diff mbox

[AArch64/ARM,3/3] Add execution tests of ARM ZIP Intrinsics

Message ID 53340313.6080806@arm.com
State New
Headers show

Commit Message

Alan Lawrence March 27, 2014, 10:53 a.m. UTC
Final patch adds new tests of the ARM ZIP 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.

All tests passing on arm-none-eabi.

gcc/testsuite/ChangeLog:
2012-03-27  Alan Lawrence  <alan.lawrence@arm.com>

	* gcc.target/arm/simd/simd.exp: New file.
	* gcc.target/arm/simd/vzipqf32_1.c: New file.
	* gcc.target/arm/simd/vzipqp16_1.c: New file.
	* gcc.target/arm/simd/vzipqp8_1.c: New file.
	* gcc.target/arm/simd/vzipqs16_1.c: New file.
	* gcc.target/arm/simd/vzipqs32_1.c: New file.
	* gcc.target/arm/simd/vzipqs8_1.c: New file.
	* gcc.target/arm/simd/vzipqu16_1.c: New file.
	* gcc.target/arm/simd/vzipqu32_1.c: New file.
	* gcc.target/arm/simd/vzipqu8_1.c: New file.
	* gcc.target/arm/simd/vzipf32_1.c: New file.
	* gcc.target/arm/simd/vzipp16_1.c: New file.
	* gcc.target/arm/simd/vzipp8_1.c: New file.
	* gcc.target/arm/simd/vzips16_1.c: New file.
	* gcc.target/arm/simd/vzips32_1.c: New file.
	* gcc.target/arm/simd/vzips8_1.c: New file.
	* gcc.target/arm/simd/vzipu16_1.c: New file.
	* gcc.target/arm/simd/vzipu32_1.c: New file.
	* gcc.target/arm/simd/vzipu8_1.c: New file.

Comments

Ramana Radhakrishnan April 30, 2014, 9:18 a.m. UTC | #1
On Thu, Mar 27, 2014 at 10:53 AM, Alan Lawrence <alan.lawrence@arm.com> wrote:
> Final patch adds new tests of the ARM ZIP 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.
>
> All tests passing on arm-none-eabi.

This is OK - thanks,

Ramana

