+++ /dev/null
-2011-02-02 Richard Sandiford <richard.sandiford@linaro.org>
-
- gcc/
- PR target/47551
- * config/arm/arm.c (coproc_secondary_reload_class): Handle
- structure modes. Don't check neon_vector_mem_operand for
- vector or structure modes.
-
- gcc/testsuite/
- PR target/47551
- * gcc.target/arm/neon-modes-2.c: New test.
-
-=== modified file 'gcc/config/arm/arm.c'
---- old/gcc/config/arm/arm.c 2011-02-21 14:04:51 +0000
-+++ new/gcc/config/arm/arm.c 2011-03-02 11:38:43 +0000
-@@ -9139,11 +9139,14 @@
- return GENERAL_REGS;
- }
-
-+ /* The neon move patterns handle all legitimate vector and struct
-+ addresses. */
- if (TARGET_NEON
-+ && MEM_P (x)
- && (GET_MODE_CLASS (mode) == MODE_VECTOR_INT
-- || GET_MODE_CLASS (mode) == MODE_VECTOR_FLOAT)
-- && neon_vector_mem_operand (x, 0))
-- return NO_REGS;
-+ || GET_MODE_CLASS (mode) == MODE_VECTOR_FLOAT
-+ || VALID_NEON_STRUCT_MODE (mode)))
-+ return NO_REGS;
-
- if (arm_coproc_mem_operand (x, wb) || s_register_operand (x, mode))
- return NO_REGS;
-
-=== added file 'gcc/testsuite/gcc.target/arm/neon-modes-2.c'
---- old/gcc/testsuite/gcc.target/arm/neon-modes-2.c 1970-01-01 00:00:00 +0000
-+++ new/gcc/testsuite/gcc.target/arm/neon-modes-2.c 2011-02-02 10:02:45 +0000
-@@ -0,0 +1,24 @@
-+/* { dg-do compile } */
-+/* { dg-require-effective-target arm_neon_ok } */
-+/* { dg-options "-O1" } */
-+/* { dg-add-options arm_neon } */
-+
-+#include "arm_neon.h"
-+
-+#define SETUP(A) x##A = vld3_u32 (ptr + A * 0x20)
-+#define MODIFY(A) x##A = vld3_lane_u32 (ptr + A * 0x20 + 0x10, x##A, 1)
-+#define STORE(A) vst3_u32 (ptr + A * 0x20, x##A)
-+
-+#define MANY(A) A (0), A (1), A (2), A (3), A (4), A (5)
-+
-+void
-+bar (uint32_t *ptr, int y)
-+{
-+ uint32x2x3_t MANY (SETUP);
-+ int *x = __builtin_alloca (y);
-+ int z[0x1000];
-+ foo (x, z);
-+ MANY (MODIFY);
-+ foo (x, z);
-+ MANY (STORE);
-+}
-