diff options
| author | Simon Pilgrim <llvm-dev@redking.me.uk> | 2017-04-29 17:15:12 +0000 |
|---|---|---|
| committer | Simon Pilgrim <llvm-dev@redking.me.uk> | 2017-04-29 17:15:12 +0000 |
| commit | 694cb2c83849e4200d670091d808c3581f5c4ee5 (patch) | |
| tree | 047aa024fbdf161bcef9709dea976ee18477aa6f /llvm/test/CodeGen/X86/avx-intrinsics-fast-isel.ll | |
| parent | ca48af3c8786ad64a1533eaabae94a05028fbbf6 (diff) | |
| download | bcm5719-llvm-694cb2c83849e4200d670091d808c3581f5c4ee5.tar.gz bcm5719-llvm-694cb2c83849e4200d670091d808c3581f5c4ee5.zip | |
[X86][AVX] Added codegen tests for _mm256_zext* helper intrinsics (PR32839)
Not great codegen, especially as VEX moves support implicit zeroing of upper bits....
llvm-svn: 301748
Diffstat (limited to 'llvm/test/CodeGen/X86/avx-intrinsics-fast-isel.ll')
| -rw-r--r-- | llvm/test/CodeGen/X86/avx-intrinsics-fast-isel.ll | 54 |
1 files changed, 54 insertions, 0 deletions
diff --git a/llvm/test/CodeGen/X86/avx-intrinsics-fast-isel.ll b/llvm/test/CodeGen/X86/avx-intrinsics-fast-isel.ll index 4a86fa22f08..1d925ff8e9b 100644 --- a/llvm/test/CodeGen/X86/avx-intrinsics-fast-isel.ll +++ b/llvm/test/CodeGen/X86/avx-intrinsics-fast-isel.ll @@ -3774,4 +3774,58 @@ define void @test_mm256_zeroupper() nounwind { } declare void @llvm.x86.avx.vzeroupper() nounwind readnone +define <4 x double> @test_mm256_zextpd128_pd256(<2 x double> %a0) nounwind { +; X32-LABEL: test_mm256_zextpd128_pd256: +; X32: # BB#0: +; X32-NEXT: # kill: %XMM0<def> %XMM0<kill> %YMM0<def> +; X32-NEXT: vxorps %xmm1, %xmm1, %xmm1 +; X32-NEXT: vinsertf128 $1, %xmm1, %ymm0, %ymm0 +; X32-NEXT: retl +; +; X64-LABEL: test_mm256_zextpd128_pd256: +; X64: # BB#0: +; X64-NEXT: # kill: %XMM0<def> %XMM0<kill> %YMM0<def> +; X64-NEXT: vxorps %xmm1, %xmm1, %xmm1 +; X64-NEXT: vinsertf128 $1, %xmm1, %ymm0, %ymm0 +; X64-NEXT: retq + %res = shufflevector <2 x double> %a0, <2 x double> zeroinitializer, <4 x i32> <i32 0, i32 1, i32 2, i32 3> + ret <4 x double> %res +} + +define <8 x float> @test_mm256_zextps128_ps256(<4 x float> %a0) nounwind { +; X32-LABEL: test_mm256_zextps128_ps256: +; X32: # BB#0: +; X32-NEXT: # kill: %XMM0<def> %XMM0<kill> %YMM0<def> +; X32-NEXT: vxorps %xmm1, %xmm1, %xmm1 +; X32-NEXT: vinsertf128 $1, %xmm1, %ymm0, %ymm0 +; X32-NEXT: retl +; +; X64-LABEL: test_mm256_zextps128_ps256: +; X64: # BB#0: +; X64-NEXT: # kill: %XMM0<def> %XMM0<kill> %YMM0<def> +; X64-NEXT: vxorps %xmm1, %xmm1, %xmm1 +; X64-NEXT: vinsertf128 $1, %xmm1, %ymm0, %ymm0 +; X64-NEXT: retq + %res = shufflevector <4 x float> %a0, <4 x float> zeroinitializer, <8 x i32> <i32 0, i32 1, i32 2, i32 3, i32 4, i32 5, i32 6, i32 7> + ret <8 x float> %res +} + +define <4 x i64> @test_mm256_zextsi128_si256(<2 x i64> %a0) nounwind { +; X32-LABEL: test_mm256_zextsi128_si256: +; X32: # BB#0: +; X32-NEXT: # kill: %XMM0<def> %XMM0<kill> %YMM0<def> +; X32-NEXT: vxorps %xmm1, %xmm1, %xmm1 +; X32-NEXT: vinsertf128 $1, %xmm1, %ymm0, %ymm0 +; X32-NEXT: retl +; +; X64-LABEL: test_mm256_zextsi128_si256: +; X64: # BB#0: +; X64-NEXT: # kill: %XMM0<def> %XMM0<kill> %YMM0<def> +; X64-NEXT: vxorps %xmm1, %xmm1, %xmm1 +; X64-NEXT: vinsertf128 $1, %xmm1, %ymm0, %ymm0 +; X64-NEXT: retq + %res = shufflevector <2 x i64> %a0, <2 x i64> zeroinitializer, <4 x i32> <i32 0, i32 1, i32 2, i32 3> + ret <4 x i64> %res +} + !0 = !{i32 1} |

