diff options
Diffstat (limited to 'clang/test/CodeGen/arm64_vLdStNum_lane.c')
| -rw-r--r-- | clang/test/CodeGen/arm64_vLdStNum_lane.c | 141 |
1 files changed, 141 insertions, 0 deletions
diff --git a/clang/test/CodeGen/arm64_vLdStNum_lane.c b/clang/test/CodeGen/arm64_vLdStNum_lane.c new file mode 100644 index 00000000000..6c4415845a6 --- /dev/null +++ b/clang/test/CodeGen/arm64_vLdStNum_lane.c @@ -0,0 +1,141 @@ +// RUN: %clang -O1 -target arm64-apple-ios7 -ffreestanding -S -o - -emit-llvm %s | FileCheck %s +// Test ARM64 SIMD load and stores of an N-element structure intrinsics + +#include <arm_neon.h> + +int64x2x2_t test_vld2q_lane_s64(const void * a1, int64x2x2_t a2) { + // CHECK: test_vld2q_lane_s64 + return vld2q_lane_s64(a1, a2, 1); + // CHECK: llvm.arm64.neon.ld2lane.v2i64.p0i8 +} + +uint64x2x2_t test_vld2q_lane_u64(const void * a1, uint64x2x2_t a2) { + // CHECK: test_vld2q_lane_u64 + return vld2q_lane_u64(a1, a2, 1); + // CHECK: llvm.arm64.neon.ld2lane.v2i64.p0i8 +} + +int64x1x2_t test_vld2_lane_s64(const void * a1, int64x1x2_t a2) { + // CHECK: test_vld2_lane_s64 + return vld2_lane_s64(a1, a2, 0); + // CHECK: llvm.arm64.neon.ld2lane.v1i64.p0i8 +} + +uint64x1x2_t test_vld2_lane_u64(const void * a1, uint64x1x2_t a2) { + // CHECK: test_vld2_lane_u64 + return vld2_lane_u64(a1, a2, 0); + // CHECK: llvm.arm64.neon.ld2lane.v1i64.p0i8 +} + +poly8x16x2_t test_vld2q_lane_p8(const void * a1, poly8x16x2_t a2) { + // CHECK: test_vld2q_lane_p8 + return vld2q_lane_p8(a1, a2, 0); + // CHECK: extractvalue {{.*}} 0{{ *$}} + // CHECK: extractvalue {{.*}} 1{{ *$}} +} + +uint8x16x2_t test_vld2q_lane_u8(const void * a1, uint8x16x2_t a2) { + // CHECK: test_vld2q_lane_u8 + return vld2q_lane_u8(a1, a2, 0); + // CHECK: llvm.arm64.neon.ld2lane.v16i8.p0i8 +} + +int64x2x3_t test_vld3q_lane_s64(const void * a1, int64x2x3_t a2) { + // CHECK: test_vld3q_lane_s64 + return vld3q_lane_s64(a1, a2, 1); + // CHECK: llvm.arm64.neon.ld3lane.v2i64.p0i8 +} + +uint64x2x3_t test_vld3q_lane_u64(const void * a1, uint64x2x3_t a2) { + // CHECK: test_vld3q_lane_u64 + return vld3q_lane_u64(a1, a2, 1); + // CHECK: llvm.arm64.neon.ld3lane.v2i64.p0i8 +} + +int64x1x3_t test_vld3_lane_s64(const void * a1, int64x1x3_t a2) { + // CHECK: test_vld3_lane_s64 + return vld3_lane_s64(a1, a2, 0); + // CHECK: llvm.arm64.neon.ld3lane.v1i64.p0i8 +} + +uint64x1x3_t test_vld3_lane_u64(const void * a1, uint64x1x3_t a2) { + // CHECK: test_vld3_lane_u64 + return vld3_lane_u64(a1, a2, 0); + // CHECK: llvm.arm64.neon.ld3lane.v1i64.p0i8 +} + +int8x8x3_t test_vld3_lane_s8(const void * a1, int8x8x3_t a2) { + // CHECK: test_vld3_lane_s8 + return vld3_lane_s8(a1, a2, 0); + // CHECK: llvm.arm64.neon.ld3lane.v8i8.p0i8 +} + +poly8x16x3_t test_vld3q_lane_p8(const void * a1, poly8x16x3_t a2) { + // CHECK: test_vld3q_lane_p8 + return vld3q_lane_p8(a1, a2, 0); + // CHECK: llvm.arm64.neon.ld3lane.v16i8.p0i8 +} + +uint8x16x3_t test_vld3q_lane_u8(const void * a1, uint8x16x3_t a2) { + // CHECK: test_vld3q_lane_u8 + return vld3q_lane_u8(a1, a2, 0); + // CHECK: llvm.arm64.neon.ld3lane.v16i8.p0i8 +} + +int64x2x4_t test_vld4q_lane_s64(const void * a1, int64x2x4_t a2) { + // CHECK: test_vld4q_lane_s64 + return vld4q_lane_s64(a1, a2, 0); + // CHECK: llvm.arm64.neon.ld4lane.v2i64.p0i8 +} + +uint64x2x4_t test_vld4q_lane_u64(const void * a1, uint64x2x4_t a2) { + // CHECK: test_vld4q_lane_u64 + return vld4q_lane_u64(a1, a2, 0); + // CHECK: llvm.arm64.neon.ld4lane.v2i64.p0i8 +} + +int64x1x4_t test_vld4_lane_s64(const void * a1, int64x1x4_t a2) { + // CHECK: test_vld4_lane_s64 + return vld4_lane_s64(a1, a2, 0); + // CHECK: llvm.arm64.neon.ld4lane.v1i64.p0i8 +} + +uint64x1x4_t test_vld4_lane_u64(const void * a1, uint64x1x4_t a2) { + // CHECK: test_vld4_lane_u64 + return vld4_lane_u64(a1, a2, 0); + // CHECK: llvm.arm64.neon.ld4lane.v1i64.p0i8 +} + +int8x8x4_t test_vld4_lane_s8(const void * a1, int8x8x4_t a2) { + // CHECK: test_vld4_lane_s8 + return vld4_lane_s8(a1, a2, 0); + // CHECK: llvm.arm64.neon.ld4lane.v8i8.p0i8 +} + +uint8x8x4_t test_vld4_lane_u8(const void * a1, uint8x8x4_t a2) { + // CHECK: test_vld4_lane_u8 + return vld4_lane_u8(a1, a2, 0); + // CHECK: llvm.arm64.neon.ld4lane.v8i8.p0i8 +} + +poly8x16x4_t test_vld4q_lane_p8(const void * a1, poly8x16x4_t a2) { + // CHECK: test_vld4q_lane_p8 + return vld4q_lane_p8(a1, a2, 0); + // CHECK: llvm.arm64.neon.ld4lane.v16i8.p0i8 +} + +int8x16x4_t test_vld4q_lane_s8(const void * a1, int8x16x4_t a2) { + // CHECK: test_vld4q_lane_s8 + return vld4q_lane_s8(a1, a2, 0); + // CHECK: extractvalue {{.*}} 0{{ *$}} + // CHECK: extractvalue {{.*}} 1{{ *$}} + // CHECK: extractvalue {{.*}} 2{{ *$}} + // CHECK: extractvalue {{.*}} 3{{ *$}} +} + +uint8x16x4_t test_vld4q_lane_u8(const void * a1, uint8x16x4_t a2) { + // CHECK: test_vld4q_lane_u8 + return vld4q_lane_u8(a1, a2, 0); + // CHECK: llvm.arm64.neon.ld4lane.v16i8.p0i8 +} + |
