1*67e74705SXin Li // REQUIRES: arm-registered-target 2*67e74705SXin Li // RUN: %clang_cc1 -triple thumbv7-apple-darwin9 \ 3*67e74705SXin Li // RUN: -target-abi apcs-gnu \ 4*67e74705SXin Li // RUN: -target-cpu cortex-a8 \ 5*67e74705SXin Li // RUN: -mfloat-abi soft \ 6*67e74705SXin Li // RUN: -target-feature +soft-float-abi \ 7*67e74705SXin Li // RUN: -ffreestanding \ 8*67e74705SXin Li // RUN: -emit-llvm -w -o - %s | FileCheck %s 9*67e74705SXin Li 10*67e74705SXin Li #include <arm_neon.h> 11*67e74705SXin Li 12*67e74705SXin Li // CHECK: define void @f0(%struct.int8x16x2_t* noalias sret %agg.result, <16 x i8> %{{.*}}, <16 x i8> %{{.*}}) f0(int8x16_t a0,int8x16_t a1)13*67e74705SXin Liint8x16x2_t f0(int8x16_t a0, int8x16_t a1) { 14*67e74705SXin Li return vzipq_s8(a0, a1); 15*67e74705SXin Li } 16*67e74705SXin Li 17*67e74705SXin Li // Test direct vector passing. 18*67e74705SXin Li 19*67e74705SXin Li typedef float T_float32x2 __attribute__ ((__vector_size__ (8))); 20*67e74705SXin Li typedef float T_float32x4 __attribute__ ((__vector_size__ (16))); 21*67e74705SXin Li typedef float T_float32x8 __attribute__ ((__vector_size__ (32))); 22*67e74705SXin Li typedef float T_float32x16 __attribute__ ((__vector_size__ (64))); 23*67e74705SXin Li 24*67e74705SXin Li // CHECK: define <2 x float> @f1_0(<2 x float> %{{.*}}) f1_0(T_float32x2 a0)25*67e74705SXin LiT_float32x2 f1_0(T_float32x2 a0) { return a0; } 26*67e74705SXin Li // CHECK: define <4 x float> @f1_1(<4 x float> %{{.*}}) f1_1(T_float32x4 a0)27*67e74705SXin LiT_float32x4 f1_1(T_float32x4 a0) { return a0; } 28*67e74705SXin Li // CHECK: define void @f1_2(<8 x float>* noalias sret %{{.*}}, <8 x float> %{{.*}}) f1_2(T_float32x8 a0)29*67e74705SXin LiT_float32x8 f1_2(T_float32x8 a0) { return a0; } 30*67e74705SXin Li // CHECK: define void @f1_3(<16 x float>* noalias sret %{{.*}}, <16 x float> %{{.*}}) f1_3(T_float32x16 a0)31*67e74705SXin LiT_float32x16 f1_3(T_float32x16 a0) { return a0; } 32