vget_lane.c: New testcase.

2015-07-03  Christophe Lyon  <christophe.lyon@linaro.org>

	* gcc.target/aarch64/advsimd-intrinsics/vget_lane.c: New testcase.

From-SVN: r225374

diff --git a/gcc/testsuite/ChangeLog b/gcc/testsuite/ChangeLog
index b6b42269009d8488e9b342701d8208af83998a90..aede20a8e508e883383f187c1dd96bba3f922cfe 100644 (file)
--- a/gcc/testsuite/ChangeLog
+++ b/gcc/testsuite/ChangeLog
@@ -1,3 +1,7 @@
+2015-07-03  Christophe Lyon  <christophe.lyon@linaro.org>
+
+       * gcc.target/aarch64/advsimd-intrinsics/vget_lane.c: New testcase.
+
 2015-07-03  James Greenhalgh  <james.greenhalgh@arm.com>
 
        PR tree-optimization/66119

diff --git a/gcc/testsuite/gcc.target/aarch64/advsimd-intrinsics/vget_lane.c b/gcc/testsuite/gcc.target/aarch64/advsimd-intrinsics/vget_lane.c
new file mode 100644 (file)
index 0000000..5806050
--- /dev/null
+++ b/gcc/testsuite/gcc.target/aarch64/advsimd-intrinsics/vget_lane.c
@@ -0,0 +1,125 @@
+#include <arm_neon.h>
+#include "arm-neon-ref.h"
+#include "compute-ref-data.h"
+
+/* Expected results.  */
+int8_t     expected_s8   = 0xf7;
+int16_t    expected_s16  = 0xfff3;
+int32_t    expected_s32  = 0xfffffff1;
+int64_t    expected_s64  = 0xfffffffffffffff0;
+uint8_t    expected_u8   = 0xf6;
+uint16_t   expected_u16  = 0xfff2;
+uint32_t   expected_u32  = 0xfffffff1;
+uint64_t   expected_u64  = 0xfffffffffffffff0;
+poly8_t    expected_p8   = 0xf6;
+poly16_t   expected_p16  = 0xfff2;
+hfloat32_t expected_f32  = 0xc1700000;
+
+int8_t     expectedq_s8  = 0xff;
+int16_t    expectedq_s16 = 0xfff5;
+int32_t    expectedq_s32 = 0xfffffff3;
+int64_t    expectedq_s64 = 0xfffffffffffffff1;
+uint8_t    expectedq_u8  = 0xfe;
+uint16_t   expectedq_u16 = 0xfff6;
+uint32_t   expectedq_u32 = 0xfffffff2;
+uint64_t   expectedq_u64 = 0xfffffffffffffff1;
+poly8_t    expectedq_p8  = 0xfe;
+poly16_t   expectedq_p16 = 0xfff6;
+hfloat32_t expectedq_f32 = 0xc1500000;
+
+int error_found = 0;
+
+#define TEST_MSG "VGET_LANE"
+void exec_vget_lane (void)
+{
+  /* vec=vget_lane(vec, lane), then store the result.  */
+#define TEST_VGET_LANE(Q, T1, T2, W, N, L)                                \
+  VAR(var, T1, W) = vget##Q##_lane_##T2##W(VECT_VAR(vector, T1, W, N), L); \
+  if (VAR(var, T1, W) != expected##Q##_##T2##W) {                         \
+    fprintf(stderr,                                                       \
+           "ERROR in %s (%s line %d in result '%s') at type %s "          \
+           "got 0x%" PRIx##W " != 0x%" PRIx##W "\n",                      \
+           TEST_MSG, __FILE__, __LINE__,                                  \
+           STR(expected##Q##_##T2##W),                                    \
+           STR(VECT_NAME(T1, W, N)),                                      \
+           VAR(var, T1, W),                                               \
+           expected##Q##_##T2##W);                                        \
+    error_found = 1;                                                      \
+  }
+
+  /* Special variant for floating-point.  */
+  union {
+    uint32_t var_int32;
+    float32_t var_float32;
+  } var_int32_float32;
+
+#define TEST_VGET_LANE_FP(Q, T1, T2, W, N, L)                             \
+  VAR(var, T1, W) = vget##Q##_lane_##T2##W(VECT_VAR(vector, T1, W, N), L); \
+  var_int##W##_float##W.var_float##W = VAR(var, T1, W);                           \
+  if (var_int##W##_float##W.var_int##W != expected##Q##_##T2##W) {        \
+    fprintf(stderr,                                                       \
+           "ERROR in %s (%s line %d in result '%s') at type %s "          \
+           "got 0x%" PRIx##W " != 0x%" PRIx##W "\n",                      \
+           TEST_MSG, __FILE__, __LINE__,                                  \
+           STR(expected##Q##_##T2##W),                                    \
+           STR(VECT_NAME(T1, W, N)),                                      \
+           var_int##W##_float##W.var_int##W,                              \
+           expected##Q##_##T2##W);                                        \
+    error_found = 1;                                                      \
+  }
+
+  DECL_VARIABLE_ALL_VARIANTS(vector);
+
+  /* Scalar variables.  */
+  VAR_DECL(var, int, 8);
+  VAR_DECL(var, int, 16);
+  VAR_DECL(var, int, 32);
+  VAR_DECL(var, int, 64);
+  VAR_DECL(var, uint, 8);
+  VAR_DECL(var, uint, 16);
+  VAR_DECL(var, uint, 32);
+  VAR_DECL(var, uint, 64);
+  VAR_DECL(var, poly, 8);
+  VAR_DECL(var, poly, 16);
+  VAR_DECL(var, float, 32);
+
+  /* Initialize input values.  */
+  TEST_MACRO_ALL_VARIANTS_2_5(VLOAD, vector, buffer);
+  VLOAD(vector, buffer, , float, f, 32, 2);
+  VLOAD(vector, buffer, q, float, f, 32, 4);
+
+  /* Choose lane arbitrarily.  */
+  TEST_VGET_LANE(, int, s, 8, 8, 7);
+  TEST_VGET_LANE(, int, s, 16, 4, 3);
+  TEST_VGET_LANE(, int, s, 32, 2, 1);
+  TEST_VGET_LANE(, int, s, 64, 1, 0);
+  TEST_VGET_LANE(, uint, u, 8, 8, 6);
+  TEST_VGET_LANE(, uint, u, 16, 4, 2);
+  TEST_VGET_LANE(, uint, u, 32, 2, 1);
+  TEST_VGET_LANE(, uint, u, 64, 1, 0);
+  TEST_VGET_LANE(, poly, p, 8, 8, 6);
+  TEST_VGET_LANE(, poly, p, 16, 4, 2);
+  TEST_VGET_LANE_FP(, float, f, 32, 2, 1);
+
+  TEST_VGET_LANE(q, int, s, 8, 16, 15);
+  TEST_VGET_LANE(q, int, s, 16, 8, 5);
+  TEST_VGET_LANE(q, int, s, 32, 4, 3);
+  TEST_VGET_LANE(q, int, s, 64, 2, 1);
+  TEST_VGET_LANE(q, uint, u, 8, 16, 14);
+  TEST_VGET_LANE(q, uint, u, 16, 8, 6);
+  TEST_VGET_LANE(q, uint, u, 32, 4, 2);
+  TEST_VGET_LANE(q, uint, u, 64, 2, 1);
+  TEST_VGET_LANE(q, poly, p, 8, 16, 14);
+  TEST_VGET_LANE(q, poly, p, 16, 8, 6);
+  TEST_VGET_LANE_FP(q, float, f, 32, 4, 3);
+}
+
+int main (void)
+{
+  exec_vget_lane ();
+
+  if (error_found)
+    abort();
+
+  return 0;
+}