diff options
| author | Adam Nemet <anemet@apple.com> | 2014-05-29 23:35:33 +0000 |
|---|---|---|
| committer | Adam Nemet <anemet@apple.com> | 2014-05-29 23:35:33 +0000 |
| commit | 23356d4d64d4511d340bc6dad1464c8a3c65473b (patch) | |
| tree | 0e67415d0396fbfbf8669a4de26d427949fe5ec0 /test/Bitcode | |
| parent | c62ba58063c3714f36486db3bea3f79049305cb5 (diff) | |
| download | llvm-23356d4d64d4511d340bc6dad1464c8a3c65473b.tar.gz llvm-23356d4d64d4511d340bc6dad1464c8a3c65473b.tar.bz2 llvm-23356d4d64d4511d340bc6dad1464c8a3c65473b.tar.xz | |
[X86] Auto-upgrade AVX1 vbroadcast intrinsics
They are replaced with the same IR that is generated for the
vector-initializers in avxintrin.h.
The test verifies that we get back the original instruction. I haven't seen
this approach to be used in other auto-upgrade tests (i.e. llc + FileCheck)
but I think it's the most direct way to test this case. I believe this should
work because llc upgrades calls during parsing. (Other tests mostly check
that assembling and disassembling yields the upgraded IR.)
git-svn-id: https://llvm.org/svn/llvm-project/llvm/trunk@209863 91177308-0d34-0410-b5e6-96231b3b80d8
Diffstat (limited to 'test/Bitcode')
| -rw-r--r-- | test/Bitcode/x86-upgrade-avx-vbroadcast.ll | 41 |
1 files changed, 41 insertions, 0 deletions
diff --git a/test/Bitcode/x86-upgrade-avx-vbroadcast.ll b/test/Bitcode/x86-upgrade-avx-vbroadcast.ll new file mode 100644 index 0000000000..d885f1cd36 --- /dev/null +++ b/test/Bitcode/x86-upgrade-avx-vbroadcast.ll @@ -0,0 +1,41 @@ +; RUN: llc -mattr=+avx < %s | FileCheck %s + +; Check that we properly upgrade the AVX vbroadcast intrinsics to IR. The +; expectation is that we should still get the original instruction back that +; maps to the intrinsic. + +target datalayout = "e-m:o-i64:64-f80:128-n8:16:32:64-S128" +target triple = "x86_64-apple-macosx10.9.0" + +; CHECK-LABEL: test_mm_broadcast_ss: +define <4 x float> @test_mm_broadcast_ss(float* readonly %__a){ +entry: + %0 = bitcast float* %__a to i8* +; CHECK: vbroadcastss (%{{.*}}), %xmm + %1 = tail call <4 x float> @llvm.x86.avx.vbroadcast.ss(i8* %0) + ret <4 x float> %1 +} + +; CHECK-LABEL: test_mm256_broadcast_sd: +define <4 x double> @test_mm256_broadcast_sd(double* readonly %__a) { +entry: + %0 = bitcast double* %__a to i8* +; CHECK: vbroadcastsd (%{{.*}}), %ymm + %1 = tail call <4 x double> @llvm.x86.avx.vbroadcast.sd.256(i8* %0) + ret <4 x double> %1 +} + +; CHECK-LABEL: test_mm256_broadcast_ss: +define <8 x float> @test_mm256_broadcast_ss(float* readonly %__a) { +entry: + %0 = bitcast float* %__a to i8* +; CHECK: vbroadcastss (%{{.*}}), %ymm + %1 = tail call <8 x float> @llvm.x86.avx.vbroadcast.ss.256(i8* %0) + ret <8 x float> %1 +} + +declare <8 x float> @llvm.x86.avx.vbroadcast.ss.256(i8*) + +declare <4 x double> @llvm.x86.avx.vbroadcast.sd.256(i8*) + +declare <4 x float> @llvm.x86.avx.vbroadcast.ss(i8*) |