1*67e74705SXin Li // RUN: %clang_cc1 -triple arm64-apple-ios7 -target-feature +neon -ffreestanding -emit-llvm -o - %s | FileCheck %s 2*67e74705SXin Li 3*67e74705SXin Li #include <arm_neon.h> 4*67e74705SXin Li rnd1(float32x2_t a)5*67e74705SXin Liint32x2_t rnd1(float32x2_t a) { return vrnd_f32(a); } 6*67e74705SXin Li // CHECK: call <2 x float> @llvm.trunc.v2f32(<2 x float> rnd3(float32x4_t a)7*67e74705SXin Liint32x4_t rnd3(float32x4_t a) { return vrndq_f32(a); } 8*67e74705SXin Li // CHECK: call <4 x float> @llvm.trunc.v4f32(<4 x float> rnd5(float64x2_t a)9*67e74705SXin Liint64x2_t rnd5(float64x2_t a) { return vrndq_f64(a); } 10*67e74705SXin Li // CHECK: call <2 x double> @llvm.trunc.v2f64(<2 x double> 11*67e74705SXin Li 12*67e74705SXin Li rnd7(float32x2_t a)13*67e74705SXin Liint32x2_t rnd7(float32x2_t a) { return vrndn_f32(a); } 14*67e74705SXin Li // CHECK: call <2 x float> @llvm.aarch64.neon.frintn.v2f32(<2 x float> rnd8(float32x4_t a)15*67e74705SXin Liint32x4_t rnd8(float32x4_t a) { return vrndnq_f32(a); } 16*67e74705SXin Li // CHECK: call <4 x float> @llvm.aarch64.neon.frintn.v4f32(<4 x float> rnd9(float64x2_t a)17*67e74705SXin Liint64x2_t rnd9(float64x2_t a) { return vrndnq_f64(a); } 18*67e74705SXin Li // CHECK: call <2 x double> @llvm.aarch64.neon.frintn.v2f64(<2 x double> rnd10(float64x2_t a)19*67e74705SXin Liint64x2_t rnd10(float64x2_t a) { return vrndnq_f64(a); } 20*67e74705SXin Li // CHECK: call <2 x double> @llvm.aarch64.neon.frintn.v2f64(<2 x double> 21*67e74705SXin Li rnd11(float32x2_t a)22*67e74705SXin Liint32x2_t rnd11(float32x2_t a) { return vrndm_f32(a); } 23*67e74705SXin Li // CHECK: call <2 x float> @llvm.floor.v2f32(<2 x float> rnd12(float32x4_t a)24*67e74705SXin Liint32x4_t rnd12(float32x4_t a) { return vrndmq_f32(a); } 25*67e74705SXin Li // CHECK: call <4 x float> @llvm.floor.v4f32(<4 x float> rnd13(float64x2_t a)26*67e74705SXin Liint64x2_t rnd13(float64x2_t a) { return vrndmq_f64(a); } 27*67e74705SXin Li // CHECK: call <2 x double> @llvm.floor.v2f64(<2 x double> rnd14(float64x2_t a)28*67e74705SXin Liint64x2_t rnd14(float64x2_t a) { return vrndmq_f64(a); } 29*67e74705SXin Li // CHECK: call <2 x double> @llvm.floor.v2f64(<2 x double> 30*67e74705SXin Li rnd15(float32x2_t a)31*67e74705SXin Liint32x2_t rnd15(float32x2_t a) { return vrndp_f32(a); } 32*67e74705SXin Li // CHECK: call <2 x float> @llvm.ceil.v2f32(<2 x float> rnd16(float32x4_t a)33*67e74705SXin Liint32x4_t rnd16(float32x4_t a) { return vrndpq_f32(a); } 34*67e74705SXin Li // CHECK: call <4 x float> @llvm.ceil.v4f32(<4 x float> rnd18(float64x2_t a)35*67e74705SXin Liint64x2_t rnd18(float64x2_t a) { return vrndpq_f64(a); } 36*67e74705SXin Li // CHECK: call <2 x double> @llvm.ceil.v2f64(<2 x double> 37*67e74705SXin Li rnd19(float32x2_t a)38*67e74705SXin Liint32x2_t rnd19(float32x2_t a) { return vrnda_f32(a); } 39*67e74705SXin Li // CHECK: call <2 x float> @llvm.round.v2f32(<2 x float> rnd20(float32x4_t a)40*67e74705SXin Liint32x4_t rnd20(float32x4_t a) { return vrndaq_f32(a); } 41*67e74705SXin Li // CHECK: call <4 x float> @llvm.round.v4f32(<4 x float> rnd22(float64x2_t a)42*67e74705SXin Liint64x2_t rnd22(float64x2_t a) { return vrndaq_f64(a); } 43*67e74705SXin Li // CHECK: call <2 x double> @llvm.round.v2f64(<2 x double> 44*67e74705SXin Li rnd23(float32x2_t a)45*67e74705SXin Liint32x2_t rnd23(float32x2_t a) { return vrndx_f32(a); } 46*67e74705SXin Li // CHECK: call <2 x float> @llvm.rint.v2f32(<2 x float> rnd24(float32x4_t a)47*67e74705SXin Liint32x4_t rnd24(float32x4_t a) { return vrndxq_f32(a); } 48*67e74705SXin Li // CHECK: call <4 x float> @llvm.rint.v4f32(<4 x float> rnd25(float64x2_t a)49*67e74705SXin Liint64x2_t rnd25(float64x2_t a) { return vrndxq_f64(a); } 50*67e74705SXin Li // CHECK: call <2 x double> @llvm.rint.v2f64(<2 x double> 51*67e74705SXin Li 52