procyberian/gcc
1
0
Fork 0
Code Issues Pull requests Projects Releases Packages Wiki Activity Actions

re PR target/47551 (ICE when reloading neon registers from out-of-range offsets)

Browse source 
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.

From-SVN: r171730
This commit is contained in:
Richard Sandiford 2011-03-30 15:00:44 +00:00 • committed by Richard Sandiford
parent a621719156
commit 159b81b00a
4 changed files with 42 additions and 3 deletions
Show stats Download patch file Download diff file Expand all files Collapse all files

7
gcc/ChangeLog
View file

@ -1,3 +1,10 @@
2011-03-30 Richard Sandiford <richard.sandiford@linaro.org>
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.
2011-03-30 Richard Sandiford <richard.sandiford@linaro.org>
Ramana Radhakrishnan <ramana.radhakrishnan@linaro.org>

9
gcc/config/arm/arm.c
View file

@ -9152,11 +9152,14 @@ coproc_secondary_reload_class (enum machine_mode mode, rtx x, bool wb)
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;

5
gcc/testsuite/ChangeLog
View file

@ -1,3 +1,8 @@
2011-03-30 Richard Sandiford <richard.sandiford@linaro.org>
PR target/47551
* gcc.target/arm/neon-modes-2.c: New test.
2011-03-30 Jakub Jelinek <jakub@redhat.com>
PR c/48305

24
gcc/testsuite/gcc.target/arm/neon-modes-2.c Normal file
View file

@ -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);
}