diff options
| author | Hannes Braun <hannes@hannesbraun.net> | 2025-02-20 15:09:41 +0100 |
|---|---|---|
| committer | Richard Earnshaw <rearnsha@arm.com> | 2025-03-05 16:19:18 +0000 |
| commit | 4d0a333ef13e2da140cd44c4941b20f48a80dc0f (patch) | |
| tree | ec5505529d213a3fbc59c4329eb46baf735fcffe | |
| parent | 81c6c99efa6a7afd3082785a9ab7fb64d2c93e1d (diff) | |
| download | gcc-4d0a333ef13e2da140cd44c4941b20f48a80dc0f.zip gcc-4d0a333ef13e2da140cd44c4941b20f48a80dc0f.tar.gz gcc-4d0a333ef13e2da140cd44c4941b20f48a80dc0f.tar.bz2 | |
arm: Fix signedness of vld1q intrinsic parms [PR118942]
vld1q_s8_x3, vld1q_s16_x3, vld1q_s8_x4 and vld1q_s16_x4 were expecting
pointers to unsigned integers. These parameters should be pointers to
signed integers.
gcc/ChangeLog:
PR target/118942
* config/arm/arm_neon.h (vld1q_s8_x3): Use int8_t instead of
uint16_t.
(vld1q_s16_x3): Use int16_t instead of uint16_t.
(vld1q_s8_x4): Likewise.
(vld1q_s16_x4): Likewise.
gcc/testsuite/ChangeLog:
PR target/118942
* gcc.target/arm/simd/vld1q_base_xN_1.c: Add -Wpointer-sign.
Signed-off-by: Hannes Braun <hannes@hannesbraun.net>
| -rw-r--r-- | gcc/config/arm/arm_neon.h | 8 | ||||
| -rw-r--r-- | gcc/testsuite/gcc.target/arm/simd/vld1q_base_xN_1.c | 2 |
2 files changed, 5 insertions, 5 deletions
diff --git a/gcc/config/arm/arm_neon.h b/gcc/config/arm/arm_neon.h index 5b1c55c..578ada8 100644 --- a/gcc/config/arm/arm_neon.h +++ b/gcc/config/arm/arm_neon.h @@ -10854,7 +10854,7 @@ vld1q_s64_x2 (const int64_t * __a) __extension__ extern __inline int8x16x3_t __attribute__ ((__always_inline__, __gnu_inline__, __artificial__)) -vld1q_s8_x3 (const uint8_t * __a) +vld1q_s8_x3 (const int8_t * __a) { union { int8x16x3_t __i; __builtin_neon_ci __o; } __rv; __rv.__o = __builtin_neon_vld1q_x3v16qi ((const __builtin_neon_qi *) __a); @@ -10863,7 +10863,7 @@ vld1q_s8_x3 (const uint8_t * __a) __extension__ extern __inline int16x8x3_t __attribute__ ((__always_inline__, __gnu_inline__, __artificial__)) -vld1q_s16_x3 (const uint16_t * __a) +vld1q_s16_x3 (const int16_t * __a) { union { int16x8x3_t __i; __builtin_neon_ci __o; } __rv; __rv.__o = __builtin_neon_vld1q_x3v8hi ((const __builtin_neon_hi *) __a); @@ -10890,7 +10890,7 @@ vld1q_s64_x3 (const int64_t * __a) __extension__ extern __inline int8x16x4_t __attribute__ ((__always_inline__, __gnu_inline__, __artificial__)) -vld1q_s8_x4 (const uint8_t * __a) +vld1q_s8_x4 (const int8_t * __a) { union { int8x16x4_t __i; __builtin_neon_xi __o; } __rv; __rv.__o = __builtin_neon_vld1q_x4v16qi ((const __builtin_neon_qi *) __a); @@ -10899,7 +10899,7 @@ vld1q_s8_x4 (const uint8_t * __a) __extension__ extern __inline int16x8x4_t __attribute__ ((__always_inline__, __gnu_inline__, __artificial__)) -vld1q_s16_x4 (const uint16_t * __a) +vld1q_s16_x4 (const int16_t * __a) { union { int16x8x4_t __i; __builtin_neon_xi __o; } __rv; __rv.__o = __builtin_neon_vld1q_x4v8hi ((const __builtin_neon_hi *) __a); diff --git a/gcc/testsuite/gcc.target/arm/simd/vld1q_base_xN_1.c b/gcc/testsuite/gcc.target/arm/simd/vld1q_base_xN_1.c index 01b29b6..c73afe2 100644 --- a/gcc/testsuite/gcc.target/arm/simd/vld1q_base_xN_1.c +++ b/gcc/testsuite/gcc.target/arm/simd/vld1q_base_xN_1.c @@ -1,6 +1,6 @@ /* { dg-do assemble } */ /* { dg-require-effective-target arm_neon_ok } */ -/* { dg-options "-save-temps -O2" } */ +/* { dg-options "-save-temps -O2 -Wpointer-sign" } */ /* { dg-add-options arm_neon } */ #include "arm_neon.h" |