aboutsummaryrefslogtreecommitdiff
path: root/gcc
diff options
context:
space:
mode:
authorAlan Lawrence <alan.lawrence@arm.com>2014-09-10 12:33:59 +0000
committerAlan Lawrence <alalaw01@gcc.gnu.org>2014-09-10 12:33:59 +0000
commitd9aa6e11227c6e21b9ef8e932ba734c73e29eaac (patch)
treed5b5118a0ddbdc7db9ef09034b3c91a9e136f282 /gcc
parent77b7d74bf69cc11794079801e9c4b7bdaa7c4b16 (diff)
downloadgcc-d9aa6e11227c6e21b9ef8e932ba734c73e29eaac.zip
gcc-d9aa6e11227c6e21b9ef8e932ba734c73e29eaac.tar.gz
gcc-d9aa6e11227c6e21b9ef8e932ba734c73e29eaac.tar.bz2
[AArch64 Testsuite] Add a test of the vldN_lane intrinsic
* gcc.target/aarch64/vldN_lane_1.c: New test. From-SVN: r215126
Diffstat (limited to 'gcc')
-rw-r--r--gcc/testsuite/ChangeLog4
-rw-r--r--gcc/testsuite/gcc.target/aarch64/vldN_lane_1.c97
2 files changed, 101 insertions, 0 deletions
diff --git a/gcc/testsuite/ChangeLog b/gcc/testsuite/ChangeLog
index e4fc660..288f335 100644
--- a/gcc/testsuite/ChangeLog
+++ b/gcc/testsuite/ChangeLog
@@ -1,3 +1,7 @@
+2014-09-10 Alan Lawrence <alan.lawrence@arm.com>
+
+ * gcc.target/aarch64/vldN_lane_1.c: New test.
+
2014-09-10 Martin Jambor <mjambor@suse.cz>
PR ipa/61654
diff --git a/gcc/testsuite/gcc.target/aarch64/vldN_lane_1.c b/gcc/testsuite/gcc.target/aarch64/vldN_lane_1.c
new file mode 100644
index 0000000..e450b7b
--- /dev/null
+++ b/gcc/testsuite/gcc.target/aarch64/vldN_lane_1.c
@@ -0,0 +1,97 @@
+/* { dg-do run } */
+/* { dg-options "-O3 -fno-inline" } */
+
+#include <arm_neon.h>
+
+extern void abort (void);
+
+#define VARIANTS(VARIANT, STRUCT) \
+VARIANT (uint8, , 8, _u8, 6, STRUCT) \
+VARIANT (uint16, , 4, _u16, 3, STRUCT) \
+VARIANT (uint32, , 2, _u32, 1, STRUCT) \
+VARIANT (uint64, , 1, _u64, 0, STRUCT) \
+VARIANT (int8, , 8, _s8, 5, STRUCT) \
+VARIANT (int16, , 4, _s16, 2, STRUCT) \
+VARIANT (int32, , 2, _s32, 0, STRUCT) \
+VARIANT (int64, , 1, _s64, 0, STRUCT) \
+VARIANT (poly8, , 8, _p8, 7, STRUCT) \
+VARIANT (poly16, , 4, _p16, 1, STRUCT) \
+VARIANT (float32, , 2, _f32, 1, STRUCT) \
+VARIANT (float64, , 1, _f64, 0, STRUCT) \
+VARIANT (uint8, q, 16, _u8, 14, STRUCT) \
+VARIANT (uint16, q, 8, _u16, 4, STRUCT) \
+VARIANT (uint32, q, 4, _u32, 3, STRUCT) \
+VARIANT (uint64, q, 2, _u64, 0, STRUCT) \
+VARIANT (int8, q, 16, _s8, 13, STRUCT) \
+VARIANT (int16, q, 8, _s16, 6, STRUCT) \
+VARIANT (int32, q, 4, _s32, 2, STRUCT) \
+VARIANT (int64, q, 2, _s64, 1, STRUCT) \
+VARIANT (poly8, q, 16, _p8, 12, STRUCT) \
+VARIANT (poly16, q, 8, _p16, 5, STRUCT) \
+VARIANT (float32, q, 4, _f32, 1, STRUCT)\
+VARIANT (float64, q, 2, _f64, 0, STRUCT)
+
+#define TESTMETH(BASE, Q, ELTS, SUFFIX, LANE, STRUCT) \
+int \
+test_vld##STRUCT##Q##_lane##SUFFIX (const BASE##_t *data, \
+ const BASE##_t *overwrite) \
+{ \
+ BASE##x##ELTS##x##STRUCT##_t vectors; \
+ BASE##_t temp[ELTS]; \
+ int i,j; \
+ for (i = 0; i < STRUCT; i++, data += ELTS) \
+ vectors.val[i] = vld1##Q##SUFFIX (data); \
+ vectors = vld##STRUCT##Q##_lane##SUFFIX (overwrite, vectors, LANE); \
+ while (--i >= 0) \
+ { \
+ vst1##Q##SUFFIX (temp, vectors.val[i]); \
+ data -= ELTS; /* Point at value loaded before vldN_lane. */ \
+ for (j = 0; j < ELTS; j++) \
+ if (temp[j] != (j == LANE ? overwrite[i] : data[j])) \
+ return 1; \
+ } \
+ return 0; \
+}
+
+
+/* Tests of vld2_dup and vld2q_dup. */
+VARIANTS (TESTMETH, 2)
+/* Tests of vld3_dup and vld3q_dup. */
+VARIANTS (TESTMETH, 3)
+/* Tests of vld4_dup and vld4q_dup. */
+VARIANTS (TESTMETH, 4)
+
+#define CHECK(BASE, Q, ELTS, SUFFIX, LANE, STRUCT) \
+ if (test_vld##STRUCT##Q##_lane##SUFFIX ((const BASE##_t *)orig_data, \
+ BASE##_data) != 0) \
+ abort ();
+
+int
+main (int argc, char **argv)
+{
+ /* Original data for all vector formats. */
+ uint64_t orig_data[8] = {0x1234567890abcdefULL, 0x13579bdf02468aceULL,
+ 0x012389ab4567cdefULL, 0xfeeddadacafe0431ULL,
+ 0x1032547698badcfeULL, 0xbadbadbadbad0badULL,
+ 0x0102030405060708ULL, 0x0f0e0d0c0b0a0908ULL};
+
+ /* Data with which vldN_lane will overwrite some of previous. */
+ uint8_t uint8_data[4] = { 7, 11, 13, 17 };
+ uint16_t uint16_data[4] = { 257, 263, 269, 271 };
+ uint32_t uint32_data[4] = { 65537, 65539, 65543, 65551 };
+ uint64_t uint64_data[4] = { 0xdeadbeefcafebabeULL, 0x0123456789abcdefULL,
+ 0xfedcba9876543210LL, 0xdeadbabecafebeefLL };
+ int8_t int8_data[4] = { -1, 3, -5, 7 };
+ int16_t int16_data[4] = { 257, -259, 261, -263 };
+ int32_t int32_data[4] = { 123456789, -987654321, -135792468, 975318642 };
+ int64_t *int64_data = (int64_t *)uint64_data;
+ poly8_t poly8_data[4] = { 0, 7, 13, 18, };
+ poly16_t poly16_data[4] = { 11111, 2222, 333, 44 };
+ float32_t float32_data[4] = { 3.14159, 2.718, 1.414, 100.0 };
+ float64_t float64_data[4] = { 1.010010001, 12345.6789, -9876.54321, 1.618 };
+
+ VARIANTS (CHECK, 2);
+ VARIANTS (CHECK, 3);
+ VARIANTS (CHECK, 4);
+ return 0;
+}