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