https://gcc.gnu.org/g:a7e0e80630abf82b16be1d1faf95bc4b5f6f807a
commit r15-5088-ga7e0e80630abf82b16be1d1faf95bc4b5f6f807a
Author: Richard Sandiford <richard.sandif...@arm.com>
Date: Mon Nov 11 12:32:15 2024 +0000
aarch64: Use braces in SVE TBL instructions
GCC previously used the older assembly syntax for SVE TBL, with no
braces around the second operand. This patch switches to the newer,
official syntax, with braces around the operand.
The initial SVE binutils submission supported both syntaxes, so there
should be no issues with backwards compatibility.
gcc/
* config/aarch64/aarch64-sve.md (@aarch64_sve_tbl<mode>): Wrap
the second operand in braces.
gcc/testsuite/
* gcc.target/aarch64/sve/acle/asm/dup_lane_bf16.c: Wrap the second
TBL operand in braces
* gcc.target/aarch64/sve/acle/asm/dup_lane_f16.c: Likewise.
* gcc.target/aarch64/sve/acle/asm/dup_lane_f32.c: Likewise.
* gcc.target/aarch64/sve/acle/asm/dup_lane_f64.c: Likewise.
* gcc.target/aarch64/sve/acle/asm/dup_lane_s16.c: Likewise.
* gcc.target/aarch64/sve/acle/asm/dup_lane_s32.c: Likewise.
* gcc.target/aarch64/sve/acle/asm/dup_lane_s64.c: Likewise.
* gcc.target/aarch64/sve/acle/asm/dup_lane_s8.c: Likewise.
* gcc.target/aarch64/sve/acle/asm/dup_lane_u16.c: Likewise.
* gcc.target/aarch64/sve/acle/asm/dup_lane_u32.c: Likewise.
* gcc.target/aarch64/sve/acle/asm/dup_lane_u64.c: Likewise.
* gcc.target/aarch64/sve/acle/asm/dup_lane_u8.c: Likewise.
* gcc.target/aarch64/sve/acle/asm/tbl_bf16.c: Likewise.
* gcc.target/aarch64/sve/acle/asm/tbl_f16.c: Likewise.
* gcc.target/aarch64/sve/acle/asm/tbl_f32.c: Likewise.
* gcc.target/aarch64/sve/acle/asm/tbl_f64.c: Likewise.
* gcc.target/aarch64/sve/acle/asm/tbl_s16.c: Likewise.
* gcc.target/aarch64/sve/acle/asm/tbl_s32.c: Likewise.
* gcc.target/aarch64/sve/acle/asm/tbl_s64.c: Likewise.
* gcc.target/aarch64/sve/acle/asm/tbl_s8.c: Likewise.
* gcc.target/aarch64/sve/acle/asm/tbl_u16.c: Likewise.
* gcc.target/aarch64/sve/acle/asm/tbl_u32.c: Likewise.
* gcc.target/aarch64/sve/acle/asm/tbl_u64.c: Likewise.
* gcc.target/aarch64/sve/acle/asm/tbl_u8.c: Likewise.
* gcc.target/aarch64/sve/slp_perm_6.c: Likewise.
* gcc.target/aarch64/sve/slp_perm_7.c: Likewise.
* gcc.target/aarch64/sve/vec_perm_1.c: Likewise.
* gcc.target/aarch64/sve/vec_perm_const_1.c: Likewise.
* gcc.target/aarch64/sve/vec_perm_const_1_overrun.c: Likewise.
* gcc.target/aarch64/sve/vec_perm_const_single_1.c: Likewise.
* gcc.target/aarch64/sve/vec_perm_single_1.c: Likewise.
* gcc.target/aarch64/sve/uzp1_1.c: Shorten the scan-assembler-nots
to just "\ttbl\".
* gcc.target/aarch64/sve/uzp2_1.c: Likewise.
Diff:
---
gcc/config/aarch64/aarch64-sve.md | 2 +-
.../gcc.target/aarch64/sve/acle/asm/dup_lane_bf16.c | 12 ++++++------
.../gcc.target/aarch64/sve/acle/asm/dup_lane_f16.c | 12 ++++++------
.../gcc.target/aarch64/sve/acle/asm/dup_lane_f32.c | 16 ++++++++--------
.../gcc.target/aarch64/sve/acle/asm/dup_lane_f64.c | 18 +++++++++---------
.../gcc.target/aarch64/sve/acle/asm/dup_lane_s16.c | 12 ++++++------
.../gcc.target/aarch64/sve/acle/asm/dup_lane_s32.c | 16 ++++++++--------
.../gcc.target/aarch64/sve/acle/asm/dup_lane_s64.c | 20 ++++++++++----------
.../gcc.target/aarch64/sve/acle/asm/dup_lane_s8.c | 8 ++++----
.../gcc.target/aarch64/sve/acle/asm/dup_lane_u16.c | 12 ++++++------
.../gcc.target/aarch64/sve/acle/asm/dup_lane_u32.c | 16 ++++++++--------
.../gcc.target/aarch64/sve/acle/asm/dup_lane_u64.c | 20 ++++++++++----------
.../gcc.target/aarch64/sve/acle/asm/dup_lane_u8.c | 8 ++++----
.../gcc.target/aarch64/sve/acle/asm/tbl_bf16.c | 6 +++---
.../gcc.target/aarch64/sve/acle/asm/tbl_f16.c | 6 +++---
.../gcc.target/aarch64/sve/acle/asm/tbl_f32.c | 6 +++---
.../gcc.target/aarch64/sve/acle/asm/tbl_f64.c | 6 +++---
.../gcc.target/aarch64/sve/acle/asm/tbl_s16.c | 6 +++---
.../gcc.target/aarch64/sve/acle/asm/tbl_s32.c | 6 +++---
.../gcc.target/aarch64/sve/acle/asm/tbl_s64.c | 6 +++---
.../gcc.target/aarch64/sve/acle/asm/tbl_s8.c | 6 +++---
.../gcc.target/aarch64/sve/acle/asm/tbl_u16.c | 6 +++---
.../gcc.target/aarch64/sve/acle/asm/tbl_u32.c | 6 +++---
.../gcc.target/aarch64/sve/acle/asm/tbl_u64.c | 6 +++---
.../gcc.target/aarch64/sve/acle/asm/tbl_u8.c | 6 +++---
gcc/testsuite/gcc.target/aarch64/sve/slp_perm_6.c | 2 +-
gcc/testsuite/gcc.target/aarch64/sve/slp_perm_7.c | 2 +-
gcc/testsuite/gcc.target/aarch64/sve/uzp1_1.c | 8 ++++----
gcc/testsuite/gcc.target/aarch64/sve/uzp2_1.c | 8 ++++----
gcc/testsuite/gcc.target/aarch64/sve/vec_perm_1.c | 8 ++++----
.../gcc.target/aarch64/sve/vec_perm_const_1.c | 8 ++++----
.../aarch64/sve/vec_perm_const_1_overrun.c | 8 ++++----
.../gcc.target/aarch64/sve/vec_perm_const_single_1.c | 8 ++++----
.../gcc.target/aarch64/sve/vec_perm_single_1.c | 8 ++++----
34 files changed, 152 insertions(+), 152 deletions(-)
diff --git a/gcc/config/aarch64/aarch64-sve.md
b/gcc/config/aarch64/aarch64-sve.md
index 06bd3e4bb2c0..0955a6976808 100644
--- a/gcc/config/aarch64/aarch64-sve.md
+++ b/gcc/config/aarch64/aarch64-sve.md
@@ -9040,7 +9040,7 @@
(match_operand:<V_INT_EQUIV> 2 "register_operand" "w")]
UNSPEC_TBL))]
"TARGET_SVE"
- "tbl\t%0.<Vetype>, %1.<Vetype>, %2.<Vetype>"
+ "tbl\t%0.<Vetype>, {%1.<Vetype>}, %2.<Vetype>"
)
;; -------------------------------------------------------------------------
diff --git a/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/dup_lane_bf16.c
b/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/dup_lane_bf16.c
index d05ad5adbb81..f328df5f2bb6 100644
--- a/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/dup_lane_bf16.c
+++ b/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/dup_lane_bf16.c
@@ -5,7 +5,7 @@
/*
** dup_lane_w0_bf16_tied1:
** mov (z[0-9]+\.h), w0
-** tbl z0\.h, z0\.h, \1
+** tbl z0\.h, {z0\.h}, \1
** ret
*/
TEST_UNIFORM_ZX (dup_lane_w0_bf16_tied1, svbfloat16_t, uint16_t,
@@ -15,7 +15,7 @@ TEST_UNIFORM_ZX (dup_lane_w0_bf16_tied1, svbfloat16_t,
uint16_t,
/*
** dup_lane_w0_bf16_untied:
** mov (z[0-9]+\.h), w0
-** tbl z0\.h, z1\.h, \1
+** tbl z0\.h, {z1\.h}, \1
** ret
*/
TEST_UNIFORM_ZX (dup_lane_w0_bf16_untied, svbfloat16_t, uint16_t,
@@ -70,7 +70,7 @@ TEST_UNIFORM_Z (dup_lane_31_bf16, svbfloat16_t,
/*
** dup_lane_32_bf16:
** mov (z[0-9]+\.h), #32
-** tbl z0\.h, z0\.h, \1
+** tbl z0\.h, {z0\.h}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_32_bf16, svbfloat16_t,
@@ -80,7 +80,7 @@ TEST_UNIFORM_Z (dup_lane_32_bf16, svbfloat16_t,
/*
** dup_lane_63_bf16:
** mov (z[0-9]+\.h), #63
-** tbl z0\.h, z0\.h, \1
+** tbl z0\.h, {z0\.h}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_63_bf16, svbfloat16_t,
@@ -90,7 +90,7 @@ TEST_UNIFORM_Z (dup_lane_63_bf16, svbfloat16_t,
/*
** dup_lane_64_bf16:
** mov (z[0-9]+\.h), #64
-** tbl z0\.h, z0\.h, \1
+** tbl z0\.h, {z0\.h}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_64_bf16, svbfloat16_t,
@@ -100,7 +100,7 @@ TEST_UNIFORM_Z (dup_lane_64_bf16, svbfloat16_t,
/*
** dup_lane_255_bf16:
** mov (z[0-9]+\.h), #255
-** tbl z0\.h, z0\.h, \1
+** tbl z0\.h, {z0\.h}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_255_bf16, svbfloat16_t,
diff --git a/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/dup_lane_f16.c
b/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/dup_lane_f16.c
index 142afbb24528..82e882d47030 100644
--- a/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/dup_lane_f16.c
+++ b/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/dup_lane_f16.c
@@ -5,7 +5,7 @@
/*
** dup_lane_w0_f16_tied1:
** mov (z[0-9]+\.h), w0
-** tbl z0\.h, z0\.h, \1
+** tbl z0\.h, {z0\.h}, \1
** ret
*/
TEST_UNIFORM_ZX (dup_lane_w0_f16_tied1, svfloat16_t, uint16_t,
@@ -15,7 +15,7 @@ TEST_UNIFORM_ZX (dup_lane_w0_f16_tied1, svfloat16_t, uint16_t,
/*
** dup_lane_w0_f16_untied:
** mov (z[0-9]+\.h), w0
-** tbl z0\.h, z1\.h, \1
+** tbl z0\.h, {z1\.h}, \1
** ret
*/
TEST_UNIFORM_ZX (dup_lane_w0_f16_untied, svfloat16_t, uint16_t,
@@ -70,7 +70,7 @@ TEST_UNIFORM_Z (dup_lane_31_f16, svfloat16_t,
/*
** dup_lane_32_f16:
** mov (z[0-9]+\.h), #32
-** tbl z0\.h, z0\.h, \1
+** tbl z0\.h, {z0\.h}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_32_f16, svfloat16_t,
@@ -80,7 +80,7 @@ TEST_UNIFORM_Z (dup_lane_32_f16, svfloat16_t,
/*
** dup_lane_63_f16:
** mov (z[0-9]+\.h), #63
-** tbl z0\.h, z0\.h, \1
+** tbl z0\.h, {z0\.h}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_63_f16, svfloat16_t,
@@ -90,7 +90,7 @@ TEST_UNIFORM_Z (dup_lane_63_f16, svfloat16_t,
/*
** dup_lane_64_f16:
** mov (z[0-9]+\.h), #64
-** tbl z0\.h, z0\.h, \1
+** tbl z0\.h, {z0\.h}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_64_f16, svfloat16_t,
@@ -100,7 +100,7 @@ TEST_UNIFORM_Z (dup_lane_64_f16, svfloat16_t,
/*
** dup_lane_255_f16:
** mov (z[0-9]+\.h), #255
-** tbl z0\.h, z0\.h, \1
+** tbl z0\.h, {z0\.h}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_255_f16, svfloat16_t,
diff --git a/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/dup_lane_f32.c
b/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/dup_lane_f32.c
index b32068a37d60..ad67aa88306f 100644
--- a/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/dup_lane_f32.c
+++ b/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/dup_lane_f32.c
@@ -5,7 +5,7 @@
/*
** dup_lane_w0_f32_tied1:
** mov (z[0-9]+\.s), w0
-** tbl z0\.s, z0\.s, \1
+** tbl z0\.s, {z0\.s}, \1
** ret
*/
TEST_UNIFORM_ZX (dup_lane_w0_f32_tied1, svfloat32_t, uint32_t,
@@ -15,7 +15,7 @@ TEST_UNIFORM_ZX (dup_lane_w0_f32_tied1, svfloat32_t, uint32_t,
/*
** dup_lane_w0_f32_untied:
** mov (z[0-9]+\.s), w0
-** tbl z0\.s, z1\.s, \1
+** tbl z0\.s, {z1\.s}, \1
** ret
*/
TEST_UNIFORM_ZX (dup_lane_w0_f32_untied, svfloat32_t, uint32_t,
@@ -52,7 +52,7 @@ TEST_UNIFORM_Z (dup_lane_15_f32, svfloat32_t,
/*
** dup_lane_16_f32:
** mov (z[0-9]+\.s), #16
-** tbl z0\.s, z0\.s, \1
+** tbl z0\.s, {z0\.s}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_16_f32, svfloat32_t,
@@ -62,7 +62,7 @@ TEST_UNIFORM_Z (dup_lane_16_f32, svfloat32_t,
/*
** dup_lane_31_f32:
** mov (z[0-9]+\.s), #31
-** tbl z0\.s, z0\.s, \1
+** tbl z0\.s, {z0\.s}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_31_f32, svfloat32_t,
@@ -72,7 +72,7 @@ TEST_UNIFORM_Z (dup_lane_31_f32, svfloat32_t,
/*
** dup_lane_32_f32:
** mov (z[0-9]+\.s), #32
-** tbl z0\.s, z0\.s, \1
+** tbl z0\.s, {z0\.s}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_32_f32, svfloat32_t,
@@ -82,7 +82,7 @@ TEST_UNIFORM_Z (dup_lane_32_f32, svfloat32_t,
/*
** dup_lane_63_f32:
** mov (z[0-9]+\.s), #63
-** tbl z0\.s, z0\.s, \1
+** tbl z0\.s, {z0\.s}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_63_f32, svfloat32_t,
@@ -92,7 +92,7 @@ TEST_UNIFORM_Z (dup_lane_63_f32, svfloat32_t,
/*
** dup_lane_64_f32:
** mov (z[0-9]+\.s), #64
-** tbl z0\.s, z0\.s, \1
+** tbl z0\.s, {z0\.s}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_64_f32, svfloat32_t,
@@ -102,7 +102,7 @@ TEST_UNIFORM_Z (dup_lane_64_f32, svfloat32_t,
/*
** dup_lane_255_f32:
** mov (z[0-9]+\.s), #255
-** tbl z0\.s, z0\.s, \1
+** tbl z0\.s, {z0\.s}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_255_f32, svfloat32_t,
diff --git a/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/dup_lane_f64.c
b/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/dup_lane_f64.c
index 64af50d0c09e..39f8e81eacb5 100644
--- a/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/dup_lane_f64.c
+++ b/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/dup_lane_f64.c
@@ -5,7 +5,7 @@
/*
** dup_lane_x0_f64_tied1:
** mov (z[0-9]+\.d), x0
-** tbl z0\.d, z0\.d, \1
+** tbl z0\.d, {z0\.d}, \1
** ret
*/
TEST_UNIFORM_ZX (dup_lane_x0_f64_tied1, svfloat64_t, uint64_t,
@@ -15,7 +15,7 @@ TEST_UNIFORM_ZX (dup_lane_x0_f64_tied1, svfloat64_t, uint64_t,
/*
** dup_lane_x0_f64_untied:
** mov (z[0-9]+\.d), x0
-** tbl z0\.d, z1\.d, \1
+** tbl z0\.d, {z1\.d}, \1
** ret
*/
TEST_UNIFORM_ZX (dup_lane_x0_f64_untied, svfloat64_t, uint64_t,
@@ -43,7 +43,7 @@ TEST_UNIFORM_Z (dup_lane_0_f64_untied, svfloat64_t,
/*
** dup_lane_15_f64:
** mov (z[0-9]+\.d), #15
-** tbl z0\.d, z0\.d, \1
+** tbl z0\.d, {z0\.d}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_15_f64, svfloat64_t,
@@ -53,7 +53,7 @@ TEST_UNIFORM_Z (dup_lane_15_f64, svfloat64_t,
/*
** dup_lane_16_f64:
** mov (z[0-9]+\.d), #16
-** tbl z0\.d, z0\.d, \1
+** tbl z0\.d, {z0\.d}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_16_f64, svfloat64_t,
@@ -63,7 +63,7 @@ TEST_UNIFORM_Z (dup_lane_16_f64, svfloat64_t,
/*
** dup_lane_31_f64:
** mov (z[0-9]+\.d), #31
-** tbl z0\.d, z0\.d, \1
+** tbl z0\.d, {z0\.d}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_31_f64, svfloat64_t,
@@ -73,7 +73,7 @@ TEST_UNIFORM_Z (dup_lane_31_f64, svfloat64_t,
/*
** dup_lane_32_f64:
** mov (z[0-9]+\.d), #32
-** tbl z0\.d, z0\.d, \1
+** tbl z0\.d, {z0\.d}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_32_f64, svfloat64_t,
@@ -83,7 +83,7 @@ TEST_UNIFORM_Z (dup_lane_32_f64, svfloat64_t,
/*
** dup_lane_63_f64:
** mov (z[0-9]+\.d), #63
-** tbl z0\.d, z0\.d, \1
+** tbl z0\.d, {z0\.d}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_63_f64, svfloat64_t,
@@ -93,7 +93,7 @@ TEST_UNIFORM_Z (dup_lane_63_f64, svfloat64_t,
/*
** dup_lane_64_f64:
** mov (z[0-9]+\.d), #64
-** tbl z0\.d, z0\.d, \1
+** tbl z0\.d, {z0\.d}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_64_f64, svfloat64_t,
@@ -103,7 +103,7 @@ TEST_UNIFORM_Z (dup_lane_64_f64, svfloat64_t,
/*
** dup_lane_255_f64:
** mov (z[0-9]+\.d), #255
-** tbl z0\.d, z0\.d, \1
+** tbl z0\.d, {z0\.d}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_255_f64, svfloat64_t,
diff --git a/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/dup_lane_s16.c
b/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/dup_lane_s16.c
index 3b6f20696fa3..2315d4969792 100644
--- a/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/dup_lane_s16.c
+++ b/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/dup_lane_s16.c
@@ -5,7 +5,7 @@
/*
** dup_lane_w0_s16_tied1:
** mov (z[0-9]+\.h), w0
-** tbl z0\.h, z0\.h, \1
+** tbl z0\.h, {z0\.h}, \1
** ret
*/
TEST_UNIFORM_ZX (dup_lane_w0_s16_tied1, svint16_t, uint16_t,
@@ -15,7 +15,7 @@ TEST_UNIFORM_ZX (dup_lane_w0_s16_tied1, svint16_t, uint16_t,
/*
** dup_lane_w0_s16_untied:
** mov (z[0-9]+\.h), w0
-** tbl z0\.h, z1\.h, \1
+** tbl z0\.h, {z1\.h}, \1
** ret
*/
TEST_UNIFORM_ZX (dup_lane_w0_s16_untied, svint16_t, uint16_t,
@@ -88,7 +88,7 @@ TEST_UNIFORM_Z (dup_lane_31_s16, svint16_t,
/*
** dup_lane_32_s16:
** mov (z[0-9]+\.h), #32
-** tbl z0\.h, z0\.h, \1
+** tbl z0\.h, {z0\.h}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_32_s16, svint16_t,
@@ -98,7 +98,7 @@ TEST_UNIFORM_Z (dup_lane_32_s16, svint16_t,
/*
** dup_lane_63_s16:
** mov (z[0-9]+\.h), #63
-** tbl z0\.h, z0\.h, \1
+** tbl z0\.h, {z0\.h}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_63_s16, svint16_t,
@@ -108,7 +108,7 @@ TEST_UNIFORM_Z (dup_lane_63_s16, svint16_t,
/*
** dup_lane_64_s16:
** mov (z[0-9]+\.h), #64
-** tbl z0\.h, z0\.h, \1
+** tbl z0\.h, {z0\.h}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_64_s16, svint16_t,
@@ -118,7 +118,7 @@ TEST_UNIFORM_Z (dup_lane_64_s16, svint16_t,
/*
** dup_lane_255_s16:
** mov (z[0-9]+\.h), #255
-** tbl z0\.h, z0\.h, \1
+** tbl z0\.h, {z0\.h}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_255_s16, svint16_t,
diff --git a/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/dup_lane_s32.c
b/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/dup_lane_s32.c
index bf597fdf66cc..98b4ff052e2e 100644
--- a/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/dup_lane_s32.c
+++ b/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/dup_lane_s32.c
@@ -5,7 +5,7 @@
/*
** dup_lane_w0_s32_tied1:
** mov (z[0-9]+\.s), w0
-** tbl z0\.s, z0\.s, \1
+** tbl z0\.s, {z0\.s}, \1
** ret
*/
TEST_UNIFORM_ZX (dup_lane_w0_s32_tied1, svint32_t, uint32_t,
@@ -15,7 +15,7 @@ TEST_UNIFORM_ZX (dup_lane_w0_s32_tied1, svint32_t, uint32_t,
/*
** dup_lane_w0_s32_untied:
** mov (z[0-9]+\.s), w0
-** tbl z0\.s, z1\.s, \1
+** tbl z0\.s, {z1\.s}, \1
** ret
*/
TEST_UNIFORM_ZX (dup_lane_w0_s32_untied, svint32_t, uint32_t,
@@ -70,7 +70,7 @@ TEST_UNIFORM_Z (dup_lane_15_s32, svint32_t,
/*
** dup_lane_16_s32:
** mov (z[0-9]+\.s), #16
-** tbl z0\.s, z0\.s, \1
+** tbl z0\.s, {z0\.s}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_16_s32, svint32_t,
@@ -80,7 +80,7 @@ TEST_UNIFORM_Z (dup_lane_16_s32, svint32_t,
/*
** dup_lane_31_s32:
** mov (z[0-9]+\.s), #31
-** tbl z0\.s, z0\.s, \1
+** tbl z0\.s, {z0\.s}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_31_s32, svint32_t,
@@ -90,7 +90,7 @@ TEST_UNIFORM_Z (dup_lane_31_s32, svint32_t,
/*
** dup_lane_32_s32:
** mov (z[0-9]+\.s), #32
-** tbl z0\.s, z0\.s, \1
+** tbl z0\.s, {z0\.s}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_32_s32, svint32_t,
@@ -100,7 +100,7 @@ TEST_UNIFORM_Z (dup_lane_32_s32, svint32_t,
/*
** dup_lane_63_s32:
** mov (z[0-9]+\.s), #63
-** tbl z0\.s, z0\.s, \1
+** tbl z0\.s, {z0\.s}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_63_s32, svint32_t,
@@ -110,7 +110,7 @@ TEST_UNIFORM_Z (dup_lane_63_s32, svint32_t,
/*
** dup_lane_64_s32:
** mov (z[0-9]+\.s), #64
-** tbl z0\.s, z0\.s, \1
+** tbl z0\.s, {z0\.s}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_64_s32, svint32_t,
@@ -120,7 +120,7 @@ TEST_UNIFORM_Z (dup_lane_64_s32, svint32_t,
/*
** dup_lane_255_s32:
** mov (z[0-9]+\.s), #255
-** tbl z0\.s, z0\.s, \1
+** tbl z0\.s, {z0\.s}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_255_s32, svint32_t,
diff --git a/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/dup_lane_s64.c
b/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/dup_lane_s64.c
index f2f3a1770cde..b9bf4ba1287d 100644
--- a/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/dup_lane_s64.c
+++ b/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/dup_lane_s64.c
@@ -5,7 +5,7 @@
/*
** dup_lane_x0_s64_tied1:
** mov (z[0-9]+\.d), x0
-** tbl z0\.d, z0\.d, \1
+** tbl z0\.d, {z0\.d}, \1
** ret
*/
TEST_UNIFORM_ZX (dup_lane_x0_s64_tied1, svint64_t, uint64_t,
@@ -15,7 +15,7 @@ TEST_UNIFORM_ZX (dup_lane_x0_s64_tied1, svint64_t, uint64_t,
/*
** dup_lane_x0_s64_untied:
** mov (z[0-9]+\.d), x0
-** tbl z0\.d, z1\.d, \1
+** tbl z0\.d, {z1\.d}, \1
** ret
*/
TEST_UNIFORM_ZX (dup_lane_x0_s64_untied, svint64_t, uint64_t,
@@ -52,7 +52,7 @@ TEST_UNIFORM_Z (dup_lane_7_s64, svint64_t,
/*
** dup_lane_8_s64:
** mov (z[0-9]+\.d), #8
-** tbl z0\.d, z0\.d, \1
+** tbl z0\.d, {z0\.d}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_8_s64, svint64_t,
@@ -62,7 +62,7 @@ TEST_UNIFORM_Z (dup_lane_8_s64, svint64_t,
/*
** dup_lane_15_s64:
** mov (z[0-9]+\.d), #15
-** tbl z0\.d, z0\.d, \1
+** tbl z0\.d, {z0\.d}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_15_s64, svint64_t,
@@ -72,7 +72,7 @@ TEST_UNIFORM_Z (dup_lane_15_s64, svint64_t,
/*
** dup_lane_16_s64:
** mov (z[0-9]+\.d), #16
-** tbl z0\.d, z0\.d, \1
+** tbl z0\.d, {z0\.d}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_16_s64, svint64_t,
@@ -82,7 +82,7 @@ TEST_UNIFORM_Z (dup_lane_16_s64, svint64_t,
/*
** dup_lane_31_s64:
** mov (z[0-9]+\.d), #31
-** tbl z0\.d, z0\.d, \1
+** tbl z0\.d, {z0\.d}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_31_s64, svint64_t,
@@ -92,7 +92,7 @@ TEST_UNIFORM_Z (dup_lane_31_s64, svint64_t,
/*
** dup_lane_32_s64:
** mov (z[0-9]+\.d), #32
-** tbl z0\.d, z0\.d, \1
+** tbl z0\.d, {z0\.d}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_32_s64, svint64_t,
@@ -102,7 +102,7 @@ TEST_UNIFORM_Z (dup_lane_32_s64, svint64_t,
/*
** dup_lane_63_s64:
** mov (z[0-9]+\.d), #63
-** tbl z0\.d, z0\.d, \1
+** tbl z0\.d, {z0\.d}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_63_s64, svint64_t,
@@ -112,7 +112,7 @@ TEST_UNIFORM_Z (dup_lane_63_s64, svint64_t,
/*
** dup_lane_64_s64:
** mov (z[0-9]+\.d), #64
-** tbl z0\.d, z0\.d, \1
+** tbl z0\.d, {z0\.d}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_64_s64, svint64_t,
@@ -122,7 +122,7 @@ TEST_UNIFORM_Z (dup_lane_64_s64, svint64_t,
/*
** dup_lane_255_s64:
** mov (z[0-9]+\.d), #255
-** tbl z0\.d, z0\.d, \1
+** tbl z0\.d, {z0\.d}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_255_s64, svint64_t,
diff --git a/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/dup_lane_s8.c
b/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/dup_lane_s8.c
index f5a07e9f3378..8de7e5597b7b 100644
--- a/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/dup_lane_s8.c
+++ b/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/dup_lane_s8.c
@@ -5,7 +5,7 @@
/*
** dup_lane_w0_s8_tied1:
** mov (z[0-9]+\.b), w0
-** tbl z0\.b, z0\.b, \1
+** tbl z0\.b, {z0\.b}, \1
** ret
*/
TEST_UNIFORM_ZX (dup_lane_w0_s8_tied1, svint8_t, uint8_t,
@@ -15,7 +15,7 @@ TEST_UNIFORM_ZX (dup_lane_w0_s8_tied1, svint8_t, uint8_t,
/*
** dup_lane_w0_s8_untied:
** mov (z[0-9]+\.b), w0
-** tbl z0\.b, z1\.b, \1
+** tbl z0\.b, {z1\.b}, \1
** ret
*/
TEST_UNIFORM_ZX (dup_lane_w0_s8_untied, svint8_t, uint8_t,
@@ -106,7 +106,7 @@ TEST_UNIFORM_Z (dup_lane_63_s8, svint8_t,
/*
** dup_lane_64_s8:
** mov (z[0-9]+\.b), #64
-** tbl z0\.b, z0\.b, \1
+** tbl z0\.b, {z0\.b}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_64_s8, svint8_t,
@@ -116,7 +116,7 @@ TEST_UNIFORM_Z (dup_lane_64_s8, svint8_t,
/*
** dup_lane_255_s8:
** mov (z[0-9]+\.b), #-1
-** tbl z0\.b, z0\.b, \1
+** tbl z0\.b, {z0\.b}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_255_s8, svint8_t,
diff --git a/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/dup_lane_u16.c
b/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/dup_lane_u16.c
index e5135caa5459..408b18338a85 100644
--- a/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/dup_lane_u16.c
+++ b/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/dup_lane_u16.c
@@ -5,7 +5,7 @@
/*
** dup_lane_w0_u16_tied1:
** mov (z[0-9]+\.h), w0
-** tbl z0\.h, z0\.h, \1
+** tbl z0\.h, {z0\.h}, \1
** ret
*/
TEST_UNIFORM_ZX (dup_lane_w0_u16_tied1, svuint16_t, uint16_t,
@@ -15,7 +15,7 @@ TEST_UNIFORM_ZX (dup_lane_w0_u16_tied1, svuint16_t, uint16_t,
/*
** dup_lane_w0_u16_untied:
** mov (z[0-9]+\.h), w0
-** tbl z0\.h, z1\.h, \1
+** tbl z0\.h, {z1\.h}, \1
** ret
*/
TEST_UNIFORM_ZX (dup_lane_w0_u16_untied, svuint16_t, uint16_t,
@@ -88,7 +88,7 @@ TEST_UNIFORM_Z (dup_lane_31_u16, svuint16_t,
/*
** dup_lane_32_u16:
** mov (z[0-9]+\.h), #32
-** tbl z0\.h, z0\.h, \1
+** tbl z0\.h, {z0\.h}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_32_u16, svuint16_t,
@@ -98,7 +98,7 @@ TEST_UNIFORM_Z (dup_lane_32_u16, svuint16_t,
/*
** dup_lane_63_u16:
** mov (z[0-9]+\.h), #63
-** tbl z0\.h, z0\.h, \1
+** tbl z0\.h, {z0\.h}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_63_u16, svuint16_t,
@@ -108,7 +108,7 @@ TEST_UNIFORM_Z (dup_lane_63_u16, svuint16_t,
/*
** dup_lane_64_u16:
** mov (z[0-9]+\.h), #64
-** tbl z0\.h, z0\.h, \1
+** tbl z0\.h, {z0\.h}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_64_u16, svuint16_t,
@@ -118,7 +118,7 @@ TEST_UNIFORM_Z (dup_lane_64_u16, svuint16_t,
/*
** dup_lane_255_u16:
** mov (z[0-9]+\.h), #255
-** tbl z0\.h, z0\.h, \1
+** tbl z0\.h, {z0\.h}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_255_u16, svuint16_t,
diff --git a/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/dup_lane_u32.c
b/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/dup_lane_u32.c
index 7e972aca70a1..d53cf056e960 100644
--- a/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/dup_lane_u32.c
+++ b/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/dup_lane_u32.c
@@ -5,7 +5,7 @@
/*
** dup_lane_w0_u32_tied1:
** mov (z[0-9]+\.s), w0
-** tbl z0\.s, z0\.s, \1
+** tbl z0\.s, {z0\.s}, \1
** ret
*/
TEST_UNIFORM_ZX (dup_lane_w0_u32_tied1, svuint32_t, uint32_t,
@@ -15,7 +15,7 @@ TEST_UNIFORM_ZX (dup_lane_w0_u32_tied1, svuint32_t, uint32_t,
/*
** dup_lane_w0_u32_untied:
** mov (z[0-9]+\.s), w0
-** tbl z0\.s, z1\.s, \1
+** tbl z0\.s, {z1\.s}, \1
** ret
*/
TEST_UNIFORM_ZX (dup_lane_w0_u32_untied, svuint32_t, uint32_t,
@@ -70,7 +70,7 @@ TEST_UNIFORM_Z (dup_lane_15_u32, svuint32_t,
/*
** dup_lane_16_u32:
** mov (z[0-9]+\.s), #16
-** tbl z0\.s, z0\.s, \1
+** tbl z0\.s, {z0\.s}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_16_u32, svuint32_t,
@@ -80,7 +80,7 @@ TEST_UNIFORM_Z (dup_lane_16_u32, svuint32_t,
/*
** dup_lane_31_u32:
** mov (z[0-9]+\.s), #31
-** tbl z0\.s, z0\.s, \1
+** tbl z0\.s, {z0\.s}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_31_u32, svuint32_t,
@@ -90,7 +90,7 @@ TEST_UNIFORM_Z (dup_lane_31_u32, svuint32_t,
/*
** dup_lane_32_u32:
** mov (z[0-9]+\.s), #32
-** tbl z0\.s, z0\.s, \1
+** tbl z0\.s, {z0\.s}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_32_u32, svuint32_t,
@@ -100,7 +100,7 @@ TEST_UNIFORM_Z (dup_lane_32_u32, svuint32_t,
/*
** dup_lane_63_u32:
** mov (z[0-9]+\.s), #63
-** tbl z0\.s, z0\.s, \1
+** tbl z0\.s, {z0\.s}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_63_u32, svuint32_t,
@@ -110,7 +110,7 @@ TEST_UNIFORM_Z (dup_lane_63_u32, svuint32_t,
/*
** dup_lane_64_u32:
** mov (z[0-9]+\.s), #64
-** tbl z0\.s, z0\.s, \1
+** tbl z0\.s, {z0\.s}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_64_u32, svuint32_t,
@@ -120,7 +120,7 @@ TEST_UNIFORM_Z (dup_lane_64_u32, svuint32_t,
/*
** dup_lane_255_u32:
** mov (z[0-9]+\.s), #255
-** tbl z0\.s, z0\.s, \1
+** tbl z0\.s, {z0\.s}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_255_u32, svuint32_t,
diff --git a/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/dup_lane_u64.c
b/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/dup_lane_u64.c
index 5097b7e96734..c6c0e8862473 100644
--- a/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/dup_lane_u64.c
+++ b/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/dup_lane_u64.c
@@ -5,7 +5,7 @@
/*
** dup_lane_x0_u64_tied1:
** mov (z[0-9]+\.d), x0
-** tbl z0\.d, z0\.d, \1
+** tbl z0\.d, {z0\.d}, \1
** ret
*/
TEST_UNIFORM_ZX (dup_lane_x0_u64_tied1, svuint64_t, uint64_t,
@@ -15,7 +15,7 @@ TEST_UNIFORM_ZX (dup_lane_x0_u64_tied1, svuint64_t, uint64_t,
/*
** dup_lane_x0_u64_untied:
** mov (z[0-9]+\.d), x0
-** tbl z0\.d, z1\.d, \1
+** tbl z0\.d, {z1\.d}, \1
** ret
*/
TEST_UNIFORM_ZX (dup_lane_x0_u64_untied, svuint64_t, uint64_t,
@@ -52,7 +52,7 @@ TEST_UNIFORM_Z (dup_lane_7_u64, svuint64_t,
/*
** dup_lane_8_u64:
** mov (z[0-9]+\.d), #8
-** tbl z0\.d, z0\.d, \1
+** tbl z0\.d, {z0\.d}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_8_u64, svuint64_t,
@@ -62,7 +62,7 @@ TEST_UNIFORM_Z (dup_lane_8_u64, svuint64_t,
/*
** dup_lane_15_u64:
** mov (z[0-9]+\.d), #15
-** tbl z0\.d, z0\.d, \1
+** tbl z0\.d, {z0\.d}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_15_u64, svuint64_t,
@@ -72,7 +72,7 @@ TEST_UNIFORM_Z (dup_lane_15_u64, svuint64_t,
/*
** dup_lane_16_u64:
** mov (z[0-9]+\.d), #16
-** tbl z0\.d, z0\.d, \1
+** tbl z0\.d, {z0\.d}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_16_u64, svuint64_t,
@@ -82,7 +82,7 @@ TEST_UNIFORM_Z (dup_lane_16_u64, svuint64_t,
/*
** dup_lane_31_u64:
** mov (z[0-9]+\.d), #31
-** tbl z0\.d, z0\.d, \1
+** tbl z0\.d, {z0\.d}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_31_u64, svuint64_t,
@@ -92,7 +92,7 @@ TEST_UNIFORM_Z (dup_lane_31_u64, svuint64_t,
/*
** dup_lane_32_u64:
** mov (z[0-9]+\.d), #32
-** tbl z0\.d, z0\.d, \1
+** tbl z0\.d, {z0\.d}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_32_u64, svuint64_t,
@@ -102,7 +102,7 @@ TEST_UNIFORM_Z (dup_lane_32_u64, svuint64_t,
/*
** dup_lane_63_u64:
** mov (z[0-9]+\.d), #63
-** tbl z0\.d, z0\.d, \1
+** tbl z0\.d, {z0\.d}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_63_u64, svuint64_t,
@@ -112,7 +112,7 @@ TEST_UNIFORM_Z (dup_lane_63_u64, svuint64_t,
/*
** dup_lane_64_u64:
** mov (z[0-9]+\.d), #64
-** tbl z0\.d, z0\.d, \1
+** tbl z0\.d, {z0\.d}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_64_u64, svuint64_t,
@@ -122,7 +122,7 @@ TEST_UNIFORM_Z (dup_lane_64_u64, svuint64_t,
/*
** dup_lane_255_u64:
** mov (z[0-9]+\.d), #255
-** tbl z0\.d, z0\.d, \1
+** tbl z0\.d, {z0\.d}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_255_u64, svuint64_t,
diff --git a/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/dup_lane_u8.c
b/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/dup_lane_u8.c
index 25fdf0acb4ae..58709f5edb82 100644
--- a/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/dup_lane_u8.c
+++ b/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/dup_lane_u8.c
@@ -5,7 +5,7 @@
/*
** dup_lane_w0_u8_tied1:
** mov (z[0-9]+\.b), w0
-** tbl z0\.b, z0\.b, \1
+** tbl z0\.b, {z0\.b}, \1
** ret
*/
TEST_UNIFORM_ZX (dup_lane_w0_u8_tied1, svuint8_t, uint8_t,
@@ -15,7 +15,7 @@ TEST_UNIFORM_ZX (dup_lane_w0_u8_tied1, svuint8_t, uint8_t,
/*
** dup_lane_w0_u8_untied:
** mov (z[0-9]+\.b), w0
-** tbl z0\.b, z1\.b, \1
+** tbl z0\.b, {z1\.b}, \1
** ret
*/
TEST_UNIFORM_ZX (dup_lane_w0_u8_untied, svuint8_t, uint8_t,
@@ -106,7 +106,7 @@ TEST_UNIFORM_Z (dup_lane_63_u8, svuint8_t,
/*
** dup_lane_64_u8:
** mov (z[0-9]+\.b), #64
-** tbl z0\.b, z0\.b, \1
+** tbl z0\.b, {z0\.b}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_64_u8, svuint8_t,
@@ -116,7 +116,7 @@ TEST_UNIFORM_Z (dup_lane_64_u8, svuint8_t,
/*
** dup_lane_255_u8:
** mov (z[0-9]+\.b), #-1
-** tbl z0\.b, z0\.b, \1
+** tbl z0\.b, {z0\.b}, \1
** ret
*/
TEST_UNIFORM_Z (dup_lane_255_u8, svuint8_t,
diff --git a/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/tbl_bf16.c
b/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/tbl_bf16.c
index 8c077d118979..379c890e9ece 100644
--- a/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/tbl_bf16.c
+++ b/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/tbl_bf16.c
@@ -4,7 +4,7 @@
/*
** tbl_bf16_tied1:
-** tbl z0\.h, z0\.h, z4\.h
+** tbl z0\.h, {z0\.h}, z4\.h
** ret
*/
TEST_DUAL_Z (tbl_bf16_tied1, svbfloat16_t, svuint16_t,
@@ -13,7 +13,7 @@ TEST_DUAL_Z (tbl_bf16_tied1, svbfloat16_t, svuint16_t,
/*
** tbl_bf16_tied2:
-** tbl z0\.h, z4\.h, z0\.h
+** tbl z0\.h, {z4\.h}, z0\.h
** ret
*/
TEST_DUAL_Z_REV (tbl_bf16_tied2, svbfloat16_t, svuint16_t,
@@ -22,7 +22,7 @@ TEST_DUAL_Z_REV (tbl_bf16_tied2, svbfloat16_t, svuint16_t,
/*
** tbl_bf16_untied:
-** tbl z0\.h, z1\.h, z4\.h
+** tbl z0\.h, {z1\.h}, z4\.h
** ret
*/
TEST_DUAL_Z (tbl_bf16_untied, svbfloat16_t, svuint16_t,
diff --git a/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/tbl_f16.c
b/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/tbl_f16.c
index 94b6104123d3..270d9d356224 100644
--- a/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/tbl_f16.c
+++ b/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/tbl_f16.c
@@ -4,7 +4,7 @@
/*
** tbl_f16_tied1:
-** tbl z0\.h, z0\.h, z4\.h
+** tbl z0\.h, {z0\.h}, z4\.h
** ret
*/
TEST_DUAL_Z (tbl_f16_tied1, svfloat16_t, svuint16_t,
@@ -13,7 +13,7 @@ TEST_DUAL_Z (tbl_f16_tied1, svfloat16_t, svuint16_t,
/*
** tbl_f16_tied2:
-** tbl z0\.h, z4\.h, z0\.h
+** tbl z0\.h, {z4\.h}, z0\.h
** ret
*/
TEST_DUAL_Z_REV (tbl_f16_tied2, svfloat16_t, svuint16_t,
@@ -22,7 +22,7 @@ TEST_DUAL_Z_REV (tbl_f16_tied2, svfloat16_t, svuint16_t,
/*
** tbl_f16_untied:
-** tbl z0\.h, z1\.h, z4\.h
+** tbl z0\.h, {z1\.h}, z4\.h
** ret
*/
TEST_DUAL_Z (tbl_f16_untied, svfloat16_t, svuint16_t,
diff --git a/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/tbl_f32.c
b/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/tbl_f32.c
index 741d3bdcf72b..f3d32745788e 100644
--- a/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/tbl_f32.c
+++ b/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/tbl_f32.c
@@ -4,7 +4,7 @@
/*
** tbl_f32_tied1:
-** tbl z0\.s, z0\.s, z4\.s
+** tbl z0\.s, {z0\.s}, z4\.s
** ret
*/
TEST_DUAL_Z (tbl_f32_tied1, svfloat32_t, svuint32_t,
@@ -13,7 +13,7 @@ TEST_DUAL_Z (tbl_f32_tied1, svfloat32_t, svuint32_t,
/*
** tbl_f32_tied2:
-** tbl z0\.s, z4\.s, z0\.s
+** tbl z0\.s, {z4\.s}, z0\.s
** ret
*/
TEST_DUAL_Z_REV (tbl_f32_tied2, svfloat32_t, svuint32_t,
@@ -22,7 +22,7 @@ TEST_DUAL_Z_REV (tbl_f32_tied2, svfloat32_t, svuint32_t,
/*
** tbl_f32_untied:
-** tbl z0\.s, z1\.s, z4\.s
+** tbl z0\.s, {z1\.s}, z4\.s
** ret
*/
TEST_DUAL_Z (tbl_f32_untied, svfloat32_t, svuint32_t,
diff --git a/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/tbl_f64.c
b/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/tbl_f64.c
index 3c24e9a59e0d..a7f81be7ca1e 100644
--- a/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/tbl_f64.c
+++ b/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/tbl_f64.c
@@ -4,7 +4,7 @@
/*
** tbl_f64_tied1:
-** tbl z0\.d, z0\.d, z4\.d
+** tbl z0\.d, {z0\.d}, z4\.d
** ret
*/
TEST_DUAL_Z (tbl_f64_tied1, svfloat64_t, svuint64_t,
@@ -13,7 +13,7 @@ TEST_DUAL_Z (tbl_f64_tied1, svfloat64_t, svuint64_t,
/*
** tbl_f64_tied2:
-** tbl z0\.d, z4\.d, z0\.d
+** tbl z0\.d, {z4\.d}, z0\.d
** ret
*/
TEST_DUAL_Z_REV (tbl_f64_tied2, svfloat64_t, svuint64_t,
@@ -22,7 +22,7 @@ TEST_DUAL_Z_REV (tbl_f64_tied2, svfloat64_t, svuint64_t,
/*
** tbl_f64_untied:
-** tbl z0\.d, z1\.d, z4\.d
+** tbl z0\.d, {z1\.d}, z4\.d
** ret
*/
TEST_DUAL_Z (tbl_f64_untied, svfloat64_t, svuint64_t,
diff --git a/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/tbl_s16.c
b/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/tbl_s16.c
index 2ec9c389a010..9dbf4bbd3072 100644
--- a/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/tbl_s16.c
+++ b/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/tbl_s16.c
@@ -4,7 +4,7 @@
/*
** tbl_s16_tied1:
-** tbl z0\.h, z0\.h, z4\.h
+** tbl z0\.h, {z0\.h}, z4\.h
** ret
*/
TEST_DUAL_Z (tbl_s16_tied1, svint16_t, svuint16_t,
@@ -13,7 +13,7 @@ TEST_DUAL_Z (tbl_s16_tied1, svint16_t, svuint16_t,
/*
** tbl_s16_tied2:
-** tbl z0\.h, z4\.h, z0\.h
+** tbl z0\.h, {z4\.h}, z0\.h
** ret
*/
TEST_DUAL_Z_REV (tbl_s16_tied2, svint16_t, svuint16_t,
@@ -22,7 +22,7 @@ TEST_DUAL_Z_REV (tbl_s16_tied2, svint16_t, svuint16_t,
/*
** tbl_s16_untied:
-** tbl z0\.h, z1\.h, z4\.h
+** tbl z0\.h, {z1\.h}, z4\.h
** ret
*/
TEST_DUAL_Z (tbl_s16_untied, svint16_t, svuint16_t,
diff --git a/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/tbl_s32.c
b/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/tbl_s32.c
index 98b2d8d8bc07..da7fa65ecb0d 100644
--- a/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/tbl_s32.c
+++ b/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/tbl_s32.c
@@ -4,7 +4,7 @@
/*
** tbl_s32_tied1:
-** tbl z0\.s, z0\.s, z4\.s
+** tbl z0\.s, {z0\.s}, z4\.s
** ret
*/
TEST_DUAL_Z (tbl_s32_tied1, svint32_t, svuint32_t,
@@ -13,7 +13,7 @@ TEST_DUAL_Z (tbl_s32_tied1, svint32_t, svuint32_t,
/*
** tbl_s32_tied2:
-** tbl z0\.s, z4\.s, z0\.s
+** tbl z0\.s, {z4\.s}, z0\.s
** ret
*/
TEST_DUAL_Z_REV (tbl_s32_tied2, svint32_t, svuint32_t,
@@ -22,7 +22,7 @@ TEST_DUAL_Z_REV (tbl_s32_tied2, svint32_t, svuint32_t,
/*
** tbl_s32_untied:
-** tbl z0\.s, z1\.s, z4\.s
+** tbl z0\.s, {z1\.s}, z4\.s
** ret
*/
TEST_DUAL_Z (tbl_s32_untied, svint32_t, svuint32_t,
diff --git a/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/tbl_s64.c
b/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/tbl_s64.c
index 0138a80d2e2f..feffce383456 100644
--- a/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/tbl_s64.c
+++ b/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/tbl_s64.c
@@ -4,7 +4,7 @@
/*
** tbl_s64_tied1:
-** tbl z0\.d, z0\.d, z4\.d
+** tbl z0\.d, {z0\.d}, z4\.d
** ret
*/
TEST_DUAL_Z (tbl_s64_tied1, svint64_t, svuint64_t,
@@ -13,7 +13,7 @@ TEST_DUAL_Z (tbl_s64_tied1, svint64_t, svuint64_t,
/*
** tbl_s64_tied2:
-** tbl z0\.d, z4\.d, z0\.d
+** tbl z0\.d, {z4\.d}, z0\.d
** ret
*/
TEST_DUAL_Z_REV (tbl_s64_tied2, svint64_t, svuint64_t,
@@ -22,7 +22,7 @@ TEST_DUAL_Z_REV (tbl_s64_tied2, svint64_t, svuint64_t,
/*
** tbl_s64_untied:
-** tbl z0\.d, z1\.d, z4\.d
+** tbl z0\.d, {z1\.d}, z4\.d
** ret
*/
TEST_DUAL_Z (tbl_s64_untied, svint64_t, svuint64_t,
diff --git a/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/tbl_s8.c
b/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/tbl_s8.c
index 7818d1b6d58d..bd974e735504 100644
--- a/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/tbl_s8.c
+++ b/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/tbl_s8.c
@@ -4,7 +4,7 @@
/*
** tbl_s8_tied1:
-** tbl z0\.b, z0\.b, z4\.b
+** tbl z0\.b, {z0\.b}, z4\.b
** ret
*/
TEST_DUAL_Z (tbl_s8_tied1, svint8_t, svuint8_t,
@@ -13,7 +13,7 @@ TEST_DUAL_Z (tbl_s8_tied1, svint8_t, svuint8_t,
/*
** tbl_s8_tied2:
-** tbl z0\.b, z4\.b, z0\.b
+** tbl z0\.b, {z4\.b}, z0\.b
** ret
*/
TEST_DUAL_Z_REV (tbl_s8_tied2, svint8_t, svuint8_t,
@@ -22,7 +22,7 @@ TEST_DUAL_Z_REV (tbl_s8_tied2, svint8_t, svuint8_t,
/*
** tbl_s8_untied:
-** tbl z0\.b, z1\.b, z4\.b
+** tbl z0\.b, {z1\.b}, z4\.b
** ret
*/
TEST_DUAL_Z (tbl_s8_untied, svint8_t, svuint8_t,
diff --git a/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/tbl_u16.c
b/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/tbl_u16.c
index f15da9211623..088a2491d623 100644
--- a/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/tbl_u16.c
+++ b/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/tbl_u16.c
@@ -4,7 +4,7 @@
/*
** tbl_u16_tied1:
-** tbl z0\.h, z0\.h, z4\.h
+** tbl z0\.h, {z0\.h}, z4\.h
** ret
*/
TEST_DUAL_Z (tbl_u16_tied1, svuint16_t, svuint16_t,
@@ -13,7 +13,7 @@ TEST_DUAL_Z (tbl_u16_tied1, svuint16_t, svuint16_t,
/*
** tbl_u16_tied2:
-** tbl z0\.h, z4\.h, z0\.h
+** tbl z0\.h, {z4\.h}, z0\.h
** ret
*/
TEST_DUAL_Z_REV (tbl_u16_tied2, svuint16_t, svuint16_t,
@@ -22,7 +22,7 @@ TEST_DUAL_Z_REV (tbl_u16_tied2, svuint16_t, svuint16_t,
/*
** tbl_u16_untied:
-** tbl z0\.h, z1\.h, z4\.h
+** tbl z0\.h, {z1\.h}, z4\.h
** ret
*/
TEST_DUAL_Z (tbl_u16_untied, svuint16_t, svuint16_t,
diff --git a/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/tbl_u32.c
b/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/tbl_u32.c
index 494300436f10..d7450004cf6f 100644
--- a/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/tbl_u32.c
+++ b/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/tbl_u32.c
@@ -4,7 +4,7 @@
/*
** tbl_u32_tied1:
-** tbl z0\.s, z0\.s, z4\.s
+** tbl z0\.s, {z0\.s}, z4\.s
** ret
*/
TEST_DUAL_Z (tbl_u32_tied1, svuint32_t, svuint32_t,
@@ -13,7 +13,7 @@ TEST_DUAL_Z (tbl_u32_tied1, svuint32_t, svuint32_t,
/*
** tbl_u32_tied2:
-** tbl z0\.s, z4\.s, z0\.s
+** tbl z0\.s, {z4\.s}, z0\.s
** ret
*/
TEST_DUAL_Z_REV (tbl_u32_tied2, svuint32_t, svuint32_t,
@@ -22,7 +22,7 @@ TEST_DUAL_Z_REV (tbl_u32_tied2, svuint32_t, svuint32_t,
/*
** tbl_u32_untied:
-** tbl z0\.s, z1\.s, z4\.s
+** tbl z0\.s, {z1\.s}, z4\.s
** ret
*/
TEST_DUAL_Z (tbl_u32_untied, svuint32_t, svuint32_t,
diff --git a/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/tbl_u64.c
b/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/tbl_u64.c
index 158990e12c01..66e41250ac22 100644
--- a/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/tbl_u64.c
+++ b/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/tbl_u64.c
@@ -4,7 +4,7 @@
/*
** tbl_u64_tied1:
-** tbl z0\.d, z0\.d, z4\.d
+** tbl z0\.d, {z0\.d}, z4\.d
** ret
*/
TEST_DUAL_Z (tbl_u64_tied1, svuint64_t, svuint64_t,
@@ -13,7 +13,7 @@ TEST_DUAL_Z (tbl_u64_tied1, svuint64_t, svuint64_t,
/*
** tbl_u64_tied2:
-** tbl z0\.d, z4\.d, z0\.d
+** tbl z0\.d, {z4\.d}, z0\.d
** ret
*/
TEST_DUAL_Z_REV (tbl_u64_tied2, svuint64_t, svuint64_t,
@@ -22,7 +22,7 @@ TEST_DUAL_Z_REV (tbl_u64_tied2, svuint64_t, svuint64_t,
/*
** tbl_u64_untied:
-** tbl z0\.d, z1\.d, z4\.d
+** tbl z0\.d, {z1\.d}, z4\.d
** ret
*/
TEST_DUAL_Z (tbl_u64_untied, svuint64_t, svuint64_t,
diff --git a/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/tbl_u8.c
b/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/tbl_u8.c
index a46309a95f17..f1a234137857 100644
--- a/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/tbl_u8.c
+++ b/gcc/testsuite/gcc.target/aarch64/sve/acle/asm/tbl_u8.c
@@ -4,7 +4,7 @@
/*
** tbl_u8_tied1:
-** tbl z0\.b, z0\.b, z4\.b
+** tbl z0\.b, {z0\.b}, z4\.b
** ret
*/
TEST_DUAL_Z (tbl_u8_tied1, svuint8_t, svuint8_t,
@@ -13,7 +13,7 @@ TEST_DUAL_Z (tbl_u8_tied1, svuint8_t, svuint8_t,
/*
** tbl_u8_tied2:
-** tbl z0\.b, z4\.b, z0\.b
+** tbl z0\.b, {z4\.b}, z0\.b
** ret
*/
TEST_DUAL_Z_REV (tbl_u8_tied2, svuint8_t, svuint8_t,
@@ -22,7 +22,7 @@ TEST_DUAL_Z_REV (tbl_u8_tied2, svuint8_t, svuint8_t,
/*
** tbl_u8_untied:
-** tbl z0\.b, z1\.b, z4\.b
+** tbl z0\.b, {z1\.b}, z4\.b
** ret
*/
TEST_DUAL_Z (tbl_u8_untied, svuint8_t, svuint8_t,
diff --git a/gcc/testsuite/gcc.target/aarch64/sve/slp_perm_6.c
b/gcc/testsuite/gcc.target/aarch64/sve/slp_perm_6.c
index 28824611be8f..1a411292409a 100644
--- a/gcc/testsuite/gcc.target/aarch64/sve/slp_perm_6.c
+++ b/gcc/testsuite/gcc.target/aarch64/sve/slp_perm_6.c
@@ -19,4 +19,4 @@ f (uint8_t *restrict a, uint8_t *restrict b)
}
}
-/* { dg-final { scan-assembler-times {\ttbl\tz[0-9]+\.b, z[0-9]+\.b,
z[0-9]+\.b\n} 1 } } */
+/* { dg-final { scan-assembler-times {\ttbl\tz[0-9]+\.b, {z[0-9]+\.b},
z[0-9]+\.b\n} 1 } } */
diff --git a/gcc/testsuite/gcc.target/aarch64/sve/slp_perm_7.c
b/gcc/testsuite/gcc.target/aarch64/sve/slp_perm_7.c
index da9e0a271a05..8dc7f1faba0d 100644
--- a/gcc/testsuite/gcc.target/aarch64/sve/slp_perm_7.c
+++ b/gcc/testsuite/gcc.target/aarch64/sve/slp_perm_7.c
@@ -19,4 +19,4 @@ f (uint8_t *restrict a, uint8_t *restrict b)
}
}
-/* { dg-final { scan-assembler {\ttbl\tz[0-9]+\.b, z[0-9]+\.b, z[0-9]+\.b\n} }
} */
+/* { dg-final { scan-assembler {\ttbl\tz[0-9]+\.b, {z[0-9]+\.b}, z[0-9]+\.b\n}
} } */
diff --git a/gcc/testsuite/gcc.target/aarch64/sve/uzp1_1.c
b/gcc/testsuite/gcc.target/aarch64/sve/uzp1_1.c
index 789fb0c28e01..84c6c6f1c606 100644
--- a/gcc/testsuite/gcc.target/aarch64/sve/uzp1_1.c
+++ b/gcc/testsuite/gcc.target/aarch64/sve/uzp1_1.c
@@ -31,10 +31,10 @@ UZP1 (vnx4sf, ((vnx4si) { 0, 2, 4, 6, 8, 10, 12, 14 }));
UZP1 (vnx8hf, ((vnx8hi) { 0, 2, 4, 6, 8, 10, 12, 14,
16, 18, 20, 22, 24, 26, 28, 30 }));
-/* { dg-final { scan-assembler-not {\ttbl\tz[0-9]+\.d, z[0-9]+\.d,
z[0-9]+\.d\n} } } */
-/* { dg-final { scan-assembler-not {\ttbl\tz[0-9]+\.s, z[0-9]+\.s,
z[0-9]+\.s\n} } } */
-/* { dg-final { scan-assembler-not {\ttbl\tz[0-9]+\.h, z[0-9]+\.h,
z[0-9]+\.h\n} } } */
-/* { dg-final { scan-assembler-not {\ttbl\tz[0-9]+\.b, z[0-9]+\.b,
z[0-9]+\.b\n} } } */
+/* { dg-final { scan-assembler-not {\ttbl\t} } } */
+/* { dg-final { scan-assembler-not {\ttbl\t} } } */
+/* { dg-final { scan-assembler-not {\ttbl\t} } } */
+/* { dg-final { scan-assembler-not {\ttbl\t} } } */
/* { dg-final { scan-assembler-times {\tuzp1\tz[0-9]+\.d, z[0-9]+\.d,
z[0-9]+\.d\n} 2 } } */
/* { dg-final { scan-assembler-times {\tuzp1\tz[0-9]+\.s, z[0-9]+\.s,
z[0-9]+\.s\n} 2 } } */
diff --git a/gcc/testsuite/gcc.target/aarch64/sve/uzp2_1.c
b/gcc/testsuite/gcc.target/aarch64/sve/uzp2_1.c
index def490daa12e..1336cafc5c7e 100644
--- a/gcc/testsuite/gcc.target/aarch64/sve/uzp2_1.c
+++ b/gcc/testsuite/gcc.target/aarch64/sve/uzp2_1.c
@@ -30,10 +30,10 @@ UZP2 (vnx4sf, ((vnx4si) { 1, 3, 5, 7, 9, 11, 13, 15 }));
UZP2 (vnx8hf, ((vnx8hi) { 1, 3, 5, 7, 9, 11, 13, 15,
17, 19, 21, 23, 25, 27, 29, 31 }));
-/* { dg-final { scan-assembler-not {\ttbl\tz[0-9]+\.d, z[0-9]+\.d,
z[0-9]+\.d\n} } } */
-/* { dg-final { scan-assembler-not {\ttbl\tz[0-9]+\.s, z[0-9]+\.s,
z[0-9]+\.s\n} } } */
-/* { dg-final { scan-assembler-not {\ttbl\tz[0-9]+\.h, z[0-9]+\.h,
z[0-9]+\.h\n} } } */
-/* { dg-final { scan-assembler-not {\ttbl\tz[0-9]+\.b, z[0-9]+\.b,
z[0-9]+\.b\n} } } */
+/* { dg-final { scan-assembler-not {\ttbl\t} } } */
+/* { dg-final { scan-assembler-not {\ttbl\t} } } */
+/* { dg-final { scan-assembler-not {\ttbl\t} } } */
+/* { dg-final { scan-assembler-not {\ttbl\t} } } */
/* { dg-final { scan-assembler-times {\tuzp2\tz[0-9]+\.d, z[0-9]+\.d,
z[0-9]+\.d\n} 2 } } */
/* { dg-final { scan-assembler-times {\tuzp2\tz[0-9]+\.s, z[0-9]+\.s,
z[0-9]+\.s\n} 2 } } */
diff --git a/gcc/testsuite/gcc.target/aarch64/sve/vec_perm_1.c
b/gcc/testsuite/gcc.target/aarch64/sve/vec_perm_1.c
index 74a48bfdd603..6b60eb02f98d 100644
--- a/gcc/testsuite/gcc.target/aarch64/sve/vec_perm_1.c
+++ b/gcc/testsuite/gcc.target/aarch64/sve/vec_perm_1.c
@@ -26,7 +26,7 @@ VEC_PERM (vnx2df, vnx2di);
VEC_PERM (vnx4sf, vnx4si);
VEC_PERM (vnx8hf, vnx8hi);
-/* { dg-final { scan-assembler-times {\ttbl\tz[0-9]+\.d, z[0-9]+\.d,
z[0-9]+\.d\n} 4 } } */
-/* { dg-final { scan-assembler-times {\ttbl\tz[0-9]+\.s, z[0-9]+\.s,
z[0-9]+\.s\n} 4 } } */
-/* { dg-final { scan-assembler-times {\ttbl\tz[0-9]+\.h, z[0-9]+\.h,
z[0-9]+\.h\n} 4 } } */
-/* { dg-final { scan-assembler-times {\ttbl\tz[0-9]+\.b, z[0-9]+\.b,
z[0-9]+\.b\n} 2 } } */
+/* { dg-final { scan-assembler-times {\ttbl\tz[0-9]+\.d, {z[0-9]+\.d},
z[0-9]+\.d\n} 4 } } */
+/* { dg-final { scan-assembler-times {\ttbl\tz[0-9]+\.s, {z[0-9]+\.s},
z[0-9]+\.s\n} 4 } } */
+/* { dg-final { scan-assembler-times {\ttbl\tz[0-9]+\.h, {z[0-9]+\.h},
z[0-9]+\.h\n} 4 } } */
+/* { dg-final { scan-assembler-times {\ttbl\tz[0-9]+\.b, {z[0-9]+\.b},
z[0-9]+\.b\n} 2 } } */
diff --git a/gcc/testsuite/gcc.target/aarch64/sve/vec_perm_const_1.c
b/gcc/testsuite/gcc.target/aarch64/sve/vec_perm_const_1.c
index 3194342f280a..548cb49200c4 100644
--- a/gcc/testsuite/gcc.target/aarch64/sve/vec_perm_const_1.c
+++ b/gcc/testsuite/gcc.target/aarch64/sve/vec_perm_const_1.c
@@ -31,7 +31,7 @@ VEC_PERM_CONST (vnx4sf, ((vnx4si) { 1, 9, 13, 11, 2, 5, 4, 2
}));
VEC_PERM_CONST (vnx8hf, ((vnx8hi) { 8, 27, 5, 4, 21, 12, 13, 0,
22, 1, 8, 9, 3, 24, 15, 1 }));
-/* { dg-final { scan-assembler-times {\ttbl\tz[0-9]+\.d, z[0-9]+\.d,
z[0-9]+\.d\n} 4 } } */
-/* { dg-final { scan-assembler-times {\ttbl\tz[0-9]+\.s, z[0-9]+\.s,
z[0-9]+\.s\n} 4 } } */
-/* { dg-final { scan-assembler-times {\ttbl\tz[0-9]+\.h, z[0-9]+\.h,
z[0-9]+\.h\n} 4 } } */
-/* { dg-final { scan-assembler-times {\ttbl\tz[0-9]+\.b, z[0-9]+\.b,
z[0-9]+\.b\n} 2 } } */
+/* { dg-final { scan-assembler-times {\ttbl\tz[0-9]+\.d, {z[0-9]+\.d},
z[0-9]+\.d\n} 4 } } */
+/* { dg-final { scan-assembler-times {\ttbl\tz[0-9]+\.s, {z[0-9]+\.s},
z[0-9]+\.s\n} 4 } } */
+/* { dg-final { scan-assembler-times {\ttbl\tz[0-9]+\.h, {z[0-9]+\.h},
z[0-9]+\.h\n} 4 } } */
+/* { dg-final { scan-assembler-times {\ttbl\tz[0-9]+\.b, {z[0-9]+\.b},
z[0-9]+\.b\n} 2 } } */
diff --git a/gcc/testsuite/gcc.target/aarch64/sve/vec_perm_const_1_overrun.c
b/gcc/testsuite/gcc.target/aarch64/sve/vec_perm_const_1_overrun.c
index b0732d0cc770..34e34696ed26 100644
--- a/gcc/testsuite/gcc.target/aarch64/sve/vec_perm_const_1_overrun.c
+++ b/gcc/testsuite/gcc.target/aarch64/sve/vec_perm_const_1_overrun.c
@@ -62,7 +62,7 @@ VEC_PERM_CONST_OVERRUN (vnx8hf, ((vnx8hi) { 8 + (32 * 3),
27 + (32 * 1),
3 + (32 * 2), 24 + (32 * 2),
15 + (32 * 1), 1 + (32 * 1) }));
-/* { dg-final { scan-assembler-times {\ttbl\tz[0-9]+\.d, z[0-9]+\.d,
z[0-9]+\.d\n} 4 } } */
-/* { dg-final { scan-assembler-times {\ttbl\tz[0-9]+\.s, z[0-9]+\.s,
z[0-9]+\.s\n} 4 } } */
-/* { dg-final { scan-assembler-times {\ttbl\tz[0-9]+\.h, z[0-9]+\.h,
z[0-9]+\.h\n} 4 } } */
-/* { dg-final { scan-assembler-times {\ttbl\tz[0-9]+\.b, z[0-9]+\.b,
z[0-9]+\.b\n} 2 } } */
+/* { dg-final { scan-assembler-times {\ttbl\tz[0-9]+\.d, {z[0-9]+\.d},
z[0-9]+\.d\n} 4 } } */
+/* { dg-final { scan-assembler-times {\ttbl\tz[0-9]+\.s, {z[0-9]+\.s},
z[0-9]+\.s\n} 4 } } */
+/* { dg-final { scan-assembler-times {\ttbl\tz[0-9]+\.h, {z[0-9]+\.h},
z[0-9]+\.h\n} 4 } } */
+/* { dg-final { scan-assembler-times {\ttbl\tz[0-9]+\.b, {z[0-9]+\.b},
z[0-9]+\.b\n} 2 } } */
diff --git a/gcc/testsuite/gcc.target/aarch64/sve/vec_perm_const_single_1.c
b/gcc/testsuite/gcc.target/aarch64/sve/vec_perm_const_single_1.c
index 61122ba11b8f..cdbd9ef8506b 100644
--- a/gcc/testsuite/gcc.target/aarch64/sve/vec_perm_const_single_1.c
+++ b/gcc/testsuite/gcc.target/aarch64/sve/vec_perm_const_single_1.c
@@ -30,7 +30,7 @@ VEC_PERM_SINGLE (vnx4sf, ((vnx4si) { 4, 5, 6, 0, 2, 7, 4, 2
}));
VEC_PERM_SINGLE (vnx8hf, ((vnx8hi) { 8, 7, 5, 4, 11, 12, 13, 0,
1, 1, 8, 9, 3, 14, 15, 1 }));
-/* { dg-final { scan-assembler-times {\ttbl\tz[0-9]+\.d, z[0-9]+\.d,
z[0-9]+\.d\n} 2 } } */
-/* { dg-final { scan-assembler-times {\ttbl\tz[0-9]+\.s, z[0-9]+\.s,
z[0-9]+\.s\n} 2 } } */
-/* { dg-final { scan-assembler-times {\ttbl\tz[0-9]+\.h, z[0-9]+\.h,
z[0-9]+\.h\n} 2 } } */
-/* { dg-final { scan-assembler-times {\ttbl\tz[0-9]+\.b, z[0-9]+\.b,
z[0-9]+\.b\n} 1 } } */
+/* { dg-final { scan-assembler-times {\ttbl\tz[0-9]+\.d, {z[0-9]+\.d},
z[0-9]+\.d\n} 2 } } */
+/* { dg-final { scan-assembler-times {\ttbl\tz[0-9]+\.s, {z[0-9]+\.s},
z[0-9]+\.s\n} 2 } } */
+/* { dg-final { scan-assembler-times {\ttbl\tz[0-9]+\.h, {z[0-9]+\.h},
z[0-9]+\.h\n} 2 } } */
+/* { dg-final { scan-assembler-times {\ttbl\tz[0-9]+\.b, {z[0-9]+\.b},
z[0-9]+\.b\n} 1 } } */
diff --git a/gcc/testsuite/gcc.target/aarch64/sve/vec_perm_single_1.c
b/gcc/testsuite/gcc.target/aarch64/sve/vec_perm_single_1.c
index 41646d3c20d2..40d6da39896e 100644
--- a/gcc/testsuite/gcc.target/aarch64/sve/vec_perm_single_1.c
+++ b/gcc/testsuite/gcc.target/aarch64/sve/vec_perm_single_1.c
@@ -25,7 +25,7 @@ VEC_PERM (vnx2df, vnx2di)
VEC_PERM (vnx4sf, vnx4si)
VEC_PERM (vnx8hf, vnx8hi)
-/* { dg-final { scan-assembler-times {\ttbl\tz[0-9]+\.d, z[0-9]+\.d,
z[0-9]+\.d\n} 2 } } */
-/* { dg-final { scan-assembler-times {\ttbl\tz[0-9]+\.s, z[0-9]+\.s,
z[0-9]+\.s\n} 2 } } */
-/* { dg-final { scan-assembler-times {\ttbl\tz[0-9]+\.h, z[0-9]+\.h,
z[0-9]+\.h\n} 2 } } */
-/* { dg-final { scan-assembler-times {\ttbl\tz[0-9]+\.b, z[0-9]+\.b,
z[0-9]+\.b\n} 1 } } */
+/* { dg-final { scan-assembler-times {\ttbl\tz[0-9]+\.d, {z[0-9]+\.d},
z[0-9]+\.d\n} 2 } } */
+/* { dg-final { scan-assembler-times {\ttbl\tz[0-9]+\.s, {z[0-9]+\.s},
z[0-9]+\.s\n} 2 } } */
+/* { dg-final { scan-assembler-times {\ttbl\tz[0-9]+\.h, {z[0-9]+\.h},
z[0-9]+\.h\n} 2 } } */
+/* { dg-final { scan-assembler-times {\ttbl\tz[0-9]+\.b, {z[0-9]+\.b},
z[0-9]+\.b\n} 1 } } */