>
> gcc/testsuite/ChangeLog:
> 2012-03-27  Alan Lawrence  <alan.lawrence@arm.com>
>
>         * gcc.target/arm/simd/simd.exp: New file.
>         * gcc.target/arm/simd/vzipqf32_1.c: New file.
>         * gcc.target/arm/simd/vzipqp16_1.c: New file.
>         * gcc.target/arm/simd/vzipqp8_1.c: New file.
>         * gcc.target/arm/simd/vzipqs16_1.c: New file.
>         * gcc.target/arm/simd/vzipqs32_1.c: New file.
>         * gcc.target/arm/simd/vzipqs8_1.c: New file.
>         * gcc.target/arm/simd/vzipqu16_1.c: New file.
>         * gcc.target/arm/simd/vzipqu32_1.c: New file.
>         * gcc.target/arm/simd/vzipqu8_1.c: New file.
>         * gcc.target/arm/simd/vzipf32_1.c: New file.
>         * gcc.target/arm/simd/vzipp16_1.c: New file.
>         * gcc.target/arm/simd/vzipp8_1.c: New file.
>         * gcc.target/arm/simd/vzips16_1.c: New file.
>         * gcc.target/arm/simd/vzips32_1.c: New file.
>         * gcc.target/arm/simd/vzips8_1.c: New file.
>         * gcc.target/arm/simd/vzipu16_1.c: New file.
>         * gcc.target/arm/simd/vzipu32_1.c: New file.
>         * gcc.target/arm/simd/vzipu8_1.c: New file.
> diff --git a/gcc/testsuite/gcc.target/arm/simd/simd.exp
> b/gcc/testsuite/gcc.target/arm/simd/simd.exp
> new file mode 100644
> index 0000000..746429d
> --- /dev/null
> +++ b/gcc/testsuite/gcc.target/arm/simd/simd.exp
> @@ -0,0 +1,35 @@
> +# Copyright (C) 1997-2014 Free Software Foundation, Inc.
> +
> +# This program is free software; you can redistribute it and/or modify
> +# it under the terms of the GNU General Public License as published by
> +# the Free Software Foundation; either version 3 of the License, or
> +# (at your option) any later version.
> +#
> +# This program is distributed in the hope that it will be useful,
> +# but WITHOUT ANY WARRANTY; without even the implied warranty of
> +# MERCHANTABILITY or FITNESS FOR A PARTICULAR PURPOSE.  See the
> +# GNU General Public License for more details.
> +#
> +# You should have received a copy of the GNU General Public License
> +# along with GCC; see the file COPYING3.  If not see
> +# <http://www.gnu.org/licenses/>.
> +
> +# GCC testsuite that uses the `dg.exp' driver.
> +
> +# Exit immediately if this isn't an ARM target.
> +if ![istarget arm*-*-*] then {
> +  return
> +}
> +
> +# Load support procs.
> +load_lib gcc-dg.exp
> +
> +# Initialize `dg'.
> +dg-init
> +
> +# Main loop.
> +dg-runtest [lsort [glob -nocomplain $srcdir/$subdir/*.\[cCS\]]] \
> +       "" ""
> +
> +# All done.
> +dg-finish
> diff --git a/gcc/testsuite/gcc.target/arm/simd/vzipf32_1.c
> b/gcc/testsuite/gcc.target/arm/simd/vzipf32_1.c
> new file mode 100644
> index 0000000..efaa96e
> --- /dev/null
> +++ b/gcc/testsuite/gcc.target/arm/simd/vzipf32_1.c
> @@ -0,0 +1,12 @@
> +/* Test the `vzipf32' 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/vzipf32.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/vzipp16_1.c
> b/gcc/testsuite/gcc.target/arm/simd/vzipp16_1.c
> new file mode 100644
> index 0000000..4154333
> --- /dev/null
> +++ b/gcc/testsuite/gcc.target/arm/simd/vzipp16_1.c
> @@ -0,0 +1,12 @@
> +/* Test the `vzipp16' 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/vzipp16.x"
> +
> +/* { dg-final { scan-assembler-times "vzip\.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/vzipp8_1.c
> b/gcc/testsuite/gcc.target/arm/simd/vzipp8_1.c
> new file mode 100644
> index 0000000..9fe2384
> --- /dev/null
> +++ b/gcc/testsuite/gcc.target/arm/simd/vzipp8_1.c
> @@ -0,0 +1,12 @@
> +/* Test the `vzipp8' 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/vzipp8.x"
> +
> +/* { dg-final { scan-assembler-times "vzip\.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/vzipqf32_1.c
> b/gcc/testsuite/gcc.target/arm/simd/vzipqf32_1.c
> new file mode 100644
> index 0000000..8c547a7
> --- /dev/null
> +++ b/gcc/testsuite/gcc.target/arm/simd/vzipqf32_1.c
> @@ -0,0 +1,12 @@
> +/* Test the `vzipQf32' 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/vzipqf32.x"
> +
> +/* { dg-final { scan-assembler-times "vzip\.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/vzipqp16_1.c
> b/gcc/testsuite/gcc.target/arm/simd/vzipqp16_1.c
> new file mode 100644
> index 0000000..e2af10b
> --- /dev/null
> +++ b/gcc/testsuite/gcc.target/arm/simd/vzipqp16_1.c
> @@ -0,0 +1,12 @@
> +/* Test the `vzipQp16' 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/vzipqp16.x"
> +
> +/* { dg-final { scan-assembler-times "vzip\.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/vzipqp8_1.c
> b/gcc/testsuite/gcc.target/arm/simd/vzipqp8_1.c
> new file mode 100644
> index 0000000..11a1329
> --- /dev/null
> +++ b/gcc/testsuite/gcc.target/arm/simd/vzipqp8_1.c
> @@ -0,0 +1,12 @@
> +/* Test the `vzipQp8' 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/vzipqp8.x"
> +
> +/* { dg-final { scan-assembler-times "vzip\.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/vzipqs16_1.c
> b/gcc/testsuite/gcc.target/arm/simd/vzipqs16_1.c
> new file mode 100644
> index 0000000..0576c00
> --- /dev/null
> +++ b/gcc/testsuite/gcc.target/arm/simd/vzipqs16_1.c
> @@ -0,0 +1,12 @@
> +/* Test the `vzipQs16' 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/vzipqs16.x"
> +
> +/* { dg-final { scan-assembler-times "vzip\.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/vzipqs32_1.c
> b/gcc/testsuite/gcc.target/arm/simd/vzipqs32_1.c
> new file mode 100644
> index 0000000..6cf2439
> --- /dev/null
> +++ b/gcc/testsuite/gcc.target/arm/simd/vzipqs32_1.c
> @@ -0,0 +1,12 @@
> +/* Test the `vzipQs32' 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/vzipqs32.x"
> +
> +/* { dg-final { scan-assembler-times "vzip\.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/vzipqs8_1.c
> b/gcc/testsuite/gcc.target/arm/simd/vzipqs8_1.c
> new file mode 100644
> index 0000000..0244374
> --- /dev/null
> +++ b/gcc/testsuite/gcc.target/arm/simd/vzipqs8_1.c
> @@ -0,0 +1,12 @@
> +/* Test the `vzipQs8' 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/vzipqs8.x"
> +
> +/* { dg-final { scan-assembler-times "vzip\.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/vzipqu16_1.c
> b/gcc/testsuite/gcc.target/arm/simd/vzipqu16_1.c
> new file mode 100644
> index 0000000..3c406f5
> --- /dev/null
> +++ b/gcc/testsuite/gcc.target/arm/simd/vzipqu16_1.c
> @@ -0,0 +1,12 @@
> +/* Test the `vzipQu16' 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/vzipqu16.x"
> +
> +/* { dg-final { scan-assembler-times "vzip\.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/vzipqu32_1.c
> b/gcc/testsuite/gcc.target/arm/simd/vzipqu32_1.c
> new file mode 100644
> index 0000000..ba1393c
> --- /dev/null
> +++ b/gcc/testsuite/gcc.target/arm/simd/vzipqu32_1.c
> @@ -0,0 +1,12 @@
> +/* Test the `vzipQu32' 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/vzipqu32.x"
> +
> +/* { dg-final { scan-assembler-times "vzip\.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/vzipqu8_1.c
> b/gcc/testsuite/gcc.target/arm/simd/vzipqu8_1.c
> new file mode 100644
> index 0000000..023ecac
> --- /dev/null
> +++ b/gcc/testsuite/gcc.target/arm/simd/vzipqu8_1.c
> @@ -0,0 +1,12 @@
> +/* Test the `vzipQu8' 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/vzipqu8.x"
> +
> +/* { dg-final { scan-assembler-times "vzip\.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/vzips16_1.c
> b/gcc/testsuite/gcc.target/arm/simd/vzips16_1.c
> new file mode 100644
> index 0000000..b6c3c2f
> --- /dev/null
> +++ b/gcc/testsuite/gcc.target/arm/simd/vzips16_1.c
> @@ -0,0 +1,12 @@
> +/* Test the `vzips16' 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/vzips16.x"
> +
> +/* { dg-final { scan-assembler-times "vzip\.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/vzips32_1.c
> b/gcc/testsuite/gcc.target/arm/simd/vzips32_1.c
> new file mode 100644
> index 0000000..1a6f170
> --- /dev/null
> +++ b/gcc/testsuite/gcc.target/arm/simd/vzips32_1.c
> @@ -0,0 +1,12 @@
> +/* Test the `vzips32' 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/vzips32.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/vzips8_1.c
> b/gcc/testsuite/gcc.target/arm/simd/vzips8_1.c
> new file mode 100644
> index 0000000..8569357
> --- /dev/null
> +++ b/gcc/testsuite/gcc.target/arm/simd/vzips8_1.c
> @@ -0,0 +1,12 @@
> +/* Test the `vzips8' 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/vzips8.x"
> +
> +/* { dg-final { scan-assembler-times "vzip\.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/vzipu16_1.c
> b/gcc/testsuite/gcc.target/arm/simd/vzipu16_1.c
> new file mode 100644
> index 0000000..23bfcc4
> --- /dev/null
> +++ b/gcc/testsuite/gcc.target/arm/simd/vzipu16_1.c
> @@ -0,0 +1,12 @@
> +/* Test the `vzipu16' 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/vzipu16.x"
> +
> +/* { dg-final { scan-assembler-times "vzip\.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/vzipu32_1.c
> b/gcc/testsuite/gcc.target/arm/simd/vzipu32_1.c
> new file mode 100644
> index 0000000..6a753f2
> --- /dev/null
> +++ b/gcc/testsuite/gcc.target/arm/simd/vzipu32_1.c
> @@ -0,0 +1,12 @@
> +/* Test the `vzipu32' 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/vzipu32.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/vzipu8_1.c
> b/gcc/testsuite/gcc.target/arm/simd/vzipu8_1.c
> new file mode 100644
> index 0000000..972af74
> --- /dev/null
> +++ b/gcc/testsuite/gcc.target/arm/simd/vzipu8_1.c
> @@ -0,0 +1,12 @@
> +/* Test the `vzipu8' 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/vzipu8.x"
> +
> +/* { dg-final { scan-assembler-times "vzip\.8\[ \t\]+\[dD\]\[0-9\]+,
> ?\[dD\]\[0-9\]+!?\(?:\[ \t\]+@\[a-zA-Z0-9 \]+\)?\n" 1 } } */
> +/* { dg-final { cleanup-saved-temps } } */
Christophe Lyon May 5, 2014, 9:26 a.m. UTC | #2
This caused:

http://gcc.gnu.org/bugzilla/show_bug.cgi?id=61062


On 30 April 2014 11:18, Ramana Radhakrishnan <ramana.gcc@googlemail.com> wrote:
> On Thu, Mar 27, 2014 at 10:53 AM, Alan Lawrence <alan.lawrence@arm.com> wrote:
>> Final patch adds new tests of the ARM ZIP 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.
>>
>> All tests passing on arm-none-eabi.
>
> This is OK - thanks,
>
> Ramana
>
>>
>> gcc/testsuite/ChangeLog:
>> 2012-03-27  Alan Lawrence  <alan.lawrence@arm.com>
>>
>>         * gcc.target/arm/simd/simd.exp: New file.
>>         * gcc.target/arm/simd/vzipqf32_1.c: New file.
>>         * gcc.target/arm/simd/vzipqp16_1.c: New file.
>>         * gcc.target/arm/simd/vzipqp8_1.c: New file.
>>         * gcc.target/arm/simd/vzipqs16_1.c: New file.
>>         * gcc.target/arm/simd/vzipqs32_1.c: New file.
>>         * gcc.target/arm/simd/vzipqs8_1.c: New file.
>>         * gcc.target/arm/simd/vzipqu16_1.c: New file.
>>         * gcc.target/arm/simd/vzipqu32_1.c: New file.
>>         * gcc.target/arm/simd/vzipqu8_1.c: New file.
>>         * gcc.target/arm/simd/vzipf32_1.c: New file.
>>         * gcc.target/arm/simd/vzipp16_1.c: New file.
>>         * gcc.target/arm/simd/vzipp8_1.c: New file.
>>         * gcc.target/arm/simd/vzips16_1.c: New file.
>>         * gcc.target/arm/simd/vzips32_1.c: New file.
>>         * gcc.target/arm/simd/vzips8_1.c: New file.
>>         * gcc.target/arm/simd/vzipu16_1.c: New file.
>>         * gcc.target/arm/simd/vzipu32_1.c: New file.
>>         * gcc.target/arm/simd/vzipu8_1.c: New file.
>> diff --git a/gcc/testsuite/gcc.target/arm/simd/simd.exp
>> b/gcc/testsuite/gcc.target/arm/simd/simd.exp
>> new file mode 100644
>> index 0000000..746429d
>> --- /dev/null
>> +++ b/gcc/testsuite/gcc.target/arm/simd/simd.exp
>> @@ -0,0 +1,35 @@
>> +# Copyright (C) 1997-2014 Free Software Foundation, Inc.
>> +
>> +# This program is free software; you can redistribute it and/or modify
>> +# it under the terms of the GNU General Public License as published by
>> +# the Free Software Foundation; either version 3 of the License, or
>> +# (at your option) any later version.
>> +#
>> +# This program is distributed in the hope that it will be useful,
>> +# but WITHOUT ANY WARRANTY; without even the implied warranty of
>> +# MERCHANTABILITY or FITNESS FOR A PARTICULAR PURPOSE.  See the
>> +# GNU General Public License for more details.
>> +#
>> +# You should have received a copy of the GNU General Public License
>> +# along with GCC; see the file COPYING3.  If not see
>> +# <http://www.gnu.org/licenses/>.
>> +
>> +# GCC testsuite that uses the `dg.exp' driver.
>> +
>> +# Exit immediately if this isn't an ARM target.
>> +if ![istarget arm*-*-*] then {
>> +  return
>> +}
>> +
>> +# Load support procs.
>> +load_lib gcc-dg.exp
>> +
>> +# Initialize `dg'.
>> +dg-init
>> +
>> +# Main loop.
>> +dg-runtest [lsort [glob -nocomplain $srcdir/$subdir/*.\[cCS\]]] \
>> +       "" ""
>> +
>> +# All done.
>> +dg-finish
>> diff --git a/gcc/testsuite/gcc.target/arm/simd/vzipf32_1.c
>> b/gcc/testsuite/gcc.target/arm/simd/vzipf32_1.c
>> new file mode 100644
>> index 0000000..efaa96e
>> --- /dev/null
>> +++ b/gcc/testsuite/gcc.target/arm/simd/vzipf32_1.c
>> @@ -0,0 +1,12 @@
>> +/* Test the `vzipf32' 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/vzipf32.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/vzipp16_1.c
>> b/gcc/testsuite/gcc.target/arm/simd/vzipp16_1.c
>> new file mode 100644
>> index 0000000..4154333
>> --- /dev/null
>> +++ b/gcc/testsuite/gcc.target/arm/simd/vzipp16_1.c
>> @@ -0,0 +1,12 @@
>> +/* Test the `vzipp16' 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/vzipp16.x"
>> +
>> +/* { dg-final { scan-assembler-times "vzip\.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/vzipp8_1.c
>> b/gcc/testsuite/gcc.target/arm/simd/vzipp8_1.c
>> new file mode 100644
>> index 0000000..9fe2384
>> --- /dev/null
>> +++ b/gcc/testsuite/gcc.target/arm/simd/vzipp8_1.c
>> @@ -0,0 +1,12 @@
>> +/* Test the `vzipp8' 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/vzipp8.x"
>> +
>> +/* { dg-final { scan-assembler-times "vzip\.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/vzipqf32_1.c
>> b/gcc/testsuite/gcc.target/arm/simd/vzipqf32_1.c
>> new file mode 100644
>> index 0000000..8c547a7
>> --- /dev/null
>> +++ b/gcc/testsuite/gcc.target/arm/simd/vzipqf32_1.c
>> @@ -0,0 +1,12 @@
>> +/* Test the `vzipQf32' 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/vzipqf32.x"
>> +
>> +/* { dg-final { scan-assembler-times "vzip\.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/vzipqp16_1.c
>> b/gcc/testsuite/gcc.target/arm/simd/vzipqp16_1.c
>> new file mode 100644
>> index 0000000..e2af10b
>> --- /dev/null
>> +++ b/gcc/testsuite/gcc.target/arm/simd/vzipqp16_1.c
>> @@ -0,0 +1,12 @@
>> +/* Test the `vzipQp16' 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/vzipqp16.x"
>> +
>> +/* { dg-final { scan-assembler-times "vzip\.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/vzipqp8_1.c
>> b/gcc/testsuite/gcc.target/arm/simd/vzipqp8_1.c
>> new file mode 100644
>> index 0000000..11a1329
>> --- /dev/null
>> +++ b/gcc/testsuite/gcc.target/arm/simd/vzipqp8_1.c
>> @@ -0,0 +1,12 @@
>> +/* Test the `vzipQp8' 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/vzipqp8.x"
>> +
>> +/* { dg-final { scan-assembler-times "vzip\.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/vzipqs16_1.c
>> b/gcc/testsuite/gcc.target/arm/simd/vzipqs16_1.c
>> new file mode 100644
>> index 0000000..0576c00
>> --- /dev/null
>> +++ b/gcc/testsuite/gcc.target/arm/simd/vzipqs16_1.c
>> @@ -0,0 +1,12 @@
>> +/* Test the `vzipQs16' 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/vzipqs16.x"
>> +
>> +/* { dg-final { scan-assembler-times "vzip\.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/vzipqs32_1.c
>> b/gcc/testsuite/gcc.target/arm/simd/vzipqs32_1.c
>> new file mode 100644
>> index 0000000..6cf2439
>> --- /dev/null
>> +++ b/gcc/testsuite/gcc.target/arm/simd/vzipqs32_1.c
>> @@ -0,0 +1,12 @@
>> +/* Test the `vzipQs32' 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/vzipqs32.x"
>> +
>> +/* { dg-final { scan-assembler-times "vzip\.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/vzipqs8_1.c
>> b/gcc/testsuite/gcc.target/arm/simd/vzipqs8_1.c
>> new file mode 100644
>> index 0000000..0244374
>> --- /dev/null
>> +++ b/gcc/testsuite/gcc.target/arm/simd/vzipqs8_1.c
>> @@ -0,0 +1,12 @@
>> +/* Test the `vzipQs8' 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/vzipqs8.x"
>> +
>> +/* { dg-final { scan-assembler-times "vzip\.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/vzipqu16_1.c
>> b/gcc/testsuite/gcc.target/arm/simd/vzipqu16_1.c
>> new file mode 100644
>> index 0000000..3c406f5
>> --- /dev/null
>> +++ b/gcc/testsuite/gcc.target/arm/simd/vzipqu16_1.c
>> @@ -0,0 +1,12 @@
>> +/* Test the `vzipQu16' 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/vzipqu16.x"
>> +
>> +/* { dg-final { scan-assembler-times "vzip\.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/vzipqu32_1.c
>> b/gcc/testsuite/gcc.target/arm/simd/vzipqu32_1.c
>> new file mode 100644
>> index 0000000..ba1393c
>> --- /dev/null
>> +++ b/gcc/testsuite/gcc.target/arm/simd/vzipqu32_1.c
>> @@ -0,0 +1,12 @@
>> +/* Test the `vzipQu32' 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/vzipqu32.x"
>> +
>> +/* { dg-final { scan-assembler-times "vzip\.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/vzipqu8_1.c
>> b/gcc/testsuite/gcc.target/arm/simd/vzipqu8_1.c
>> new file mode 100644
>> index 0000000..023ecac
>> --- /dev/null
>> +++ b/gcc/testsuite/gcc.target/arm/simd/vzipqu8_1.c
>> @@ -0,0 +1,12 @@
>> +/* Test the `vzipQu8' 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/vzipqu8.x"
>> +
>> +/* { dg-final { scan-assembler-times "vzip\.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/vzips16_1.c
>> b/gcc/testsuite/gcc.target/arm/simd/vzips16_1.c
>> new file mode 100644
>> index 0000000..b6c3c2f
>> --- /dev/null
>> +++ b/gcc/testsuite/gcc.target/arm/simd/vzips16_1.c
>> @@ -0,0 +1,12 @@
>> +/* Test the `vzips16' 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/vzips16.x"
>> +
>> +/* { dg-final { scan-assembler-times "vzip\.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/vzips32_1.c
>> b/gcc/testsuite/gcc.target/arm/simd/vzips32_1.c
>> new file mode 100644
>> index 0000000..1a6f170
>> --- /dev/null
>> +++ b/gcc/testsuite/gcc.target/arm/simd/vzips32_1.c
>> @@ -0,0 +1,12 @@
>> +/* Test the `vzips32' 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/vzips32.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/vzips8_1.c
>> b/gcc/testsuite/gcc.target/arm/simd/vzips8_1.c
>> new file mode 100644
>> index 0000000..8569357
>> --- /dev/null
>> +++ b/gcc/testsuite/gcc.target/arm/simd/vzips8_1.c
>> @@ -0,0 +1,12 @@
>> +/* Test the `vzips8' 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/vzips8.x"
>> +
>> +/* { dg-final { scan-assembler-times "vzip\.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/vzipu16_1.c
>> b/gcc/testsuite/gcc.target/arm/simd/vzipu16_1.c
>> new file mode 100644
>> index 0000000..23bfcc4
>> --- /dev/null
>> +++ b/gcc/testsuite/gcc.target/arm/simd/vzipu16_1.c
>> @@ -0,0 +1,12 @@
>> +/* Test the `vzipu16' 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/vzipu16.x"
>> +
>> +/* { dg-final { scan-assembler-times "vzip\.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/vzipu32_1.c
>> b/gcc/testsuite/gcc.target/arm/simd/vzipu32_1.c
>> new file mode 100644
>> index 0000000..6a753f2
>> --- /dev/null
>> +++ b/gcc/testsuite/gcc.target/arm/simd/vzipu32_1.c
>> @@ -0,0 +1,12 @@
>> +/* Test the `vzipu32' 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/vzipu32.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/vzipu8_1.c
>> b/gcc/testsuite/gcc.target/arm/simd/vzipu8_1.c
>> new file mode 100644
>> index 0000000..972af74
>> --- /dev/null
>> +++ b/gcc/testsuite/gcc.target/arm/simd/vzipu8_1.c
>> @@ -0,0 +1,12 @@
>> +/* Test the `vzipu8' 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/vzipu8.x"
>> +
>> +/* { dg-final { scan-assembler-times "vzip\.8\[ \t\]+\[dD\]\[0-9\]+,
>> ?\[dD\]\[0-9\]+!?\(?:\[ \t\]+@\[a-zA-Z0-9 \]+\)?\n" 1 } } */
>> +/* { dg-final { cleanup-saved-temps } } */
Alan Lawrence May 6, 2014, 2:16 p.m. UTC | #3
Right. Tests appear correct and problem is in arm_neon.h. I'll work on a fix.

Cheers, Alan

Christophe Lyon wrote:
> This caused:
> 
> http://gcc.gnu.org/bugzilla/show_bug.cgi?id=61062
> 
> 
> On 30 April 2014 11:18, Ramana Radhakrishnan <ramana.gcc@googlemail.com> wrote:
>> On Thu, Mar 27, 2014 at 10:53 AM, Alan Lawrence <alan.lawrence@arm.com> wrote:
>>> Final patch adds new tests of the ARM ZIP 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.
>>>
>>> All tests passing on arm-none-eabi.
>> This is OK - thanks,
>>
>> Ramana
>>
>>> gcc/testsuite/ChangeLog:
>>> 2012-03-27  Alan Lawrence  <alan.lawrence@arm.com>
>>>
>>>         * gcc.target/arm/simd/simd.exp: New file.
>>>         * gcc.target/arm/simd/vzipqf32_1.c: New file.
>>>         * gcc.target/arm/simd/vzipqp16_1.c: New file.
>>>         * gcc.target/arm/simd/vzipqp8_1.c: New file.
>>>         * gcc.target/arm/simd/vzipqs16_1.c: New file.
>>>         * gcc.target/arm/simd/vzipqs32_1.c: New file.
>>>         * gcc.target/arm/simd/vzipqs8_1.c: New file.
>>>         * gcc.target/arm/simd/vzipqu16_1.c: New file.
>>>         * gcc.target/arm/simd/vzipqu32_1.c: New file.
>>>         * gcc.target/arm/simd/vzipqu8_1.c: New file.
>>>         * gcc.target/arm/simd/vzipf32_1.c: New file.
>>>         * gcc.target/arm/simd/vzipp16_1.c: New file.
>>>         * gcc.target/arm/simd/vzipp8_1.c: New file.
>>>         * gcc.target/arm/simd/vzips16_1.c: New file.
>>>         * gcc.target/arm/simd/vzips32_1.c: New file.
>>>         * gcc.target/arm/simd/vzips8_1.c: New file.
>>>         * gcc.target/arm/simd/vzipu16_1.c: New file.
>>>         * gcc.target/arm/simd/vzipu32_1.c: New file.
>>>         * gcc.target/arm/simd/vzipu8_1.c: New file.
>>> diff --git a/gcc/testsuite/gcc.target/arm/simd/simd.exp
>>> b/gcc/testsuite/gcc.target/arm/simd/simd.exp
>>> new file mode 100644
>>> index 0000000..746429d
>>> --- /dev/null
>>> +++ b/gcc/testsuite/gcc.target/arm/simd/simd.exp
>>> @@ -0,0 +1,35 @@
>>> +# Copyright (C) 1997-2014 Free Software Foundation, Inc.
>>> +
>>> +# This program is free software; you can redistribute it and/or modify
>>> +# it under the terms of the GNU General Public License as published by
>>> +# the Free Software Foundation; either version 3 of the License, or
>>> +# (at your option) any later version.
>>> +#
>>> +# This program is distributed in the hope that it will be useful,
>>> +# but WITHOUT ANY WARRANTY; without even the implied warranty of
>>> +# MERCHANTABILITY or FITNESS FOR A PARTICULAR PURPOSE.  See the
>>> +# GNU General Public License for more details.
>>> +#
>>> +# You should have received a copy of the GNU General Public License
>>> +# along with GCC; see the file COPYING3.  If not see
>>> +# <http://www.gnu.org/licenses/>.
>>> +
>>> +# GCC testsuite that uses the `dg.exp' driver.
>>> +
>>> +# Exit immediately if this isn't an ARM target.
>>> +if ![istarget arm*-*-*] then {
>>> +  return
>>> +}
>>> +
>>> +# Load support procs.
>>> +load_lib gcc-dg.exp
>>> +
>>> +# Initialize `dg'.
>>> +dg-init
>>> +
>>> +# Main loop.
>>> +dg-runtest [lsort [glob -nocomplain $srcdir/$subdir/*.\[cCS\]]] \
>>> +       "" ""
>>> +
>>> +# All done.
>>> +dg-finish
>>> diff --git a/gcc/testsuite/gcc.target/arm/simd/vzipf32_1.c
>>> b/gcc/testsuite/gcc.target/arm/simd/vzipf32_1.c
>>> new file mode 100644
>>> index 0000000..efaa96e
>>> --- /dev/null
>>> +++ b/gcc/testsuite/gcc.target/arm/simd/vzipf32_1.c
>>> @@ -0,0 +1,12 @@
>>> +/* Test the `vzipf32' 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/vzipf32.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/vzipp16_1.c
>>> b/gcc/testsuite/gcc.target/arm/simd/vzipp16_1.c
>>> new file mode 100644
>>> index 0000000..4154333
>>> --- /dev/null
>>> +++ b/gcc/testsuite/gcc.target/arm/simd/vzipp16_1.c
>>> @@ -0,0 +1,12 @@
>>> +/* Test the `vzipp16' 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/vzipp16.x"
>>> +
>>> +/* { dg-final { scan-assembler-times "vzip\.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/vzipp8_1.c
>>> b/gcc/testsuite/gcc.target/arm/simd/vzipp8_1.c
>>> new file mode 100644
>>> index 0000000..9fe2384
>>> --- /dev/null
>>> +++ b/gcc/testsuite/gcc.target/arm/simd/vzipp8_1.c
>>> @@ -0,0 +1,12 @@
>>> +/* Test the `vzipp8' 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/vzipp8.x"
>>> +
>>> +/* { dg-final { scan-assembler-times "vzip\.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/vzipqf32_1.c
>>> b/gcc/testsuite/gcc.target/arm/simd/vzipqf32_1.c
>>> new file mode 100644
>>> index 0000000..8c547a7
>>> --- /dev/null
>>> +++ b/gcc/testsuite/gcc.target/arm/simd/vzipqf32_1.c
>>> @@ -0,0 +1,12 @@
>>> +/* Test the `vzipQf32' 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/vzipqf32.x"
>>> +
>>> +/* { dg-final { scan-assembler-times "vzip\.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/vzipqp16_1.c
>>> b/gcc/testsuite/gcc.target/arm/simd/vzipqp16_1.c
>>> new file mode 100644
>>> index 0000000..e2af10b
>>> --- /dev/null
>>> +++ b/gcc/testsuite/gcc.target/arm/simd/vzipqp16_1.c
>>> @@ -0,0 +1,12 @@
>>> +/* Test the `vzipQp16' 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/vzipqp16.x"
>>> +
>>> +/* { dg-final { scan-assembler-times "vzip\.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/vzipqp8_1.c
>>> b/gcc/testsuite/gcc.target/arm/simd/vzipqp8_1.c
>>> new file mode 100644
>>> index 0000000..11a1329
>>> --- /dev/null
>>> +++ b/gcc/testsuite/gcc.target/arm/simd/vzipqp8_1.c
>>> @@ -0,0 +1,12 @@
>>> +/* Test the `vzipQp8' 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/vzipqp8.x"
>>> +
>>> +/* { dg-final { scan-assembler-times "vzip\.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/vzipqs16_1.c
>>> b/gcc/testsuite/gcc.target/arm/simd/vzipqs16_1.c
>>> new file mode 100644
>>> index 0000000..0576c00
>>> --- /dev/null
>>> +++ b/gcc/testsuite/gcc.target/arm/simd/vzipqs16_1.c
>>> @@ -0,0 +1,12 @@
>>> +/* Test the `vzipQs16' 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/vzipqs16.x"
>>> +
>>> +/* { dg-final { scan-assembler-times "vzip\.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/vzipqs32_1.c
>>> b/gcc/testsuite/gcc.target/arm/simd/vzipqs32_1.c
>>> new file mode 100644
>>> index 0000000..6cf2439
>>> --- /dev/null
>>> +++ b/gcc/testsuite/gcc.target/arm/simd/vzipqs32_1.c
>>> @@ -0,0 +1,12 @@
>>> +/* Test the `vzipQs32' 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/vzipqs32.x"
>>> +
>>> +/* { dg-final { scan-assembler-times "vzip\.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/vzipqs8_1.c
>>> b/gcc/testsuite/gcc.target/arm/simd/vzipqs8_1.c
>>> new file mode 100644
>>> index 0000000..0244374
>>> --- /dev/null
>>> +++ b/gcc/testsuite/gcc.target/arm/simd/vzipqs8_1.c
>>> @@ -0,0 +1,12 @@
>>> +/* Test the `vzipQs8' 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/vzipqs8.x"
>>> +
>>> +/* { dg-final { scan-assembler-times "vzip\.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/vzipqu16_1.c
>>> b/gcc/testsuite/gcc.target/arm/simd/vzipqu16_1.c
>>> new file mode 100644
>>> index 0000000..3c406f5
>>> --- /dev/null
>>> +++ b/gcc/testsuite/gcc.target/arm/simd/vzipqu16_1.c
>>> @@ -0,0 +1,12 @@
>>> +/* Test the `vzipQu16' 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/vzipqu16.x"
>>> +
>>> +/* { dg-final { scan-assembler-times "vzip\.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/vzipqu32_1.c
>>> b/gcc/testsuite/gcc.target/arm/simd/vzipqu32_1.c
>>> new file mode 100644
>>> index 0000000..ba1393c
>>> --- /dev/null
>>> +++ b/gcc/testsuite/gcc.target/arm/simd/vzipqu32_1.c
>>> @@ -0,0 +1,12 @@
>>> +/* Test the `vzipQu32' 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/vzipqu32.x"
>>> +
>>> +/* { dg-final { scan-assembler-times "vzip\.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/vzipqu8_1.c
>>> b/gcc/testsuite/gcc.target/arm/simd/vzipqu8_1.c
>>> new file mode 100644
>>> index 0000000..023ecac
>>> --- /dev/null
>>> +++ b/gcc/testsuite/gcc.target/arm/simd/vzipqu8_1.c
>>> @@ -0,0 +1,12 @@
>>> +/* Test the `vzipQu8' 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/vzipqu8.x"
>>> +
>>> +/* { dg-final { scan-assembler-times "vzip\.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/vzips16_1.c
>>> b/gcc/testsuite/gcc.target/arm/simd/vzips16_1.c
>>> new file mode 100644
>>> index 0000000..b6c3c2f
>>> --- /dev/null
>>> +++ b/gcc/testsuite/gcc.target/arm/simd/vzips16_1.c
>>> @@ -0,0 +1,12 @@
>>> +/* Test the `vzips16' 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/vzips16.x"
>>> +
>>> +/* { dg-final { scan-assembler-times "vzip\.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/vzips32_1.c
>>> b/gcc/testsuite/gcc.target/arm/simd/vzips32_1.c
>>> new file mode 100644
>>> index 0000000..1a6f170
>>> --- /dev/null
>>> +++ b/gcc/testsuite/gcc.target/arm/simd/vzips32_1.c
>>> @@ -0,0 +1,12 @@
>>> +/* Test the `vzips32' 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/vzips32.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/vzips8_1.c
>>> b/gcc/testsuite/gcc.target/arm/simd/vzips8_1.c
>>> new file mode 100644
>>> index 0000000..8569357
>>> --- /dev/null
>>> +++ b/gcc/testsuite/gcc.target/arm/simd/vzips8_1.c
>>> @@ -0,0 +1,12 @@
>>> +/* Test the `vzips8' 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/vzips8.x"
>>> +
>>> +/* { dg-final { scan-assembler-times "vzip\.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/vzipu16_1.c
>>> b/gcc/testsuite/gcc.target/arm/simd/vzipu16_1.c
>>> new file mode 100644
>>> index 0000000..23bfcc4
>>> --- /dev/null
>>> +++ b/gcc/testsuite/gcc.target/arm/simd/vzipu16_1.c
>>> @@ -0,0 +1,12 @@
>>> +/* Test the `vzipu16' 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/vzipu16.x"
>>> +
>>> +/* { dg-final { scan-assembler-times "vzip\.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/vzipu32_1.c
>>> b/gcc/testsuite/gcc.target/arm/simd/vzipu32_1.c
>>> new file mode 100644
>>> index 0000000..6a753f2
>>> --- /dev/null
>>> +++ b/gcc/testsuite/gcc.target/arm/simd/vzipu32_1.c
>>> @@ -0,0 +1,12 @@
>>> +/* Test the `vzipu32' 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/vzipu32.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/vzipu8_1.c
>>> b/gcc/testsuite/gcc.target/arm/simd/vzipu8_1.c
>>> new file mode 100644
>>> index 0000000..972af74
>>> --- /dev/null
>>> +++ b/gcc/testsuite/gcc.target/arm/simd/vzipu8_1.c
>>> @@ -0,0 +1,12 @@
>>> +/* Test the `vzipu8' 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/vzipu8.x"
>>> +
>>> +/* { dg-final { scan-assembler-times "vzip\.8\[ \t\]+\[dD\]\[0-9\]+,
>>> ?\[dD\]\[0-9\]+!?\(?:\[ \t\]+@\[a-zA-Z0-9 \]+\)?\n" 1 } } */
>>> +/* { dg-final { cleanup-saved-temps } } */
>
diff mbox

Patch

diff --git a/gcc/testsuite/gcc.target/arm/simd/simd.exp b/gcc/testsuite/gcc.target/arm/simd/simd.exp
new file mode 100644
index 0000000..746429d
--- /dev/null
+++ b/gcc/testsuite/gcc.target/arm/simd/simd.exp
@@ -0,0 +1,35 @@ 
+# Copyright (C) 1997-2014 Free Software Foundation, Inc.
+
+# This program is free software; you can redistribute it and/or modify
+# it under the terms of the GNU General Public License as published by
+# the Free Software Foundation; either version 3 of the License, or
+# (at your option) any later version.
+#
+# This program is distributed in the hope that it will be useful,
+# but WITHOUT ANY WARRANTY; without even the implied warranty of
+# MERCHANTABILITY or FITNESS FOR A PARTICULAR PURPOSE.  See the
+# GNU General Public License for more details.
+#
+# You should have received a copy of the GNU General Public License
+# along with GCC; see the file COPYING3.  If not see
+# <http://www.gnu.org/licenses/>.
+
+# GCC testsuite that uses the `dg.exp' driver.
+
+# Exit immediately if this isn't an ARM target.
+if ![istarget arm*-*-*] then {
+  return
+}
+
+# Load support procs.
+load_lib gcc-dg.exp
+
+# Initialize `dg'.
+dg-init
+
+# Main loop.
+dg-runtest [lsort [glob -nocomplain $srcdir/$subdir/*.\[cCS\]]] \
+	"" ""
+
+# All done.
+dg-finish
diff --git a/gcc/testsuite/gcc.target/arm/simd/vzipf32_1.c b/gcc/testsuite/gcc.target/arm/simd/vzipf32_1.c
new file mode 100644
index 0000000..efaa96e
--- /dev/null
+++ b/gcc/testsuite/gcc.target/arm/simd/vzipf32_1.c
@@ -0,0 +1,12 @@ 
+/* Test the `vzipf32' 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/vzipf32.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/vzipp16_1.c b/gcc/testsuite/gcc.target/arm/simd/vzipp16_1.c
new file mode 100644
index 0000000..4154333
--- /dev/null
+++ b/gcc/testsuite/gcc.target/arm/simd/vzipp16_1.c
@@ -0,0 +1,12 @@ 
+/* Test the `vzipp16' 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/vzipp16.x"
+
+/* { dg-final { scan-assembler-times "vzip\.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/vzipp8_1.c b/gcc/testsuite/gcc.target/arm/simd/vzipp8_1.c
new file mode 100644
index 0000000..9fe2384
--- /dev/null
+++ b/gcc/testsuite/gcc.target/arm/simd/vzipp8_1.c
@@ -0,0 +1,12 @@ 
+/* Test the `vzipp8' 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/vzipp8.x"
+
+/* { dg-final { scan-assembler-times "vzip\.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/vzipqf32_1.c b/gcc/testsuite/gcc.target/arm/simd/vzipqf32_1.c
new file mode 100644
index 0000000..8c547a7
--- /dev/null
+++ b/gcc/testsuite/gcc.target/arm/simd/vzipqf32_1.c
@@ -0,0 +1,12 @@ 
+/* Test the `vzipQf32' 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/vzipqf32.x"
+
+/* { dg-final { scan-assembler-times "vzip\.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/vzipqp16_1.c b/gcc/testsuite/gcc.target/arm/simd/vzipqp16_1.c
new file mode 100644
index 0000000..e2af10b
--- /dev/null
+++ b/gcc/testsuite/gcc.target/arm/simd/vzipqp16_1.c
@@ -0,0 +1,12 @@ 
+/* Test the `vzipQp16' 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/vzipqp16.x"
+
+/* { dg-final { scan-assembler-times "vzip\.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/vzipqp8_1.c b/gcc/testsuite/gcc.target/arm/simd/vzipqp8_1.c
new file mode 100644
index 0000000..11a1329
--- /dev/null
+++ b/gcc/testsuite/gcc.target/arm/simd/vzipqp8_1.c
@@ -0,0 +1,12 @@ 
+/* Test the `vzipQp8' 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/vzipqp8.x"
+
+/* { dg-final { scan-assembler-times "vzip\.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/vzipqs16_1.c b/gcc/testsuite/gcc.target/arm/simd/vzipqs16_1.c
new file mode 100644
index 0000000..0576c00
--- /dev/null
+++ b/gcc/testsuite/gcc.target/arm/simd/vzipqs16_1.c
@@ -0,0 +1,12 @@ 
+/* Test the `vzipQs16' 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/vzipqs16.x"
+
+/* { dg-final { scan-assembler-times "vzip\.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/vzipqs32_1.c b/gcc/testsuite/gcc.target/arm/simd/vzipqs32_1.c
new file mode 100644
index 0000000..6cf2439
--- /dev/null
+++ b/gcc/testsuite/gcc.target/arm/simd/vzipqs32_1.c
@@ -0,0 +1,12 @@ 
+/* Test the `vzipQs32' 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/vzipqs32.x"
+
+/* { dg-final { scan-assembler-times "vzip\.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/vzipqs8_1.c b/gcc/testsuite/gcc.target/arm/simd/vzipqs8_1.c
new file mode 100644
index 0000000..0244374
--- /dev/null
+++ b/gcc/testsuite/gcc.target/arm/simd/vzipqs8_1.c
@@ -0,0 +1,12 @@ 
+/* Test the `vzipQs8' 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/vzipqs8.x"
+
+/* { dg-final { scan-assembler-times "vzip\.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/vzipqu16_1.c b/gcc/testsuite/gcc.target/arm/simd/vzipqu16_1.c
new file mode 100644
index 0000000..3c406f5
--- /dev/null
+++ b/gcc/testsuite/gcc.target/arm/simd/vzipqu16_1.c
@@ -0,0 +1,12 @@ 
+/* Test the `vzipQu16' 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/vzipqu16.x"
+
+/* { dg-final { scan-assembler-times "vzip\.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/vzipqu32_1.c b/gcc/testsuite/gcc.target/arm/simd/vzipqu32_1.c
new file mode 100644
index 0000000..ba1393c
--- /dev/null
+++ b/gcc/testsuite/gcc.target/arm/simd/vzipqu32_1.c
@@ -0,0 +1,12 @@ 
+/* Test the `vzipQu32' 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/vzipqu32.x"
+
+/* { dg-final { scan-assembler-times "vzip\.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/vzipqu8_1.c b/gcc/testsuite/gcc.target/arm/simd/vzipqu8_1.c
new file mode 100644
index 0000000..023ecac
--- /dev/null
+++ b/gcc/testsuite/gcc.target/arm/simd/vzipqu8_1.c
@@ -0,0 +1,12 @@ 
+/* Test the `vzipQu8' 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/vzipqu8.x"
+
+/* { dg-final { scan-assembler-times "vzip\.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/vzips16_1.c b/gcc/testsuite/gcc.target/arm/simd/vzips16_1.c
new file mode 100644
index 0000000..b6c3c2f
--- /dev/null
+++ b/gcc/testsuite/gcc.target/arm/simd/vzips16_1.c
@@ -0,0 +1,12 @@ 
+/* Test the `vzips16' 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/vzips16.x"
+
+/* { dg-final { scan-assembler-times "vzip\.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/vzips32_1.c b/gcc/testsuite/gcc.target/arm/simd/vzips32_1.c
new file mode 100644
index 0000000..1a6f170
--- /dev/null
+++ b/gcc/testsuite/gcc.target/arm/simd/vzips32_1.c
@@ -0,0 +1,12 @@ 
+/* Test the `vzips32' 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/vzips32.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/vzips8_1.c b/gcc/testsuite/gcc.target/arm/simd/vzips8_1.c
new file mode 100644
index 0000000..8569357
--- /dev/null
+++ b/gcc/testsuite/gcc.target/arm/simd/vzips8_1.c
@@ -0,0 +1,12 @@ 
+/* Test the `vzips8' 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/vzips8.x"
+
+/* { dg-final { scan-assembler-times "vzip\.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/vzipu16_1.c b/gcc/testsuite/gcc.target/arm/simd/vzipu16_1.c
new file mode 100644
index 0000000..23bfcc4
--- /dev/null
+++ b/gcc/testsuite/gcc.target/arm/simd/vzipu16_1.c
@@ -0,0 +1,12 @@ 
+/* Test the `vzipu16' 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/vzipu16.x"
+
+/* { dg-final { scan-assembler-times "vzip\.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/vzipu32_1.c b/gcc/testsuite/gcc.target/arm/simd/vzipu32_1.c
new file mode 100644
index 0000000..6a753f2
--- /dev/null
+++ b/gcc/testsuite/gcc.target/arm/simd/vzipu32_1.c
@@ -0,0 +1,12 @@ 
+/* Test the `vzipu32' 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/vzipu32.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/vzipu8_1.c b/gcc/testsuite/gcc.target/arm/simd/vzipu8_1.c
new file mode 100644
index 0000000..972af74
--- /dev/null
+++ b/gcc/testsuite/gcc.target/arm/simd/vzipu8_1.c
@@ -0,0 +1,12 @@ 
+/* Test the `vzipu8' 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/vzipu8.x"
+
+/* { dg-final { scan-assembler-times "vzip\.8\[ \t\]+\[dD\]\[0-9\]+, ?\[dD\]\[0-9\]+!?\(?:\[ \t\]+@\[a-zA-Z0-9 \]+\)?\n" 1 } } */
+/* { dg-final { cleanup-saved-temps } } */