1/* Test vld1 and vst1 maintain consistent indexing. */ 2/* { dg-do run } */ 3/* { dg-options "-O3" } */ 4#include <arm_neon.h> 5 6extern void abort (void); 7 8#define TESTMETH(TYPE, NUM, BASETYPE, SUFFIX) \ 9int __attribute__ ((noinline)) \ 10test_vld1_vst1##SUFFIX () \ 11{ \ 12 TYPE vec; \ 13 int i = 0; \ 14 BASETYPE src[NUM]; \ 15 BASETYPE dest[NUM]; \ 16 for (i = 0; i < NUM; i++) \ 17 src[i] = 2*i + 1; \ 18 asm volatile ("":::"memory"); \ 19 vec = vld1 ## SUFFIX (src); \ 20 asm volatile ("":::"memory"); \ 21 vst1 ## SUFFIX (dest, vec); \ 22 asm volatile ("":::"memory"); \ 23 for (i = 0; i < NUM; i++) \ 24 if (src[i] != dest[i]) \ 25 return 1; \ 26 return 0; \ 27} 28 29#define VARIANTS(THING) \ 30THING (int8x8_t, 8, int8_t, _s8) \ 31THING (uint8x8_t, 8, uint8_t, _u8) \ 32THING (int16x4_t, 4, int16_t, _s16) \ 33THING (uint16x4_t, 4, uint16_t, _u16) \ 34THING (int32x2_t, 2, int32_t, _s32) \ 35THING (uint32x2_t, 2, uint32_t, _u32) \ 36THING (float32x2_t, 2, float32_t, _f32) \ 37THING (int8x16_t, 16, int8_t, q_s8) \ 38THING (uint8x16_t, 16, uint8_t, q_u8) \ 39THING (int16x8_t, 8, int16_t, q_s16) \ 40THING (uint16x8_t, 8, uint16_t, q_u16) \ 41THING (int32x4_t, 4, int32_t, q_s32) \ 42THING (uint32x4_t, 4, uint32_t, q_u32) \ 43THING (int64x2_t, 2, int64_t, q_s64) \ 44THING (uint64x2_t, 2, uint64_t, q_u64) \ 45THING (float64x2_t, 2, float64_t, q_f64) 46 47VARIANTS (TESTMETH) 48 49#define DOTEST(TYPE, NUM, BASETYPE, SUFFIX) \ 50 if (test_vld1_vst1##SUFFIX ()) \ 51 abort (); 52 53int 54main () 55{ 56 VARIANTS (DOTEST); 57 return 0; 58} 59