|| mode == TImode
|| mode == TFmode
|| (BYTES_BIG_ENDIAN && advsimd_struct_p));
-
/* If we are dealing with ADDR_QUERY_LDP_STP_N that means the incoming mode
corresponds to the actual size of the memory being loaded/stored and the
mode of the corresponding addressing mode is half of that. */
mode = DFmode;
bool allow_reg_index_p = (!load_store_pair_p
- && (known_lt (GET_MODE_SIZE (mode), 16)
+ && ((vec_flags == 0
+ && known_lt (GET_MODE_SIZE (mode), 16))
|| vec_flags == VEC_ADVSIMD
|| vec_flags & VEC_SVE_DATA));
- /* For SVE, only accept [Rn], [Rn, Rm, LSL #shift] and
- [Rn, #offset, MUL VL]. */
+ /* For SVE, only accept [Rn], [Rn, #offset, MUL VL] and [Rn, Rm, LSL #shift].
+ The latter is not valid for SVE predicates, and that's rejected through
+ allow_reg_index_p above. */
if ((vec_flags & (VEC_SVE_DATA | VEC_SVE_PRED)) != 0
&& (code != REG && code != PLUS))
return false;
--- /dev/null
+/* PR target/102252. */
+/* { dg-do assemble { target aarch64_asm_sve_ok } } */
+/* { dg-options "-march=armv8.2-a+sve -msve-vector-bits=512" } */
+
+/* We used to generate invalid assembly for SVE predicate loads. */
+
+#include <arm_sve.h>
+
+class SimdBool
+{
+private:
+ typedef svbool_t simdInternalType_ __attribute__((arm_sve_vector_bits(512)));
+
+public:
+ SimdBool() {}
+
+ simdInternalType_ simdInternal_;
+
+};
+
+static svfloat32_t selectByMask(svfloat32_t a, SimdBool m) {
+ return svsel_f32(m.simdInternal_, a, svdup_f32(0.0));
+}
+
+struct s {
+ SimdBool array[1];
+};
+
+
+
+void foo(struct s* const work, int offset)
+{
+ svfloat32_t tz_S0;
+
+ tz_S0 = selectByMask(tz_S0, work->array[offset]);
+}
+