1  /* { dg-do run } */
       2  /* { dg-options "-O3 -std=c99" } */
       3  
       4  #include <arm_neon.h>
       5  
       6  extern void abort (void);
       7  
       8  #define VARIANTS(VARIANT)				\
       9  VARIANT (uint8_t, 8, uint8x8_t, uint8x16_t, u8)		\
      10  VARIANT (uint16_t, 4, uint16x4_t, uint16x8_t, u16)	\
      11  VARIANT (uint32_t, 2, uint32x2_t, uint32x4_t, u32)	\
      12  VARIANT (uint64_t, 1, uint64x1_t, uint64x2_t, u64)	\
      13  VARIANT (int8_t, 8, int8x8_t, int8x16_t, s8)		\
      14  VARIANT (int16_t, 4, int16x4_t, int16x8_t, s16)		\
      15  VARIANT (int32_t, 2, int32x2_t, int32x4_t, s32)		\
      16  VARIANT (int64_t, 1, int64x1_t, int64x2_t, s64)		\
      17  VARIANT (float16_t, 4, float16x4_t, float16x8_t, f16)	\
      18  VARIANT (float32_t, 2, float32x2_t, float32x4_t, f32)	\
      19  VARIANT (float64_t, 1, float64x1_t, float64x2_t, f64)
      20  
      21  
      22  #define TESTMETH(BASETYPE, NUM64, TYPE64, TYPE128, SUFFIX)	\
      23  int								\
      24  test_vget_low_ ##SUFFIX (BASETYPE *data)			\
      25  {								\
      26    BASETYPE temp [NUM64];					\
      27    TYPE128 vec = vld1q_##SUFFIX (data);				\
      28    TYPE64 high = vget_high_##SUFFIX (vec);			\
      29    vst1_##SUFFIX (temp, high);					\
      30    for (int i = 0; i < NUM64; i++)				\
      31      if (temp[i] != data[i + NUM64])				\
      32        return 1;							\
      33    return 0;							\
      34  }
      35  
      36  VARIANTS (TESTMETH)
      37  
      38  #define CHECK(BASETYPE, NUM64, TYPE64, TYPE128, SUFFIX)		\
      39    if (test_vget_low_##SUFFIX (BASETYPE ## _ ## data) != 0)	\
      40      abort ();
      41  
      42  int
      43  main (int argc, char **argv)
      44  {
      45    uint8_t uint8_t_data[16] =
      46        { 1, 2, 3, 5, 7, 11, 13, 17, 19, 23, 29, 31, 37, 41, 43, 47 };
      47    uint16_t uint16_t_data[8] = { 1, 22, 333, 4444, 55555, 6666, 777, 88 };
      48    uint32_t uint32_t_data[4] = { 65537, 11, 70000, 23 };
      49    uint64_t uint64_t_data[2] = { 0xdeadbeefcafebabeULL, 0x0123456789abcdefULL };
      50    int8_t int8_t_data[16] =
      51        { -1, -3, -5, -7, 9, -11, -13, 15, -17, -19, 21, -23, 25, 27, -29, -31 };
      52    int16_t int16_t_data[8] = { -17, 19, 3, -999, 44048, 505, 9999, 1000};
      53    int32_t int32_t_data[4] = { 123456789, -987654321, -135792468, 975318642 };
      54    int64_t int64_t_data[2] = {0xfedcba9876543210LL, 0xdeadbabecafebeefLL };
      55    float16_t float16_t_data[8] = { 1.25, 4.5, 7.875, 2.3125, 5.675, 8.875,
      56        3.6875, 6.75};
      57    float32_t float32_t_data[4] = { 3.14159, 2.718, 1.414, 100.0 };
      58    float64_t float64_t_data[2] = { 1.01001000100001, 12345.6789 };
      59  
      60    VARIANTS (CHECK);
      61  
      62    return 0;
      63  }