From: Tim Northover Date: Tue, 1 Apr 2014 10:37:47 +0000 (+0000) Subject: ARM64: add missing ldN/stN intrinsics and enable tests. X-Git-Url: https://granicus.if.org/sourcecode?a=commitdiff_plain;h=11b8e17d8b1de0588ad0afce7b0b30f8446e4c30;p=clang ARM64: add missing ldN/stN intrinsics and enable tests. git-svn-id: https://llvm.org/svn/llvm-project/cfe/trunk@205296 91177308-0d34-0410-b5e6-96231b3b80d8 --- diff --git a/lib/CodeGen/CGBuiltin.cpp b/lib/CodeGen/CGBuiltin.cpp index c743b68d21..9b321b9bf5 100644 --- a/lib/CodeGen/CGBuiltin.cpp +++ b/lib/CodeGen/CGBuiltin.cpp @@ -6552,7 +6552,8 @@ Value *CodeGenFunction::EmitARM64BuiltinExpr(unsigned BuiltinID, llvm::PointerType::getUnqual(Ops[1]->getType())); return Builder.CreateStore(Ops[1], Ops[0]); } - case NEON::BI__builtin_neon_vld2_dup_v: { + case NEON::BI__builtin_neon_vld2_dup_v: + case NEON::BI__builtin_neon_vld2q_dup_v: { llvm::Type *PTy = llvm::PointerType::getUnqual(VTy->getElementType()); Ops[1] = Builder.CreateBitCast(Ops[1], PTy); @@ -6563,7 +6564,8 @@ Value *CodeGenFunction::EmitARM64BuiltinExpr(unsigned BuiltinID, llvm::PointerType::getUnqual(Ops[1]->getType())); return Builder.CreateStore(Ops[1], Ops[0]); } - case NEON::BI__builtin_neon_vld3_dup_v: { + case NEON::BI__builtin_neon_vld3_dup_v: + case NEON::BI__builtin_neon_vld3q_dup_v: { llvm::Type *PTy = llvm::PointerType::getUnqual(VTy->getElementType()); Ops[1] = Builder.CreateBitCast(Ops[1], PTy); @@ -6574,7 +6576,8 @@ Value *CodeGenFunction::EmitARM64BuiltinExpr(unsigned BuiltinID, llvm::PointerType::getUnqual(Ops[1]->getType())); return Builder.CreateStore(Ops[1], Ops[0]); } - case NEON::BI__builtin_neon_vld4_dup_v: { + case NEON::BI__builtin_neon_vld4_dup_v: + case NEON::BI__builtin_neon_vld4q_dup_v: { llvm::Type *PTy = llvm::PointerType::getUnqual(VTy->getElementType()); Ops[1] = Builder.CreateBitCast(Ops[1], PTy); diff --git a/test/CodeGen/aarch64-neon-ldst-one.c b/test/CodeGen/aarch64-neon-ldst-one.c index 737810ee18..2d63628e9b 100644 --- a/test/CodeGen/aarch64-neon-ldst-one.c +++ b/test/CodeGen/aarch64-neon-ldst-one.c @@ -1,2077 +1,2052 @@ // REQUIRES: aarch64-registered-target +// REQUIRES: arm64-registered-target // RUN: %clang_cc1 -triple aarch64-none-linux-gnu -target-feature +neon \ // RUN: -ffp-contract=fast -S -O3 -o - %s | FileCheck %s +// RUN: %clang_cc1 -triple arm64-none-linux-gnu \ +// RUN: -ffp-contract=fast -S -O3 -o - %s | FileCheck %s #include uint8x16_t test_vld1q_dup_u8(uint8_t *a) { // CHECK-LABEL: test_vld1q_dup_u8 return vld1q_dup_u8(a); - // CHECK: ld1r {v{{[0-9]+}}.16b}, [{{x[0-9]+|sp}}] + // CHECK: ld1r {{{ *v[0-9]+.16b *}}}, [{{x[0-9]+|sp}}] } uint16x8_t test_vld1q_dup_u16(uint16_t *a) { // CHECK-LABEL: test_vld1q_dup_u16 return vld1q_dup_u16(a); - // CHECK: ld1r {v{{[0-9]+}}.8h}, [{{x[0-9]+|sp}}] + // CHECK: ld1r {{{ *v[0-9]+.8h *}}}, [{{x[0-9]+|sp}}] } uint32x4_t test_vld1q_dup_u32(uint32_t *a) { // CHECK-LABEL: test_vld1q_dup_u32 return vld1q_dup_u32(a); - // CHECK: ld1r {v{{[0-9]+}}.4s}, [{{x[0-9]+|sp}}] + // CHECK: ld1r {{{ *v[0-9]+.4s *}}}, [{{x[0-9]+|sp}}] } uint64x2_t test_vld1q_dup_u64(uint64_t *a) { // CHECK-LABEL: test_vld1q_dup_u64 return vld1q_dup_u64(a); - // CHECK: ld1r {v{{[0-9]+}}.2d}, [{{x[0-9]+|sp}}] + // CHECK: ld1r {{{ *v[0-9]+.2d *}}}, [{{x[0-9]+|sp}}] } int8x16_t test_vld1q_dup_s8(int8_t *a) { // CHECK-LABEL: test_vld1q_dup_s8 return vld1q_dup_s8(a); - // CHECK: ld1r {v{{[0-9]+}}.16b}, [{{x[0-9]+|sp}}] + // CHECK: ld1r {{{ *v[0-9]+.16b *}}}, [{{x[0-9]+|sp}}] } int16x8_t test_vld1q_dup_s16(int16_t *a) { // CHECK-LABEL: test_vld1q_dup_s16 return vld1q_dup_s16(a); - // CHECK: ld1r {v{{[0-9]+}}.8h}, [{{x[0-9]+|sp}}] + // CHECK: ld1r {{{ *v[0-9]+.8h *}}}, [{{x[0-9]+|sp}}] } int32x4_t test_vld1q_dup_s32(int32_t *a) { // CHECK-LABEL: test_vld1q_dup_s32 return vld1q_dup_s32(a); - // CHECK: ld1r {v{{[0-9]+}}.4s}, [{{x[0-9]+|sp}}] + // CHECK: ld1r {{{ *v[0-9]+.4s *}}}, [{{x[0-9]+|sp}}] } int64x2_t test_vld1q_dup_s64(int64_t *a) { // CHECK-LABEL: test_vld1q_dup_s64 return vld1q_dup_s64(a); - // CHECK: ld1r {v{{[0-9]+}}.2d}, [{{x[0-9]+|sp}}] + // CHECK: ld1r {{{ *v[0-9]+.2d *}}}, [{{x[0-9]+|sp}}] } float16x8_t test_vld1q_dup_f16(float16_t *a) { // CHECK-LABEL: test_vld1q_dup_f16 return vld1q_dup_f16(a); - // CHECK: ld1r {v{{[0-9]+}}.8h}, [{{x[0-9]+|sp}}] + // CHECK: ld1r {{{ *v[0-9]+.8h *}}}, [{{x[0-9]+|sp}}] } float32x4_t test_vld1q_dup_f32(float32_t *a) { // CHECK-LABEL: test_vld1q_dup_f32 return vld1q_dup_f32(a); - // CHECK: ld1r {v{{[0-9]+}}.4s}, [{{x[0-9]+|sp}}] + // CHECK: ld1r {{{ *v[0-9]+.4s *}}}, [{{x[0-9]+|sp}}] } float64x2_t test_vld1q_dup_f64(float64_t *a) { // CHECK-LABEL: test_vld1q_dup_f64 return vld1q_dup_f64(a); - // CHECK: ld1r {v{{[0-9]+}}.2d}, [{{x[0-9]+|sp}}] + // CHECK: ld1r {{{ *v[0-9]+.2d *}}}, [{{x[0-9]+|sp}}] } poly8x16_t test_vld1q_dup_p8(poly8_t *a) { // CHECK-LABEL: test_vld1q_dup_p8 return vld1q_dup_p8(a); - // CHECK: ld1r {v{{[0-9]+}}.16b}, [{{x[0-9]+|sp}}] + // CHECK: ld1r {{{ *v[0-9]+.16b *}}}, [{{x[0-9]+|sp}}] } poly16x8_t test_vld1q_dup_p16(poly16_t *a) { // CHECK-LABEL: test_vld1q_dup_p16 return vld1q_dup_p16(a); - // CHECK: ld1r {v{{[0-9]+}}.8h}, [{{x[0-9]+|sp}}] + // CHECK: ld1r {{{ *v[0-9]+.8h *}}}, [{{x[0-9]+|sp}}] } poly64x2_t test_vld1q_dup_p64(poly64_t *a) { // CHECK-LABEL: test_vld1q_dup_p64 return vld1q_dup_p64(a); - // CHECK: ld1r {v{{[0-9]+}}.2d}, [{{x[0-9]+|sp}}] + // CHECK: ld1r {{{ *v[0-9]+.2d *}}}, [{{x[0-9]+|sp}}] } uint8x8_t test_vld1_dup_u8(uint8_t *a) { // CHECK-LABEL: test_vld1_dup_u8 return vld1_dup_u8(a); - // CHECK: ld1r {v{{[0-9]+}}.8b}, [{{x[0-9]+|sp}}] + // CHECK: ld1r {{{ *v[0-9]+.8b *}}}, [{{x[0-9]+|sp}}] } uint16x4_t test_vld1_dup_u16(uint16_t *a) { // CHECK-LABEL: test_vld1_dup_u16 return vld1_dup_u16(a); - // CHECK: ld1r {v{{[0-9]+}}.4h}, [{{x[0-9]+|sp}}] + // CHECK: ld1r {{{ *v[0-9]+.4h *}}}, [{{x[0-9]+|sp}}] } uint32x2_t test_vld1_dup_u32(uint32_t *a) { // CHECK-LABEL: test_vld1_dup_u32 return vld1_dup_u32(a); - // CHECK: ld1r {v{{[0-9]+}}.2s}, [{{x[0-9]+|sp}}] + // CHECK: ld1r {{{ *v[0-9]+.2s *}}}, [{{x[0-9]+|sp}}] } uint64x1_t test_vld1_dup_u64(uint64_t *a) { // CHECK-LABEL: test_vld1_dup_u64 return vld1_dup_u64(a); - // CHECK: ld1r {v{{[0-9]+}}.1d}, [{{x[0-9]+|sp}}] + // CHECK: {{ld1r {v[0-9]+.1d}|ldr d[0-9]+}}, [{{x[0-9]+|sp}}] } int8x8_t test_vld1_dup_s8(int8_t *a) { // CHECK-LABEL: test_vld1_dup_s8 return vld1_dup_s8(a); - // CHECK: ld1r {v{{[0-9]+}}.8b}, [{{x[0-9]+|sp}}] + // CHECK: ld1r {{{ *v[0-9]+.8b *}}}, [{{x[0-9]+|sp}}] } int16x4_t test_vld1_dup_s16(int16_t *a) { // CHECK-LABEL: test_vld1_dup_s16 return vld1_dup_s16(a); - // CHECK: ld1r {v{{[0-9]+}}.4h}, [{{x[0-9]+|sp}}] + // CHECK: ld1r {{{ *v[0-9]+.4h *}}}, [{{x[0-9]+|sp}}] } int32x2_t test_vld1_dup_s32(int32_t *a) { // CHECK-LABEL: test_vld1_dup_s32 return vld1_dup_s32(a); - // CHECK: ld1r {v{{[0-9]+}}.2s}, [{{x[0-9]+|sp}}] + // CHECK: ld1r {{{ *v[0-9]+.2s *}}}, [{{x[0-9]+|sp}}] } int64x1_t test_vld1_dup_s64(int64_t *a) { // CHECK-LABEL: test_vld1_dup_s64 return vld1_dup_s64(a); - // CHECK: ld1r {v{{[0-9]+}}.1d}, [{{x[0-9]+|sp}}] + // CHECK: {{ld1r {v[0-9]+.1d}|ldr d[0-9]+}}, [{{x[0-9]+|sp}}] } float16x4_t test_vld1_dup_f16(float16_t *a) { // CHECK-LABEL: test_vld1_dup_f16 return vld1_dup_f16(a); - // CHECK: ld1r {v{{[0-9]+}}.4h}, [{{x[0-9]+|sp}}] + // CHECK: ld1r {{{ *v[0-9]+.4h *}}}, [{{x[0-9]+|sp}}] } float32x2_t test_vld1_dup_f32(float32_t *a) { // CHECK-LABEL: test_vld1_dup_f32 return vld1_dup_f32(a); - // CHECK: ld1r {v{{[0-9]+}}.2s}, [{{x[0-9]+|sp}}] + // CHECK: ld1r {{{ *v[0-9]+.2s *}}}, [{{x[0-9]+|sp}}] } float64x1_t test_vld1_dup_f64(float64_t *a) { // CHECK-LABEL: test_vld1_dup_f64 return vld1_dup_f64(a); - // CHECK: ld1r {v{{[0-9]+}}.1d}, [{{x[0-9]+|sp}}] + // CHECK: {{ld1r {v[0-9]+.1d}|ldr d[0-9]+}}, [{{x[0-9]+|sp}}] } poly8x8_t test_vld1_dup_p8(poly8_t *a) { // CHECK-LABEL: test_vld1_dup_p8 return vld1_dup_p8(a); - // CHECK: ld1r {v{{[0-9]+}}.8b}, [{{x[0-9]+|sp}}] + // CHECK: ld1r {{{ *v[0-9]+.8b *}}}, [{{x[0-9]+|sp}}] } poly16x4_t test_vld1_dup_p16(poly16_t *a) { // CHECK-LABEL: test_vld1_dup_p16 return vld1_dup_p16(a); - // CHECK: ld1r {v{{[0-9]+}}.4h}, [{{x[0-9]+|sp}}] + // CHECK: ld1r {{{ *v[0-9]+.4h *}}}, [{{x[0-9]+|sp}}] } poly64x1_t test_vld1_dup_p64(poly64_t *a) { // CHECK-LABEL: test_vld1_dup_p64 return vld1_dup_p64(a); - // CHECK: ld1r {v{{[0-9]+}}.1d}, [{{x[0-9]+|sp}}] + // CHECK: {{ld1r {v[0-9]+.1d}|ldr d[0-9]+}}, [{{x[0-9]+|sp}}] } uint8x16x2_t test_vld2q_dup_u8(uint8_t *a) { // CHECK-LABEL: test_vld2q_dup_u8 return vld2q_dup_u8(a); - // CHECK: ld2r {v{{[0-9]+}}.16b, v{{[0-9]+}}.16b}, [{{x[0-9]+|sp}}] + // CHECK: ld2r {{{ *v[0-9]+.16b, v[0-9]+.16b *}}}, [{{x[0-9]+|sp}}] } uint16x8x2_t test_vld2q_dup_u16(uint16_t *a) { // CHECK-LABEL: test_vld2q_dup_u16 return vld2q_dup_u16(a); - // CHECK: ld2r {v{{[0-9]+}}.8h, v{{[0-9]+}}.8h}, [{{x[0-9]+|sp}}] + // CHECK: ld2r {{{ *v[0-9]+.8h, v[0-9]+.8h *}}}, [{{x[0-9]+|sp}}] } uint32x4x2_t test_vld2q_dup_u32(uint32_t *a) { // CHECK-LABEL: test_vld2q_dup_u32 return vld2q_dup_u32(a); - // CHECK: ld2r {v{{[0-9]+}}.4s, v{{[0-9]+}}.4s}, [{{x[0-9]+|sp}}] + // CHECK: ld2r {{{ *v[0-9]+.4s, v[0-9]+.4s *}}}, [{{x[0-9]+|sp}}] } uint64x2x2_t test_vld2q_dup_u64(uint64_t *a) { // CHECK-LABEL: test_vld2q_dup_u64 return vld2q_dup_u64(a); - // CHECK: ld2r {v{{[0-9]+}}.2d, v{{[0-9]+}}.2d}, [{{x[0-9]+|sp}}] + // CHECK: ld2r {{{ *v[0-9]+.2d, v[0-9]+.2d *}}}, [{{x[0-9]+|sp}}] } int8x16x2_t test_vld2q_dup_s8(int8_t *a) { // CHECK-LABEL: test_vld2q_dup_s8 return vld2q_dup_s8(a); - // CHECK: ld2r {v{{[0-9]+}}.16b, v{{[0-9]+}}.16b}, [{{x[0-9]+|sp}}] + // CHECK: ld2r {{{ *v[0-9]+.16b, v[0-9]+.16b *}}}, [{{x[0-9]+|sp}}] } int16x8x2_t test_vld2q_dup_s16(int16_t *a) { // CHECK-LABEL: test_vld2q_dup_s16 return vld2q_dup_s16(a); - // CHECK: ld2r {v{{[0-9]+}}.8h, v{{[0-9]+}}.8h}, [{{x[0-9]+|sp}}] + // CHECK: ld2r {{{ *v[0-9]+.8h, v[0-9]+.8h *}}}, [{{x[0-9]+|sp}}] } int32x4x2_t test_vld2q_dup_s32(int32_t *a) { // CHECK-LABEL: test_vld2q_dup_s32 return vld2q_dup_s32(a); - // CHECK: ld2r {v{{[0-9]+}}.4s, v{{[0-9]+}}.4s}, [{{x[0-9]+|sp}}] + // CHECK: ld2r {{{ *v[0-9]+.4s, v[0-9]+.4s *}}}, [{{x[0-9]+|sp}}] } int64x2x2_t test_vld2q_dup_s64(int64_t *a) { // CHECK-LABEL: test_vld2q_dup_s64 return vld2q_dup_s64(a); - // CHECK: ld2r {v{{[0-9]+}}.2d, v{{[0-9]+}}.2d}, [{{x[0-9]+|sp}}] + // CHECK: ld2r {{{ *v[0-9]+.2d, v[0-9]+.2d *}}}, [{{x[0-9]+|sp}}] } float16x8x2_t test_vld2q_dup_f16(float16_t *a) { // CHECK-LABEL: test_vld2q_dup_f16 return vld2q_dup_f16(a); - // CHECK: ld2r {v{{[0-9]+}}.8h, v{{[0-9]+}}.8h}, [{{x[0-9]+|sp}}] + // CHECK: ld2r {{{ *v[0-9]+.8h, v[0-9]+.8h *}}}, [{{x[0-9]+|sp}}] } float32x4x2_t test_vld2q_dup_f32(float32_t *a) { // CHECK-LABEL: test_vld2q_dup_f32 return vld2q_dup_f32(a); - // CHECK: ld2r {v{{[0-9]+}}.4s, v{{[0-9]+}}.4s}, [{{x[0-9]+|sp}}] + // CHECK: ld2r {{{ *v[0-9]+.4s, v[0-9]+.4s *}}}, [{{x[0-9]+|sp}}] } float64x2x2_t test_vld2q_dup_f64(float64_t *a) { // CHECK-LABEL: test_vld2q_dup_f64 return vld2q_dup_f64(a); - // CHECK: ld2r {v{{[0-9]+}}.2d, v{{[0-9]+}}.2d}, [{{x[0-9]+|sp}}] + // CHECK: ld2r {{{ *v[0-9]+.2d, v[0-9]+.2d *}}}, [{{x[0-9]+|sp}}] } poly8x16x2_t test_vld2q_dup_p8(poly8_t *a) { // CHECK-LABEL: test_vld2q_dup_p8 return vld2q_dup_p8(a); - // CHECK: ld2r {v{{[0-9]+}}.16b, v{{[0-9]+}}.16b}, [{{x[0-9]+|sp}}] + // CHECK: ld2r {{{ *v[0-9]+.16b, v[0-9]+.16b *}}}, [{{x[0-9]+|sp}}] } poly16x8x2_t test_vld2q_dup_p16(poly16_t *a) { // CHECK-LABEL: test_vld2q_dup_p16 return vld2q_dup_p16(a); - // CHECK: ld2r {v{{[0-9]+}}.8h, v{{[0-9]+}}.8h}, [{{x[0-9]+|sp}}] + // CHECK: ld2r {{{ *v[0-9]+.8h, v[0-9]+.8h *}}}, [{{x[0-9]+|sp}}] } poly64x2x2_t test_vld2q_dup_p64(poly64_t *a) { // CHECK-LABEL: test_vld2q_dup_p64 return vld2q_dup_p64(a); - // CHECK: ld2r {v{{[0-9]+}}.2d, v{{[0-9]+}}.2d}, [{{x[0-9]+|sp}}] + // CHECK: ld2r {{{ *v[0-9]+.2d, v[0-9]+.2d *}}}, [{{x[0-9]+|sp}}] } uint8x8x2_t test_vld2_dup_u8(uint8_t *a) { // CHECK-LABEL: test_vld2_dup_u8 return vld2_dup_u8(a); - // CHECK: ld2r {v{{[0-9]+}}.8b, v{{[0-9]+}}.8b}, [{{x[0-9]+|sp}}] + // CHECK: ld2r {{{ *v[0-9]+.8b, v[0-9]+.8b *}}}, [{{x[0-9]+|sp}}] } uint16x4x2_t test_vld2_dup_u16(uint16_t *a) { // CHECK-LABEL: test_vld2_dup_u16 return vld2_dup_u16(a); - // CHECK: ld2r {v{{[0-9]+}}.4h, v{{[0-9]+}}.4h}, [{{x[0-9]+|sp}}] + // CHECK: ld2r {{{ *v[0-9]+.4h, v[0-9]+.4h *}}}, [{{x[0-9]+|sp}}] } uint32x2x2_t test_vld2_dup_u32(uint32_t *a) { // CHECK-LABEL: test_vld2_dup_u32 return vld2_dup_u32(a); - // CHECK: ld2r {v{{[0-9]+}}.2s, v{{[0-9]+}}.2s}, [{{x[0-9]+|sp}}] + // CHECK: ld2r {{{ *v[0-9]+.2s, v[0-9]+.2s *}}}, [{{x[0-9]+|sp}}] } uint64x1x2_t test_vld2_dup_u64(uint64_t *a) { // CHECK-LABEL: test_vld2_dup_u64 return vld2_dup_u64(a); - // CHECK: ld1 {v{{[0-9]+}}.1d, v{{[0-9]+}}.1d}, [{{x[0-9]+|sp}}] + // CHECK: {{ld1|ld2r}} {{{ *v[0-9]+.1d, v[0-9]+.1d *}}}, [{{x[0-9]+|sp}}] } int8x8x2_t test_vld2_dup_s8(int8_t *a) { // CHECK-LABEL: test_vld2_dup_s8 return vld2_dup_s8(a); - // CHECK: ld2r {v{{[0-9]+}}.8b, v{{[0-9]+}}.8b}, [{{x[0-9]+|sp}}] + // CHECK: ld2r {{{ *v[0-9]+.8b, v[0-9]+.8b *}}}, [{{x[0-9]+|sp}}] } int16x4x2_t test_vld2_dup_s16(int16_t *a) { // CHECK-LABEL: test_vld2_dup_s16 return vld2_dup_s16(a); - // CHECK: ld2r {v{{[0-9]+}}.4h, v{{[0-9]+}}.4h}, [{{x[0-9]+|sp}}] + // CHECK: ld2r {{{ *v[0-9]+.4h, v[0-9]+.4h *}}}, [{{x[0-9]+|sp}}] } int32x2x2_t test_vld2_dup_s32(int32_t *a) { // CHECK-LABEL: test_vld2_dup_s32 return vld2_dup_s32(a); - // CHECK: ld2r {v{{[0-9]+}}.2s, v{{[0-9]+}}.2s}, [{{x[0-9]+|sp}}] + // CHECK: ld2r {{{ *v[0-9]+.2s, v[0-9]+.2s *}}}, [{{x[0-9]+|sp}}] } int64x1x2_t test_vld2_dup_s64(int64_t *a) { // CHECK-LABEL: test_vld2_dup_s64 return vld2_dup_s64(a); - // CHECK: ld1 {v{{[0-9]+}}.1d, v{{[0-9]+}}.1d}, [{{x[0-9]+|sp}}] + // CHECK: {{ld1|ld2r}} {{{ *v[0-9]+.1d, v[0-9]+.1d *}}}, [{{x[0-9]+|sp}}] } float16x4x2_t test_vld2_dup_f16(float16_t *a) { // CHECK-LABEL: test_vld2_dup_f16 return vld2_dup_f16(a); - // CHECK: ld2r {v{{[0-9]+}}.4h, v{{[0-9]+}}.4h}, [{{x[0-9]+|sp}}] + // CHECK: ld2r {{{ *v[0-9]+.4h, v[0-9]+.4h *}}}, [{{x[0-9]+|sp}}] } float32x2x2_t test_vld2_dup_f32(float32_t *a) { // CHECK-LABEL: test_vld2_dup_f32 return vld2_dup_f32(a); - // CHECK: ld2r {v{{[0-9]+}}.2s, v{{[0-9]+}}.2s}, [{{x[0-9]+|sp}}] + // CHECK: ld2r {{{ *v[0-9]+.2s, v[0-9]+.2s *}}}, [{{x[0-9]+|sp}}] } float64x1x2_t test_vld2_dup_f64(float64_t *a) { // CHECK-LABEL: test_vld2_dup_f64 return vld2_dup_f64(a); - // CHECK: ld1 {v{{[0-9]+}}.1d, v{{[0-9]+}}.1d}, [{{x[0-9]+|sp}}] + // CHECK: {{ld1|ld2r}} {{{ *v[0-9]+.1d, v[0-9]+.1d *}}}, [{{x[0-9]+|sp}}] } poly8x8x2_t test_vld2_dup_p8(poly8_t *a) { // CHECK-LABEL: test_vld2_dup_p8 return vld2_dup_p8(a); - // CHECK: ld2r {v{{[0-9]+}}.8b, v{{[0-9]+}}.8b}, [{{x[0-9]+|sp}}] + // CHECK: ld2r {{{ *v[0-9]+.8b, v[0-9]+.8b *}}}, [{{x[0-9]+|sp}}] } poly16x4x2_t test_vld2_dup_p16(poly16_t *a) { // CHECK-LABEL: test_vld2_dup_p16 return vld2_dup_p16(a); - // CHECK: ld2r {v{{[0-9]+}}.4h, v{{[0-9]+}}.4h}, [{{x[0-9]+|sp}}] + // CHECK: ld2r {{{ *v[0-9]+.4h, v[0-9]+.4h *}}}, [{{x[0-9]+|sp}}] } poly64x1x2_t test_vld2_dup_p64(poly64_t *a) { // CHECK-LABEL: test_vld2_dup_p64 return vld2_dup_p64(a); - // CHECK: ld1 {v{{[0-9]+}}.1d, v{{[0-9]+}}.1d}, [{{x[0-9]+|sp}}] + // CHECK: {{ld1|ld2r}} {{{ *v[0-9]+.1d, v[0-9]+.1d *}}}, [{{x[0-9]+|sp}}] } uint8x16x3_t test_vld3q_dup_u8(uint8_t *a) { // CHECK-LABEL: test_vld3q_dup_u8 return vld3q_dup_u8(a); - // CHECK: ld3r {v{{[0-9]+}}.16b, v{{[0-9]+}}.16b, v{{[0-9]+}}.16b}, + // CHECK: ld3r {{{ *v[0-9]+.16b, v[0-9]+.16b, v[0-9]+.16b *}}}, // [{{x[0-9]+|sp}}] } uint16x8x3_t test_vld3q_dup_u16(uint16_t *a) { // CHECK-LABEL: test_vld3q_dup_u16 return vld3q_dup_u16(a); - // CHECK: ld3r {v{{[0-9]+}}.8h, v{{[0-9]+}}.8h, v{{[0-9]+}}.8h}, + // CHECK: ld3r {{{ *v[0-9]+.8h, v[0-9]+.8h, v[0-9]+.8h *}}}, // [{{x[0-9]+|sp}}] } uint32x4x3_t test_vld3q_dup_u32(uint32_t *a) { // CHECK-LABEL: test_vld3q_dup_u32 return vld3q_dup_u32(a); - // CHECK: ld3r {v{{[0-9]+}}.4s, v{{[0-9]+}}.4s, v{{[0-9]+}}.4s}, + // CHECK: ld3r {{{ *v[0-9]+.4s, v[0-9]+.4s, v[0-9]+.4s *}}}, // [{{x[0-9]+|sp}}] } uint64x2x3_t test_vld3q_dup_u64(uint64_t *a) { // CHECK-LABEL: test_vld3q_dup_u64 return vld3q_dup_u64(a); - // CHECK: ld3r {v{{[0-9]+}}.2d, v{{[0-9]+}}.2d, v{{[0-9]+}}.2d}, + // CHECK: ld3r {{{ *v[0-9]+.2d, v[0-9]+.2d, v[0-9]+.2d *}}}, // [{{x[0-9]+|sp}}] } int8x16x3_t test_vld3q_dup_s8(int8_t *a) { // CHECK-LABEL: test_vld3q_dup_s8 return vld3q_dup_s8(a); - // CHECK: ld3r {v{{[0-9]+}}.16b, v{{[0-9]+}}.16b, v{{[0-9]+}}.16b}, + // CHECK: ld3r {{{ *v[0-9]+.16b, v[0-9]+.16b, v[0-9]+.16b *}}}, // [{{x[0-9]+|sp}}] } int16x8x3_t test_vld3q_dup_s16(int16_t *a) { // CHECK-LABEL: test_vld3q_dup_s16 return vld3q_dup_s16(a); - // CHECK: ld3r {v{{[0-9]+}}.8h, v{{[0-9]+}}.8h, v{{[0-9]+}}.8h}, + // CHECK: ld3r {{{ *v[0-9]+.8h, v[0-9]+.8h, v[0-9]+.8h *}}}, // [{{x[0-9]+|sp}}] } int32x4x3_t test_vld3q_dup_s32(int32_t *a) { // CHECK-LABEL: test_vld3q_dup_s32 return vld3q_dup_s32(a); - // CHECK: ld3r {v{{[0-9]+}}.4s, v{{[0-9]+}}.4s, v{{[0-9]+}}.4s}, + // CHECK: ld3r {{{ *v[0-9]+.4s, v[0-9]+.4s, v[0-9]+.4s *}}}, // [{{x[0-9]+|sp}}] } int64x2x3_t test_vld3q_dup_s64(int64_t *a) { // CHECK-LABEL: test_vld3q_dup_s64 return vld3q_dup_s64(a); - // CHECK: ld3r {v{{[0-9]+}}.2d, v{{[0-9]+}}.2d, v{{[0-9]+}}.2d}, + // CHECK: ld3r {{{ *v[0-9]+.2d, v[0-9]+.2d, v[0-9]+.2d *}}}, // [{{x[0-9]+|sp}}] } float16x8x3_t test_vld3q_dup_f16(float16_t *a) { // CHECK-LABEL: test_vld3q_dup_f16 return vld3q_dup_f16(a); - // CHECK: ld3r {v{{[0-9]+}}.8h, v{{[0-9]+}}.8h, v{{[0-9]+}}.8h}, + // CHECK: ld3r {{{ *v[0-9]+.8h, v[0-9]+.8h, v[0-9]+.8h *}}}, // [{{x[0-9]+|sp}}] } float32x4x3_t test_vld3q_dup_f32(float32_t *a) { // CHECK-LABEL: test_vld3q_dup_f32 return vld3q_dup_f32(a); - // CHECK: ld3r {v{{[0-9]+}}.4s, v{{[0-9]+}}.4s, v{{[0-9]+}}.4s}, + // CHECK: ld3r {{{ *v[0-9]+.4s, v[0-9]+.4s, v[0-9]+.4s *}}}, // [{{x[0-9]+|sp}}] } float64x2x3_t test_vld3q_dup_f64(float64_t *a) { // CHECK-LABEL: test_vld3q_dup_f64 return vld3q_dup_f64(a); - // CHECK: ld3r {v{{[0-9]+}}.2d, v{{[0-9]+}}.2d, v{{[0-9]+}}.2d}, + // CHECK: ld3r {{{ *v[0-9]+.2d, v[0-9]+.2d, v[0-9]+.2d *}}}, // [{{x[0-9]+|sp}}] } poly8x16x3_t test_vld3q_dup_p8(poly8_t *a) { // CHECK-LABEL: test_vld3q_dup_p8 return vld3q_dup_p8(a); - // CHECK: ld3r {v{{[0-9]+}}.16b, v{{[0-9]+}}.16b, v{{[0-9]+}}.16b}, + // CHECK: ld3r {{{ *v[0-9]+.16b, v[0-9]+.16b, v[0-9]+.16b *}}}, // [{{x[0-9]+|sp}}] } poly16x8x3_t test_vld3q_dup_p16(poly16_t *a) { // CHECK-LABEL: test_vld3q_dup_p16 return vld3q_dup_p16(a); - // CHECK: ld3r {v{{[0-9]+}}.8h, v{{[0-9]+}}.8h, v{{[0-9]+}}.8h}, + // CHECK: ld3r {{{ *v[0-9]+.8h, v[0-9]+.8h, v[0-9]+.8h *}}}, // [{{x[0-9]+|sp}}] } poly64x2x3_t test_vld3q_dup_p64(poly64_t *a) { // CHECK-LABEL: test_vld3q_dup_p64 return vld3q_dup_p64(a); - // CHECK: ld3r {v{{[0-9]+}}.2d, v{{[0-9]+}}.2d, v{{[0-9]+}}.2d}, + // CHECK: ld3r {{{ *v[0-9]+.2d, v[0-9]+.2d, v[0-9]+.2d *}}}, // [{{x[0-9]+|sp}}] } uint8x8x3_t test_vld3_dup_u8(uint8_t *a) { // CHECK-LABEL: test_vld3_dup_u8 return vld3_dup_u8(a); - // CHECK: ld3r {v{{[0-9]+}}.8b, v{{[0-9]+}}.8b, v{{[0-9]+}}.8b}, + // CHECK: ld3r {{{ *v[0-9]+.8b, v[0-9]+.8b, v[0-9]+.8b *}}}, // [{{x[0-9]+|sp}}] } uint16x4x3_t test_vld3_dup_u16(uint16_t *a) { // CHECK-LABEL: test_vld3_dup_u16 return vld3_dup_u16(a); - // CHECK: ld3r {v{{[0-9]+}}.4h, v{{[0-9]+}}.4h, v{{[0-9]+}}.4h}, + // CHECK: ld3r {{{ *v[0-9]+.4h, v[0-9]+.4h, v[0-9]+.4h *}}}, // [{{x[0-9]+|sp}}] } uint32x2x3_t test_vld3_dup_u32(uint32_t *a) { // CHECK-LABEL: test_vld3_dup_u32 return vld3_dup_u32(a); - // CHECK: ld3r {v{{[0-9]+}}.2s, v{{[0-9]+}}.2s, v{{[0-9]+}}.2s}, + // CHECK: ld3r {{{ *v[0-9]+.2s, v[0-9]+.2s, v[0-9]+.2s *}}}, // [{{x[0-9]+|sp}}] } uint64x1x3_t test_vld3_dup_u64(uint64_t *a) { // CHECK-LABEL: test_vld3_dup_u64 return vld3_dup_u64(a); - // CHECK: ld1 {v{{[0-9]+}}.1d, v{{[0-9]+}}.1d, v{{[0-9]+}}.1d}, + // CHECK: {{ld1|ld3r}} {{{ *v[0-9]+.1d, v[0-9]+.1d, v[0-9]+.1d *}}}, // [{{x[0-9]+|sp}}] } int8x8x3_t test_vld3_dup_s8(int8_t *a) { // CHECK-LABEL: test_vld3_dup_s8 return vld3_dup_s8(a); - // CHECK: ld3r {v{{[0-9]+}}.8b, v{{[0-9]+}}.8b, v{{[0-9]+}}.8b}, + // CHECK: ld3r {{{ *v[0-9]+.8b, v[0-9]+.8b, v[0-9]+.8b *}}}, // [{{x[0-9]+|sp}}] } int16x4x3_t test_vld3_dup_s16(int16_t *a) { // CHECK-LABEL: test_vld3_dup_s16 return vld3_dup_s16(a); - // CHECK: ld3r {v{{[0-9]+}}.4h, v{{[0-9]+}}.4h, v{{[0-9]+}}.4h}, + // CHECK: ld3r {{{ *v[0-9]+.4h, v[0-9]+.4h, v[0-9]+.4h *}}}, // [{{x[0-9]+|sp}}] } int32x2x3_t test_vld3_dup_s32(int32_t *a) { // CHECK-LABEL: test_vld3_dup_s32 return vld3_dup_s32(a); - // CHECK: ld3r {v{{[0-9]+}}.2s, v{{[0-9]+}}.2s, v{{[0-9]+}}.2s}, + // CHECK: ld3r {{{ *v[0-9]+.2s, v[0-9]+.2s, v[0-9]+.2s *}}}, // [{{x[0-9]+|sp}}] } int64x1x3_t test_vld3_dup_s64(int64_t *a) { // CHECK-LABEL: test_vld3_dup_s64 return vld3_dup_s64(a); - // CHECK: ld1 {v{{[0-9]+}}.1d, v{{[0-9]+}}.1d, v{{[0-9]+}}.1d}, + // CHECK: {{ld1|ld3r}} {{{ *v[0-9]+.1d, v[0-9]+.1d, v[0-9]+.1d *}}}, // [{{x[0-9]+|sp}}] } float16x4x3_t test_vld3_dup_f16(float16_t *a) { // CHECK-LABEL: test_vld3_dup_f16 return vld3_dup_f16(a); - // CHECK: ld3r {v{{[0-9]+}}.4h, v{{[0-9]+}}.4h, v{{[0-9]+}}.4h}, + // CHECK: ld3r {{{ *v[0-9]+.4h, v[0-9]+.4h, v[0-9]+.4h *}}}, // [{{x[0-9]+|sp}}] } float32x2x3_t test_vld3_dup_f32(float32_t *a) { // CHECK-LABEL: test_vld3_dup_f32 return vld3_dup_f32(a); - // CHECK: ld3r {v{{[0-9]+}}.2s, v{{[0-9]+}}.2s, v{{[0-9]+}}.2s}, + // CHECK: ld3r {{{ *v[0-9]+.2s, v[0-9]+.2s, v[0-9]+.2s *}}}, // [{{x[0-9]+|sp}}] } float64x1x3_t test_vld3_dup_f64(float64_t *a) { // CHECK-LABEL: test_vld3_dup_f64 return vld3_dup_f64(a); - // CHECK: ld1 {v{{[0-9]+}}.1d, v{{[0-9]+}}.1d, v{{[0-9]+}}.1d}, + // CHECK: {{ld1|ld3r}} {{{ *v[0-9]+.1d, v[0-9]+.1d, v[0-9]+.1d *}}}, // [{{x[0-9]+|sp}}] } poly8x8x3_t test_vld3_dup_p8(poly8_t *a) { // CHECK-LABEL: test_vld3_dup_p8 return vld3_dup_p8(a); - // CHECK: ld3r {v{{[0-9]+}}.8b, v{{[0-9]+}}.8b, v{{[0-9]+}}.8b}, + // CHECK: ld3r {{{ *v[0-9]+.8b, v[0-9]+.8b, v[0-9]+.8b *}}}, // [{{x[0-9]+|sp}}] } poly16x4x3_t test_vld3_dup_p16(poly16_t *a) { // CHECK-LABEL: test_vld3_dup_p16 return vld3_dup_p16(a); - // CHECK: ld3r {v{{[0-9]+}}.4h, v{{[0-9]+}}.4h, v{{[0-9]+}}.4h}, + // CHECK: ld3r {{{ *v[0-9]+.4h, v[0-9]+.4h, v[0-9]+.4h *}}}, // [{{x[0-9]+|sp}}] } poly64x1x3_t test_vld3_dup_p64(poly64_t *a) { // CHECK-LABEL: test_vld3_dup_p64 return vld3_dup_p64(a); - // CHECK: ld1 {v{{[0-9]+}}.1d, v{{[0-9]+}}.1d, v{{[0-9]+}}.1d}, + // CHECK: {{ld1|ld3r}} {{{ *v[0-9]+.1d, v[0-9]+.1d, v[0-9]+.1d *}}}, // [{{x[0-9]+|sp}}] } uint8x16x4_t test_vld4q_dup_u8(uint8_t *a) { // CHECK-LABEL: test_vld4q_dup_u8 return vld4q_dup_u8(a); - // CHECK: ld4r {v{{[0-9]+}}.16b, v{{[0-9]+}}.16b, v{{[0-9]+}}.16b, - // v{{[0-9]+}}.16b}, [{{x[0-9]+|sp}}] + // CHECK: ld4r {{{ *v[0-9]+.16b, v[0-9]+.16b, v[0-9]+.16b, v[0-9]+.16b *}}}, [{{x[0-9]+|sp}}] } uint16x8x4_t test_vld4q_dup_u16(uint16_t *a) { // CHECK-LABEL: test_vld4q_dup_u16 return vld4q_dup_u16(a); - // CHECK: ld4r {v{{[0-9]+}}.8h, v{{[0-9]+}}.8h, v{{[0-9]+}}.8h, - // v{{[0-9]+}}.8h}, [{{x[0-9]+|sp}}] + // CHECK: ld4r {{{ *v[0-9]+.8h, v[0-9]+.8h, v[0-9]+.8h, v[0-9]+.8h *}}}, [{{x[0-9]+|sp}}] } uint32x4x4_t test_vld4q_dup_u32(uint32_t *a) { // CHECK-LABEL: test_vld4q_dup_u32 return vld4q_dup_u32(a); - // CHECK: ld4r {v{{[0-9]+}}.4s, v{{[0-9]+}}.4s, v{{[0-9]+}}.4s, - // v{{[0-9]+}}.4s}, [{{x[0-9]+|sp}}] + // CHECK: ld4r {{{ *v[0-9]+.4s, v[0-9]+.4s, v[0-9]+.4s, v[0-9]+.4s *}}}, [{{x[0-9]+|sp}}] } uint64x2x4_t test_vld4q_dup_u64(uint64_t *a) { // CHECK-LABEL: test_vld4q_dup_u64 return vld4q_dup_u64(a); - // CHECK: ld4r {v{{[0-9]+}}.2d, v{{[0-9]+}}.2d, v{{[0-9]+}}.2d, - // v{{[0-9]+}}.2d}, [{{x[0-9]+|sp}}] + // CHECK: ld4r {{{ *v[0-9]+.2d, v[0-9]+.2d, v[0-9]+.2d, v[0-9]+.2d *}}}, [{{x[0-9]+|sp}}] } int8x16x4_t test_vld4q_dup_s8(int8_t *a) { // CHECK-LABEL: test_vld4q_dup_s8 return vld4q_dup_s8(a); - // CHECK: ld4r {v{{[0-9]+}}.16b, v{{[0-9]+}}.16b, v{{[0-9]+}}.16b, - // v{{[0-9]+}}.16b}, [{{x[0-9]+|sp}}] + // CHECK: ld4r {{{ *v[0-9]+.16b, v[0-9]+.16b, v[0-9]+.16b, v[0-9]+.16b *}}}, [{{x[0-9]+|sp}}] } int16x8x4_t test_vld4q_dup_s16(int16_t *a) { // CHECK-LABEL: test_vld4q_dup_s16 return vld4q_dup_s16(a); - // CHECK: ld4r {v{{[0-9]+}}.8h, v{{[0-9]+}}.8h, v{{[0-9]+}}.8h, - // v{{[0-9]+}}.8h}, [{{x[0-9]+|sp}}] + // CHECK: ld4r {{{ *v[0-9]+.8h, v[0-9]+.8h, v[0-9]+.8h, v[0-9]+.8h *}}}, [{{x[0-9]+|sp}}] } int32x4x4_t test_vld4q_dup_s32(int32_t *a) { // CHECK-LABEL: test_vld4q_dup_s32 return vld4q_dup_s32(a); - // CHECK: ld4r {v{{[0-9]+}}.4s, v{{[0-9]+}}.4s, v{{[0-9]+}}.4s, - // v{{[0-9]+}}.4s}, [{{x[0-9]+|sp}}] + // CHECK: ld4r {{{ *v[0-9]+.4s, v[0-9]+.4s, v[0-9]+.4s, v[0-9]+.4s *}}}, [{{x[0-9]+|sp}}] } int64x2x4_t test_vld4q_dup_s64(int64_t *a) { // CHECK-LABEL: test_vld4q_dup_s64 return vld4q_dup_s64(a); - // CHECK: ld4r {v{{[0-9]+}}.2d, v{{[0-9]+}}.2d, v{{[0-9]+}}.2d, - // v{{[0-9]+}}.2d}, [{{x[0-9]+|sp}}] + // CHECK: ld4r {{{ *v[0-9]+.2d, v[0-9]+.2d, v[0-9]+.2d, v[0-9]+.2d *}}}, [{{x[0-9]+|sp}}] } float16x8x4_t test_vld4q_dup_f16(float16_t *a) { // CHECK-LABEL: test_vld4q_dup_f16 return vld4q_dup_f16(a); - // CHECK: ld4r {v{{[0-9]+}}.8h, v{{[0-9]+}}.8h, v{{[0-9]+}}.8h, - // v{{[0-9]+}}.8h}, [{{x[0-9]+|sp}}] + // CHECK: ld4r {{{ *v[0-9]+.8h, v[0-9]+.8h, v[0-9]+.8h, v[0-9]+.8h *}}}, [{{x[0-9]+|sp}}] } float32x4x4_t test_vld4q_dup_f32(float32_t *a) { // CHECK-LABEL: test_vld4q_dup_f32 return vld4q_dup_f32(a); - // CHECK: ld4r {v{{[0-9]+}}.4s, v{{[0-9]+}}.4s, v{{[0-9]+}}.4s, - // v{{[0-9]+}}.4s}, [{{x[0-9]+|sp}}] + // CHECK: ld4r {{{ *v[0-9]+.4s, v[0-9]+.4s, v[0-9]+.4s, v[0-9]+.4s *}}}, [{{x[0-9]+|sp}}] } float64x2x4_t test_vld4q_dup_f64(float64_t *a) { // CHECK-LABEL: test_vld4q_dup_f64 return vld4q_dup_f64(a); - // CHECK: ld4r {v{{[0-9]+}}.2d, v{{[0-9]+}}.2d, v{{[0-9]+}}.2d, - // v{{[0-9]+}}.4s}, [{{x[0-9]+|sp}}] + // CHECK: ld4r {{{ *v[0-9]+.2d, v[0-9]+.2d, v[0-9]+.2d, v[0-9]+.2d *}}}, [{{x[0-9]+|sp}}] } poly8x16x4_t test_vld4q_dup_p8(poly8_t *a) { // CHECK-LABEL: test_vld4q_dup_p8 return vld4q_dup_p8(a); - // CHECK: ld4r {v{{[0-9]+}}.16b, v{{[0-9]+}}.16b, v{{[0-9]+}}.16b, - // v{{[0-9]+}}.16b}, [{{x[0-9]+|sp}}] + // CHECK: ld4r {{{ *v[0-9]+.16b, v[0-9]+.16b, v[0-9]+.16b, v[0-9]+.16b *}}}, [{{x[0-9]+|sp}}] } poly16x8x4_t test_vld4q_dup_p16(poly16_t *a) { // CHECK-LABEL: test_vld4q_dup_p16 return vld4q_dup_p16(a); - // CHECK: ld4r {v{{[0-9]+}}.8h, v{{[0-9]+}}.8h, v{{[0-9]+}}.8h, - // v{{[0-9]+}}.8h}, [{{x[0-9]+|sp}}] + // CHECK: ld4r {{{ *v[0-9]+.8h, v[0-9]+.8h, v[0-9]+.8h, v[0-9]+.8h *}}}, [{{x[0-9]+|sp}}] } poly64x2x4_t test_vld4q_dup_p64(poly64_t *a) { // CHECK-LABEL: test_vld4q_dup_p64 return vld4q_dup_p64(a); - // CHECK: ld4r {v{{[0-9]+}}.2d, v{{[0-9]+}}.2d, v{{[0-9]+}}.2d, - // v{{[0-9]+}}.2d}, [{{x[0-9]+|sp}}] + // CHECK: ld4r {{{ *v[0-9]+.2d, v[0-9]+.2d, v[0-9]+.2d, v[0-9]+.2d *}}}, [{{x[0-9]+|sp}}] } uint8x8x4_t test_vld4_dup_u8(uint8_t *a) { // CHECK-LABEL: test_vld4_dup_u8 return vld4_dup_u8(a); - // CHECK: ld4r {v{{[0-9]+}}.8b, v{{[0-9]+}}.8b, v{{[0-9]+}}.8b, - // v{{[0-9]+}}.8b}, [{{x[0-9]+|sp}}] + // CHECK: ld4r {{{ *v[0-9]+.8b, v[0-9]+.8b, v[0-9]+.8b, v[0-9]+.8b *}}}, [{{x[0-9]+|sp}}] } uint16x4x4_t test_vld4_dup_u16(uint16_t *a) { // CHECK-LABEL: test_vld4_dup_u16 return vld4_dup_u16(a); - // CHECK: ld4r {v{{[0-9]+}}.4h, v{{[0-9]+}}.4h, v{{[0-9]+}}.4h, - // v{{[0-9]+}}.4h}, [{{x[0-9]+|sp}}] + // CHECK: ld4r {{{ *v[0-9]+.4h, v[0-9]+.4h, v[0-9]+.4h, v[0-9]+.4h *}}}, [{{x[0-9]+|sp}}] } uint32x2x4_t test_vld4_dup_u32(uint32_t *a) { // CHECK-LABEL: test_vld4_dup_u32 return vld4_dup_u32(a); - // CHECK: ld4r {v{{[0-9]+}}.2s, v{{[0-9]+}}.2s, v{{[0-9]+}}.2s, - // v{{[0-9]+}}.2s}, [{{x[0-9]+|sp}}] + // CHECK: ld4r {{{ *v[0-9]+.2s, v[0-9]+.2s, v[0-9]+.2s, v[0-9]+.2s *}}}, [{{x[0-9]+|sp}}] } uint64x1x4_t test_vld4_dup_u64(uint64_t *a) { // CHECK-LABEL: test_vld4_dup_u64 return vld4_dup_u64(a); - // CHECK: ld1 {v{{[0-9]+}}.1d, v{{[0-9]+}}.1d, v{{[0-9]+}}.1d, - // v{{[0-9]+}}.1d}, [{{x[0-9]+|sp}}] + // CHECK: {{ld1|ld4r}} {{{ *v[0-9]+.1d, v[0-9]+.1d, v[0-9]+.1d, v[0-9]+.1d *}}}, [{{x[0-9]+|sp}}] } int8x8x4_t test_vld4_dup_s8(int8_t *a) { // CHECK-LABEL: test_vld4_dup_s8 return vld4_dup_s8(a); - // CHECK: ld4r {v{{[0-9]+}}.8b, v{{[0-9]+}}.8b, v{{[0-9]+}}.8b, - // v{{[0-9]+}}.8b}, [{{x[0-9]+|sp}}] + // CHECK: ld4r {{{ *v[0-9]+.8b, v[0-9]+.8b, v[0-9]+.8b, v[0-9]+.8b *}}}, [{{x[0-9]+|sp}}] } int16x4x4_t test_vld4_dup_s16(int16_t *a) { // CHECK-LABEL: test_vld4_dup_s16 return vld4_dup_s16(a); - // CHECK: ld4r {v{{[0-9]+}}.4h, v{{[0-9]+}}.4h, v{{[0-9]+}}.4h, - // v{{[0-9]+}}.4h}, [{{x[0-9]+|sp}}] + // CHECK: ld4r {{{ *v[0-9]+.4h, v[0-9]+.4h, v[0-9]+.4h, v[0-9]+.4h *}}}, [{{x[0-9]+|sp}}] } int32x2x4_t test_vld4_dup_s32(int32_t *a) { // CHECK-LABEL: test_vld4_dup_s32 return vld4_dup_s32(a); - // CHECK: ld4r {v{{[0-9]+}}.2s, v{{[0-9]+}}.2s, v{{[0-9]+}}.2s, - // v{{[0-9]+}}.2s}, [{{x[0-9]+|sp}}] + // CHECK: ld4r {{{ *v[0-9]+.2s, v[0-9]+.2s, v[0-9]+.2s, v[0-9]+.2s *}}}, [{{x[0-9]+|sp}}] } int64x1x4_t test_vld4_dup_s64(int64_t *a) { // CHECK-LABEL: test_vld4_dup_s64 return vld4_dup_s64(a); - // CHECK: ld1 {v{{[0-9]+}}.1d, v{{[0-9]+}}.1d, v{{[0-9]+}}.1d, - // v{{[0-9]+}}.1d}, [{{x[0-9]+|sp}}] + // CHECK: {{ld1|ld4r}} {{{ *v[0-9]+.1d, v[0-9]+.1d, v[0-9]+.1d, v[0-9]+.1d *}}}, [{{x[0-9]+|sp}}] } float16x4x4_t test_vld4_dup_f16(float16_t *a) { // CHECK-LABEL: test_vld4_dup_f16 return vld4_dup_f16(a); - // CHECK: ld4r {v{{[0-9]+}}.4h, v{{[0-9]+}}.4h, v{{[0-9]+}}.4h, - // v{{[0-9]+}}.4h}, [{{x[0-9]+|sp}}] + // CHECK: ld4r {{{ *v[0-9]+.4h, v[0-9]+.4h, v[0-9]+.4h, v[0-9]+.4h *}}}, [{{x[0-9]+|sp}}] } float32x2x4_t test_vld4_dup_f32(float32_t *a) { // CHECK-LABEL: test_vld4_dup_f32 return vld4_dup_f32(a); - // CHECK: ld4r {v{{[0-9]+}}.2s, v{{[0-9]+}}.2s, v{{[0-9]+}}.2s, - // v{{[0-9]+}}.2s}, [{{x[0-9]+|sp}}] + // CHECK: ld4r {{{ *v[0-9]+.2s, v[0-9]+.2s, v[0-9]+.2s, v[0-9]+.2s *}}}, [{{x[0-9]+|sp}}] } float64x1x4_t test_vld4_dup_f64(float64_t *a) { // CHECK-LABEL: test_vld4_dup_f64 return vld4_dup_f64(a); - // CHECK: ld1 {v{{[0-9]+}}.1d, v{{[0-9]+}}.1d, v{{[0-9]+}}.1d, - // v{{[0-9]+}}.1d}, [{{x[0-9]+|sp}}] + // CHECK: {{ld1|ld4r}} {{{ *v[0-9]+.1d, v[0-9]+.1d, v[0-9]+.1d, v[0-9]+.1d *}}}, [{{x[0-9]+|sp}}] } poly8x8x4_t test_vld4_dup_p8(poly8_t *a) { // CHECK-LABEL: test_vld4_dup_p8 return vld4_dup_p8(a); - // CHECK: ld4r {v{{[0-9]+}}.8b, v{{[0-9]+}}.8b, v{{[0-9]+}}.8b, - // v{{[0-9]+}}.8b}, [{{x[0-9]+|sp}}] + // CHECK: ld4r {{{ *v[0-9]+.8b, v[0-9]+.8b, v[0-9]+.8b, v[0-9]+.8b *}}}, [{{x[0-9]+|sp}}] } poly16x4x4_t test_vld4_dup_p16(poly16_t *a) { // CHECK-LABEL: test_vld4_dup_p16 return vld4_dup_p16(a); - // CHECK: ld4r {v{{[0-9]+}}.4h, v{{[0-9]+}}.4h, v{{[0-9]+}}.4h, - // v{{[0-9]+}}.4h}, [{{x[0-9]+|sp}}] + // CHECK: ld4r {{{ *v[0-9]+.4h, v[0-9]+.4h, v[0-9]+.4h, v[0-9]+.4h *}}}, [{{x[0-9]+|sp}}] } poly64x1x4_t test_vld4_dup_p64(poly64_t *a) { // CHECK-LABEL: test_vld4_dup_p64 return vld4_dup_p64(a); - // CHECK: ld1 {v{{[0-9]+}}.1d, v{{[0-9]+}}.1d, v{{[0-9]+}}.1d, - // v{{[0-9]+}}.1d}, [{{x[0-9]+|sp}}] + // CHECK: {{ld1|ld4r}} {{{ *v[0-9]+.1d, v[0-9]+.1d, v[0-9]+.1d, v[0-9]+.1d *}}}, [{{x[0-9]+|sp}}] } uint8x16_t test_vld1q_lane_u8(uint8_t *a, uint8x16_t b) { // CHECK-LABEL: test_vld1q_lane_u8 return vld1q_lane_u8(a, b, 15); - // CHECK: ld1 {v{{[0-9]+}}.b}[15], [{{x[0-9]+|sp}}] + // CHECK: ld1 {{{ *v[0-9]+.b *}}}[15], [{{x[0-9]+|sp}}] } uint16x8_t test_vld1q_lane_u16(uint16_t *a, uint16x8_t b) { // CHECK-LABEL: test_vld1q_lane_u16 return vld1q_lane_u16(a, b, 7); - // CHECK: ld1 {v{{[0-9]+}}.h}[7], [{{x[0-9]+|sp}}] + // CHECK: ld1 {{{ *v[0-9]+.h *}}}[7], [{{x[0-9]+|sp}}] } uint32x4_t test_vld1q_lane_u32(uint32_t *a, uint32x4_t b) { // CHECK-LABEL: test_vld1q_lane_u32 return vld1q_lane_u32(a, b, 3); - // CHECK: ld1 {v{{[0-9]+}}.s}[3], [{{x[0-9]+|sp}}] + // CHECK: ld1 {{{ *v[0-9]+.s *}}}[3], [{{x[0-9]+|sp}}] } uint64x2_t test_vld1q_lane_u64(uint64_t *a, uint64x2_t b) { // CHECK-LABEL: test_vld1q_lane_u64 return vld1q_lane_u64(a, b, 1); - // CHECK: ld1 {v{{[0-9]+}}.d}[1], [{{x[0-9]+|sp}}] + // CHECK: ld1 {{{ *v[0-9]+.d *}}}[1], [{{x[0-9]+|sp}}] } int8x16_t test_vld1q_lane_s8(int8_t *a, int8x16_t b) { // CHECK-LABEL: test_vld1q_lane_s8 return vld1q_lane_s8(a, b, 15); - // CHECK: ld1 {v{{[0-9]+}}.b}[15], [{{x[0-9]+|sp}}] + // CHECK: ld1 {{{ *v[0-9]+.b *}}}[15], [{{x[0-9]+|sp}}] } int16x8_t test_vld1q_lane_s16(int16_t *a, int16x8_t b) { // CHECK-LABEL: test_vld1q_lane_s16 return vld1q_lane_s16(a, b, 7); - // CHECK: ld1 {v{{[0-9]+}}.h}[7], [{{x[0-9]+|sp}}] + // CHECK: ld1 {{{ *v[0-9]+.h *}}}[7], [{{x[0-9]+|sp}}] } int32x4_t test_vld1q_lane_s32(int32_t *a, int32x4_t b) { // CHECK-LABEL: test_vld1q_lane_s32 return vld1q_lane_s32(a, b, 3); - // CHECK: ld1 {v{{[0-9]+}}.s}[3], [{{x[0-9]+|sp}}] + // CHECK: ld1 {{{ *v[0-9]+.s *}}}[3], [{{x[0-9]+|sp}}] } int64x2_t test_vld1q_lane_s64(int64_t *a, int64x2_t b) { // CHECK-LABEL: test_vld1q_lane_s64 return vld1q_lane_s64(a, b, 1); - // CHECK: ld1 {v{{[0-9]+}}.d}[1], [{{x[0-9]+|sp}}] + // CHECK: ld1 {{{ *v[0-9]+.d *}}}[1], [{{x[0-9]+|sp}}] } float16x8_t test_vld1q_lane_f16(float16_t *a, float16x8_t b) { // CHECK-LABEL: test_vld1q_lane_f16 return vld1q_lane_f16(a, b, 7); - // CHECK: ld1 {v{{[0-9]+}}.h}[7], [{{x[0-9]+|sp}}] + // CHECK: ld1 {{{ *v[0-9]+.h *}}}[7], [{{x[0-9]+|sp}}] } float32x4_t test_vld1q_lane_f32(float32_t *a, float32x4_t b) { // CHECK-LABEL: test_vld1q_lane_f32 return vld1q_lane_f32(a, b, 3); - // CHECK: ld1 {v{{[0-9]+}}.s}[3], [{{x[0-9]+|sp}}] + // CHECK: ld1 {{{ *v[0-9]+.s *}}}[3], [{{x[0-9]+|sp}}] } float64x2_t test_vld1q_lane_f64(float64_t *a, float64x2_t b) { // CHECK-LABEL: test_vld1q_lane_f64 return vld1q_lane_f64(a, b, 1); - // CHECK: ld1 {v{{[0-9]+}}.d}[1], [{{x[0-9]+|sp}}] + // CHECK: ld1 {{{ *v[0-9]+.d *}}}[1], [{{x[0-9]+|sp}}] } poly8x16_t test_vld1q_lane_p8(poly8_t *a, poly8x16_t b) { // CHECK-LABEL: test_vld1q_lane_p8 return vld1q_lane_p8(a, b, 15); - // CHECK: ld1 {v{{[0-9]+}}.b}[15], [{{x[0-9]+|sp}}] + // CHECK: ld1 {{{ *v[0-9]+.b *}}}[15], [{{x[0-9]+|sp}}] } poly16x8_t test_vld1q_lane_p16(poly16_t *a, poly16x8_t b) { // CHECK-LABEL: test_vld1q_lane_p16 return vld1q_lane_p16(a, b, 7); - // CHECK: ld1 {v{{[0-9]+}}.h}[7], [{{x[0-9]+|sp}}] + // CHECK: ld1 {{{ *v[0-9]+.h *}}}[7], [{{x[0-9]+|sp}}] } poly64x2_t test_vld1q_lane_p64(poly64_t *a, poly64x2_t b) { // CHECK-LABEL: test_vld1q_lane_p64 return vld1q_lane_p64(a, b, 1); - // CHECK: ld1 {v{{[0-9]+}}.d}[1], [{{x[0-9]+|sp}}] + // CHECK: ld1 {{{ *v[0-9]+.d *}}}[1], [{{x[0-9]+|sp}}] } uint8x8_t test_vld1_lane_u8(uint8_t *a, uint8x8_t b) { // CHECK-LABEL: test_vld1_lane_u8 return vld1_lane_u8(a, b, 7); - // CHECK: ld1 {v{{[0-9]+}}.b}[7], [{{x[0-9]+|sp}}] + // CHECK: ld1 {{{ *v[0-9]+.b *}}}[7], [{{x[0-9]+|sp}}] } uint16x4_t test_vld1_lane_u16(uint16_t *a, uint16x4_t b) { // CHECK-LABEL: test_vld1_lane_u16 return vld1_lane_u16(a, b, 3); - // CHECK: ld1 {v{{[0-9]+}}.h}[3], [{{x[0-9]+|sp}}] + // CHECK: ld1 {{{ *v[0-9]+.h *}}}[3], [{{x[0-9]+|sp}}] } uint32x2_t test_vld1_lane_u32(uint32_t *a, uint32x2_t b) { // CHECK-LABEL: test_vld1_lane_u32 return vld1_lane_u32(a, b, 1); - // CHECK: ld1 {v{{[0-9]+}}.s}[1], [{{x[0-9]+|sp}}] + // CHECK: ld1 {{{ *v[0-9]+.s *}}}[1], [{{x[0-9]+|sp}}] } uint64x1_t test_vld1_lane_u64(uint64_t *a, uint64x1_t b) { // CHECK-LABEL: test_vld1_lane_u64 return vld1_lane_u64(a, b, 0); - // CHECK: ld1r {v{{[0-9]+}}.1d}, [{{x[0-9]+|sp}}] + // CHECK: {{ld1r {v[0-9]+.1d}|ldr d[0-9]+}}, [{{x[0-9]+|sp}}] } int8x8_t test_vld1_lane_s8(int8_t *a, int8x8_t b) { // CHECK-LABEL: test_vld1_lane_s8 return vld1_lane_s8(a, b, 7); - // CHECK: ld1 {v{{[0-9]+}}.b}[7], [{{x[0-9]+|sp}}] + // CHECK: ld1 {{{ *v[0-9]+.b *}}}[7], [{{x[0-9]+|sp}}] } int16x4_t test_vld1_lane_s16(int16_t *a, int16x4_t b) { // CHECK-LABEL: test_vld1_lane_s16 return vld1_lane_s16(a, b, 3); - // CHECK: ld1 {v{{[0-9]+}}.h}[3], [{{x[0-9]+|sp}}] + // CHECK: ld1 {{{ *v[0-9]+.h *}}}[3], [{{x[0-9]+|sp}}] } int32x2_t test_vld1_lane_s32(int32_t *a, int32x2_t b) { // CHECK-LABEL: test_vld1_lane_s32 return vld1_lane_s32(a, b, 1); - // CHECK: ld1 {v{{[0-9]+}}.s}[1], [{{x[0-9]+|sp}}] + // CHECK: ld1 {{{ *v[0-9]+.s *}}}[1], [{{x[0-9]+|sp}}] } int64x1_t test_vld1_lane_s64(int64_t *a, int64x1_t b) { // CHECK-LABEL: test_vld1_lane_s64 return vld1_lane_s64(a, b, 0); - // CHECK: ld1r {v{{[0-9]+}}.1d}, [{{x[0-9]+|sp}}] + // CHECK: {{ld1r {v[0-9]+.1d}|ldr d[0-9]+}}, [{{x[0-9]+|sp}}] } float16x4_t test_vld1_lane_f16(float16_t *a, float16x4_t b) { // CHECK-LABEL: test_vld1_lane_f16 return vld1_lane_f16(a, b, 3); - // CHECK: ld1 {v{{[0-9]+}}.h}[3], [{{x[0-9]+|sp}}] + // CHECK: ld1 {{{ *v[0-9]+.h *}}}[3], [{{x[0-9]+|sp}}] } float32x2_t test_vld1_lane_f32(float32_t *a, float32x2_t b) { // CHECK-LABEL: test_vld1_lane_f32 return vld1_lane_f32(a, b, 1); - // CHECK: ld1 {v{{[0-9]+}}.s}[1], [{{x[0-9]+|sp}}] + // CHECK: ld1 {{{ *v[0-9]+.s *}}}[1], [{{x[0-9]+|sp}}] } float64x1_t test_vld1_lane_f64(float64_t *a, float64x1_t b) { // CHECK-LABEL: test_vld1_lane_f64 return vld1_lane_f64(a, b, 0); - // CHECK: ld1r {v{{[0-9]+}}.1d}, [{{x[0-9]+|sp}}] + // CHECK: {{ld1r {v[0-9]+.1d}|ldr d[0-9]+}}, [{{x[0-9]+|sp}}] } poly8x8_t test_vld1_lane_p8(poly8_t *a, poly8x8_t b) { // CHECK-LABEL: test_vld1_lane_p8 return vld1_lane_p8(a, b, 7); - // CHECK: ld1 {v{{[0-9]+}}.b}[7], [{{x[0-9]+|sp}}] + // CHECK: ld1 {{{ *v[0-9]+.b *}}}[7], [{{x[0-9]+|sp}}] } poly16x4_t test_vld1_lane_p16(poly16_t *a, poly16x4_t b) { // CHECK-LABEL: test_vld1_lane_p16 return vld1_lane_p16(a, b, 3); - // CHECK: ld1 {v{{[0-9]+}}.h}[3], [{{x[0-9]+|sp}}] + // CHECK: ld1 {{{ *v[0-9]+.h *}}}[3], [{{x[0-9]+|sp}}] } poly64x1_t test_vld1_lane_p64(poly64_t *a, poly64x1_t b) { // CHECK-LABEL: test_vld1_lane_p64 return vld1_lane_p64(a, b, 0); - // CHECK: ld1r {v{{[0-9]+}}.1d}, [{{x[0-9]+|sp}}] + // CHECK: {{ld1r {v[0-9]+.1d}|ldr d[0-9]+}}, [{{x[0-9]+|sp}}] } int8x16x2_t test_vld2q_lane_s8(int8_t const * ptr, int8x16x2_t src) { // CHECK-LABEL: test_vld2q_lane_s8 - return vld2q_lane_s8(ptr, src, 15); - // CHECK: ld2 {{{v[0-9]+}}.b, {{v[0-9]+}}.b}[15], [x0] + return vld2q_lane_s8(ptr, src, 15); + // CHECK: ld2 {{{ *v[0-9]+.b, v[0-9]+.b *}}}[15], [x0] } uint8x16x2_t test_vld2q_lane_u8(uint8_t const * ptr, uint8x16x2_t src) { // CHECK-LABEL: test_vld2q_lane_u8 - return vld2q_lane_u8(ptr, src, 15); - // CHECK: ld2 {{{v[0-9]+}}.b, {{v[0-9]+}}.b}[15], [x0] + return vld2q_lane_u8(ptr, src, 15); + // CHECK: ld2 {{{ *v[0-9]+.b, v[0-9]+.b *}}}[15], [x0] } poly8x16x2_t test_vld2q_lane_p8(poly8_t const * ptr, poly8x16x2_t src) { // CHECK-LABEL: test_vld2q_lane_p8 - return vld2q_lane_p8(ptr, src, 15); - // CHECK: ld2 {{{v[0-9]+}}.b, {{v[0-9]+}}.b}[15], [x0] + return vld2q_lane_p8(ptr, src, 15); + // CHECK: ld2 {{{ *v[0-9]+.b, v[0-9]+.b *}}}[15], [x0] } int8x16x3_t test_vld3q_lane_s8(int8_t const * ptr, int8x16x3_t src) { // CHECK-LABEL: test_vld3q_lane_s8 return vld3q_lane_s8(ptr, src, 15); - // CHECK: ld3 {{{v[0-9]+}}.b, {{v[0-9]+}}.b, {{v[0-9]+}}.b}[15], [x0] + // CHECK: ld3 {{{ *v[0-9]+.b, v[0-9]+.b, v[0-9]+.b *}}}[15], [x0] } uint8x16x3_t test_vld3q_lane_u8(uint8_t const * ptr, uint8x16x3_t src) { // CHECK-LABEL: test_vld3q_lane_u8 return vld3q_lane_u8(ptr, src, 15); - // CHECK: ld3 {{{v[0-9]+}}.b, {{v[0-9]+}}.b, {{v[0-9]+}}.b}[15], [x0] + // CHECK: ld3 {{{ *v[0-9]+.b, v[0-9]+.b, v[0-9]+.b *}}}[15], [x0] } uint16x8x2_t test_vld2q_lane_u16(uint16_t *a, uint16x8x2_t b) { // CHECK-LABEL: test_vld2q_lane_u16 return vld2q_lane_u16(a, b, 7); - // CHECK: ld2 {v{{[0-9]+}}.h, v{{[0-9]+}}.h}[7], [{{x[0-9]+|sp}}] + // CHECK: ld2 {{{ *v[0-9]+.h, v[0-9]+.h *}}}[7], [{{x[0-9]+|sp}}] } uint32x4x2_t test_vld2q_lane_u32(uint32_t *a, uint32x4x2_t b) { // CHECK-LABEL: test_vld2q_lane_u32 return vld2q_lane_u32(a, b, 3); - // CHECK: ld2 {v{{[0-9]+}}.s, v{{[0-9]+}}.s}[3], [{{x[0-9]+|sp}}] + // CHECK: ld2 {{{ *v[0-9]+.s, v[0-9]+.s *}}}[3], [{{x[0-9]+|sp}}] } uint64x2x2_t test_vld2q_lane_u64(uint64_t *a, uint64x2x2_t b) { // CHECK-LABEL: test_vld2q_lane_u64 return vld2q_lane_u64(a, b, 1); - // CHECK: ld2 {v{{[0-9]+}}.d, v{{[0-9]+}}.d}[1], [{{x[0-9]+|sp}}] + // CHECK: ld2 {{{ *v[0-9]+.d, v[0-9]+.d *}}}[1], [{{x[0-9]+|sp}}] } int16x8x2_t test_vld2q_lane_s16(int16_t *a, int16x8x2_t b) { // CHECK-LABEL: test_vld2q_lane_s16 return vld2q_lane_s16(a, b, 7); - // CHECK: ld2 {v{{[0-9]+}}.h, v{{[0-9]+}}.h}[7], [{{x[0-9]+|sp}}] + // CHECK: ld2 {{{ *v[0-9]+.h, v[0-9]+.h *}}}[7], [{{x[0-9]+|sp}}] } int32x4x2_t test_vld2q_lane_s32(int32_t *a, int32x4x2_t b) { // CHECK-LABEL: test_vld2q_lane_s32 return vld2q_lane_s32(a, b, 3); - // CHECK: ld2 {v{{[0-9]+}}.s, v{{[0-9]+}}.s}[3], [{{x[0-9]+|sp}}] + // CHECK: ld2 {{{ *v[0-9]+.s, v[0-9]+.s *}}}[3], [{{x[0-9]+|sp}}] } int64x2x2_t test_vld2q_lane_s64(int64_t *a, int64x2x2_t b) { // CHECK-LABEL: test_vld2q_lane_s64 return vld2q_lane_s64(a, b, 1); - // CHECK: ld2 {v{{[0-9]+}}.d, v{{[0-9]+}}.d}[1], [{{x[0-9]+|sp}}] + // CHECK: ld2 {{{ *v[0-9]+.d, v[0-9]+.d *}}}[1], [{{x[0-9]+|sp}}] } float16x8x2_t test_vld2q_lane_f16(float16_t *a, float16x8x2_t b) { // CHECK-LABEL: test_vld2q_lane_f16 return vld2q_lane_f16(a, b, 7); - // CHECK: ld2 {v{{[0-9]+}}.h, v{{[0-9]+}}.h}[7], [{{x[0-9]+|sp}}] + // CHECK: ld2 {{{ *v[0-9]+.h, v[0-9]+.h *}}}[7], [{{x[0-9]+|sp}}] } float32x4x2_t test_vld2q_lane_f32(float32_t *a, float32x4x2_t b) { // CHECK-LABEL: test_vld2q_lane_f32 return vld2q_lane_f32(a, b, 3); - // CHECK: ld2 {v{{[0-9]+}}.s, v{{[0-9]+}}.s}[3], [{{x[0-9]+|sp}}] + // CHECK: ld2 {{{ *v[0-9]+.s, v[0-9]+.s *}}}[3], [{{x[0-9]+|sp}}] } float64x2x2_t test_vld2q_lane_f64(float64_t *a, float64x2x2_t b) { // CHECK-LABEL: test_vld2q_lane_f64 return vld2q_lane_f64(a, b, 1); - // CHECK: ld2 {v{{[0-9]+}}.d, v{{[0-9]+}}.d}[1], [{{x[0-9]+|sp}}] + // CHECK: ld2 {{{ *v[0-9]+.d, v[0-9]+.d *}}}[1], [{{x[0-9]+|sp}}] } poly16x8x2_t test_vld2q_lane_p16(poly16_t *a, poly16x8x2_t b) { // CHECK-LABEL: test_vld2q_lane_p16 return vld2q_lane_p16(a, b, 7); - // CHECK: ld2 {v{{[0-9]+}}.h, v{{[0-9]+}}.h}[7], [{{x[0-9]+|sp}}] + // CHECK: ld2 {{{ *v[0-9]+.h, v[0-9]+.h *}}}[7], [{{x[0-9]+|sp}}] } poly64x2x2_t test_vld2q_lane_p64(poly64_t *a, poly64x2x2_t b) { // CHECK-LABEL: test_vld2q_lane_p64 return vld2q_lane_p64(a, b, 1); - // CHECK: ld2 {v{{[0-9]+}}.d, v{{[0-9]+}}.d}[1], [{{x[0-9]+|sp}}] + // CHECK: ld2 {{{ *v[0-9]+.d, v[0-9]+.d *}}}[1], [{{x[0-9]+|sp}}] } uint8x8x2_t test_vld2_lane_u8(uint8_t *a, uint8x8x2_t b) { // CHECK-LABEL: test_vld2_lane_u8 return vld2_lane_u8(a, b, 7); - // CHECK: ld2 {v{{[0-9]+}}.b, v{{[0-9]+}}.b}[7], [{{x[0-9]+|sp}}] + // CHECK: ld2 {{{ *v[0-9]+.b, v[0-9]+.b *}}}[7], [{{x[0-9]+|sp}}] } uint16x4x2_t test_vld2_lane_u16(uint16_t *a, uint16x4x2_t b) { // CHECK-LABEL: test_vld2_lane_u16 return vld2_lane_u16(a, b, 3); - // CHECK: ld2 {v{{[0-9]+}}.h, v{{[0-9]+}}.h}[3], [{{x[0-9]+|sp}}] + // CHECK: ld2 {{{ *v[0-9]+.h, v[0-9]+.h *}}}[3], [{{x[0-9]+|sp}}] } uint32x2x2_t test_vld2_lane_u32(uint32_t *a, uint32x2x2_t b) { // CHECK-LABEL: test_vld2_lane_u32 return vld2_lane_u32(a, b, 1); - // CHECK: ld2 {v{{[0-9]+}}.s, v{{[0-9]+}}.s}[1], [{{x[0-9]+|sp}}] + // CHECK: ld2 {{{ *v[0-9]+.s, v[0-9]+.s *}}}[1], [{{x[0-9]+|sp}}] } uint64x1x2_t test_vld2_lane_u64(uint64_t *a, uint64x1x2_t b) { // CHECK-LABEL: test_vld2_lane_u64 return vld2_lane_u64(a, b, 0); - // CHECK: ld2 {v{{[0-9]+}}.d, v{{[0-9]+}}.d}[0], [{{x[0-9]+|sp}}] + // CHECK: ld2 {{{ *v[0-9]+.d, v[0-9]+.d *}}}[0], [{{x[0-9]+|sp}}] } int8x8x2_t test_vld2_lane_s8(int8_t *a, int8x8x2_t b) { // CHECK-LABEL: test_vld2_lane_s8 return vld2_lane_s8(a, b, 7); - // CHECK: ld2 {v{{[0-9]+}}.b, v{{[0-9]+}}.b}[7], [{{x[0-9]+|sp}}] + // CHECK: ld2 {{{ *v[0-9]+.b, v[0-9]+.b *}}}[7], [{{x[0-9]+|sp}}] } int16x4x2_t test_vld2_lane_s16(int16_t *a, int16x4x2_t b) { // CHECK-LABEL: test_vld2_lane_s16 return vld2_lane_s16(a, b, 3); - // CHECK: ld2 {v{{[0-9]+}}.h, v{{[0-9]+}}.h}[3], [{{x[0-9]+|sp}}] + // CHECK: ld2 {{{ *v[0-9]+.h, v[0-9]+.h *}}}[3], [{{x[0-9]+|sp}}] } int32x2x2_t test_vld2_lane_s32(int32_t *a, int32x2x2_t b) { // CHECK-LABEL: test_vld2_lane_s32 return vld2_lane_s32(a, b, 1); - // CHECK: ld2 {v{{[0-9]+}}.s, v{{[0-9]+}}.s}[1], [{{x[0-9]+|sp}}] + // CHECK: ld2 {{{ *v[0-9]+.s, v[0-9]+.s *}}}[1], [{{x[0-9]+|sp}}] } int64x1x2_t test_vld2_lane_s64(int64_t *a, int64x1x2_t b) { // CHECK-LABEL: test_vld2_lane_s64 return vld2_lane_s64(a, b, 0); - // CHECK: ld2 {v{{[0-9]+}}.d, v{{[0-9]+}}.d}[0], [{{x[0-9]+|sp}}] + // CHECK: ld2 {{{ *v[0-9]+.d, v[0-9]+.d *}}}[0], [{{x[0-9]+|sp}}] } float16x4x2_t test_vld2_lane_f16(float16_t *a, float16x4x2_t b) { // CHECK-LABEL: test_vld2_lane_f16 return vld2_lane_f16(a, b, 3); - // CHECK: ld2 {v{{[0-9]+}}.h, v{{[0-9]+}}.h}[3], [{{x[0-9]+|sp}}] + // CHECK: ld2 {{{ *v[0-9]+.h, v[0-9]+.h *}}}[3], [{{x[0-9]+|sp}}] } float32x2x2_t test_vld2_lane_f32(float32_t *a, float32x2x2_t b) { // CHECK-LABEL: test_vld2_lane_f32 return vld2_lane_f32(a, b, 1); - // CHECK: ld2 {v{{[0-9]+}}.s, v{{[0-9]+}}.s}[1], [{{x[0-9]+|sp}}] + // CHECK: ld2 {{{ *v[0-9]+.s, v[0-9]+.s *}}}[1], [{{x[0-9]+|sp}}] } float64x1x2_t test_vld2_lane_f64(float64_t *a, float64x1x2_t b) { // CHECK-LABEL: test_vld2_lane_f64 return vld2_lane_f64(a, b, 0); - // CHECK: ld2 {v{{[0-9]+}}.d, v{{[0-9]+}}.d}[0], [{{x[0-9]+|sp}}] + // CHECK: ld2 {{{ *v[0-9]+.d, v[0-9]+.d *}}}[0], [{{x[0-9]+|sp}}] } poly8x8x2_t test_vld2_lane_p8(poly8_t *a, poly8x8x2_t b) { // CHECK-LABEL: test_vld2_lane_p8 return vld2_lane_p8(a, b, 7); - // CHECK: ld2 {v{{[0-9]+}}.b, v{{[0-9]+}}.b}[7], [{{x[0-9]+|sp}}] + // CHECK: ld2 {{{ *v[0-9]+.b, v[0-9]+.b *}}}[7], [{{x[0-9]+|sp}}] } poly16x4x2_t test_vld2_lane_p16(poly16_t *a, poly16x4x2_t b) { // CHECK-LABEL: test_vld2_lane_p16 return vld2_lane_p16(a, b, 3); - // CHECK: ld2 {v{{[0-9]+}}.h, v{{[0-9]+}}.h}[3], [{{x[0-9]+|sp}}] + // CHECK: ld2 {{{ *v[0-9]+.h, v[0-9]+.h *}}}[3], [{{x[0-9]+|sp}}] } poly64x1x2_t test_vld2_lane_p64(poly64_t *a, poly64x1x2_t b) { // CHECK-LABEL: test_vld2_lane_p64 return vld2_lane_p64(a, b, 0); - // CHECK: ld2 {v{{[0-9]+}}.d, v{{[0-9]+}}.d}[0], [{{x[0-9]+|sp}}] + // CHECK: ld2 {{{ *v[0-9]+.d, v[0-9]+.d *}}}[0], [{{x[0-9]+|sp}}] } uint16x8x3_t test_vld3q_lane_u16(uint16_t *a, uint16x8x3_t b) { // CHECK-LABEL: test_vld3q_lane_u16 return vld3q_lane_u16(a, b, 7); - // CHECK: ld3 {v{{[0-9]+}}.h, v{{[0-9]+}}.h, v{{[0-9]+}}.h}[7], [{{x[0-9]+|sp}}] + // CHECK: ld3 {{{ *v[0-9]+.h, v[0-9]+.h, v[0-9]+.h *}}}[7], [{{x[0-9]+|sp}}] } uint32x4x3_t test_vld3q_lane_u32(uint32_t *a, uint32x4x3_t b) { // CHECK-LABEL: test_vld3q_lane_u32 return vld3q_lane_u32(a, b, 3); - // CHECK: ld3 {v{{[0-9]+}}.s, v{{[0-9]+}}.s, v{{[0-9]+}}.s}[3], [{{x[0-9]+|sp}}] + // CHECK: ld3 {{{ *v[0-9]+.s, v[0-9]+.s, v[0-9]+.s *}}}[3], [{{x[0-9]+|sp}}] } uint64x2x3_t test_vld3q_lane_u64(uint64_t *a, uint64x2x3_t b) { // CHECK-LABEL: test_vld3q_lane_u64 return vld3q_lane_u64(a, b, 1); - // CHECK: ld3 {v{{[0-9]+}}.d, v{{[0-9]+}}.d, v{{[0-9]+}}.d}[1], [{{x[0-9]+|sp}}] + // CHECK: ld3 {{{ *v[0-9]+.d, v[0-9]+.d, v[0-9]+.d *}}}[1], [{{x[0-9]+|sp}}] } int16x8x3_t test_vld3q_lane_s16(int16_t *a, int16x8x3_t b) { // CHECK-LABEL: test_vld3q_lane_s16 return vld3q_lane_s16(a, b, 7); - // CHECK: ld3 {v{{[0-9]+}}.h, v{{[0-9]+}}.h, v{{[0-9]+}}.h}[7], [{{x[0-9]+|sp}}] + // CHECK: ld3 {{{ *v[0-9]+.h, v[0-9]+.h, v[0-9]+.h *}}}[7], [{{x[0-9]+|sp}}] } int32x4x3_t test_vld3q_lane_s32(int32_t *a, int32x4x3_t b) { // CHECK-LABEL: test_vld3q_lane_s32 return vld3q_lane_s32(a, b, 3); - // CHECK: ld3 {v{{[0-9]+}}.s, v{{[0-9]+}}.s, v{{[0-9]+}}.s}[3], [{{x[0-9]+|sp}}] + // CHECK: ld3 {{{ *v[0-9]+.s, v[0-9]+.s, v[0-9]+.s *}}}[3], [{{x[0-9]+|sp}}] } int64x2x3_t test_vld3q_lane_s64(int64_t *a, int64x2x3_t b) { // CHECK-LABEL: test_vld3q_lane_s64 return vld3q_lane_s64(a, b, 1); - // CHECK: ld3 {v{{[0-9]+}}.d, v{{[0-9]+}}.d, v{{[0-9]+}}.d}[1], [{{x[0-9]+|sp}}] + // CHECK: ld3 {{{ *v[0-9]+.d, v[0-9]+.d, v[0-9]+.d *}}}[1], [{{x[0-9]+|sp}}] } float16x8x3_t test_vld3q_lane_f16(float16_t *a, float16x8x3_t b) { // CHECK-LABEL: test_vld3q_lane_f16 return vld3q_lane_f16(a, b, 7); - // CHECK: ld3 {v{{[0-9]+}}.h, v{{[0-9]+}}.h, v{{[0-9]+}}.h}[7], [{{x[0-9]+|sp}}] + // CHECK: ld3 {{{ *v[0-9]+.h, v[0-9]+.h, v[0-9]+.h *}}}[7], [{{x[0-9]+|sp}}] } float32x4x3_t test_vld3q_lane_f32(float32_t *a, float32x4x3_t b) { // CHECK-LABEL: test_vld3q_lane_f32 return vld3q_lane_f32(a, b, 3); - // CHECK: ld3 {v{{[0-9]+}}.s, v{{[0-9]+}}.s, v{{[0-9]+}}.s}[3], [{{x[0-9]+|sp}}] + // CHECK: ld3 {{{ *v[0-9]+.s, v[0-9]+.s, v[0-9]+.s *}}}[3], [{{x[0-9]+|sp}}] } float64x2x3_t test_vld3q_lane_f64(float64_t *a, float64x2x3_t b) { // CHECK-LABEL: test_vld3q_lane_f64 return vld3q_lane_f64(a, b, 1); - // CHECK: ld3 {v{{[0-9]+}}.d, v{{[0-9]+}}.d, v{{[0-9]+}}.d}[1], [{{x[0-9]+|sp}}] + // CHECK: ld3 {{{ *v[0-9]+.d, v[0-9]+.d, v[0-9]+.d *}}}[1], [{{x[0-9]+|sp}}] } poly8x16x3_t test_vld3q_lane_p8(poly8_t *a, poly8x16x3_t b) { // CHECK-LABEL: test_vld3q_lane_p8 return vld3q_lane_p8(a, b, 15); - // CHECK: ld3 {v{{[0-9]+}}.b, v{{[0-9]+}}.b, v{{[0-9]+}}.b}[15], [{{x[0-9]+|sp}}] + // CHECK: ld3 {{{ *v[0-9]+.b, v[0-9]+.b, v[0-9]+.b *}}}[15], [{{x[0-9]+|sp}}] } poly16x8x3_t test_vld3q_lane_p16(poly16_t *a, poly16x8x3_t b) { // CHECK-LABEL: test_vld3q_lane_p16 return vld3q_lane_p16(a, b, 7); - // CHECK: ld3 {v{{[0-9]+}}.h, v{{[0-9]+}}.h, v{{[0-9]+}}.h}[7], [{{x[0-9]+|sp}}] + // CHECK: ld3 {{{ *v[0-9]+.h, v[0-9]+.h, v[0-9]+.h *}}}[7], [{{x[0-9]+|sp}}] } poly64x2x3_t test_vld3q_lane_p64(poly64_t *a, poly64x2x3_t b) { // CHECK-LABEL: test_vld3q_lane_p64 return vld3q_lane_p64(a, b, 1); - // CHECK: ld3 {v{{[0-9]+}}.d, v{{[0-9]+}}.d, v{{[0-9]+}}.d}[1], [{{x[0-9]+|sp}}] + // CHECK: ld3 {{{ *v[0-9]+.d, v[0-9]+.d, v[0-9]+.d *}}}[1], [{{x[0-9]+|sp}}] } uint8x8x3_t test_vld3_lane_u8(uint8_t *a, uint8x8x3_t b) { // CHECK-LABEL: test_vld3_lane_u8 return vld3_lane_u8(a, b, 7); - // CHECK: ld3 {v{{[0-9]+}}.b, v{{[0-9]+}}.b, v{{[0-9]+}}.b}[7], [{{x[0-9]+|sp}}] + // CHECK: ld3 {{{ *v[0-9]+.b, v[0-9]+.b, v[0-9]+.b *}}}[7], [{{x[0-9]+|sp}}] } uint16x4x3_t test_vld3_lane_u16(uint16_t *a, uint16x4x3_t b) { // CHECK-LABEL: test_vld3_lane_u16 return vld3_lane_u16(a, b, 3); - // CHECK: ld3 {v{{[0-9]+}}.h, v{{[0-9]+}}.h, v{{[0-9]+}}.h}[3], [{{x[0-9]+|sp}}] + // CHECK: ld3 {{{ *v[0-9]+.h, v[0-9]+.h, v[0-9]+.h *}}}[3], [{{x[0-9]+|sp}}] } uint32x2x3_t test_vld3_lane_u32(uint32_t *a, uint32x2x3_t b) { // CHECK-LABEL: test_vld3_lane_u32 return vld3_lane_u32(a, b, 1); - // CHECK: ld3 {v{{[0-9]+}}.s, v{{[0-9]+}}.s, v{{[0-9]+}}.s}[1], [{{x[0-9]+|sp}}] + // CHECK: ld3 {{{ *v[0-9]+.s, v[0-9]+.s, v[0-9]+.s *}}}[1], [{{x[0-9]+|sp}}] } uint64x1x3_t test_vld3_lane_u64(uint64_t *a, uint64x1x3_t b) { // CHECK-LABEL: test_vld3_lane_u64 return vld3_lane_u64(a, b, 0); - // CHECK: ld3 {v{{[0-9]+}}.d, v{{[0-9]+}}.d, v{{[0-9]+}}.d}[0], [{{x[0-9]+|sp}}] + // CHECK: ld3 {{{ *v[0-9]+.d, v[0-9]+.d, v[0-9]+.d *}}}[0], [{{x[0-9]+|sp}}] } int8x8x3_t test_vld3_lane_s8(int8_t *a, int8x8x3_t b) { // CHECK-LABEL: test_vld3_lane_s8 return vld3_lane_s8(a, b, 7); - // CHECK: ld3 {v{{[0-9]+}}.b, v{{[0-9]+}}.b, v{{[0-9]+}}.b}[7], [{{x[0-9]+|sp}}] + // CHECK: ld3 {{{ *v[0-9]+.b, v[0-9]+.b, v[0-9]+.b *}}}[7], [{{x[0-9]+|sp}}] } int16x4x3_t test_vld3_lane_s16(int16_t *a, int16x4x3_t b) { // CHECK-LABEL: test_vld3_lane_s16 return vld3_lane_s16(a, b, 3); - // CHECK: ld3 {v{{[0-9]+}}.h, v{{[0-9]+}}.h, v{{[0-9]+}}.h}[3], [{{x[0-9]+|sp}}] + // CHECK: ld3 {{{ *v[0-9]+.h, v[0-9]+.h, v[0-9]+.h *}}}[3], [{{x[0-9]+|sp}}] } int32x2x3_t test_vld3_lane_s32(int32_t *a, int32x2x3_t b) { // CHECK-LABEL: test_vld3_lane_s32 return vld3_lane_s32(a, b, 1); - // CHECK: ld3 {v{{[0-9]+}}.s, v{{[0-9]+}}.s, v{{[0-9]+}}.s}[1], [{{x[0-9]+|sp}}] + // CHECK: ld3 {{{ *v[0-9]+.s, v[0-9]+.s, v[0-9]+.s *}}}[1], [{{x[0-9]+|sp}}] } int64x1x3_t test_vld3_lane_s64(int64_t *a, int64x1x3_t b) { // CHECK-LABEL: test_vld3_lane_s64 return vld3_lane_s64(a, b, 0); - // CHECK: ld3 {v{{[0-9]+}}.d, v{{[0-9]+}}.d, v{{[0-9]+}}.d}[0], [{{x[0-9]+|sp}}] + // CHECK: ld3 {{{ *v[0-9]+.d, v[0-9]+.d, v[0-9]+.d *}}}[0], [{{x[0-9]+|sp}}] } float16x4x3_t test_vld3_lane_f16(float16_t *a, float16x4x3_t b) { // CHECK-LABEL: test_vld3_lane_f16 return vld3_lane_f16(a, b, 3); - // CHECK: ld3 {v{{[0-9]+}}.h, v{{[0-9]+}}.h, v{{[0-9]+}}.h}[3], [{{x[0-9]+|sp}}] + // CHECK: ld3 {{{ *v[0-9]+.h, v[0-9]+.h, v[0-9]+.h *}}}[3], [{{x[0-9]+|sp}}] } float32x2x3_t test_vld3_lane_f32(float32_t *a, float32x2x3_t b) { // CHECK-LABEL: test_vld3_lane_f32 return vld3_lane_f32(a, b, 1); - // CHECK: ld3 {v{{[0-9]+}}.s, v{{[0-9]+}}.s, v{{[0-9]+}}.s}[1], [{{x[0-9]+|sp}}] + // CHECK: ld3 {{{ *v[0-9]+.s, v[0-9]+.s, v[0-9]+.s *}}}[1], [{{x[0-9]+|sp}}] } float64x1x3_t test_vld3_lane_f64(float64_t *a, float64x1x3_t b) { // CHECK-LABEL: test_vld3_lane_f64 return vld3_lane_f64(a, b, 0); - // CHECK: ld3 {v{{[0-9]+}}.d, v{{[0-9]+}}.d, v{{[0-9]+}}.d}[0], [{{x[0-9]+|sp}}] + // CHECK: ld3 {{{ *v[0-9]+.d, v[0-9]+.d, v[0-9]+.d *}}}[0], [{{x[0-9]+|sp}}] } poly8x8x3_t test_vld3_lane_p8(poly8_t *a, poly8x8x3_t b) { // CHECK-LABEL: test_vld3_lane_p8 return vld3_lane_p8(a, b, 7); - // CHECK: ld3 {v{{[0-9]+}}.b, v{{[0-9]+}}.b, v{{[0-9]+}}.b}[7], [{{x[0-9]+|sp}}] + // CHECK: ld3 {{{ *v[0-9]+.b, v[0-9]+.b, v[0-9]+.b *}}}[7], [{{x[0-9]+|sp}}] } poly16x4x3_t test_vld3_lane_p16(poly16_t *a, poly16x4x3_t b) { // CHECK-LABEL: test_vld3_lane_p16 return vld3_lane_p16(a, b, 3); - // CHECK: ld3 {v{{[0-9]+}}.h, v{{[0-9]+}}.h, v{{[0-9]+}}.h}[3], [{{x[0-9]+|sp}}] + // CHECK: ld3 {{{ *v[0-9]+.h, v[0-9]+.h, v[0-9]+.h *}}}[3], [{{x[0-9]+|sp}}] } poly64x1x3_t test_vld3_lane_p64(poly64_t *a, poly64x1x3_t b) { // CHECK-LABEL: test_vld3_lane_p64 return vld3_lane_p64(a, b, 0); - // CHECK: ld3 {v{{[0-9]+}}.d, v{{[0-9]+}}.d, v{{[0-9]+}}.d}[0], [{{x[0-9]+|sp}}] + // CHECK: ld3 {{{ *v[0-9]+.d, v[0-9]+.d, v[0-9]+.d *}}}[0], [{{x[0-9]+|sp}}] } uint8x16x4_t test_vld4q_lane_u8(uint8_t *a, uint8x16x4_t b) { // CHECK-LABEL: test_vld4q_lane_u8 return vld4q_lane_u8(a, b, 15); - // CHECK: ld4 {v{{[0-9]+}}.b, v{{[0-9]+}}.b, v{{[0-9]+}}.b, v{{[0-9]+}}.b}[15], [{{x[0-9]+|sp}}] + // CHECK: ld4 {{{ *v[0-9]+.b, v[0-9]+.b, v[0-9]+.b, v[0-9]+.b *}}}[15], [{{x[0-9]+|sp}}] } uint16x8x4_t test_vld4q_lane_u16(uint16_t *a, uint16x8x4_t b) { // CHECK-LABEL: test_vld4q_lane_u16 return vld4q_lane_u16(a, b, 7); - // CHECK: ld4 {v{{[0-9]+}}.h, v{{[0-9]+}}.h, v{{[0-9]+}}.h, v{{[0-9]+}}.h}[7], [{{x[0-9]+|sp}}] + // CHECK: ld4 {{{ *v[0-9]+.h, v[0-9]+.h, v[0-9]+.h, v[0-9]+.h *}}}[7], [{{x[0-9]+|sp}}] } uint32x4x4_t test_vld4q_lane_u32(uint32_t *a, uint32x4x4_t b) { // CHECK-LABEL: test_vld4q_lane_u32 return vld4q_lane_u32(a, b, 3); - // CHECK: ld4 {v{{[0-9]+}}.s, v{{[0-9]+}}.s, v{{[0-9]+}}.s, v{{[0-9]+}}.s}[3], [{{x[0-9]+|sp}}] + // CHECK: ld4 {{{ *v[0-9]+.s, v[0-9]+.s, v[0-9]+.s, v[0-9]+.s *}}}[3], [{{x[0-9]+|sp}}] } uint64x2x4_t test_vld4q_lane_u64(uint64_t *a, uint64x2x4_t b) { // CHECK-LABEL: test_vld4q_lane_u64 return vld4q_lane_u64(a, b, 1); - // CHECK: ld4 {v{{[0-9]+}}.d, v{{[0-9]+}}.d, v{{[0-9]+}}.d, v{{[0-9]+}}.d}[1], [{{x[0-9]+|sp}}] + // CHECK: ld4 {{{ *v[0-9]+.d, v[0-9]+.d, v[0-9]+.d, v[0-9]+.d *}}}[1], [{{x[0-9]+|sp}}] } int8x16x4_t test_vld4q_lane_s8(int8_t *a, int8x16x4_t b) { // CHECK-LABEL: test_vld4q_lane_s8 return vld4q_lane_s8(a, b, 15); - // CHECK: ld4 {v{{[0-9]+}}.b, v{{[0-9]+}}.b, v{{[0-9]+}}.b, v{{[0-9]+}}.b}[15], [{{x[0-9]+|sp}}] + // CHECK: ld4 {{{ *v[0-9]+.b, v[0-9]+.b, v[0-9]+.b, v[0-9]+.b *}}}[15], [{{x[0-9]+|sp}}] } int16x8x4_t test_vld4q_lane_s16(int16_t *a, int16x8x4_t b) { // CHECK-LABEL: test_vld4q_lane_s16 return vld4q_lane_s16(a, b, 7); - // CHECK: ld4 {v{{[0-9]+}}.h, v{{[0-9]+}}.h, v{{[0-9]+}}.h, v{{[0-9]+}}.h}[7], [{{x[0-9]+|sp}}] + // CHECK: ld4 {{{ *v[0-9]+.h, v[0-9]+.h, v[0-9]+.h, v[0-9]+.h *}}}[7], [{{x[0-9]+|sp}}] } int32x4x4_t test_vld4q_lane_s32(int32_t *a, int32x4x4_t b) { // CHECK-LABEL: test_vld4q_lane_s32 return vld4q_lane_s32(a, b, 3); - // CHECK: ld4 {v{{[0-9]+}}.s, v{{[0-9]+}}.s, v{{[0-9]+}}.s, v{{[0-9]+}}.s}[3], [{{x[0-9]+|sp}}] + // CHECK: ld4 {{{ *v[0-9]+.s, v[0-9]+.s, v[0-9]+.s, v[0-9]+.s *}}}[3], [{{x[0-9]+|sp}}] } int64x2x4_t test_vld4q_lane_s64(int64_t *a, int64x2x4_t b) { // CHECK-LABEL: test_vld4q_lane_s64 return vld4q_lane_s64(a, b, 1); - // CHECK: ld4 {v{{[0-9]+}}.d, v{{[0-9]+}}.d, v{{[0-9]+}}.d, v{{[0-9]+}}.d}[1], [{{x[0-9]+|sp}}] + // CHECK: ld4 {{{ *v[0-9]+.d, v[0-9]+.d, v[0-9]+.d, v[0-9]+.d *}}}[1], [{{x[0-9]+|sp}}] } float16x8x4_t test_vld4q_lane_f16(float16_t *a, float16x8x4_t b) { // CHECK-LABEL: test_vld4q_lane_f16 return vld4q_lane_f16(a, b, 7); - // CHECK: ld4 {v{{[0-9]+}}.h, v{{[0-9]+}}.h, v{{[0-9]+}}.h, v{{[0-9]+}}.h}[7], [{{x[0-9]+|sp}}] + // CHECK: ld4 {{{ *v[0-9]+.h, v[0-9]+.h, v[0-9]+.h, v[0-9]+.h *}}}[7], [{{x[0-9]+|sp}}] } float32x4x4_t test_vld4q_lane_f32(float32_t *a, float32x4x4_t b) { // CHECK-LABEL: test_vld4q_lane_f32 return vld4q_lane_f32(a, b, 3); - // CHECK: ld4 {v{{[0-9]+}}.s, v{{[0-9]+}}.s, v{{[0-9]+}}.s, v{{[0-9]+}}.s}[3], [{{x[0-9]+|sp}}] + // CHECK: ld4 {{{ *v[0-9]+.s, v[0-9]+.s, v[0-9]+.s, v[0-9]+.s *}}}[3], [{{x[0-9]+|sp}}] } float64x2x4_t test_vld4q_lane_f64(float64_t *a, float64x2x4_t b) { // CHECK-LABEL: test_vld4q_lane_f64 return vld4q_lane_f64(a, b, 1); - // CHECK: ld4 {v{{[0-9]+}}.d, v{{[0-9]+}}.d, v{{[0-9]+}}.d, v{{[0-9]+}}.d}[1], [{{x[0-9]+|sp}}] + // CHECK: ld4 {{{ *v[0-9]+.d, v[0-9]+.d, v[0-9]+.d, v[0-9]+.d *}}}[1], [{{x[0-9]+|sp}}] } poly8x16x4_t test_vld4q_lane_p8(poly8_t *a, poly8x16x4_t b) { // CHECK-LABEL: test_vld4q_lane_p8 return vld4q_lane_p8(a, b, 15); - // CHECK: ld4 {v{{[0-9]+}}.b, v{{[0-9]+}}.b, v{{[0-9]+}}.b, v{{[0-9]+}}.b}[15], [{{x[0-9]+|sp}}] + // CHECK: ld4 {{{ *v[0-9]+.b, v[0-9]+.b, v[0-9]+.b, v[0-9]+.b *}}}[15], [{{x[0-9]+|sp}}] } poly16x8x4_t test_vld4q_lane_p16(poly16_t *a, poly16x8x4_t b) { // CHECK-LABEL: test_vld4q_lane_p16 return vld4q_lane_p16(a, b, 7); - // CHECK: ld4 {v{{[0-9]+}}.h, v{{[0-9]+}}.h, v{{[0-9]+}}.h, v{{[0-9]+}}.h}[7], [{{x[0-9]+|sp}}] + // CHECK: ld4 {{{ *v[0-9]+.h, v[0-9]+.h, v[0-9]+.h, v[0-9]+.h *}}}[7], [{{x[0-9]+|sp}}] } poly64x2x4_t test_vld4q_lane_p64(poly64_t *a, poly64x2x4_t b) { // CHECK-LABEL: test_vld4q_lane_p64 return vld4q_lane_p64(a, b, 1); - // CHECK: ld4 {v{{[0-9]+}}.d, v{{[0-9]+}}.d, v{{[0-9]+}}.d, v{{[0-9]+}}.d}[1], [{{x[0-9]+|sp}}] + // CHECK: ld4 {{{ *v[0-9]+.d, v[0-9]+.d, v[0-9]+.d, v[0-9]+.d *}}}[1], [{{x[0-9]+|sp}}] } uint8x8x4_t test_vld4_lane_u8(uint8_t *a, uint8x8x4_t b) { // CHECK-LABEL: test_vld4_lane_u8 return vld4_lane_u8(a, b, 7); - // CHECK: ld4 {v{{[0-9]+}}.b, v{{[0-9]+}}.b, v{{[0-9]+}}.b, v{{[0-9]+}}.b}[7], [{{x[0-9]+|sp}}] + // CHECK: ld4 {{{ *v[0-9]+.b, v[0-9]+.b, v[0-9]+.b, v[0-9]+.b *}}}[7], [{{x[0-9]+|sp}}] } uint16x4x4_t test_vld4_lane_u16(uint16_t *a, uint16x4x4_t b) { // CHECK-LABEL: test_vld4_lane_u16 return vld4_lane_u16(a, b, 3); - // CHECK: ld4 {v{{[0-9]+}}.h, v{{[0-9]+}}.h, v{{[0-9]+}}.h, v{{[0-9]+}}.h}[3], [{{x[0-9]+|sp}}] + // CHECK: ld4 {{{ *v[0-9]+.h, v[0-9]+.h, v[0-9]+.h, v[0-9]+.h *}}}[3], [{{x[0-9]+|sp}}] } uint32x2x4_t test_vld4_lane_u32(uint32_t *a, uint32x2x4_t b) { // CHECK-LABEL: test_vld4_lane_u32 return vld4_lane_u32(a, b, 1); - // CHECK: ld4 {v{{[0-9]+}}.s, v{{[0-9]+}}.s, v{{[0-9]+}}.s, v{{[0-9]+}}.s}[1], [{{x[0-9]+|sp}}] + // CHECK: ld4 {{{ *v[0-9]+.s, v[0-9]+.s, v[0-9]+.s, v[0-9]+.s *}}}[1], [{{x[0-9]+|sp}}] } uint64x1x4_t test_vld4_lane_u64(uint64_t *a, uint64x1x4_t b) { // CHECK-LABEL: test_vld4_lane_u64 return vld4_lane_u64(a, b, 0); - // CHECK: ld4 {v{{[0-9]+}}.d, v{{[0-9]+}}.d, v{{[0-9]+}}.d, v{{[0-9]+}}.d}[0], [{{x[0-9]+|sp}}] + // CHECK: ld4 {{{ *v[0-9]+.d, v[0-9]+.d, v[0-9]+.d, v[0-9]+.d *}}}[0], [{{x[0-9]+|sp}}] } int8x8x4_t test_vld4_lane_s8(int8_t *a, int8x8x4_t b) { // CHECK-LABEL: test_vld4_lane_s8 return vld4_lane_s8(a, b, 7); - // CHECK: ld4 {v{{[0-9]+}}.b, v{{[0-9]+}}.b, v{{[0-9]+}}.b, v{{[0-9]+}}.b}[7], [{{x[0-9]+|sp}}] + // CHECK: ld4 {{{ *v[0-9]+.b, v[0-9]+.b, v[0-9]+.b, v[0-9]+.b *}}}[7], [{{x[0-9]+|sp}}] } int16x4x4_t test_vld4_lane_s16(int16_t *a, int16x4x4_t b) { // CHECK-LABEL: test_vld4_lane_s16 return vld4_lane_s16(a, b, 3); - // CHECK: ld4 {v{{[0-9]+}}.h, v{{[0-9]+}}.h, v{{[0-9]+}}.h, v{{[0-9]+}}.h}[3], [{{x[0-9]+|sp}}] + // CHECK: ld4 {{{ *v[0-9]+.h, v[0-9]+.h, v[0-9]+.h, v[0-9]+.h *}}}[3], [{{x[0-9]+|sp}}] } int32x2x4_t test_vld4_lane_s32(int32_t *a, int32x2x4_t b) { // CHECK-LABEL: test_vld4_lane_s32 return vld4_lane_s32(a, b, 1); - // CHECK: ld4 {v{{[0-9]+}}.s, v{{[0-9]+}}.s, v{{[0-9]+}}.s, v{{[0-9]+}}.s}[1], [{{x[0-9]+|sp}}] + // CHECK: ld4 {{{ *v[0-9]+.s, v[0-9]+.s, v[0-9]+.s, v[0-9]+.s *}}}[1], [{{x[0-9]+|sp}}] } int64x1x4_t test_vld4_lane_s64(int64_t *a, int64x1x4_t b) { // CHECK-LABEL: test_vld4_lane_s64 return vld4_lane_s64(a, b, 0); - // CHECK: ld4 {v{{[0-9]+}}.d, v{{[0-9]+}}.d, v{{[0-9]+}}.d, v{{[0-9]+}}.d}[0], [{{x[0-9]+|sp}}] + // CHECK: ld4 {{{ *v[0-9]+.d, v[0-9]+.d, v[0-9]+.d, v[0-9]+.d *}}}[0], [{{x[0-9]+|sp}}] } float16x4x4_t test_vld4_lane_f16(float16_t *a, float16x4x4_t b) { // CHECK-LABEL: test_vld4_lane_f16 return vld4_lane_f16(a, b, 3); - // CHECK: ld4 {v{{[0-9]+}}.h, v{{[0-9]+}}.h, v{{[0-9]+}}.h, v{{[0-9]+}}.h}[3], [{{x[0-9]+|sp}}] + // CHECK: ld4 {{{ *v[0-9]+.h, v[0-9]+.h, v[0-9]+.h, v[0-9]+.h *}}}[3], [{{x[0-9]+|sp}}] } float32x2x4_t test_vld4_lane_f32(float32_t *a, float32x2x4_t b) { // CHECK-LABEL: test_vld4_lane_f32 return vld4_lane_f32(a, b, 1); - // CHECK: ld4 {v{{[0-9]+}}.s, v{{[0-9]+}}.s, v{{[0-9]+}}.s, v{{[0-9]+}}.s}[1], [{{x[0-9]+|sp}}] + // CHECK: ld4 {{{ *v[0-9]+.s, v[0-9]+.s, v[0-9]+.s, v[0-9]+.s *}}}[1], [{{x[0-9]+|sp}}] } float64x1x4_t test_vld4_lane_f64(float64_t *a, float64x1x4_t b) { // CHECK-LABEL: test_vld4_lane_f64 return vld4_lane_f64(a, b, 0); - // CHECK: ld4 {v{{[0-9]+}}.d, v{{[0-9]+}}.d, v{{[0-9]+}}.d, v{{[0-9]+}}.d}[0], [{{x[0-9]+|sp}}] + // CHECK: ld4 {{{ *v[0-9]+.d, v[0-9]+.d, v[0-9]+.d, v[0-9]+.d *}}}[0], [{{x[0-9]+|sp}}] } poly8x8x4_t test_vld4_lane_p8(poly8_t *a, poly8x8x4_t b) { // CHECK-LABEL: test_vld4_lane_p8 return vld4_lane_p8(a, b, 7); - // CHECK: ld4 {v{{[0-9]+}}.b, v{{[0-9]+}}.b, v{{[0-9]+}}.b, v{{[0-9]+}}.b}[7], [{{x[0-9]+|sp}}] + // CHECK: ld4 {{{ *v[0-9]+.b, v[0-9]+.b, v[0-9]+.b, v[0-9]+.b *}}}[7], [{{x[0-9]+|sp}}] } poly16x4x4_t test_vld4_lane_p16(poly16_t *a, poly16x4x4_t b) { // CHECK-LABEL: test_vld4_lane_p16 return vld4_lane_p16(a, b, 3); - // CHECK: ld4 {v{{[0-9]+}}.h, v{{[0-9]+}}.h, v{{[0-9]+}}.h, v{{[0-9]+}}.h}[3], [{{x[0-9]+|sp}}] + // CHECK: ld4 {{{ *v[0-9]+.h, v[0-9]+.h, v[0-9]+.h, v[0-9]+.h *}}}[3], [{{x[0-9]+|sp}}] } poly64x1x4_t test_vld4_lane_p64(poly64_t *a, poly64x1x4_t b) { // CHECK-LABEL: test_vld4_lane_p64 return vld4_lane_p64(a, b, 0); - // CHECK: ld4 {v{{[0-9]+}}.d, v{{[0-9]+}}.d, v{{[0-9]+}}.d, v{{[0-9]+}}.d}[0], [{{x[0-9]+|sp}}] + // CHECK: ld4 {{{ *v[0-9]+.d, v[0-9]+.d, v[0-9]+.d, v[0-9]+.d *}}}[0], [{{x[0-9]+|sp}}] } void test_vst1q_lane_u8(uint8_t *a, uint8x16_t b) { // CHECK-LABEL: test_vst1q_lane_u8 vst1q_lane_u8(a, b, 15); - // CHECK: st1 {v{{[0-9]+}}.b}[15], [{{x[0-9]+|sp}}] + // CHECK: st1 {{{ *v[0-9]+.b *}}}[15], [{{x[0-9]+|sp}}] } void test_vst1q_lane_u16(uint16_t *a, uint16x8_t b) { // CHECK-LABEL: test_vst1q_lane_u16 vst1q_lane_u16(a, b, 7); - // CHECK: st1 {v{{[0-9]+}}.h}[7], [{{x[0-9]+|sp}}] + // CHECK: st1 {{{ *v[0-9]+.h *}}}[7], [{{x[0-9]+|sp}}] } void test_vst1q_lane_u32(uint32_t *a, uint32x4_t b) { // CHECK-LABEL: test_vst1q_lane_u32 vst1q_lane_u32(a, b, 3); - // CHECK: st1 {v{{[0-9]+}}.s}[3], [{{x[0-9]+|sp}}] + // CHECK: st1 {{{ *v[0-9]+.s *}}}[3], [{{x[0-9]+|sp}}] } void test_vst1q_lane_u64(uint64_t *a, uint64x2_t b) { // CHECK-LABEL: test_vst1q_lane_u64 vst1q_lane_u64(a, b, 1); - // CHECK: st1 {v{{[0-9]+}}.d}[1], [{{x[0-9]+|sp}}] + // CHECK: st1 {{{ *v[0-9]+.d *}}}[1], [{{x[0-9]+|sp}}] } void test_vst1q_lane_s8(int8_t *a, int8x16_t b) { // CHECK-LABEL: test_vst1q_lane_s8 vst1q_lane_s8(a, b, 15); - // CHECK: st1 {v{{[0-9]+}}.b}[15], [{{x[0-9]+|sp}}] + // CHECK: st1 {{{ *v[0-9]+.b *}}}[15], [{{x[0-9]+|sp}}] } void test_vst1q_lane_s16(int16_t *a, int16x8_t b) { // CHECK-LABEL: test_vst1q_lane_s16 vst1q_lane_s16(a, b, 7); - // CHECK: st1 {v{{[0-9]+}}.h}[7], [{{x[0-9]+|sp}}] + // CHECK: st1 {{{ *v[0-9]+.h *}}}[7], [{{x[0-9]+|sp}}] } void test_vst1q_lane_s32(int32_t *a, int32x4_t b) { // CHECK-LABEL: test_vst1q_lane_s32 vst1q_lane_s32(a, b, 3); - // CHECK: st1 {v{{[0-9]+}}.s}[3], [{{x[0-9]+|sp}}] + // CHECK: st1 {{{ *v[0-9]+.s *}}}[3], [{{x[0-9]+|sp}}] } void test_vst1q_lane_s64(int64_t *a, int64x2_t b) { // CHECK-LABEL: test_vst1q_lane_s64 vst1q_lane_s64(a, b, 1); - // CHECK: st1 {v{{[0-9]+}}.d}[1], [{{x[0-9]+|sp}}] + // CHECK: st1 {{{ *v[0-9]+.d *}}}[1], [{{x[0-9]+|sp}}] } void test_vst1q_lane_f16(float16_t *a, float16x8_t b) { // CHECK-LABEL: test_vst1q_lane_f16 vst1q_lane_f16(a, b, 7); - // CHECK: st1 {v{{[0-9]+}}.h}[7], [{{x[0-9]+|sp}}] + // CHECK: st1 {{{ *v[0-9]+.h *}}}[7], [{{x[0-9]+|sp}}] } void test_vst1q_lane_f32(float32_t *a, float32x4_t b) { // CHECK-LABEL: test_vst1q_lane_f32 vst1q_lane_f32(a, b, 3); - // CHECK: st1 {v{{[0-9]+}}.s}[3], [{{x[0-9]+|sp}}] + // CHECK: st1 {{{ *v[0-9]+.s *}}}[3], [{{x[0-9]+|sp}}] } void test_vst1q_lane_f64(float64_t *a, float64x2_t b) { // CHECK-LABEL: test_vst1q_lane_f64 vst1q_lane_f64(a, b, 1); - // CHECK: st1 {v{{[0-9]+}}.d}[1], [{{x[0-9]+|sp}}] + // CHECK: st1 {{{ *v[0-9]+.d *}}}[1], [{{x[0-9]+|sp}}] } -poly8x16_t test_vst1q_lane_p8(poly8_t *a, poly8x16_t b) { +void test_vst1q_lane_p8(poly8_t *a, poly8x16_t b) { // CHECK-LABEL: test_vst1q_lane_p8 vst1q_lane_p8(a, b, 15); - // CHECK: st1 {v{{[0-9]+}}.b}[15], [{{x[0-9]+|sp}}] + // CHECK: st1 {{{ *v[0-9]+.b *}}}[15], [{{x[0-9]+|sp}}] } void test_vst1q_lane_p16(poly16_t *a, poly16x8_t b) { // CHECK-LABEL: test_vst1q_lane_p16 vst1q_lane_p16(a, b, 7); - // CHECK: st1 {v{{[0-9]+}}.h}[7], [{{x[0-9]+|sp}}] + // CHECK: st1 {{{ *v[0-9]+.h *}}}[7], [{{x[0-9]+|sp}}] } void test_vst1q_lane_p64(poly64_t *a, poly64x2_t b) { // CHECK-LABEL: test_vst1q_lane_p64 vst1q_lane_p64(a, b, 1); - // CHECK: st1 {v{{[0-9]+}}.d}[1], [{{x[0-9]+|sp}}] + // CHECK: st1 {{{ *v[0-9]+.d *}}}[1], [{{x[0-9]+|sp}}] } void test_vst1_lane_u8(uint8_t *a, uint8x8_t b) { // CHECK-LABEL: test_vst1_lane_u8 vst1_lane_u8(a, b, 7); - // CHECK: st1 {v{{[0-9]+}}.b}[7], [{{x[0-9]+|sp}}] + // CHECK: st1 {{{ *v[0-9]+.b *}}}[7], [{{x[0-9]+|sp}}] } void test_vst1_lane_u16(uint16_t *a, uint16x4_t b) { // CHECK-LABEL: test_vst1_lane_u16 vst1_lane_u16(a, b, 3); - // CHECK: st1 {v{{[0-9]+}}.h}[3], [{{x[0-9]+|sp}}] + // CHECK: st1 {{{ *v[0-9]+.h *}}}[3], [{{x[0-9]+|sp}}] } void test_vst1_lane_u32(uint32_t *a, uint32x2_t b) { // CHECK-LABEL: test_vst1_lane_u32 vst1_lane_u32(a, b, 1); - // CHECK: st1 {v{{[0-9]+}}.s}[1], [{{x[0-9]+|sp}}] + // CHECK: st1 {{{ *v[0-9]+.s *}}}[1], [{{x[0-9]+|sp}}] } void test_vst1_lane_u64(uint64_t *a, uint64x1_t b) { // CHECK-LABEL: test_vst1_lane_u64 vst1_lane_u64(a, b, 0); - // CHECK: st1 {v{{[0-9]+}}.d}[0], [{{x[0-9]+|sp}}] + // CHECK: st1 {{{ *v[0-9]+.d *}}}[0], [{{x[0-9]+|sp}}] } void test_vst1_lane_s8(int8_t *a, int8x8_t b) { // CHECK-LABEL: test_vst1_lane_s8 vst1_lane_s8(a, b, 7); - // CHECK: st1 {v{{[0-9]+}}.b}[7], [{{x[0-9]+|sp}}] + // CHECK: st1 {{{ *v[0-9]+.b *}}}[7], [{{x[0-9]+|sp}}] } void test_vst1_lane_s16(int16_t *a, int16x4_t b) { // CHECK-LABEL: test_vst1_lane_s16 vst1_lane_s16(a, b, 3); - // CHECK: st1 {v{{[0-9]+}}.h}[3], [{{x[0-9]+|sp}}] + // CHECK: st1 {{{ *v[0-9]+.h *}}}[3], [{{x[0-9]+|sp}}] } void test_vst1_lane_s32(int32_t *a, int32x2_t b) { // CHECK-LABEL: test_vst1_lane_s32 vst1_lane_s32(a, b, 1); - // CHECK: st1 {v{{[0-9]+}}.s}[1], [{{x[0-9]+|sp}}] + // CHECK: st1 {{{ *v[0-9]+.s *}}}[1], [{{x[0-9]+|sp}}] } void test_vst1_lane_s64(int64_t *a, int64x1_t b) { // CHECK-LABEL: test_vst1_lane_s64 vst1_lane_s64(a, b, 0); - // CHECK: st1 {v{{[0-9]+}}.d}[0], [{{x[0-9]+|sp}}] + // CHECK: st1 {{{ *v[0-9]+.d *}}}[0], [{{x[0-9]+|sp}}] } void test_vst1_lane_f16(float16_t *a, float16x4_t b) { // CHECK-LABEL: test_vst1_lane_f16 vst1_lane_f16(a, b, 3); - // CHECK: st1 {v{{[0-9]+}}.h}[3], [{{x[0-9]+|sp}}] + // CHECK: st1 {{{ *v[0-9]+.h *}}}[3], [{{x[0-9]+|sp}}] } void test_vst1_lane_f32(float32_t *a, float32x2_t b) { // CHECK-LABEL: test_vst1_lane_f32 vst1_lane_f32(a, b, 1); - // CHECK: st1 {v{{[0-9]+}}.s}[1], [{{x[0-9]+|sp}}] + // CHECK: st1 {{{ *v[0-9]+.s *}}}[1], [{{x[0-9]+|sp}}] } void test_vst1_lane_f64(float64_t *a, float64x1_t b) { // CHECK-LABEL: test_vst1_lane_f64 vst1_lane_f64(a, b, 0); - // CHECK: st1 {v{{[0-9]+}}.d}[0], [{{x[0-9]+|sp}}] + // CHECK: {{st1 {v[0-9]+.d}\[0]|str d[0-9]+}}, [{{x[0-9]+|sp}}] } void test_vst1_lane_p8(poly8_t *a, poly8x8_t b) { // CHECK-LABEL: test_vst1_lane_p8 vst1_lane_p8(a, b, 7); - // CHECK: st1 {v{{[0-9]+}}.b}[7], [{{x[0-9]+|sp}}] + // CHECK: st1 {{{ *v[0-9]+.b *}}}[7], [{{x[0-9]+|sp}}] } void test_vst1_lane_p16(poly16_t *a, poly16x4_t b) { // CHECK-LABEL: test_vst1_lane_p16 vst1_lane_p16(a, b, 3); - // CHECK: st1 {v{{[0-9]+}}.h}[3], [{{x[0-9]+|sp}}] + // CHECK: st1 {{{ *v[0-9]+.h *}}}[3], [{{x[0-9]+|sp}}] } void test_vst1_lane_p64(poly64_t *a, poly64x1_t b) { // CHECK-LABEL: test_vst1_lane_p64 vst1_lane_p64(a, b, 0); - // CHECK: st1 {v{{[0-9]+}}.d}[0], [{{x[0-9]+|sp}}] + // CHECK: st1 {{{ *v[0-9]+.d *}}}[0], [{{x[0-9]+|sp}}] } void test_vst2q_lane_u8(uint8_t *a, uint8x16x2_t b) { // CHECK-LABEL: test_vst2q_lane_u8 vst2q_lane_u8(a, b, 15); - // CHECK: st2 {v{{[0-9]+}}.b, v{{[0-9]+}}.b}[15], [{{x[0-9]+|sp}}] + // CHECK: st2 {{{ *v[0-9]+.b, v[0-9]+.b *}}}[15], [{{x[0-9]+|sp}}] } void test_vst2q_lane_u16(uint16_t *a, uint16x8x2_t b) { // CHECK-LABEL: test_vst2q_lane_u16 vst2q_lane_u16(a, b, 7); - // CHECK: st2 {v{{[0-9]+}}.h, v{{[0-9]+}}.h}[7], [{{x[0-9]+|sp}}] + // CHECK: st2 {{{ *v[0-9]+.h, v[0-9]+.h *}}}[7], [{{x[0-9]+|sp}}] } void test_vst2q_lane_u32(uint32_t *a, uint32x4x2_t b) { // CHECK-LABEL: test_vst2q_lane_u32 vst2q_lane_u32(a, b, 3); - // CHECK: st2 {v{{[0-9]+}}.s, v{{[0-9]+}}.s}[3], [{{x[0-9]+|sp}}] + // CHECK: st2 {{{ *v[0-9]+.s, v[0-9]+.s *}}}[3], [{{x[0-9]+|sp}}] } void test_vst2q_lane_u64(uint64_t *a, uint64x2x2_t b) { // CHECK-LABEL: test_vst2q_lane_u64 vst2q_lane_u64(a, b, 1); - // CHECK: st2 {v{{[0-9]+}}.d, v{{[0-9]+}}.d}[1], [{{x[0-9]+|sp}}] + // CHECK: st2 {{{ *v[0-9]+.d, v[0-9]+.d *}}}[1], [{{x[0-9]+|sp}}] } void test_vst2q_lane_s8(int8_t *a, int8x16x2_t b) { // CHECK-LABEL: test_vst2q_lane_s8 vst2q_lane_s8(a, b, 15); - // CHECK: st2 {v{{[0-9]+}}.b, v{{[0-9]+}}.b}[15], [{{x[0-9]+|sp}}] + // CHECK: st2 {{{ *v[0-9]+.b, v[0-9]+.b *}}}[15], [{{x[0-9]+|sp}}] } void test_vst2q_lane_s16(int16_t *a, int16x8x2_t b) { // CHECK-LABEL: test_vst2q_lane_s16 vst2q_lane_s16(a, b, 7); - // CHECK: st2 {v{{[0-9]+}}.h, v{{[0-9]+}}.h}[7], [{{x[0-9]+|sp}}] + // CHECK: st2 {{{ *v[0-9]+.h, v[0-9]+.h *}}}[7], [{{x[0-9]+|sp}}] } void test_vst2q_lane_s32(int32_t *a, int32x4x2_t b) { // CHECK-LABEL: test_vst2q_lane_s32 vst2q_lane_s32(a, b, 3); - // CHECK: st2 {v{{[0-9]+}}.s, v{{[0-9]+}}.s}[3], [{{x[0-9]+|sp}}] + // CHECK: st2 {{{ *v[0-9]+.s, v[0-9]+.s *}}}[3], [{{x[0-9]+|sp}}] } void test_vst2q_lane_s64(int64_t *a, int64x2x2_t b) { // CHECK-LABEL: test_vst2q_lane_s64 vst2q_lane_s64(a, b, 1); - // CHECK: st2 {v{{[0-9]+}}.d, v{{[0-9]+}}.d}[1], [{{x[0-9]+|sp}}] + // CHECK: st2 {{{ *v[0-9]+.d, v[0-9]+.d *}}}[1], [{{x[0-9]+|sp}}] } void test_vst2q_lane_f16(float16_t *a, float16x8x2_t b) { // CHECK-LABEL: test_vst2q_lane_f16 vst2q_lane_f16(a, b, 7); - // CHECK: st2 {v{{[0-9]+}}.h, v{{[0-9]+}}.h}[7], [{{x[0-9]+|sp}}] + // CHECK: st2 {{{ *v[0-9]+.h, v[0-9]+.h *}}}[7], [{{x[0-9]+|sp}}] } void test_vst2q_lane_f32(float32_t *a, float32x4x2_t b) { // CHECK-LABEL: test_vst2q_lane_f32 vst2q_lane_f32(a, b, 3); - // CHECK: st2 {v{{[0-9]+}}.s, v{{[0-9]+}}.s}[3], [{{x[0-9]+|sp}}] + // CHECK: st2 {{{ *v[0-9]+.s, v[0-9]+.s *}}}[3], [{{x[0-9]+|sp}}] } void test_vst2q_lane_f64(float64_t *a, float64x2x2_t b) { // CHECK-LABEL: test_vst2q_lane_f64 vst2q_lane_f64(a, b, 1); - // CHECK: st2 {v{{[0-9]+}}.d, v{{[0-9]+}}.d}[1], [{{x[0-9]+|sp}}] + // CHECK: st2 {{{ *v[0-9]+.d, v[0-9]+.d *}}}[1], [{{x[0-9]+|sp}}] } void test_vst2q_lane_p8(poly8_t *a, poly8x16x2_t b) { // CHECK-LABEL: test_vst2q_lane_p8 vst2q_lane_p8(a, b, 15); - // CHECK: st2 {v{{[0-9]+}}.b, v{{[0-9]+}}.b}[15], [{{x[0-9]+|sp}}] + // CHECK: st2 {{{ *v[0-9]+.b, v[0-9]+.b *}}}[15], [{{x[0-9]+|sp}}] } void test_vst2q_lane_p16(poly16_t *a, poly16x8x2_t b) { // CHECK-LABEL: test_vst2q_lane_p16 vst2q_lane_p16(a, b, 7); - // CHECK: st2 {v{{[0-9]+}}.h, v{{[0-9]+}}.h}[7], [{{x[0-9]+|sp}}] + // CHECK: st2 {{{ *v[0-9]+.h, v[0-9]+.h *}}}[7], [{{x[0-9]+|sp}}] } void test_vst2q_lane_p64(poly64_t *a, poly64x2x2_t b) { // CHECK-LABEL: test_vst2q_lane_p64 vst2q_lane_p64(a, b, 1); - // CHECK: st2 {v{{[0-9]+}}.d, v{{[0-9]+}}.d}[1], [{{x[0-9]+|sp}}] + // CHECK: st2 {{{ *v[0-9]+.d, v[0-9]+.d *}}}[1], [{{x[0-9]+|sp}}] } void test_vst2_lane_u8(uint8_t *a, uint8x8x2_t b) { // CHECK-LABEL: test_vst2_lane_u8 vst2_lane_u8(a, b, 7); - // CHECK: st2 {v{{[0-9]+}}.b, v{{[0-9]+}}.b}[7], [{{x[0-9]+|sp}}] + // CHECK: st2 {{{ *v[0-9]+.b, v[0-9]+.b *}}}[7], [{{x[0-9]+|sp}}] } void test_vst2_lane_u16(uint16_t *a, uint16x4x2_t b) { // CHECK-LABEL: test_vst2_lane_u16 vst2_lane_u16(a, b, 3); - // CHECK: st2 {v{{[0-9]+}}.h, v{{[0-9]+}}.h}[3], [{{x[0-9]+|sp}}] + // CHECK: st2 {{{ *v[0-9]+.h, v[0-9]+.h *}}}[3], [{{x[0-9]+|sp}}] } void test_vst2_lane_u32(uint32_t *a, uint32x2x2_t b) { // CHECK-LABEL: test_vst2_lane_u32 vst2_lane_u32(a, b, 1); - // CHECK: st2 {v{{[0-9]+}}.s, v{{[0-9]+}}.s}[1], [{{x[0-9]+|sp}}] + // CHECK: st2 {{{ *v[0-9]+.s, v[0-9]+.s *}}}[1], [{{x[0-9]+|sp}}] } void test_vst2_lane_u64(uint64_t *a, uint64x1x2_t b) { // CHECK-LABEL: test_vst2_lane_u64 vst2_lane_u64(a, b, 0); - // CHECK: st2 {v{{[0-9]+}}.d, v{{[0-9]+}}.d}[0], [{{x[0-9]+|sp}}] + // CHECK: st2 {{{ *v[0-9]+.d, v[0-9]+.d *}}}[0], [{{x[0-9]+|sp}}] } void test_vst2_lane_s8(int8_t *a, int8x8x2_t b) { // CHECK-LABEL: test_vst2_lane_s8 vst2_lane_s8(a, b, 7); - // CHECK: st2 {v{{[0-9]+}}.b, v{{[0-9]+}}.b}[7], [{{x[0-9]+|sp}}] + // CHECK: st2 {{{ *v[0-9]+.b, v[0-9]+.b *}}}[7], [{{x[0-9]+|sp}}] } void test_vst2_lane_s16(int16_t *a, int16x4x2_t b) { // CHECK-LABEL: test_vst2_lane_s16 vst2_lane_s16(a, b, 3); - // CHECK: st2 {v{{[0-9]+}}.h, v{{[0-9]+}}.h}[3], [{{x[0-9]+|sp}}] + // CHECK: st2 {{{ *v[0-9]+.h, v[0-9]+.h *}}}[3], [{{x[0-9]+|sp}}] } void test_vst2_lane_s32(int32_t *a, int32x2x2_t b) { // CHECK-LABEL: test_vst2_lane_s32 vst2_lane_s32(a, b, 1); - // CHECK: st2 {v{{[0-9]+}}.s, v{{[0-9]+}}.s}[1], [{{x[0-9]+|sp}}] + // CHECK: st2 {{{ *v[0-9]+.s, v[0-9]+.s *}}}[1], [{{x[0-9]+|sp}}] } void test_vst2_lane_s64(int64_t *a, int64x1x2_t b) { // CHECK-LABEL: test_vst2_lane_s64 vst2_lane_s64(a, b, 0); - // CHECK: st2 {v{{[0-9]+}}.d, v{{[0-9]+}}.d}[0], [{{x[0-9]+|sp}}] + // CHECK: st2 {{{ *v[0-9]+.d, v[0-9]+.d *}}}[0], [{{x[0-9]+|sp}}] } void test_vst2_lane_f16(float16_t *a, float16x4x2_t b) { // CHECK-LABEL: test_vst2_lane_f16 vst2_lane_f16(a, b, 3); - // CHECK: st2 {v{{[0-9]+}}.h, v{{[0-9]+}}.h}[3], [{{x[0-9]+|sp}}] + // CHECK: st2 {{{ *v[0-9]+.h, v[0-9]+.h *}}}[3], [{{x[0-9]+|sp}}] } void test_vst2_lane_f32(float32_t *a, float32x2x2_t b) { // CHECK-LABEL: test_vst2_lane_f32 vst2_lane_f32(a, b, 1); - // CHECK: st2 {v{{[0-9]+}}.s, v{{[0-9]+}}.s}[1], [{{x[0-9]+|sp}}] + // CHECK: st2 {{{ *v[0-9]+.s, v[0-9]+.s *}}}[1], [{{x[0-9]+|sp}}] } void test_vst2_lane_f64(float64_t *a, float64x1x2_t b) { // CHECK-LABEL: test_vst2_lane_f64 vst2_lane_f64(a, b, 0); - // CHECK: st2 {v{{[0-9]+}}.d, v{{[0-9]+}}.d}[0], [{{x[0-9]+|sp}}] + // CHECK: st2 {{{ *v[0-9]+.d, v[0-9]+.d *}}}[0], [{{x[0-9]+|sp}}] } void test_vst2_lane_p8(poly8_t *a, poly8x8x2_t b) { // CHECK-LABEL: test_vst2_lane_p8 vst2_lane_p8(a, b, 7); - // CHECK: st2 {v{{[0-9]+}}.b, v{{[0-9]+}}.b}[7], [{{x[0-9]+|sp}}] + // CHECK: st2 {{{ *v[0-9]+.b, v[0-9]+.b *}}}[7], [{{x[0-9]+|sp}}] } void test_vst2_lane_p16(poly16_t *a, poly16x4x2_t b) { // CHECK-LABEL: test_vst2_lane_p16 vst2_lane_p16(a, b, 3); - // CHECK: st2 {v{{[0-9]+}}.h, v{{[0-9]+}}.h}[3], [{{x[0-9]+|sp}}] + // CHECK: st2 {{{ *v[0-9]+.h, v[0-9]+.h *}}}[3], [{{x[0-9]+|sp}}] } void test_vst2_lane_p64(poly64_t *a, poly64x1x2_t b) { // CHECK-LABEL: test_vst2_lane_p64 vst2_lane_p64(a, b, 0); - // CHECK: st2 {v{{[0-9]+}}.d, v{{[0-9]+}}.d}[0], [{{x[0-9]+|sp}}] + // CHECK: st2 {{{ *v[0-9]+.d, v[0-9]+.d *}}}[0], [{{x[0-9]+|sp}}] } void test_vst3q_lane_u8(uint8_t *a, uint8x16x3_t b) { // CHECK-LABEL: test_vst3q_lane_u8 vst3q_lane_u8(a, b, 15); - // CHECK: st3 {v{{[0-9]+}}.b, v{{[0-9]+}}.b, v{{[0-9]+}}.b}[15], [{{x[0-9]+|sp}}] + // CHECK: st3 {{{ *v[0-9]+.b, v[0-9]+.b, v[0-9]+.b *}}}[15], [{{x[0-9]+|sp}}] } void test_vst3q_lane_u16(uint16_t *a, uint16x8x3_t b) { // CHECK-LABEL: test_vst3q_lane_u16 vst3q_lane_u16(a, b, 7); - // CHECK: st3 {v{{[0-9]+}}.h, v{{[0-9]+}}.h, v{{[0-9]+}}.h}[7], [{{x[0-9]+|sp}}] + // CHECK: st3 {{{ *v[0-9]+.h, v[0-9]+.h, v[0-9]+.h *}}}[7], [{{x[0-9]+|sp}}] } void test_vst3q_lane_u32(uint32_t *a, uint32x4x3_t b) { // CHECK-LABEL: test_vst3q_lane_u32 vst3q_lane_u32(a, b, 3); - // CHECK: st3 {v{{[0-9]+}}.s, v{{[0-9]+}}.s, v{{[0-9]+}}.s}[3], [{{x[0-9]+|sp}}] + // CHECK: st3 {{{ *v[0-9]+.s, v[0-9]+.s, v[0-9]+.s *}}}[3], [{{x[0-9]+|sp}}] } void test_vst3q_lane_u64(uint64_t *a, uint64x2x3_t b) { // CHECK-LABEL: test_vst3q_lane_u64 vst3q_lane_u64(a, b, 1); - // CHECK: st3 {v{{[0-9]+}}.d, v{{[0-9]+}}.d, v{{[0-9]+}}.d}[1], [{{x[0-9]+|sp}}] + // CHECK: st3 {{{ *v[0-9]+.d, v[0-9]+.d, v[0-9]+.d *}}}[1], [{{x[0-9]+|sp}}] } void test_vst3q_lane_s8(int8_t *a, int8x16x3_t b) { // CHECK-LABEL: test_vst3q_lane_s8 vst3q_lane_s8(a, b, 15); - // CHECK: st3 {v{{[0-9]+}}.b, v{{[0-9]+}}.b, v{{[0-9]+}}.b}[15], [{{x[0-9]+|sp}}] + // CHECK: st3 {{{ *v[0-9]+.b, v[0-9]+.b, v[0-9]+.b *}}}[15], [{{x[0-9]+|sp}}] } void test_vst3q_lane_s16(int16_t *a, int16x8x3_t b) { // CHECK-LABEL: test_vst3q_lane_s16 vst3q_lane_s16(a, b, 7); - // CHECK: st3 {v{{[0-9]+}}.h, v{{[0-9]+}}.h, v{{[0-9]+}}.h}[7], [{{x[0-9]+|sp}}] + // CHECK: st3 {{{ *v[0-9]+.h, v[0-9]+.h, v[0-9]+.h *}}}[7], [{{x[0-9]+|sp}}] } void test_vst3q_lane_s32(int32_t *a, int32x4x3_t b) { // CHECK-LABEL: test_vst3q_lane_s32 vst3q_lane_s32(a, b, 3); - // CHECK: st3 {v{{[0-9]+}}.s, v{{[0-9]+}}.s, v{{[0-9]+}}.s}[3], [{{x[0-9]+|sp}}] + // CHECK: st3 {{{ *v[0-9]+.s, v[0-9]+.s, v[0-9]+.s *}}}[3], [{{x[0-9]+|sp}}] } void test_vst3q_lane_s64(int64_t *a, int64x2x3_t b) { // CHECK-LABEL: test_vst3q_lane_s64 vst3q_lane_s64(a, b, 1); - // CHECK: st3 {v{{[0-9]+}}.d, v{{[0-9]+}}.d, v{{[0-9]+}}.d}[1], [{{x[0-9]+|sp}}] + // CHECK: st3 {{{ *v[0-9]+.d, v[0-9]+.d, v[0-9]+.d *}}}[1], [{{x[0-9]+|sp}}] } void test_vst3q_lane_f16(float16_t *a, float16x8x3_t b) { // CHECK-LABEL: test_vst3q_lane_f16 vst3q_lane_f16(a, b, 7); - // CHECK: st3 {v{{[0-9]+}}.h, v{{[0-9]+}}.h, v{{[0-9]+}}.h}[7], [{{x[0-9]+|sp}}] + // CHECK: st3 {{{ *v[0-9]+.h, v[0-9]+.h, v[0-9]+.h *}}}[7], [{{x[0-9]+|sp}}] } void test_vst3q_lane_f32(float32_t *a, float32x4x3_t b) { // CHECK-LABEL: test_vst3q_lane_f32 vst3q_lane_f32(a, b, 3); - // CHECK: st3 {v{{[0-9]+}}.s, v{{[0-9]+}}.s, v{{[0-9]+}}.s}[3], [{{x[0-9]+|sp}}] + // CHECK: st3 {{{ *v[0-9]+.s, v[0-9]+.s, v[0-9]+.s *}}}[3], [{{x[0-9]+|sp}}] } void test_vst3q_lane_f64(float64_t *a, float64x2x3_t b) { // CHECK-LABEL: test_vst3q_lane_f64 vst3q_lane_f64(a, b, 1); - // CHECK: st3 {v{{[0-9]+}}.d, v{{[0-9]+}}.d, v{{[0-9]+}}.d}[1], [{{x[0-9]+|sp}}] + // CHECK: st3 {{{ *v[0-9]+.d, v[0-9]+.d, v[0-9]+.d *}}}[1], [{{x[0-9]+|sp}}] } void test_vst3q_lane_p8(poly8_t *a, poly8x16x3_t b) { // CHECK-LABEL: test_vst3q_lane_p8 vst3q_lane_p8(a, b, 15); - // CHECK: st3 {v{{[0-9]+}}.b, v{{[0-9]+}}.b, v{{[0-9]+}}.b}[15], [{{x[0-9]+|sp}}] + // CHECK: st3 {{{ *v[0-9]+.b, v[0-9]+.b, v[0-9]+.b *}}}[15], [{{x[0-9]+|sp}}] } void test_vst3q_lane_p16(poly16_t *a, poly16x8x3_t b) { // CHECK-LABEL: test_vst3q_lane_p16 vst3q_lane_p16(a, b, 7); - // CHECK: st3 {v{{[0-9]+}}.h, v{{[0-9]+}}.h, v{{[0-9]+}}.h}[7], [{{x[0-9]+|sp}}] + // CHECK: st3 {{{ *v[0-9]+.h, v[0-9]+.h, v[0-9]+.h *}}}[7], [{{x[0-9]+|sp}}] } void test_vst3q_lane_p64(poly64_t *a, poly64x2x3_t b) { // CHECK-LABEL: test_vst3q_lane_p64 vst3q_lane_p64(a, b, 1); - // CHECK: st3 {v{{[0-9]+}}.d, v{{[0-9]+}}.d, v{{[0-9]+}}.d}[1], [{{x[0-9]+|sp}}] + // CHECK: st3 {{{ *v[0-9]+.d, v[0-9]+.d, v[0-9]+.d *}}}[1], [{{x[0-9]+|sp}}] } void test_vst3_lane_u8(uint8_t *a, uint8x8x3_t b) { // CHECK-LABEL: test_vst3_lane_u8 vst3_lane_u8(a, b, 7); - // CHECK: st3 {v{{[0-9]+}}.b, v{{[0-9]+}}.b, v{{[0-9]+}}.b}[7], [{{x[0-9]+|sp}}] + // CHECK: st3 {{{ *v[0-9]+.b, v[0-9]+.b, v[0-9]+.b *}}}[7], [{{x[0-9]+|sp}}] } void test_vst3_lane_u16(uint16_t *a, uint16x4x3_t b) { // CHECK-LABEL: test_vst3_lane_u16 vst3_lane_u16(a, b, 3); - // CHECK: st3 {v{{[0-9]+}}.h, v{{[0-9]+}}.h, v{{[0-9]+}}.h}[3], [{{x[0-9]+|sp}}] + // CHECK: st3 {{{ *v[0-9]+.h, v[0-9]+.h, v[0-9]+.h *}}}[3], [{{x[0-9]+|sp}}] } void test_vst3_lane_u32(uint32_t *a, uint32x2x3_t b) { // CHECK-LABEL: test_vst3_lane_u32 vst3_lane_u32(a, b, 1); - // CHECK: st3 {v{{[0-9]+}}.s, v{{[0-9]+}}.s, v{{[0-9]+}}.s}[1], [{{x[0-9]+|sp}}] + // CHECK: st3 {{{ *v[0-9]+.s, v[0-9]+.s, v[0-9]+.s *}}}[1], [{{x[0-9]+|sp}}] } void test_vst3_lane_u64(uint64_t *a, uint64x1x3_t b) { // CHECK-LABEL: test_vst3_lane_u64 vst3_lane_u64(a, b, 0); - // CHECK: st3 {v{{[0-9]+}}.d, v{{[0-9]+}}.d, v{{[0-9]+}}.d}[0], [{{x[0-9]+|sp}}] + // CHECK: st3 {{{ *v[0-9]+.d, v[0-9]+.d, v[0-9]+.d *}}}[0], [{{x[0-9]+|sp}}] } void test_vst3_lane_s8(int8_t *a, int8x8x3_t b) { // CHECK-LABEL: test_vst3_lane_s8 vst3_lane_s8(a, b, 7); - // CHECK: st3 {v{{[0-9]+}}.b, v{{[0-9]+}}.b, v{{[0-9]+}}.b}[7], [{{x[0-9]+|sp}}] + // CHECK: st3 {{{ *v[0-9]+.b, v[0-9]+.b, v[0-9]+.b *}}}[7], [{{x[0-9]+|sp}}] } void test_vst3_lane_s16(int16_t *a, int16x4x3_t b) { // CHECK-LABEL: test_vst3_lane_s16 vst3_lane_s16(a, b, 3); - // CHECK: st3 {v{{[0-9]+}}.h, v{{[0-9]+}}.h, v{{[0-9]+}}.h}[3], [{{x[0-9]+|sp}}] + // CHECK: st3 {{{ *v[0-9]+.h, v[0-9]+.h, v[0-9]+.h *}}}[3], [{{x[0-9]+|sp}}] } void test_vst3_lane_s32(int32_t *a, int32x2x3_t b) { // CHECK-LABEL: test_vst3_lane_s32 vst3_lane_s32(a, b, 1); - // CHECK: st3 {v{{[0-9]+}}.s, v{{[0-9]+}}.s, v{{[0-9]+}}.s}[1], [{{x[0-9]+|sp}}] + // CHECK: st3 {{{ *v[0-9]+.s, v[0-9]+.s, v[0-9]+.s *}}}[1], [{{x[0-9]+|sp}}] } void test_vst3_lane_s64(int64_t *a, int64x1x3_t b) { // CHECK-LABEL: test_vst3_lane_s64 vst3_lane_s64(a, b, 0); - // CHECK: st3 {v{{[0-9]+}}.d, v{{[0-9]+}}.d, v{{[0-9]+}}.d}[0], [{{x[0-9]+|sp}}] + // CHECK: st3 {{{ *v[0-9]+.d, v[0-9]+.d, v[0-9]+.d *}}}[0], [{{x[0-9]+|sp}}] } void test_vst3_lane_f16(float16_t *a, float16x4x3_t b) { // CHECK-LABEL: test_vst3_lane_f16 vst3_lane_f16(a, b, 3); - // CHECK: st3 {v{{[0-9]+}}.h, v{{[0-9]+}}.h, v{{[0-9]+}}.h}[3], [{{x[0-9]+|sp}}] + // CHECK: st3 {{{ *v[0-9]+.h, v[0-9]+.h, v[0-9]+.h *}}}[3], [{{x[0-9]+|sp}}] } void test_vst3_lane_f32(float32_t *a, float32x2x3_t b) { // CHECK-LABEL: test_vst3_lane_f32 vst3_lane_f32(a, b, 1); - // CHECK: st3 {v{{[0-9]+}}.s, v{{[0-9]+}}.s, v{{[0-9]+}}.s}[1], [{{x[0-9]+|sp}}] + // CHECK: st3 {{{ *v[0-9]+.s, v[0-9]+.s, v[0-9]+.s *}}}[1], [{{x[0-9]+|sp}}] } void test_vst3_lane_f64(float64_t *a, float64x1x3_t b) { // CHECK-LABEL: test_vst3_lane_f64 vst3_lane_f64(a, b, 0); - // CHECK: st3 {v{{[0-9]+}}.d, v{{[0-9]+}}.d, v{{[0-9]+}}.d}[0], [{{x[0-9]+|sp}}] + // CHECK: st3 {{{ *v[0-9]+.d, v[0-9]+.d, v[0-9]+.d *}}}[0], [{{x[0-9]+|sp}}] } void test_vst3_lane_p8(poly8_t *a, poly8x8x3_t b) { // CHECK-LABEL: test_vst3_lane_p8 vst3_lane_p8(a, b, 7); - // CHECK: st3 {v{{[0-9]+}}.b, v{{[0-9]+}}.b, v{{[0-9]+}}.b}[7], [{{x[0-9]+|sp}}] + // CHECK: st3 {{{ *v[0-9]+.b, v[0-9]+.b, v[0-9]+.b *}}}[7], [{{x[0-9]+|sp}}] } void test_vst3_lane_p16(poly16_t *a, poly16x4x3_t b) { // CHECK-LABEL: test_vst3_lane_p16 vst3_lane_p16(a, b, 3); - // CHECK: st3 {v{{[0-9]+}}.h, v{{[0-9]+}}.h, v{{[0-9]+}}.h}[3], [{{x[0-9]+|sp}}] + // CHECK: st3 {{{ *v[0-9]+.h, v[0-9]+.h, v[0-9]+.h *}}}[3], [{{x[0-9]+|sp}}] } void test_vst3_lane_p64(poly64_t *a, poly64x1x3_t b) { // CHECK-LABEL: test_vst3_lane_p64 vst3_lane_p64(a, b, 0); - // CHECK: st3 {v{{[0-9]+}}.d, v{{[0-9]+}}.d, v{{[0-9]+}}.d}[0], [{{x[0-9]+|sp}}] + // CHECK: st3 {{{ *v[0-9]+.d, v[0-9]+.d, v[0-9]+.d *}}}[0], [{{x[0-9]+|sp}}] } -void test_vst4q_lane_u8(uint16_t *a, uint8x16x4_t b) { +void test_vst4q_lane_u8(uint8_t *a, uint8x16x4_t b) { // CHECK-LABEL: test_vst4q_lane_u8 vst4q_lane_u8(a, b, 15); - // CHECK: st4 {v{{[0-9]+}}.b, v{{[0-9]+}}.b, v{{[0-9]+}}.b, v{{[0-9]+}}.b}[15], [{{x[0-9]+|sp}}] + // CHECK: st4 {{{ *v[0-9]+.b, v[0-9]+.b, v[0-9]+.b, v[0-9]+.b *}}}[15], [{{x[0-9]+|sp}}] } void test_vst4q_lane_u16(uint16_t *a, uint16x8x4_t b) { // CHECK-LABEL: test_vst4q_lane_u16 vst4q_lane_u16(a, b, 7); - // CHECK: st4 {v{{[0-9]+}}.h, v{{[0-9]+}}.h, v{{[0-9]+}}.h, v{{[0-9]+}}.h}[7], [{{x[0-9]+|sp}}] + // CHECK: st4 {{{ *v[0-9]+.h, v[0-9]+.h, v[0-9]+.h, v[0-9]+.h *}}}[7], [{{x[0-9]+|sp}}] } void test_vst4q_lane_u32(uint32_t *a, uint32x4x4_t b) { // CHECK-LABEL: test_vst4q_lane_u32 vst4q_lane_u32(a, b, 3); - // CHECK: st4 {v{{[0-9]+}}.s, v{{[0-9]+}}.s, v{{[0-9]+}}.s, v{{[0-9]+}}.s}[3], [{{x[0-9]+|sp}}] + // CHECK: st4 {{{ *v[0-9]+.s, v[0-9]+.s, v[0-9]+.s, v[0-9]+.s *}}}[3], [{{x[0-9]+|sp}}] } void test_vst4q_lane_u64(uint64_t *a, uint64x2x4_t b) { // CHECK-LABEL: test_vst4q_lane_u64 vst4q_lane_u64(a, b, 1); - // CHECK: st4 {v{{[0-9]+}}.d, v{{[0-9]+}}.d, v{{[0-9]+}}.d, v{{[0-9]+}}.d}[1], [{{x[0-9]+|sp}}] + // CHECK: st4 {{{ *v[0-9]+.d, v[0-9]+.d, v[0-9]+.d, v[0-9]+.d *}}}[1], [{{x[0-9]+|sp}}] } -void test_vst4q_lane_s8(int16_t *a, int8x16x4_t b) { +void test_vst4q_lane_s8(int8_t *a, int8x16x4_t b) { // CHECK-LABEL: test_vst4q_lane_s8 vst4q_lane_s8(a, b, 15); - // CHECK: st4 {v{{[0-9]+}}.b, v{{[0-9]+}}.b, v{{[0-9]+}}.b, v{{[0-9]+}}.b}[15], [{{x[0-9]+|sp}}] + // CHECK: st4 {{{ *v[0-9]+.b, v[0-9]+.b, v[0-9]+.b, v[0-9]+.b *}}}[15], [{{x[0-9]+|sp}}] } void test_vst4q_lane_s16(int16_t *a, int16x8x4_t b) { // CHECK-LABEL: test_vst4q_lane_s16 vst4q_lane_s16(a, b, 7); - // CHECK: st4 {v{{[0-9]+}}.h, v{{[0-9]+}}.h, v{{[0-9]+}}.h, v{{[0-9]+}}.h}[7], [{{x[0-9]+|sp}}] + // CHECK: st4 {{{ *v[0-9]+.h, v[0-9]+.h, v[0-9]+.h, v[0-9]+.h *}}}[7], [{{x[0-9]+|sp}}] } void test_vst4q_lane_s32(int32_t *a, int32x4x4_t b) { // CHECK-LABEL: test_vst4q_lane_s32 vst4q_lane_s32(a, b, 3); - // CHECK: st4 {v{{[0-9]+}}.s, v{{[0-9]+}}.s, v{{[0-9]+}}.s, v{{[0-9]+}}.s}[3], [{{x[0-9]+|sp}}] + // CHECK: st4 {{{ *v[0-9]+.s, v[0-9]+.s, v[0-9]+.s, v[0-9]+.s *}}}[3], [{{x[0-9]+|sp}}] } void test_vst4q_lane_s64(int64_t *a, int64x2x4_t b) { // CHECK-LABEL: test_vst4q_lane_s64 vst4q_lane_s64(a, b, 1); - // CHECK: st4 {v{{[0-9]+}}.d, v{{[0-9]+}}.d, v{{[0-9]+}}.d, v{{[0-9]+}}.d}[1], [{{x[0-9]+|sp}}] + // CHECK: st4 {{{ *v[0-9]+.d, v[0-9]+.d, v[0-9]+.d, v[0-9]+.d *}}}[1], [{{x[0-9]+|sp}}] } void test_vst4q_lane_f16(float16_t *a, float16x8x4_t b) { // CHECK-LABEL: test_vst4q_lane_f16 vst4q_lane_f16(a, b, 7); - // CHECK: st4 {v{{[0-9]+}}.h, v{{[0-9]+}}.h, v{{[0-9]+}}.h, v{{[0-9]+}}.h}[7], [{{x[0-9]+|sp}}] + // CHECK: st4 {{{ *v[0-9]+.h, v[0-9]+.h, v[0-9]+.h, v[0-9]+.h *}}}[7], [{{x[0-9]+|sp}}] } void test_vst4q_lane_f32(float32_t *a, float32x4x4_t b) { // CHECK-LABEL: test_vst4q_lane_f32 vst4q_lane_f32(a, b, 3); - // CHECK: st4 {v{{[0-9]+}}.s, v{{[0-9]+}}.s, v{{[0-9]+}}.s, v{{[0-9]+}}.s}[3], [{{x[0-9]+|sp}}] + // CHECK: st4 {{{ *v[0-9]+.s, v[0-9]+.s, v[0-9]+.s, v[0-9]+.s *}}}[3], [{{x[0-9]+|sp}}] } void test_vst4q_lane_f64(float64_t *a, float64x2x4_t b) { // CHECK-LABEL: test_vst4q_lane_f64 vst4q_lane_f64(a, b, 1); - // CHECK: st4 {v{{[0-9]+}}.d, v{{[0-9]+}}.d, v{{[0-9]+}}.d, v{{[0-9]+}}.d}[1], [{{x[0-9]+|sp}}] + // CHECK: st4 {{{ *v[0-9]+.d, v[0-9]+.d, v[0-9]+.d, v[0-9]+.d *}}}[1], [{{x[0-9]+|sp}}] } -void test_vst4q_lane_p8(poly16_t *a, poly8x16x4_t b) { +void test_vst4q_lane_p8(poly8_t *a, poly8x16x4_t b) { // CHECK-LABEL: test_vst4q_lane_p8 vst4q_lane_p8(a, b, 15); - // CHECK: st4 {v{{[0-9]+}}.b, v{{[0-9]+}}.b, v{{[0-9]+}}.b, v{{[0-9]+}}.b}[15], [{{x[0-9]+|sp}}] + // CHECK: st4 {{{ *v[0-9]+.b, v[0-9]+.b, v[0-9]+.b, v[0-9]+.b *}}}[15], [{{x[0-9]+|sp}}] } void test_vst4q_lane_p16(poly16_t *a, poly16x8x4_t b) { // CHECK-LABEL: test_vst4q_lane_p16 vst4q_lane_p16(a, b, 7); - // CHECK: st4 {v{{[0-9]+}}.h, v{{[0-9]+}}.h, v{{[0-9]+}}.h, v{{[0-9]+}}.h}[7], [{{x[0-9]+|sp}}] + // CHECK: st4 {{{ *v[0-9]+.h, v[0-9]+.h, v[0-9]+.h, v[0-9]+.h *}}}[7], [{{x[0-9]+|sp}}] } void test_vst4q_lane_p64(poly64_t *a, poly64x2x4_t b) { // CHECK-LABEL: test_vst4q_lane_p64 vst4q_lane_p64(a, b, 1); - // CHECK: st4 {v{{[0-9]+}}.d, v{{[0-9]+}}.d, v{{[0-9]+}}.d, v{{[0-9]+}}.d}[1], [{{x[0-9]+|sp}}] + // CHECK: st4 {{{ *v[0-9]+.d, v[0-9]+.d, v[0-9]+.d, v[0-9]+.d *}}}[1], [{{x[0-9]+|sp}}] } void test_vst4_lane_u8(uint8_t *a, uint8x8x4_t b) { // CHECK-LABEL: test_vst4_lane_u8 vst4_lane_u8(a, b, 7); - // CHECK: st4 {v{{[0-9]+}}.b, v{{[0-9]+}}.b, v{{[0-9]+}}.b, v{{[0-9]+}}.b}[7], [{{x[0-9]+|sp}}] + // CHECK: st4 {{{ *v[0-9]+.b, v[0-9]+.b, v[0-9]+.b, v[0-9]+.b *}}}[7], [{{x[0-9]+|sp}}] } void test_vst4_lane_u16(uint16_t *a, uint16x4x4_t b) { // CHECK-LABEL: test_vst4_lane_u16 vst4_lane_u16(a, b, 3); - // CHECK: st4 {v{{[0-9]+}}.h, v{{[0-9]+}}.h, v{{[0-9]+}}.h, v{{[0-9]+}}.h}[3], [{{x[0-9]+|sp}}] + // CHECK: st4 {{{ *v[0-9]+.h, v[0-9]+.h, v[0-9]+.h, v[0-9]+.h *}}}[3], [{{x[0-9]+|sp}}] } void test_vst4_lane_u32(uint32_t *a, uint32x2x4_t b) { // CHECK-LABEL: test_vst4_lane_u32 vst4_lane_u32(a, b, 1); - // CHECK: st4 {v{{[0-9]+}}.s, v{{[0-9]+}}.s, v{{[0-9]+}}.s, v{{[0-9]+}}.s}[1], [{{x[0-9]+|sp}}] + // CHECK: st4 {{{ *v[0-9]+.s, v[0-9]+.s, v[0-9]+.s, v[0-9]+.s *}}}[1], [{{x[0-9]+|sp}}] } void test_vst4_lane_u64(uint64_t *a, uint64x1x4_t b) { // CHECK-LABEL: test_vst4_lane_u64 vst4_lane_u64(a, b, 0); - // CHECK: st4 {v{{[0-9]+}}.d, v{{[0-9]+}}.d, v{{[0-9]+}}.d, v{{[0-9]+}}.d}[0], [{{x[0-9]+|sp}}] + // CHECK: st4 {{{ *v[0-9]+.d, v[0-9]+.d, v[0-9]+.d, v[0-9]+.d *}}}[0], [{{x[0-9]+|sp}}] } void test_vst4_lane_s8(int8_t *a, int8x8x4_t b) { // CHECK-LABEL: test_vst4_lane_s8 vst4_lane_s8(a, b, 7); - // CHECK: st4 {v{{[0-9]+}}.b, v{{[0-9]+}}.b, v{{[0-9]+}}.b, v{{[0-9]+}}.b}[7], [{{x[0-9]+|sp}}] + // CHECK: st4 {{{ *v[0-9]+.b, v[0-9]+.b, v[0-9]+.b, v[0-9]+.b *}}}[7], [{{x[0-9]+|sp}}] } void test_vst4_lane_s16(int16_t *a, int16x4x4_t b) { // CHECK-LABEL: test_vst4_lane_s16 vst4_lane_s16(a, b, 3); - // CHECK: st4 {v{{[0-9]+}}.h, v{{[0-9]+}}.h, v{{[0-9]+}}.h, v{{[0-9]+}}.h}[3], [{{x[0-9]+|sp}}] + // CHECK: st4 {{{ *v[0-9]+.h, v[0-9]+.h, v[0-9]+.h, v[0-9]+.h *}}}[3], [{{x[0-9]+|sp}}] } void test_vst4_lane_s32(int32_t *a, int32x2x4_t b) { // CHECK-LABEL: test_vst4_lane_s32 vst4_lane_s32(a, b, 1); - // CHECK: st4 {v{{[0-9]+}}.s, v{{[0-9]+}}.s, v{{[0-9]+}}.s, v{{[0-9]+}}.s}[1], [{{x[0-9]+|sp}}] + // CHECK: st4 {{{ *v[0-9]+.s, v[0-9]+.s, v[0-9]+.s, v[0-9]+.s *}}}[1], [{{x[0-9]+|sp}}] } void test_vst4_lane_s64(int64_t *a, int64x1x4_t b) { // CHECK-LABEL: test_vst4_lane_s64 vst4_lane_s64(a, b, 0); - // CHECK: st4 {v{{[0-9]+}}.d, v{{[0-9]+}}.d, v{{[0-9]+}}.d, v{{[0-9]+}}.d}[0], [{{x[0-9]+|sp}}] + // CHECK: st4 {{{ *v[0-9]+.d, v[0-9]+.d, v[0-9]+.d, v[0-9]+.d *}}}[0], [{{x[0-9]+|sp}}] } void test_vst4_lane_f16(float16_t *a, float16x4x4_t b) { // CHECK-LABEL: test_vst4_lane_f16 vst4_lane_f16(a, b, 3); - // CHECK: st4 {v{{[0-9]+}}.h, v{{[0-9]+}}.h, v{{[0-9]+}}.h, v{{[0-9]+}}.h}[3], [{{x[0-9]+|sp}}] + // CHECK: st4 {{{ *v[0-9]+.h, v[0-9]+.h, v[0-9]+.h, v[0-9]+.h *}}}[3], [{{x[0-9]+|sp}}] } void test_vst4_lane_f32(float32_t *a, float32x2x4_t b) { // CHECK-LABEL: test_vst4_lane_f32 vst4_lane_f32(a, b, 1); - // CHECK: st4 {v{{[0-9]+}}.s, v{{[0-9]+}}.s, v{{[0-9]+}}.s, v{{[0-9]+}}.s}[1], [{{x[0-9]+|sp}}] + // CHECK: st4 {{{ *v[0-9]+.s, v[0-9]+.s, v[0-9]+.s, v[0-9]+.s *}}}[1], [{{x[0-9]+|sp}}] } void test_vst4_lane_f64(float64_t *a, float64x1x4_t b) { // CHECK-LABEL: test_vst4_lane_f64 vst4_lane_f64(a, b, 0); - // CHECK: st4 {v{{[0-9]+}}.d, v{{[0-9]+}}.d, v{{[0-9]+}}.d, v{{[0-9]+}}.d}[0], [{{x[0-9]+|sp}}] + // CHECK: st4 {{{ *v[0-9]+.d, v[0-9]+.d, v[0-9]+.d, v[0-9]+.d *}}}[0], [{{x[0-9]+|sp}}] } void test_vst4_lane_p8(poly8_t *a, poly8x8x4_t b) { // CHECK-LABEL: test_vst4_lane_p8 vst4_lane_p8(a, b, 7); - // CHECK: st4 {v{{[0-9]+}}.b, v{{[0-9]+}}.b, v{{[0-9]+}}.b, v{{[0-9]+}}.b}[7], [{{x[0-9]+|sp}}] + // CHECK: st4 {{{ *v[0-9]+.b, v[0-9]+.b, v[0-9]+.b, v[0-9]+.b *}}}[7], [{{x[0-9]+|sp}}] } void test_vst4_lane_p16(poly16_t *a, poly16x4x4_t b) { // CHECK-LABEL: test_vst4_lane_p16 vst4_lane_p16(a, b, 3); - // CHECK: st4 {v{{[0-9]+}}.h, v{{[0-9]+}}.h, v{{[0-9]+}}.h, v{{[0-9]+}}.h}[3], [{{x[0-9]+|sp}}] + // CHECK: st4 {{{ *v[0-9]+.h, v[0-9]+.h, v[0-9]+.h, v[0-9]+.h *}}}[3], [{{x[0-9]+|sp}}] } void test_vst4_lane_p64(poly64_t *a, poly64x1x4_t b) { // CHECK-LABEL: test_vst4_lane_p64 vst4_lane_p64(a, b, 0); - // CHECK: st4 {v{{[0-9]+}}.d, v{{[0-9]+}}.d, v{{[0-9]+}}.d, v{{[0-9]+}}.d}[0], [{{x[0-9]+|sp}}] + // CHECK: st4 {{{ *v[0-9]+.d, v[0-9]+.d, v[0-9]+.d, v[0-9]+.d *}}}[0], [{{x[0-9]+|sp}}] }