xref: /minix3/external/bsd/llvm/dist/clang/test/CodeGen/arm-neon-vcvtX.c (revision 0a6a1f1d05b60e214de2f05a7310ddd1f0e590e7)
1*0a6a1f1dSLionel Sambuc // RUN: %clang_cc1 -triple thumbv8-linux-gnueabihf -target-cpu cortex-a57 -ffreestanding -O1 -emit-llvm %s -o - | FileCheck %s
2*0a6a1f1dSLionel Sambuc 
3*0a6a1f1dSLionel Sambuc #include <arm_neon.h>
4*0a6a1f1dSLionel Sambuc 
test_vcvta_s32_f32(float32x2_t a)5*0a6a1f1dSLionel Sambuc int32x2_t test_vcvta_s32_f32(float32x2_t a) {
6*0a6a1f1dSLionel Sambuc   // CHECK-LABEL: test_vcvta_s32_f32
7*0a6a1f1dSLionel Sambuc   // CHECK-LABEL: call <2 x i32> @llvm.arm.neon.vcvtas.v2i32.v2f32(<2 x float> %a)
8*0a6a1f1dSLionel Sambuc   return vcvta_s32_f32(a);
9*0a6a1f1dSLionel Sambuc }
10*0a6a1f1dSLionel Sambuc 
test_vcvta_u32_f32(float32x2_t a)11*0a6a1f1dSLionel Sambuc uint32x2_t test_vcvta_u32_f32(float32x2_t a) {
12*0a6a1f1dSLionel Sambuc   // CHECK-LABEL: test_vcvta_u32_f32
13*0a6a1f1dSLionel Sambuc   // CHECK-LABEL: call <2 x i32> @llvm.arm.neon.vcvtau.v2i32.v2f32(<2 x float> %a)
14*0a6a1f1dSLionel Sambuc   return vcvta_u32_f32(a);
15*0a6a1f1dSLionel Sambuc }
16*0a6a1f1dSLionel Sambuc 
test_vcvtaq_s32_f32(float32x4_t a)17*0a6a1f1dSLionel Sambuc int32x4_t test_vcvtaq_s32_f32(float32x4_t a) {
18*0a6a1f1dSLionel Sambuc   // CHECK-LABEL: test_vcvtaq_s32_f32
19*0a6a1f1dSLionel Sambuc   // CHECK-LABEL: call <4 x i32> @llvm.arm.neon.vcvtas.v4i32.v4f32(<4 x float> %a)
20*0a6a1f1dSLionel Sambuc   return vcvtaq_s32_f32(a);
21*0a6a1f1dSLionel Sambuc }
22*0a6a1f1dSLionel Sambuc 
test_vcvtaq_u32_f32(float32x4_t a)23*0a6a1f1dSLionel Sambuc uint32x4_t test_vcvtaq_u32_f32(float32x4_t a) {
24*0a6a1f1dSLionel Sambuc   // CHECK-LABEL: test_vcvtaq_u32_f32
25*0a6a1f1dSLionel Sambuc   // CHECK-LABEL: call <4 x i32> @llvm.arm.neon.vcvtau.v4i32.v4f32(<4 x float> %a)
26*0a6a1f1dSLionel Sambuc   return vcvtaq_u32_f32(a);
27*0a6a1f1dSLionel Sambuc }
28*0a6a1f1dSLionel Sambuc 
test_vcvtn_s32_f32(float32x2_t a)29*0a6a1f1dSLionel Sambuc int32x2_t test_vcvtn_s32_f32(float32x2_t a) {
30*0a6a1f1dSLionel Sambuc   // CHECK-LABEL: test_vcvtn_s32_f32
31*0a6a1f1dSLionel Sambuc   // CHECK-LABEL: call <2 x i32> @llvm.arm.neon.vcvtns.v2i32.v2f32(<2 x float> %a)
32*0a6a1f1dSLionel Sambuc   return vcvtn_s32_f32(a);
33*0a6a1f1dSLionel Sambuc }
34*0a6a1f1dSLionel Sambuc 
test_vcvtn_u32_f32(float32x2_t a)35*0a6a1f1dSLionel Sambuc uint32x2_t test_vcvtn_u32_f32(float32x2_t a) {
36*0a6a1f1dSLionel Sambuc   // CHECK-LABEL: test_vcvtn_u32_f32
37*0a6a1f1dSLionel Sambuc   // CHECK-LABEL: call <2 x i32> @llvm.arm.neon.vcvtnu.v2i32.v2f32(<2 x float> %a)
38*0a6a1f1dSLionel Sambuc   return vcvtn_u32_f32(a);
39*0a6a1f1dSLionel Sambuc }
40*0a6a1f1dSLionel Sambuc 
test_vcvtnq_s32_f32(float32x4_t a)41*0a6a1f1dSLionel Sambuc int32x4_t test_vcvtnq_s32_f32(float32x4_t a) {
42*0a6a1f1dSLionel Sambuc   // CHECK-LABEL: test_vcvtnq_s32_f32
43*0a6a1f1dSLionel Sambuc   // CHECK-LABEL: call <4 x i32> @llvm.arm.neon.vcvtns.v4i32.v4f32(<4 x float> %a)
44*0a6a1f1dSLionel Sambuc   return vcvtnq_s32_f32(a);
45*0a6a1f1dSLionel Sambuc }
46*0a6a1f1dSLionel Sambuc 
test_vcvtnq_u32_f32(float32x4_t a)47*0a6a1f1dSLionel Sambuc uint32x4_t test_vcvtnq_u32_f32(float32x4_t a) {
48*0a6a1f1dSLionel Sambuc   // CHECK-LABEL: test_vcvtnq_u32_f32
49*0a6a1f1dSLionel Sambuc   // CHECK-LABEL: call <4 x i32> @llvm.arm.neon.vcvtnu.v4i32.v4f32(<4 x float> %a)
50*0a6a1f1dSLionel Sambuc   return vcvtnq_u32_f32(a);
51*0a6a1f1dSLionel Sambuc }
52*0a6a1f1dSLionel Sambuc 
test_vcvtp_s32_f32(float32x2_t a)53*0a6a1f1dSLionel Sambuc int32x2_t test_vcvtp_s32_f32(float32x2_t a) {
54*0a6a1f1dSLionel Sambuc   // CHECK-LABEL: test_vcvtp_s32_f32
55*0a6a1f1dSLionel Sambuc   // CHECK-LABEL: call <2 x i32> @llvm.arm.neon.vcvtps.v2i32.v2f32(<2 x float> %a)
56*0a6a1f1dSLionel Sambuc   return vcvtp_s32_f32(a);
57*0a6a1f1dSLionel Sambuc }
58*0a6a1f1dSLionel Sambuc 
test_vcvtp_u32_f32(float32x2_t a)59*0a6a1f1dSLionel Sambuc uint32x2_t test_vcvtp_u32_f32(float32x2_t a) {
60*0a6a1f1dSLionel Sambuc   // CHECK-LABEL: test_vcvtp_u32_f32
61*0a6a1f1dSLionel Sambuc   // CHECK-LABEL: call <2 x i32> @llvm.arm.neon.vcvtpu.v2i32.v2f32(<2 x float> %a)
62*0a6a1f1dSLionel Sambuc   return vcvtp_u32_f32(a);
63*0a6a1f1dSLionel Sambuc }
64*0a6a1f1dSLionel Sambuc 
test_vcvtpq_s32_f32(float32x4_t a)65*0a6a1f1dSLionel Sambuc int32x4_t test_vcvtpq_s32_f32(float32x4_t a) {
66*0a6a1f1dSLionel Sambuc   // CHECK-LABEL: test_vcvtpq_s32_f32
67*0a6a1f1dSLionel Sambuc   // CHECK-LABEL: call <4 x i32> @llvm.arm.neon.vcvtps.v4i32.v4f32(<4 x float> %a)
68*0a6a1f1dSLionel Sambuc   return vcvtpq_s32_f32(a);
69*0a6a1f1dSLionel Sambuc }
70*0a6a1f1dSLionel Sambuc 
test_vcvtpq_u32_f32(float32x4_t a)71*0a6a1f1dSLionel Sambuc uint32x4_t test_vcvtpq_u32_f32(float32x4_t a) {
72*0a6a1f1dSLionel Sambuc   // CHECK-LABEL: test_vcvtpq_u32_f32
73*0a6a1f1dSLionel Sambuc   // CHECK-LABEL: call <4 x i32> @llvm.arm.neon.vcvtpu.v4i32.v4f32(<4 x float> %a)
74*0a6a1f1dSLionel Sambuc   return vcvtpq_u32_f32(a);
75*0a6a1f1dSLionel Sambuc }
76*0a6a1f1dSLionel Sambuc 
test_vcvtm_s32_f32(float32x2_t a)77*0a6a1f1dSLionel Sambuc int32x2_t test_vcvtm_s32_f32(float32x2_t a) {
78*0a6a1f1dSLionel Sambuc   // CHECK-LABEL: test_vcvtm_s32_f32
79*0a6a1f1dSLionel Sambuc   // CHECK-LABEL: call <2 x i32> @llvm.arm.neon.vcvtms.v2i32.v2f32(<2 x float> %a)
80*0a6a1f1dSLionel Sambuc   return vcvtm_s32_f32(a);
81*0a6a1f1dSLionel Sambuc }
82*0a6a1f1dSLionel Sambuc 
test_vcvtm_u32_f32(float32x2_t a)83*0a6a1f1dSLionel Sambuc uint32x2_t test_vcvtm_u32_f32(float32x2_t a) {
84*0a6a1f1dSLionel Sambuc   // CHECK-LABEL: test_vcvtm_u32_f32
85*0a6a1f1dSLionel Sambuc   // CHECK-LABEL: call <2 x i32> @llvm.arm.neon.vcvtmu.v2i32.v2f32(<2 x float> %a)
86*0a6a1f1dSLionel Sambuc   return vcvtm_u32_f32(a);
87*0a6a1f1dSLionel Sambuc }
88*0a6a1f1dSLionel Sambuc 
test_vcvtmq_s32_f32(float32x4_t a)89*0a6a1f1dSLionel Sambuc int32x4_t test_vcvtmq_s32_f32(float32x4_t a) {
90*0a6a1f1dSLionel Sambuc   // CHECK-LABEL: test_vcvtmq_s32_f32
91*0a6a1f1dSLionel Sambuc   // CHECK-LABEL: call <4 x i32> @llvm.arm.neon.vcvtms.v4i32.v4f32(<4 x float> %a)
92*0a6a1f1dSLionel Sambuc   return vcvtmq_s32_f32(a);
93*0a6a1f1dSLionel Sambuc }
94*0a6a1f1dSLionel Sambuc 
test_vcvtmq_u32_f32(float32x4_t a)95*0a6a1f1dSLionel Sambuc uint32x4_t test_vcvtmq_u32_f32(float32x4_t a) {
96*0a6a1f1dSLionel Sambuc   // CHECK-LABEL: test_vcvtmq_u32_f32
97*0a6a1f1dSLionel Sambuc   // CHECK-LABEL: call <4 x i32> @llvm.arm.neon.vcvtmu.v4i32.v4f32(<4 x float> %a)
98*0a6a1f1dSLionel Sambuc   return vcvtmq_u32_f32(a);
99*0a6a1f1dSLionel Sambuc }
100