16bcf27bb9a4b5c3f79cb44c0e4654a6d7619ad89Stephen Hines// RUN: %clang_cc1 -O1 -triple arm64-apple-ios7 -target-feature +neon -ffreestanding -S -o - -emit-llvm %s | FileCheck %s
2651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines
3651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines#include <arm_neon.h>
4651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines
5651f13cea278ec967336033dd032faef0e9fc2ecStephen Hinesfloat64x2_t test_vcvt_f64_f32(float32x2_t x) {
6651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines  // CHECK-LABEL: test_vcvt_f64_f32
7651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines  return vcvt_f64_f32(x);
8651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines  // CHECK: fpext <2 x float> {{%.*}} to <2 x double>
9651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines  // CHECK-NEXT: ret
10651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines}
11651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines
12651f13cea278ec967336033dd032faef0e9fc2ecStephen Hinesfloat64x2_t test_vcvt_high_f64_f32(float32x4_t x) {
13651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines  // CHECK-LABEL: test_vcvt_high_f64_f32
14651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines  return vcvt_high_f64_f32(x);
15651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines  // CHECK: [[HIGH:%.*]] = shufflevector <4 x float> {{%.*}}, <4 x float> undef, <2 x i32> <i32 2, i32 3>
16651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines  // CHECK-NEXT: fpext <2 x float> [[HIGH]] to <2 x double>
17651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines  // CHECK-NEXT: ret
18651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines}
19651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines
20651f13cea278ec967336033dd032faef0e9fc2ecStephen Hinesfloat32x2_t test_vcvt_f32_f64(float64x2_t v) {
21651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines  // CHECK: test_vcvt_f32_f64
22651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines  return vcvt_f32_f64(v);
23651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines  // CHECK: fptrunc <2 x double> {{%.*}} to <2 x float>
24651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines  // CHECK-NEXT: ret
25651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines}
26651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines
27651f13cea278ec967336033dd032faef0e9fc2ecStephen Hinesfloat32x4_t test_vcvt_high_f32_f64(float32x2_t x, float64x2_t v) {
28651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines  // CHECK: test_vcvt_high_f32_f64
29651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines  return vcvt_high_f32_f64(x, v);
30651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines  // CHECK: [[TRUNC:%.*]] = fptrunc <2 x double> {{.*}} to <2 x float>
31651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines  // CHECK-NEXT: shufflevector <2 x float> {{.*}}, <2 x float> [[TRUNC]], <4 x i32> <i32 0, i32 1, i32 2, i32 3>
32651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines  // CHECK-NEXT: ret
33651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines}
34651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines
35651f13cea278ec967336033dd032faef0e9fc2ecStephen Hinesfloat32x2_t test_vcvtx_f32_f64(float64x2_t v) {
36651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines  // CHECK: test_vcvtx_f32_f64
37651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines  return vcvtx_f32_f64(v);
386bcf27bb9a4b5c3f79cb44c0e4654a6d7619ad89Stephen Hines  // CHECK: llvm.aarch64.neon.fcvtxn.v2f32.v2f64
39651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines  // CHECK-NEXT: ret
40651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines}
41651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines
42651f13cea278ec967336033dd032faef0e9fc2ecStephen Hinesfloat32x4_t test_vcvtx_high_f32_f64(float32x2_t x, float64x2_t v) {
43651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines  // CHECK: test_vcvtx_high_f32_f64
44651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines  return vcvtx_high_f32_f64(x, v);
456bcf27bb9a4b5c3f79cb44c0e4654a6d7619ad89Stephen Hines  // CHECK: llvm.aarch64.neon.fcvtxn.v2f32.v2f64
46651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines  // CHECK: shufflevector
47ef8225444452a1486bd721f3285301fe84643b00Stephen Hines  // CHECK: ret
48651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines}
49