diff options
| author | Prathamesh Kulkarni <prathamesh.kulkarni@linaro.org> | 2016-01-27 11:04:56 +0100 |
|---|---|---|
| committer | Linaro Code Review <review@review.linaro.org> | 2016-02-05 13:30:50 +0000 |
| commit | d5106e0dda5823c21c3b5887c507805b22cc0214 (patch) | |
| tree | be71eb778b2de64c35ef1a4df5bbd590d70d6013 /gcc | |
| parent | 5c396c068ea497f58494239b49c1122d123d8733 (diff) | |
gcc/
Backport from trunk r232668.
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.
gcc/testsuite/
Backport from trunk r232668.
PR target/69187
PR target/65624
* gcc.target/arm/pr69187.c: New test.
Change-Id: Iff2377c7356b5167553afda438e1b41e802bddf0
Diffstat (limited to 'gcc')
| -rw-r--r-- | gcc/config/arm/arm-builtins.c | 2 | ||||
| -rw-r--r-- | gcc/testsuite/gcc.target/arm/pr69187.c | 19 |
2 files changed, 20 insertions, 1 deletions
diff --git a/gcc/config/arm/arm-builtins.c b/gcc/config/arm/arm-builtins.c index e961ee8b424..a70cb536792 100644 --- a/gcc/config/arm/arm-builtins.c +++ b/gcc/config/arm/arm-builtins.c @@ -2249,7 +2249,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/gcc.target/arm/pr69187.c b/gcc/testsuite/gcc.target/arm/pr69187.c new file mode 100644 index 00000000000..9992a6954b1 --- /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); +} |