gcc/testsuite/gcc.target/aarch64/vldN_lane_1.c

   1 /* { dg-do run } */
   2 /* { dg-options "-O3 -fno-inline" } */
   3
   4 #include <arm_neon.h>
   5
   6 extern void abort (void);
   7
   8 #define VARIANTS(VARIANT, STRUCT)       \
   9 VARIANT (uint8, , 8, _u8, 6, STRUCT)    \
  10 VARIANT (uint16, , 4, _u16, 3, STRUCT)  \
  11 VARIANT (uint32, , 2, _u32, 1, STRUCT)  \
  12 VARIANT (uint64, , 1, _u64, 0, STRUCT)  \
  13 VARIANT (int8, , 8, _s8, 5, STRUCT)     \
  14 VARIANT (int16, , 4, _s16, 2, STRUCT)   \
  15 VARIANT (int32, , 2, _s32, 0, STRUCT)   \
  16 VARIANT (int64, , 1, _s64, 0, STRUCT)   \
  17 VARIANT (poly8, , 8, _p8, 7, STRUCT)    \
  18 VARIANT (poly16, , 4, _p16, 1, STRUCT)  \
  19 VARIANT (float32, , 2, _f32, 1, STRUCT) \
  20 VARIANT (float64, , 1, _f64, 0, STRUCT) \
  21 VARIANT (uint8, q, 16, _u8, 14, STRUCT) \
  22 VARIANT (uint16, q, 8, _u16, 4, STRUCT) \
  23 VARIANT (uint32, q, 4, _u32, 3, STRUCT) \
  24 VARIANT (uint64, q, 2, _u64, 0, STRUCT) \
  25 VARIANT (int8, q, 16, _s8, 13, STRUCT)  \
  26 VARIANT (int16, q, 8, _s16, 6, STRUCT)  \
  27 VARIANT (int32, q, 4, _s32, 2, STRUCT)  \
  28 VARIANT (int64, q, 2, _s64, 1, STRUCT)  \
  29 VARIANT (poly8, q, 16, _p8, 12, STRUCT) \
  30 VARIANT (poly16, q, 8, _p16, 5, STRUCT) \
  31 VARIANT (float32, q, 4, _f32, 1, STRUCT)\
  32 VARIANT (float64, q, 2, _f64, 0, STRUCT)
  33
  34 #define TESTMETH(BASE, Q, ELTS, SUFFIX, LANE, STRUCT)                   \
  35 int                                                                     \
  36 test_vld##STRUCT##Q##_lane##SUFFIX (const BASE##_t *data,               \
  37                                      const BASE##_t *overwrite)         \
  38 {                                                                       \
  39   BASE##x##ELTS##x##STRUCT##_t vectors;                                 \
  40   BASE##_t temp[ELTS];                                                  \
  41   int i,j;                                                              \
  42   for (i = 0; i < STRUCT; i++, data += ELTS)                            \
  43     vectors.val[i] = vld1##Q##SUFFIX (data);                            \
  44   vectors = vld##STRUCT##Q##_lane##SUFFIX (overwrite, vectors, LANE);   \
  45   while (--i >= 0)                                                      \
  46     {                                                                   \
  47       vst1##Q##SUFFIX (temp, vectors.val[i]);                           \
  48       data -= ELTS; /* Point at value loaded before vldN_lane.  */      \
  49       for (j = 0; j < ELTS; j++)                                        \
  50         if (temp[j] != (j == LANE ? overwrite[i] : data[j]))            \
  51           return 1;                                                     \
  52     }                                                                   \
  53   return 0;                                                             \
  54 }
  55
  56
  57 /* Tests of vld2_dup and vld2q_dup.  */
  58 VARIANTS (TESTMETH, 2)
  59 /* Tests of vld3_dup and vld3q_dup.  */
  60 VARIANTS (TESTMETH, 3)
  61 /* Tests of vld4_dup and vld4q_dup.  */
  62 VARIANTS (TESTMETH, 4)
  63
  64 #define CHECK(BASE, Q, ELTS, SUFFIX, LANE, STRUCT)                      \
  65   if (test_vld##STRUCT##Q##_lane##SUFFIX ((const BASE##_t *)orig_data,  \
  66                                                 BASE##_data) != 0)      \
  67     abort ();
  68
  69 int
  70 main (int argc, char **argv)
  71 {
  72   /* Original data for all vector formats.  */
  73   uint64_t orig_data[8] = {0x1234567890abcdefULL, 0x13579bdf02468aceULL,
  74                            0x012389ab4567cdefULL, 0xfeeddadacafe0431ULL,
  75                            0x1032547698badcfeULL, 0xbadbadbadbad0badULL,
  76                            0x0102030405060708ULL, 0x0f0e0d0c0b0a0908ULL};
  77
  78   /* Data with which vldN_lane will overwrite some of previous.  */
  79   uint8_t uint8_data[4] = { 7, 11, 13, 17 };
  80   uint16_t uint16_data[4] = { 257, 263, 269, 271 };
  81   uint32_t uint32_data[4] = { 65537, 65539, 65543, 65551 };
  82   uint64_t uint64_data[4] = { 0xdeadbeefcafebabeULL, 0x0123456789abcdefULL,
  83                               0xfedcba9876543210LL, 0xdeadbabecafebeefLL };
  84   int8_t int8_data[4] = { -1, 3, -5, 7 };
  85   int16_t int16_data[4] = { 257, -259, 261, -263 };
  86   int32_t int32_data[4] = { 123456789, -987654321, -135792468, 975318642 };
  87   int64_t *int64_data = (int64_t *)uint64_data;
  88   poly8_t poly8_data[4] = { 0, 7, 13, 18, };
  89   poly16_t poly16_data[4] = { 11111, 2222, 333, 44 };
  90   float32_t float32_data[4] = { 3.14159, 2.718, 1.414, 100.0 };
  91   float64_t float64_data[4] = { 1.010010001, 12345.6789, -9876.54321, 1.618 };
  92
  93   VARIANTS (CHECK, 2);
  94   VARIANTS (CHECK, 3);
  95   VARIANTS (CHECK, 4);
  96   return 0;
  97 }