1  /* { dg-do run } */
       2  /* { dg-options "-O3" } */
       3  
       4  #include <arm_neon.h>
       5  
       6  extern void abort (void);
       7  
       8  #define TESTMETH(BASE, ELTS, STRUCT, SUFFIX)		\
       9  int __attribute__ ((noinline))				\
      10  test_vst##STRUCT##SUFFIX ()				\
      11  {							\
      12    BASE##_t src[ELTS * STRUCT];				\
      13    BASE##_t dest[ELTS * STRUCT];				\
      14    BASE##x##ELTS##x##STRUCT##_t vectors;			\
      15    int i,j;						\
      16    for (i = 0; i < STRUCT * ELTS; i++)			\
      17      src [i] = (BASE##_t) 2*i + 1;			\
      18    for (i = 0; i < STRUCT; i++)				\
      19      vectors.val[i] = vld1##SUFFIX (&src[i*ELTS]);	\
      20    asm volatile ("" : : : "memory");			\
      21    vst##STRUCT##SUFFIX (dest, vectors);			\
      22    asm volatile ("" : : : "memory");			\
      23    for (i = 0; i < STRUCT; i++)				\
      24      {							\
      25        for (j = 0; j < ELTS; j++)			\
      26          if (src[i*ELTS + j] != dest[i + STRUCT*j])	\
      27            return 1;					\
      28      }							\
      29    return 0;						\
      30  }
      31  
      32  #define VARIANTS(VARIANT, STRUCT)	\
      33  VARIANT (uint8, 8, STRUCT, _u8)		\
      34  VARIANT (uint16, 4, STRUCT, _u16)	\
      35  VARIANT (uint32, 2, STRUCT, _u32)	\
      36  VARIANT (uint64, 1, STRUCT, _u64)	\
      37  VARIANT (int8, 8, STRUCT, _s8)		\
      38  VARIANT (int16, 4, STRUCT, _s16)	\
      39  VARIANT (int32, 2, STRUCT, _s32)	\
      40  VARIANT (int64, 1, STRUCT, _s64)	\
      41  VARIANT (poly8, 8, STRUCT, _p8)		\
      42  VARIANT (poly16, 4, STRUCT, _p16)	\
      43  VARIANT (float32, 2, STRUCT, _f32)	\
      44  VARIANT (float64, 1, STRUCT, _f64)	\
      45  VARIANT (uint8, 16, STRUCT, q_u8)	\
      46  VARIANT (uint16, 8, STRUCT, q_u16)	\
      47  VARIANT (uint32, 4, STRUCT, q_u32)	\
      48  VARIANT (uint64, 2, STRUCT, q_u64)	\
      49  VARIANT (int8, 16, STRUCT, q_s8)	\
      50  VARIANT (int16, 8, STRUCT, q_s16)	\
      51  VARIANT (int32, 4, STRUCT, q_s32)	\
      52  VARIANT (int64, 2, STRUCT, q_s64)	\
      53  VARIANT (poly8, 16, STRUCT, q_p8)	\
      54  VARIANT (poly16, 8, STRUCT, q_p16)	\
      55  VARIANT (float32, 4, STRUCT, q_f32)	\
      56  VARIANT (float64, 2, STRUCT, q_f64)
      57  
      58  /* Tests of vst2 and vst2q.  */
      59  VARIANTS (TESTMETH, 2)
      60  /* Tests of vst3 and vst3q.  */
      61  VARIANTS (TESTMETH, 3)
      62  /* Tests of vst4 and vst4q.  */
      63  VARIANTS (TESTMETH, 4)
      64  
      65  #define CHECK(BASE, ELTS, STRUCT, SUFFIX)	\
      66    if (test_vst##STRUCT##SUFFIX () != 0)		\
      67      abort ();
      68  
      69  int
      70  main (int argc, char **argv)
      71  {
      72    VARIANTS (CHECK, 2)
      73    VARIANTS (CHECK, 3)
      74    VARIANTS (CHECK, 4)
      75    return 0;
      76  }