blob: d885f1cd364f699e66054c27d0122b3789613d84 (
plain)
1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
20
21
22
23
24
25
26
27
28
29
30
31
32
33
34
35
36
37
38
39
40
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*)
|
