This is the mail archive of the gcc-patches@gcc.gnu.org mailing list for the GCC project.
Index Nav:	[Date Index] [Subject Index] [Author Index] [Thread Index]
Message Nav:	[Date Prev] [Date Next]	[Thread Prev] [Thread Next]
Other format:	[Raw text]
Re: [AArch64/ARM 3/3] Add execution tests of ARM UZP Intrinsics

From: Ramana Radhakrishnan <ramana dot gcc at googlemail dot com>
To: Alan Lawrence <alan dot lawrence at arm dot com>
Cc: "gcc-patches at gcc dot gnu dot org" <gcc-patches at gcc dot gnu dot org>
Date: Wed, 30 Apr 2014 10:20:26 +0100
Subject: Re: [AArch64/ARM 3/3] Add execution tests of ARM UZP Intrinsics
Authentication-results: sourceware.org; auth=none
References: <53345CA6 dot 70202 at arm dot com> <53345FA1 dot 5000708 at arm dot com>
Reply-to: ramrad01 at arm dot com
On Thu, Mar 27, 2014 at 5:28 PM, Alan Lawrence <alan.lawrence@arm.com> wrote:
> inal patch in series, adds new tests of the ARM UZP Intrinsics (subsuming
> the autogenerated ones in testsuite/gcc.target/arm/neon/), that also check
> the execution results, reusing the test bodies introduced into AArch64 in
> the first patch.
>
> Tests use gcc.target/arm/simd/simd.exp from corresponding patch for ZIP
> Intrinsics, will commit that first.
>
> All tests passing on arm-none-eabi.


Ok if no regressions.

