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