maxjhandsome
/
llvm-project
forked from OSchip/llvm-project
1
0
Fork 0
Code Issues Pull Requests Packages Releases Wiki Activity
llvm-project/clang/test/CodeGen/arm-vector-arguments.c

31 lines
1.2 KiB
C
Raw Normal View History

IRgen/ABI/ARM: Trust the backend to pass vectors correctly for the given ABI. - Therefore, we can lower out the NEON wrapper structs and pass the vectors directly. This makes a huge difference in the cleanliness of the IR after optimization. - I will trust, but verify, via future ABITest testing (for APCS-GNU, at least). llvm-svn: 114618
2010-09-23 09:54:28 +08:00
// RUN: %clang_cc1 -triple thumbv7-apple-darwin9 \
// RUN: -target-abi apcs-gnu \
// RUN: -target-cpu cortex-a8 \
// RUN: -mfloat-abi soft \
// RUN: -target-feature +soft-float-abi \
Tweak test to pass -ffreestanding, to avoid platform dependent header issues. llvm-svn: 114627
2010-09-23 12:40:10 +08:00
// RUN: -ffreestanding \
IRgen/ABI/ARM: Trust the backend to pass vectors correctly for the given ABI. - Therefore, we can lower out the NEON wrapper structs and pass the vectors directly. This makes a huge difference in the cleanliness of the IR after optimization. - I will trust, but verify, via future ABITest testing (for APCS-GNU, at least). llvm-svn: 114618
2010-09-23 09:54:28 +08:00
// RUN: -emit-llvm -w -o - %s | FileCheck %s
#include <arm_neon.h>
Track whether an AggValueSlot is potentially aliased, and do not emit call results into potentially aliased slots. This allows us to properly mark indirect return slots as noalias, at the cost of requiring an extra memcpy when assigning an aggregate call result into a l-value. It also brings us into compliance with the x86-64 ABI. llvm-svn: 138599
2011-08-26 07:04:34 +08:00
// CHECK: define void @f0(%struct.int8x16x2_t* noalias sret %agg.result, <16 x i8> %{{.*}}, <16 x i8> %{{.*}})
Re-enable test with modifications for Neon vector changes in clang. I mistakenly thought that this was checking for vector name mangling, but it is not. Since we're no longer wrapping Neon vectors in structs, this test can just return a vector directly. There are already other tests for that, so just to make this interesting, change the test to return a struct of two vectors. llvm-svn: 119434
2010-11-17 08:44:53 +08:00
int8x16x2_t f0(int8x16_t a0, int8x16_t a1) {
return vzipq_s8(a0, a1);
IRgen/ABI/ARM: Trust the backend to pass vectors correctly for the given ABI. - Therefore, we can lower out the NEON wrapper structs and pass the vectors directly. This makes a huge difference in the cleanliness of the IR after optimization. - I will trust, but verify, via future ABITest testing (for APCS-GNU, at least). llvm-svn: 114618
2010-09-23 09:54:28 +08:00
}
IRgen/ABI/ARM: Return large vectors in memory. llvm-svn: 114619
2010-09-23 09:54:32 +08:00
// Test direct vector passing.
typedef float T_float32x2 __attribute__ ((__vector_size__ (8)));
typedef float T_float32x4 __attribute__ ((__vector_size__ (16)));
typedef float T_float32x8 __attribute__ ((__vector_size__ (32)));
typedef float T_float32x16 __attribute__ ((__vector_size__ (64)));
// CHECK: define <2 x float> @f1_0(<2 x float> %{{.*}})
T_float32x2 f1_0(T_float32x2 a0) { return a0; }
// CHECK: define <4 x float> @f1_1(<4 x float> %{{.*}})
T_float32x4 f1_1(T_float32x4 a0) { return a0; }
Track whether an AggValueSlot is potentially aliased, and do not emit call results into potentially aliased slots. This allows us to properly mark indirect return slots as noalias, at the cost of requiring an extra memcpy when assigning an aggregate call result into a l-value. It also brings us into compliance with the x86-64 ABI. llvm-svn: 138599
2011-08-26 07:04:34 +08:00
// CHECK: define void @f1_2(<8 x float>* noalias sret %{{.*}}, <8 x float> %{{.*}})
IRgen/ABI/ARM: Return large vectors in memory. llvm-svn: 114619
2010-09-23 09:54:32 +08:00
T_float32x8 f1_2(T_float32x8 a0) { return a0; }
Track whether an AggValueSlot is potentially aliased, and do not emit call results into potentially aliased slots. This allows us to properly mark indirect return slots as noalias, at the cost of requiring an extra memcpy when assigning an aggregate call result into a l-value. It also brings us into compliance with the x86-64 ABI. llvm-svn: 138599
2011-08-26 07:04:34 +08:00
// CHECK: define void @f1_3(<16 x float>* noalias sret %{{.*}}, <16 x float> %{{.*}})
IRgen/ABI/ARM: Return large vectors in memory. llvm-svn: 114619
2010-09-23 09:54:32 +08:00
T_float32x16 f1_3(T_float32x16 a0) { return a0; }