gcc/testsuite/
authoryroux <yroux@138bc75d-0d04-0410-961f-82ee72b054a4>
Thu, 4 Dec 2014 13:51:49 +0000 (13:51 +0000)
committeryroux <yroux@138bc75d-0d04-0410-961f-82ee72b054a4>
Thu, 4 Dec 2014 13:51:49 +0000 (13:51 +0000)
2014-12-04  Yvan Roux  <yvan.roux@linaro.org>

Backport from trunk r215129.
2014-09-10  Alan Lawrence  <alan.lawrence@arm.com>

* gcc.target/aarch64/vstN_1.c: New test.

git-svn-id: svn+ssh://gcc.gnu.org/svn/gcc/branches/linaro/gcc-4_9-branch@218364 138bc75d-0d04-0410-961f-82ee72b054a4

gcc/testsuite/ChangeLog.linaro
gcc/testsuite/gcc.target/aarch64/vstN_1.c [new file with mode: 0644]

index bc32cc6..ae6f09e 100644 (file)
@@ -1,5 +1,12 @@
 2014-12-04  Yvan Roux  <yvan.roux@linaro.org>
 
+       Backport from trunk r215129.
+       2014-09-10  Alan Lawrence  <alan.lawrence@arm.com>
+
+       * gcc.target/aarch64/vstN_1.c: New test.
+
+2014-12-04  Yvan Roux  <yvan.roux@linaro.org>
+
        Backport from trunk r215126.
        2014-09-10  Alan Lawrence  <alan.lawrence@arm.com>
 
diff --git a/gcc/testsuite/gcc.target/aarch64/vstN_1.c b/gcc/testsuite/gcc.target/aarch64/vstN_1.c
new file mode 100644 (file)
index 0000000..9c166b7
--- /dev/null
@@ -0,0 +1,76 @@
+/* { dg-do run } */
+/* { dg-options "-O3" } */
+
+#include <arm_neon.h>
+
+extern void abort (void);
+
+#define TESTMETH(BASE, ELTS, STRUCT, SUFFIX)           \
+int __attribute__ ((noinline))                         \
+test_vst##STRUCT##SUFFIX ()                            \
+{                                                      \
+  BASE##_t src[ELTS * STRUCT];                         \
+  BASE##_t dest[ELTS * STRUCT];                                \
+  BASE##x##ELTS##x##STRUCT##_t vectors;                        \
+  int i,j;                                             \
+  for (i = 0; i < STRUCT * ELTS; i++)                  \
+    src [i] = (BASE##_t) 2*i + 1;                      \
+  for (i = 0; i < STRUCT; i++)                         \
+    vectors.val[i] = vld1##SUFFIX (&src[i*ELTS]);      \
+  asm volatile ("" : : : "memory");                    \
+  vst##STRUCT##SUFFIX (dest, vectors);                 \
+  asm volatile ("" : : : "memory");                    \
+  for (i = 0; i < STRUCT; i++)                         \
+    {                                                  \
+      for (j = 0; j < ELTS; j++)                       \
+        if (src[i*ELTS + j] != dest[i + STRUCT*j])     \
+          return 1;                                    \
+    }                                                  \
+  return 0;                                            \
+}
+
+#define VARIANTS(VARIANT, STRUCT)      \
+VARIANT (uint8, 8, STRUCT, _u8)                \
+VARIANT (uint16, 4, STRUCT, _u16)      \
+VARIANT (uint32, 2, STRUCT, _u32)      \
+VARIANT (uint64, 1, STRUCT, _u64)      \
+VARIANT (int8, 8, STRUCT, _s8)         \
+VARIANT (int16, 4, STRUCT, _s16)       \
+VARIANT (int32, 2, STRUCT, _s32)       \
+VARIANT (int64, 1, STRUCT, _s64)       \
+VARIANT (poly8, 8, STRUCT, _p8)                \
+VARIANT (poly16, 4, STRUCT, _p16)      \
+VARIANT (float32, 2, STRUCT, _f32)     \
+VARIANT (float64, 1, STRUCT, _f64)     \
+VARIANT (uint8, 16, STRUCT, q_u8)      \
+VARIANT (uint16, 8, STRUCT, q_u16)     \
+VARIANT (uint32, 4, STRUCT, q_u32)     \
+VARIANT (uint64, 2, STRUCT, q_u64)     \
+VARIANT (int8, 16, STRUCT, q_s8)       \
+VARIANT (int16, 8, STRUCT, q_s16)      \
+VARIANT (int32, 4, STRUCT, q_s32)      \
+VARIANT (int64, 2, STRUCT, q_s64)      \
+VARIANT (poly8, 16, STRUCT, q_p8)      \
+VARIANT (poly16, 8, STRUCT, q_p16)     \
+VARIANT (float32, 4, STRUCT, q_f32)    \
+VARIANT (float64, 2, STRUCT, q_f64)
+
+/* Tests of vst2 and vst2q.  */
+VARIANTS (TESTMETH, 2)
+/* Tests of vst3 and vst3q.  */
+VARIANTS (TESTMETH, 3)
+/* Tests of vst4 and vst4q.  */
+VARIANTS (TESTMETH, 4)
+
+#define CHECK(BASE, ELTS, STRUCT, SUFFIX)      \
+  if (test_vst##STRUCT##SUFFIX () != 0)                \
+    abort ();
+
+int
+main (int argc, char **argv)
+{
+  VARIANTS (CHECK, 2)
+  VARIANTS (CHECK, 3)
+  VARIANTS (CHECK, 4)
+  return 0;
+}