Ramana
>
> gcc/testsuite/ChangeLog:
> 2014-03-27  Alan Lawrence  <alan.lawrence@arm.com>
>
>     * gcc.target/arm/simd/vuzpqf32_1.c: New file.
>     * gcc.target/arm/simd/vuzpqp16_1.c: New file.
>     * gcc.target/arm/simd/vuzpqp8_1.c: New file.
>     * gcc.target/arm/simd/vuzpqs16_1.c: New file.
>     * gcc.target/arm/simd/vuzpqs32_1.c: New file.
>     * gcc.target/arm/simd/vuzpqs8_1.c: New file.
>     * gcc.target/arm/simd/vuzpqu16_1.c: New file.
>     * gcc.target/arm/simd/vuzpqu32_1.c: New file.
>     * gcc.target/arm/simd/vuzpqu8_1.c: New file.
>     * gcc.target/arm/simd/vuzpf32_1.c: New file.
>     * gcc.target/arm/simd/vuzpp16_1.c: New file.
>     * gcc.target/arm/simd/vuzpp8_1.c: New file.
>     * gcc.target/arm/simd/vuzps16_1.c: New file.
>     * gcc.target/arm/simd/vuzps32_1.c: New file.
>     * gcc.target/arm/simd/vuzps8_1.c: New file.
>     * gcc.target/arm/simd/vuzpu16_1.c: New file.
>     * gcc.target/arm/simd/vuzpu32_1.c: New file.
>     * gcc.target/arm/simd/vuzpu8_1.c: New file.
>
>
> diff --git a/gcc/testsuite/gcc.target/arm/simd/vuzpf32_1.c
> b/gcc/testsuite/gcc.target/arm/simd/vuzpf32_1.c
> new file mode 100644
> index 0000000..723c86a
> --- /dev/null
> +++ b/gcc/testsuite/gcc.target/arm/simd/vuzpf32_1.c
> @@ -0,0 +1,12 @@
> +/* Test the `vuzpf32' ARM Neon intrinsic.  */
> +
> +/* { dg-do run } */
> +/* { dg-require-effective-target arm_neon_ok } */
> +/* { dg-options "-save-temps -O1 -fno-inline" } */
> +/* { dg-add-options arm_neon } */
> +
> +#include "arm_neon.h"
> +#include "../../aarch64/simd/vuzpf32.x"
> +
> +/* { dg-final { scan-assembler-times "vuzp\.32\[ \t\]+\[dD\]\[0-9\]+,
> ?\[dD\]\[0-9\]+!?\(?:\[ \t\]+@\[a-zA-Z0-9 \]+\)?\n" 1 } } */
> +/* { dg-final { cleanup-saved-temps } } */
> diff --git a/gcc/testsuite/gcc.target/arm/simd/vuzpp16_1.c
> b/gcc/testsuite/gcc.target/arm/simd/vuzpp16_1.c
> new file mode 100644
> index 0000000..c7ad757
> --- /dev/null
> +++ b/gcc/testsuite/gcc.target/arm/simd/vuzpp16_1.c
> @@ -0,0 +1,12 @@
> +/* Test the `vuzpp16' ARM Neon intrinsic.  */
> +
> +/* { dg-do run } */
> +/* { dg-require-effective-target arm_neon_ok } */
> +/* { dg-options "-save-temps -O1 -fno-inline" } */
> +/* { dg-add-options arm_neon } */
> +
> +#include "arm_neon.h"
> +#include "../../aarch64/simd/vuzpp16.x"
> +
> +/* { dg-final { scan-assembler-times "vuzp\.16\[ \t\]+\[dD\]\[0-9\]+,
> ?\[dD\]\[0-9\]+!?\(?:\[ \t\]+@\[a-zA-Z0-9 \]+\)?\n" 1 } } */
> +/* { dg-final { cleanup-saved-temps } } */
> diff --git a/gcc/testsuite/gcc.target/arm/simd/vuzpp8_1.c
> b/gcc/testsuite/gcc.target/arm/simd/vuzpp8_1.c
> new file mode 100644
> index 0000000..670b550
> --- /dev/null
> +++ b/gcc/testsuite/gcc.target/arm/simd/vuzpp8_1.c
> @@ -0,0 +1,12 @@
> +/* Test the `vuzpp8' ARM Neon intrinsic.  */
> +
> +/* { dg-do run } */
> +/* { dg-require-effective-target arm_neon_ok } */
> +/* { dg-options "-save-temps -O1 -fno-inline" } */
> +/* { dg-add-options arm_neon } */
> +
> +#include "arm_neon.h"
> +#include "../../aarch64/simd/vuzpp8.x"
> +
> +/* { dg-final { scan-assembler-times "vuzp\.8\[ \t\]+\[dD\]\[0-9\]+,
> ?\[dD\]\[0-9\]+!?\(?:\[ \t\]+@\[a-zA-Z0-9 \]+\)?\n" 1 } } */
> +/* { dg-final { cleanup-saved-temps } } */
> diff --git a/gcc/testsuite/gcc.target/arm/simd/vuzpqf32_1.c
> b/gcc/testsuite/gcc.target/arm/simd/vuzpqf32_1.c
> new file mode 100644
> index 0000000..53147f1
> --- /dev/null
> +++ b/gcc/testsuite/gcc.target/arm/simd/vuzpqf32_1.c
> @@ -0,0 +1,12 @@
> +/* Test the `vuzpQf32' ARM Neon intrinsic.  */
> +
> +/* { dg-do run } */
> +/* { dg-require-effective-target arm_neon_ok } */
> +/* { dg-options "-save-temps -O1 -fno-inline" } */
> +/* { dg-add-options arm_neon } */
> +
> +#include "arm_neon.h"
> +#include "../../aarch64/simd/vuzpqf32.x"
> +
> +/* { dg-final { scan-assembler-times "vuzp\.32\[ \t\]+\[qQ\]\[0-9\]+,
> ?\[qQ\]\[0-9\]+!?\(?:\[ \t\]+@\[a-zA-Z0-9 \]+\)?\n" 1 } } */
> +/* { dg-final { cleanup-saved-temps } } */
> diff --git a/gcc/testsuite/gcc.target/arm/simd/vuzpqp16_1.c
> b/gcc/testsuite/gcc.target/arm/simd/vuzpqp16_1.c
> new file mode 100644
> index 0000000..feef15a
> --- /dev/null
> +++ b/gcc/testsuite/gcc.target/arm/simd/vuzpqp16_1.c
> @@ -0,0 +1,12 @@
> +/* Test the `vuzpQp16' ARM Neon intrinsic.  */
> +
> +/* { dg-do run } */
> +/* { dg-require-effective-target arm_neon_ok } */
> +/* { dg-options "-save-temps -O1 -fno-inline" } */
> +/* { dg-add-options arm_neon } */
> +
> +#include "arm_neon.h"
> +#include "../../aarch64/simd/vuzpqp16.x"
> +
> +/* { dg-final { scan-assembler-times "vuzp\.16\[ \t\]+\[qQ\]\[0-9\]+,
> ?\[qQ\]\[0-9\]+!?\(?:\[ \t\]+@\[a-zA-Z0-9 \]+\)?\n" 1 } } */
> +/* { dg-final { cleanup-saved-temps } } */
> diff --git a/gcc/testsuite/gcc.target/arm/simd/vuzpqp8_1.c
> b/gcc/testsuite/gcc.target/arm/simd/vuzpqp8_1.c
> new file mode 100644
> index 0000000..db98f35
> --- /dev/null
> +++ b/gcc/testsuite/gcc.target/arm/simd/vuzpqp8_1.c
> @@ -0,0 +1,12 @@
> +/* Test the `vuzpQp8' ARM Neon intrinsic.  */
> +
> +/* { dg-do run } */
> +/* { dg-require-effective-target arm_neon_ok } */
> +/* { dg-options "-save-temps -O1 -fno-inline" } */
> +/* { dg-add-options arm_neon } */
> +
> +#include "arm_neon.h"
> +#include "../../aarch64/simd/vuzpqp8.x"
> +
> +/* { dg-final { scan-assembler-times "vuzp\.8\[ \t\]+\[qQ\]\[0-9\]+,
> ?\[qQ\]\[0-9\]+!?\(?:\[ \t\]+@\[a-zA-Z0-9 \]+\)?\n" 1 } } */
> +/* { dg-final { cleanup-saved-temps } } */
> diff --git a/gcc/testsuite/gcc.target/arm/simd/vuzpqs16_1.c
> b/gcc/testsuite/gcc.target/arm/simd/vuzpqs16_1.c
> new file mode 100644
> index 0000000..808d562
> --- /dev/null
> +++ b/gcc/testsuite/gcc.target/arm/simd/vuzpqs16_1.c
> @@ -0,0 +1,12 @@
> +/* Test the `vuzpQs16' ARM Neon intrinsic.  */
> +
> +/* { dg-do run } */
> +/* { dg-require-effective-target arm_neon_ok } */
> +/* { dg-options "-save-temps -O1 -fno-inline" } */
> +/* { dg-add-options arm_neon } */
> +
> +#include "arm_neon.h"
> +#include "../../aarch64/simd/vuzpqs16.x"
> +
> +/* { dg-final { scan-assembler-times "vuzp\.16\[ \t\]+\[qQ\]\[0-9\]+,
> ?\[qQ\]\[0-9\]+!?\(?:\[ \t\]+@\[a-zA-Z0-9 \]+\)?\n" 1 } } */
> +/* { dg-final { cleanup-saved-temps } } */
> diff --git a/gcc/testsuite/gcc.target/arm/simd/vuzpqs32_1.c
> b/gcc/testsuite/gcc.target/arm/simd/vuzpqs32_1.c
> new file mode 100644
> index 0000000..7adf5f9
> --- /dev/null
> +++ b/gcc/testsuite/gcc.target/arm/simd/vuzpqs32_1.c
> @@ -0,0 +1,12 @@
> +/* Test the `vuzpQs32' ARM Neon intrinsic.  */
> +
> +/* { dg-do run } */
> +/* { dg-require-effective-target arm_neon_ok } */
> +/* { dg-options "-save-temps -O1 -fno-inline" } */
> +/* { dg-add-options arm_neon } */
> +
> +#include "arm_neon.h"
> +#include "../../aarch64/simd/vuzpqs32.x"
> +
> +/* { dg-final { scan-assembler-times "vuzp\.32\[ \t\]+\[qQ\]\[0-9\]+,
> ?\[qQ\]\[0-9\]+!?\(?:\[ \t\]+@\[a-zA-Z0-9 \]+\)?\n" 1 } } */
> +/* { dg-final { cleanup-saved-temps } } */
> diff --git a/gcc/testsuite/gcc.target/arm/simd/vuzpqs8_1.c
> b/gcc/testsuite/gcc.target/arm/simd/vuzpqs8_1.c
> new file mode 100644
> index 0000000..9d0256a
> --- /dev/null
> +++ b/gcc/testsuite/gcc.target/arm/simd/vuzpqs8_1.c
> @@ -0,0 +1,12 @@
> +/* Test the `vuzpQs8' ARM Neon intrinsic.  */
> +
> +/* { dg-do run } */
> +/* { dg-require-effective-target arm_neon_ok } */
> +/* { dg-options "-save-temps -O1 -fno-inline" } */
> +/* { dg-add-options arm_neon } */
> +
> +#include "arm_neon.h"
> +#include "../../aarch64/simd/vuzpqs8.x"
> +
> +/* { dg-final { scan-assembler-times "vuzp\.8\[ \t\]+\[qQ\]\[0-9\]+,
> ?\[qQ\]\[0-9\]+!?\(?:\[ \t\]+@\[a-zA-Z0-9 \]+\)?\n" 1 } } */
> +/* { dg-final { cleanup-saved-temps } } */
> diff --git a/gcc/testsuite/gcc.target/arm/simd/vuzpqu16_1.c
> b/gcc/testsuite/gcc.target/arm/simd/vuzpqu16_1.c
> new file mode 100644
> index 0000000..23106ed
> --- /dev/null
> +++ b/gcc/testsuite/gcc.target/arm/simd/vuzpqu16_1.c
> @@ -0,0 +1,12 @@
> +/* Test the `vuzpQu16' ARM Neon intrinsic.  */
> +
> +/* { dg-do run } */
> +/* { dg-require-effective-target arm_neon_ok } */
> +/* { dg-options "-save-temps -O1 -fno-inline" } */
> +/* { dg-add-options arm_neon } */
> +
> +#include "arm_neon.h"
> +#include "../../aarch64/simd/vuzpqu16.x"
> +
> +/* { dg-final { scan-assembler-times "vuzp\.16\[ \t\]+\[qQ\]\[0-9\]+,
> ?\[qQ\]\[0-9\]+!?\(?:\[ \t\]+@\[a-zA-Z0-9 \]+\)?\n" 1 } } */
> +/* { dg-final { cleanup-saved-temps } } */
> diff --git a/gcc/testsuite/gcc.target/arm/simd/vuzpqu32_1.c
> b/gcc/testsuite/gcc.target/arm/simd/vuzpqu32_1.c
> new file mode 100644
> index 0000000..0002fdf
> --- /dev/null
> +++ b/gcc/testsuite/gcc.target/arm/simd/vuzpqu32_1.c
> @@ -0,0 +1,12 @@
> +/* Test the `vuzpQu32' ARM Neon intrinsic.  */
> +
> +/* { dg-do run } */
> +/* { dg-require-effective-target arm_neon_ok } */
> +/* { dg-options "-save-temps -O1 -fno-inline" } */
> +/* { dg-add-options arm_neon } */
> +
> +#include "arm_neon.h"
> +#include "../../aarch64/simd/vuzpqu32.x"
> +
> +/* { dg-final { scan-assembler-times "vuzp\.32\[ \t\]+\[qQ\]\[0-9\]+,
> ?\[qQ\]\[0-9\]+!?\(?:\[ \t\]+@\[a-zA-Z0-9 \]+\)?\n" 1 } } */
> +/* { dg-final { cleanup-saved-temps } } */
> diff --git a/gcc/testsuite/gcc.target/arm/simd/vuzpqu8_1.c
> b/gcc/testsuite/gcc.target/arm/simd/vuzpqu8_1.c
> new file mode 100644
> index 0000000..f8d19dc
> --- /dev/null
> +++ b/gcc/testsuite/gcc.target/arm/simd/vuzpqu8_1.c
> @@ -0,0 +1,12 @@
> +/* Test the `vuzpQu8' ARM Neon intrinsic.  */
> +
> +/* { dg-do run } */
> +/* { dg-require-effective-target arm_neon_ok } */
> +/* { dg-options "-save-temps -O1 -fno-inline" } */
> +/* { dg-add-options arm_neon } */
> +
> +#include "arm_neon.h"
> +#include "../../aarch64/simd/vuzpqu8.x"
> +
> +/* { dg-final { scan-assembler-times "vuzp\.8\[ \t\]+\[qQ\]\[0-9\]+,
> ?\[qQ\]\[0-9\]+!?\(?:\[ \t\]+@\[a-zA-Z0-9 \]+\)?\n" 1 } } */
> +/* { dg-final { cleanup-saved-temps } } */
> diff --git a/gcc/testsuite/gcc.target/arm/simd/vuzps16_1.c
> b/gcc/testsuite/gcc.target/arm/simd/vuzps16_1.c
> new file mode 100644
> index 0000000..6e3f2eb
> --- /dev/null
> +++ b/gcc/testsuite/gcc.target/arm/simd/vuzps16_1.c
> @@ -0,0 +1,12 @@
> +/* Test the `vuzps16' ARM Neon intrinsic.  */
> +
> +/* { dg-do run } */
> +/* { dg-require-effective-target arm_neon_ok } */
> +/* { dg-options "-save-temps -O1 -fno-inline" } */
> +/* { dg-add-options arm_neon } */
> +
> +#include "arm_neon.h"
> +#include "../../aarch64/simd/vuzps16.x"
> +
> +/* { dg-final { scan-assembler-times "vuzp\.16\[ \t\]+\[dD\]\[0-9\]+,
> ?\[dD\]\[0-9\]+!?\(?:\[ \t\]+@\[a-zA-Z0-9 \]+\)?\n" 1 } } */
> +/* { dg-final { cleanup-saved-temps } } */
> diff --git a/gcc/testsuite/gcc.target/arm/simd/vuzps32_1.c
> b/gcc/testsuite/gcc.target/arm/simd/vuzps32_1.c
> new file mode 100644
> index 0000000..372c393
> --- /dev/null
> +++ b/gcc/testsuite/gcc.target/arm/simd/vuzps32_1.c
> @@ -0,0 +1,12 @@
> +/* Test the `vuzps32' ARM Neon intrinsic.  */
> +
> +/* { dg-do run } */
> +/* { dg-require-effective-target arm_neon_ok } */
> +/* { dg-options "-save-temps -O1 -fno-inline" } */
> +/* { dg-add-options arm_neon } */
> +
> +#include "arm_neon.h"
> +#include "../../aarch64/simd/vuzps32.x"
> +
> +/* { dg-final { scan-assembler-times "vuzp\.32\[ \t\]+\[dD\]\[0-9\]+,
> ?\[dD\]\[0-9\]+!?\(?:\[ \t\]+@\[a-zA-Z0-9 \]+\)?\n" 1 } } */
> +/* { dg-final { cleanup-saved-temps } } */
> diff --git a/gcc/testsuite/gcc.target/arm/simd/vuzps8_1.c
> b/gcc/testsuite/gcc.target/arm/simd/vuzps8_1.c
> new file mode 100644
> index 0000000..3338477
> --- /dev/null
> +++ b/gcc/testsuite/gcc.target/arm/simd/vuzps8_1.c
> @@ -0,0 +1,12 @@
> +/* Test the `vuzps8' ARM Neon intrinsic.  */
> +
> +/* { dg-do run } */
> +/* { dg-require-effective-target arm_neon_ok } */
> +/* { dg-options "-save-temps -O1 -fno-inline" } */
> +/* { dg-add-options arm_neon } */
> +
> +#include "arm_neon.h"
> +#include "../../aarch64/simd/vuzps8.x"
> +
> +/* { dg-final { scan-assembler-times "vuzp\.8\[ \t\]+\[dD\]\[0-9\]+,
> ?\[dD\]\[0-9\]+!?\(?:\[ \t\]+@\[a-zA-Z0-9 \]+\)?\n" 1 } } */
> +/* { dg-final { cleanup-saved-temps } } */
> diff --git a/gcc/testsuite/gcc.target/arm/simd/vuzpu16_1.c
> b/gcc/testsuite/gcc.target/arm/simd/vuzpu16_1.c
> new file mode 100644
> index 0000000..378b5a9
> --- /dev/null
> +++ b/gcc/testsuite/gcc.target/arm/simd/vuzpu16_1.c
> @@ -0,0 +1,12 @@
> +/* Test the `vuzpu16' ARM Neon intrinsic.  */
> +
> +/* { dg-do run } */
> +/* { dg-require-effective-target arm_neon_ok } */
> +/* { dg-options "-save-temps -O1 -fno-inline" } */
> +/* { dg-add-options arm_neon } */
> +
> +#include "arm_neon.h"
> +#include "../../aarch64/simd/vuzpu16.x"
> +
> +/* { dg-final { scan-assembler-times "vuzp\.16\[ \t\]+\[dD\]\[0-9\]+,
> ?\[dD\]\[0-9\]+!?\(?:\[ \t\]+@\[a-zA-Z0-9 \]+\)?\n" 1 } } */
> +/* { dg-final { cleanup-saved-temps } } */
> diff --git a/gcc/testsuite/gcc.target/arm/simd/vuzpu32_1.c
> b/gcc/testsuite/gcc.target/arm/simd/vuzpu32_1.c
> new file mode 100644
> index 0000000..ebb0d6b
> --- /dev/null
> +++ b/gcc/testsuite/gcc.target/arm/simd/vuzpu32_1.c
> @@ -0,0 +1,12 @@
> +/* Test the `vuzpu32' ARM Neon intrinsic.  */
> +
> +/* { dg-do run } */
> +/* { dg-require-effective-target arm_neon_ok } */
> +/* { dg-options "-save-temps -O1 -fno-inline" } */
> +/* { dg-add-options arm_neon } */
> +
> +#include "arm_neon.h"
> +#include "../../aarch64/simd/vuzpu32.x"
> +
> +/* { dg-final { scan-assembler-times "vuzp\.32\[ \t\]+\[dD\]\[0-9\]+,
> ?\[dD\]\[0-9\]+!?\(?:\[ \t\]+@\[a-zA-Z0-9 \]+\)?\n" 1 } } */
> +/* { dg-final { cleanup-saved-temps } } */
> diff --git a/gcc/testsuite/gcc.target/arm/simd/vuzpu8_1.c
> b/gcc/testsuite/gcc.target/arm/simd/vuzpu8_1.c
> new file mode 100644
> index 0000000..82719a5
> --- /dev/null
> +++ b/gcc/testsuite/gcc.target/arm/simd/vuzpu8_1.c
> @@ -0,0 +1,12 @@
> +/* Test the `vuzpu8' ARM Neon intrinsic.  */
> +
> +/* { dg-do run } */
> +/* { dg-require-effective-target arm_neon_ok } */
> +/* { dg-options "-save-temps -O1 -fno-inline" } */
> +/* { dg-add-options arm_neon } */
> +
> +#include "arm_neon.h"
> +#include "../../aarch64/simd/vuzpu8.x"
> +
> +/* { dg-final { scan-assembler-times "vuzp\.8\[ \t\]+\[dD\]\[0-9\]+,
> ?\[dD\]\[0-9\]+!?\(?:\[ \t\]+@\[a-zA-Z0-9 \]+\)?\n" 1 } } */
> +/* { dg-final { cleanup-saved-temps } } */
Index Nav:	[Date Index] [Subject Index] [Author Index] [Thread Index]
Message Nav:	[Date Prev] [Date Next]	[Thread Prev] [Thread Next]