diff options
| author | Stefan Sørensen <stefan.sorensen@spectralink.com> | 2016-01-21 10:52:46 +0100 |
|---|---|---|
| committer | Jakub Jelinek <jakub@gcc.gnu.org> | 2016-01-21 10:52:46 +0100 |
| commit | 6d31cc758baf6756d0627da19b546625709176c6 (patch) | |
| tree | 9949c3da10b212ccb72cdb22a8c552466be16162 /gcc | |
| parent | b929b47014eb64cfc5d9ed3539fc7ef80134211e (diff) | |
| download | gcc-6d31cc758baf6756d0627da19b546625709176c6.zip gcc-6d31cc758baf6756d0627da19b546625709176c6.tar.gz gcc-6d31cc758baf6756d0627da19b546625709176c6.tar.bz2 | |
re PR target/69187 (ICE: Aborted when native compiling neon code with __builtin_neon_vmlals_lanev4hi)
PR target/69187
PR target/65624
* config/arm/arm-builtins.c (arm_expand_neon_builtin): Increase
args array size by one to avoid buffer overflow.
* gcc.target/arm/pr69187.c: New test.
From-SVN: r232668
Diffstat (limited to 'gcc')
| -rw-r--r-- | gcc/ChangeLog | 8 | ||||
| -rw-r--r-- | gcc/config/arm/arm-builtins.c | 2 | ||||
| -rw-r--r-- | gcc/testsuite/ChangeLog | 4 | ||||
| -rw-r--r-- | gcc/testsuite/gcc.target/arm/pr69187.c | 19 |
4 files changed, 32 insertions, 1 deletions
diff --git a/gcc/ChangeLog b/gcc/ChangeLog index 2ea6938..a17a403 100644 --- a/gcc/ChangeLog +++ b/gcc/ChangeLog @@ -1,3 +1,11 @@ +2016-01-21 Stefan Sørensen <stefan.sorensen@spectralink.com> + Jakub Jelinek <jakub@redhat.com> + + PR target/69187 + PR target/65624 + * config/arm/arm-builtins.c (arm_expand_neon_builtin): Increase + args array size by one to avoid buffer overflow. + 2016-01-21 Marcin Kościelnicki <koriakin@0x04.net> * config/s390/s390.md (pool_section_start): Use switch_to_section diff --git a/gcc/config/arm/arm-builtins.c b/gcc/config/arm/arm-builtins.c index db6b29d..90fb40f 100644 --- a/gcc/config/arm/arm-builtins.c +++ b/gcc/config/arm/arm-builtins.c @@ -2246,7 +2246,7 @@ arm_expand_neon_builtin (int fcode, tree exp, rtx target) neon_builtin_datum *d = &neon_builtin_data[fcode - ARM_BUILTIN_NEON_PATTERN_START]; enum insn_code icode = d->code; - builtin_arg args[SIMD_MAX_BUILTIN_ARGS]; + builtin_arg args[SIMD_MAX_BUILTIN_ARGS + 1]; int num_args = insn_data[d->code].n_operands; int is_void = 0; int k; diff --git a/gcc/testsuite/ChangeLog b/gcc/testsuite/ChangeLog index a6bc40c..3ef65ab 100644 --- a/gcc/testsuite/ChangeLog +++ b/gcc/testsuite/ChangeLog @@ -1,5 +1,9 @@ 2016-01-21 Jakub Jelinek <jakub@redhat.com> + PR target/69187 + PR target/65624 + * gcc.target/arm/pr69187.c: New test. + PR c++/69355 * g++.dg/torture/pr69355.C: New test. diff --git a/gcc/testsuite/gcc.target/arm/pr69187.c b/gcc/testsuite/gcc.target/arm/pr69187.c new file mode 100644 index 0000000..9992a69 --- /dev/null +++ b/gcc/testsuite/gcc.target/arm/pr69187.c @@ -0,0 +1,19 @@ +/* PR target/69187 */ +/* { dg-do compile } */ +/* { dg-require-effective-target arm_neon } */ +/* { dg-options "-O0" } */ +/* { dg-add-options arm_neon } */ + +#include <arm_neon.h> + +int32x4_t +foo (void) +{ + int32x4_t vector_int32x4; + int16x4_t vector3_int16x4; + int16x4_t vector4_int16x4; + static int32_t buffer_int32x4[32]; + + vector_int32x4 = vld1q_s32(buffer_int32x4); + return vqdmlsl_lane_s16(vector_int32x4, vector3_int16x4, vector4_int16x4, 0); +} |