OpenE2K
/
gcc
2
0
Fork 0
Code Issues Pull Requests Projects Releases Wiki Activity

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
This commit is contained in:
Stefan Sørensen 2016-01-21 10:52:46 +01:00 committed by Jakub Jelinek
parent b929b47014
commit 6d31cc758b
4 changed files with 32 additions and 1 deletions
Show Stats Download Patch File Download Diff File Expand all files Collapse all files

8
gcc/ChangeLog
View File

@ -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

2
gcc/config/arm/arm-builtins.c
View File

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

4
gcc/testsuite/ChangeLog
View File

@ -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.

19
gcc/testsuite/gcc.target/arm/pr69187.c Normal file
View File

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