748 lines
29 KiB
C
748 lines
29 KiB
C
// RUN: %clang_cc1 -triple arm64-apple-ios7 -target-feature +neon -target-abi darwinpcs -ffreestanding -emit-llvm -w -o - %s | FileCheck %s
|
|
|
|
// CHECK: define signext i8 @f0()
|
|
char f0(void) {
|
|
return 0;
|
|
}
|
|
|
|
// Struct as return type. Aggregates <= 16 bytes are passed directly and round
|
|
// up to multiple of 8 bytes.
|
|
// CHECK: define i64 @f1()
|
|
struct s1 { char f0; };
|
|
struct s1 f1(void) {}
|
|
|
|
// CHECK: define i64 @f2()
|
|
struct s2 { short f0; };
|
|
struct s2 f2(void) {}
|
|
|
|
// CHECK: define i64 @f3()
|
|
struct s3 { int f0; };
|
|
struct s3 f3(void) {}
|
|
|
|
// CHECK: define i64 @f4()
|
|
struct s4 { struct s4_0 { int f0; } f0; };
|
|
struct s4 f4(void) {}
|
|
|
|
// CHECK: define i64 @f5()
|
|
struct s5 { struct { } f0; int f1; };
|
|
struct s5 f5(void) {}
|
|
|
|
// CHECK: define i64 @f6()
|
|
struct s6 { int f0[1]; };
|
|
struct s6 f6(void) {}
|
|
|
|
// CHECK: define void @f7()
|
|
struct s7 { struct { int : 0; } f0; };
|
|
struct s7 f7(void) {}
|
|
|
|
// CHECK: define void @f8()
|
|
struct s8 { struct { int : 0; } f0[1]; };
|
|
struct s8 f8(void) {}
|
|
|
|
// CHECK: define i64 @f9()
|
|
struct s9 { int f0; int : 0; };
|
|
struct s9 f9(void) {}
|
|
|
|
// CHECK: define i64 @f10()
|
|
struct s10 { int f0; int : 0; int : 0; };
|
|
struct s10 f10(void) {}
|
|
|
|
// CHECK: define i64 @f11()
|
|
struct s11 { int : 0; int f0; };
|
|
struct s11 f11(void) {}
|
|
|
|
// CHECK: define i64 @f12()
|
|
union u12 { char f0; short f1; int f2; };
|
|
union u12 f12(void) {}
|
|
|
|
// Homogeneous Aggregate as return type will be passed directly.
|
|
// CHECK: define %struct.s13 @f13()
|
|
struct s13 { float f0; };
|
|
struct s13 f13(void) {}
|
|
// CHECK: define %union.u14 @f14()
|
|
union u14 { float f0; };
|
|
union u14 f14(void) {}
|
|
|
|
// CHECK: define void @f15()
|
|
void f15(struct s7 a0) {}
|
|
|
|
// CHECK: define void @f16()
|
|
void f16(struct s8 a0) {}
|
|
|
|
// CHECK: define i64 @f17()
|
|
struct s17 { short f0 : 13; char f1 : 4; };
|
|
struct s17 f17(void) {}
|
|
|
|
// CHECK: define i64 @f18()
|
|
struct s18 { short f0; char f1 : 4; };
|
|
struct s18 f18(void) {}
|
|
|
|
// CHECK: define i64 @f19()
|
|
struct s19 { int f0; struct s8 f1; };
|
|
struct s19 f19(void) {}
|
|
|
|
// CHECK: define i64 @f20()
|
|
struct s20 { struct s8 f1; int f0; };
|
|
struct s20 f20(void) {}
|
|
|
|
// CHECK: define i64 @f21()
|
|
struct s21 { struct {} f1; int f0 : 4; };
|
|
struct s21 f21(void) {}
|
|
|
|
// CHECK: define i64 @f22()
|
|
// CHECK: define i64 @f23()
|
|
// CHECK: define i64 @f24()
|
|
// CHECK: define [2 x i64] @f25()
|
|
// CHECK: define { float, float } @f26()
|
|
// CHECK: define { double, double } @f27()
|
|
_Complex char f22(void) {}
|
|
_Complex short f23(void) {}
|
|
_Complex int f24(void) {}
|
|
_Complex long long f25(void) {}
|
|
_Complex float f26(void) {}
|
|
_Complex double f27(void) {}
|
|
|
|
// CHECK: define i64 @f28()
|
|
struct s28 { _Complex char f0; };
|
|
struct s28 f28() {}
|
|
|
|
// CHECK: define i64 @f29()
|
|
struct s29 { _Complex short f0; };
|
|
struct s29 f29() {}
|
|
|
|
// CHECK: define i64 @f30()
|
|
struct s30 { _Complex int f0; };
|
|
struct s30 f30() {}
|
|
|
|
struct s31 { char x; };
|
|
void f31(struct s31 s) { }
|
|
// CHECK: define void @f31(i64 %s.coerce)
|
|
// CHECK: %s = alloca %struct.s31, align 1
|
|
// CHECK: trunc i64 %s.coerce to i8
|
|
// CHECK: store i8 %{{.*}},
|
|
|
|
struct s32 { double x; };
|
|
void f32(struct s32 s) { }
|
|
// CHECK: @f32([1 x double] %{{.*}})
|
|
|
|
// A composite type larger than 16 bytes should be passed indirectly.
|
|
struct s33 { char buf[32*32]; };
|
|
void f33(struct s33 s) { }
|
|
// CHECK: define void @f33(%struct.s33* %s)
|
|
|
|
struct s34 { char c; };
|
|
void f34(struct s34 s);
|
|
void g34(struct s34 *s) { f34(*s); }
|
|
// CHECK: @g34(%struct.s34* %s)
|
|
// CHECK: %[[a:.*]] = load i8, i8* %{{.*}}
|
|
// CHECK: zext i8 %[[a]] to i64
|
|
// CHECK: call void @f34(i64 %{{.*}})
|
|
|
|
/*
|
|
* Check that va_arg accesses stack according to ABI alignment
|
|
*/
|
|
long long t1(int i, ...) {
|
|
// CHECK: t1
|
|
__builtin_va_list ap;
|
|
__builtin_va_start(ap, i);
|
|
// CHECK-NOT: add i32 %{{.*}} 7
|
|
// CHECK-NOT: and i32 %{{.*}} -8
|
|
long long ll = __builtin_va_arg(ap, long long);
|
|
__builtin_va_end(ap);
|
|
return ll;
|
|
}
|
|
double t2(int i, ...) {
|
|
// CHECK: t2
|
|
__builtin_va_list ap;
|
|
__builtin_va_start(ap, i);
|
|
// CHECK-NOT: add i32 %{{.*}} 7
|
|
// CHECK-NOT: and i32 %{{.*}} -8
|
|
double ll = __builtin_va_arg(ap, double);
|
|
__builtin_va_end(ap);
|
|
return ll;
|
|
}
|
|
|
|
#include <arm_neon.h>
|
|
|
|
// Homogeneous Vector Aggregate as return type and argument type.
|
|
// CHECK: define %struct.int8x16x2_t @f0_0(<16 x i8> %{{.*}}, <16 x i8> %{{.*}})
|
|
int8x16x2_t f0_0(int8x16_t a0, int8x16_t a1) {
|
|
return vzipq_s8(a0, a1);
|
|
}
|
|
|
|
// 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; }
|
|
// Vector with length bigger than 16-byte is illegal and is passed indirectly.
|
|
// CHECK: define void @f1_2(<8 x float>* noalias sret %{{.*}}, <8 x float>* %0)
|
|
T_float32x8 f1_2(T_float32x8 a0) { return a0; }
|
|
// CHECK: define void @f1_3(<16 x float>* noalias sret %{{.*}}, <16 x float>* %0)
|
|
T_float32x16 f1_3(T_float32x16 a0) { return a0; }
|
|
|
|
// Testing alignment with aggregates: HFA, aggregates with size <= 16 bytes and
|
|
// aggregates with size > 16 bytes.
|
|
struct s35
|
|
{
|
|
float v[4]; //Testing HFA.
|
|
} __attribute__((aligned(16)));
|
|
typedef struct s35 s35_with_align;
|
|
|
|
typedef __attribute__((neon_vector_type(4))) float float32x4_t;
|
|
float32x4_t f35(int i, s35_with_align s1, s35_with_align s2) {
|
|
// CHECK: define <4 x float> @f35(i32 %i, [4 x float] %s1.coerce, [4 x float] %s2.coerce)
|
|
// CHECK: %s1 = alloca %struct.s35, align 16
|
|
// CHECK: %s2 = alloca %struct.s35, align 16
|
|
// CHECK: %[[a:.*]] = bitcast %struct.s35* %s1 to <4 x float>*
|
|
// CHECK: load <4 x float>, <4 x float>* %[[a]], align 16
|
|
// CHECK: %[[b:.*]] = bitcast %struct.s35* %s2 to <4 x float>*
|
|
// CHECK: load <4 x float>, <4 x float>* %[[b]], align 16
|
|
float32x4_t v = vaddq_f32(*(float32x4_t *)&s1,
|
|
*(float32x4_t *)&s2);
|
|
return v;
|
|
}
|
|
|
|
struct s36
|
|
{
|
|
int v[4]; //Testing 16-byte aggregate.
|
|
} __attribute__((aligned(16)));
|
|
typedef struct s36 s36_with_align;
|
|
|
|
typedef __attribute__((neon_vector_type(4))) int int32x4_t;
|
|
int32x4_t f36(int i, s36_with_align s1, s36_with_align s2) {
|
|
// CHECK: define <4 x i32> @f36(i32 %i, i128 %s1.coerce, i128 %s2.coerce)
|
|
// CHECK: %s1 = alloca %struct.s36, align 16
|
|
// CHECK: %s2 = alloca %struct.s36, align 16
|
|
// CHECK: store i128 %s1.coerce, i128* %{{.*}}, align 16
|
|
// CHECK: store i128 %s2.coerce, i128* %{{.*}}, align 16
|
|
// CHECK: %[[a:.*]] = bitcast %struct.s36* %s1 to <4 x i32>*
|
|
// CHECK: load <4 x i32>, <4 x i32>* %[[a]], align 16
|
|
// CHECK: %[[b:.*]] = bitcast %struct.s36* %s2 to <4 x i32>*
|
|
// CHECK: load <4 x i32>, <4 x i32>* %[[b]], align 16
|
|
int32x4_t v = vaddq_s32(*(int32x4_t *)&s1,
|
|
*(int32x4_t *)&s2);
|
|
return v;
|
|
}
|
|
|
|
struct s37
|
|
{
|
|
int v[18]; //Testing large aggregate.
|
|
} __attribute__((aligned(16)));
|
|
typedef struct s37 s37_with_align;
|
|
|
|
int32x4_t f37(int i, s37_with_align s1, s37_with_align s2) {
|
|
// CHECK: define <4 x i32> @f37(i32 %i, %struct.s37* %s1, %struct.s37* %s2)
|
|
// CHECK: %[[a:.*]] = bitcast %struct.s37* %s1 to <4 x i32>*
|
|
// CHECK: load <4 x i32>, <4 x i32>* %[[a]], align 16
|
|
// CHECK: %[[b:.*]] = bitcast %struct.s37* %s2 to <4 x i32>*
|
|
// CHECK: load <4 x i32>, <4 x i32>* %[[b]], align 16
|
|
int32x4_t v = vaddq_s32(*(int32x4_t *)&s1,
|
|
*(int32x4_t *)&s2);
|
|
return v;
|
|
}
|
|
s37_with_align g37;
|
|
int32x4_t caller37() {
|
|
// CHECK: caller37
|
|
// CHECK: %[[a:.*]] = alloca %struct.s37, align 16
|
|
// CHECK: %[[b:.*]] = alloca %struct.s37, align 16
|
|
// CHECK: call void @llvm.memcpy
|
|
// CHECK: call void @llvm.memcpy
|
|
// CHECK: call <4 x i32> @f37(i32 3, %struct.s37* %[[a]], %struct.s37* %[[b]])
|
|
return f37(3, g37, g37);
|
|
}
|
|
|
|
// rdar://problem/12648441
|
|
// Test passing structs with size < 8, < 16 and > 16
|
|
// with alignment of 16 and without
|
|
|
|
// structs with size <= 8 bytes, without alignment attribute
|
|
// passed as i64 regardless of the align attribute
|
|
struct s38
|
|
{
|
|
int i;
|
|
short s;
|
|
};
|
|
typedef struct s38 s38_no_align;
|
|
// passing structs in registers
|
|
__attribute__ ((noinline))
|
|
int f38(int i, s38_no_align s1, s38_no_align s2) {
|
|
// CHECK: define i32 @f38(i32 %i, i64 %s1.coerce, i64 %s2.coerce)
|
|
// CHECK: %s1 = alloca %struct.s38, align 4
|
|
// CHECK: %s2 = alloca %struct.s38, align 4
|
|
// CHECK: store i64 %s1.coerce, i64* %{{.*}}, align 4
|
|
// CHECK: store i64 %s2.coerce, i64* %{{.*}}, align 4
|
|
// CHECK: getelementptr inbounds %struct.s38, %struct.s38* %s1, i32 0, i32 0
|
|
// CHECK: getelementptr inbounds %struct.s38, %struct.s38* %s2, i32 0, i32 0
|
|
// CHECK: getelementptr inbounds %struct.s38, %struct.s38* %s1, i32 0, i32 1
|
|
// CHECK: getelementptr inbounds %struct.s38, %struct.s38* %s2, i32 0, i32 1
|
|
return s1.i + s2.i + i + s1.s + s2.s;
|
|
}
|
|
s38_no_align g38;
|
|
s38_no_align g38_2;
|
|
int caller38() {
|
|
// CHECK: define i32 @caller38()
|
|
// CHECK: %[[a:.*]] = load i64, i64* bitcast (%struct.s38* @g38 to i64*), align 4
|
|
// CHECK: %[[b:.*]] = load i64, i64* bitcast (%struct.s38* @g38_2 to i64*), align 4
|
|
// CHECK: call i32 @f38(i32 3, i64 %[[a]], i64 %[[b]])
|
|
return f38(3, g38, g38_2);
|
|
}
|
|
// passing structs on stack
|
|
__attribute__ ((noinline))
|
|
int f38_stack(int i, int i2, int i3, int i4, int i5, int i6, int i7, int i8,
|
|
int i9, s38_no_align s1, s38_no_align s2) {
|
|
// CHECK: define i32 @f38_stack(i32 %i, i32 %i2, i32 %i3, i32 %i4, i32 %i5, i32 %i6, i32 %i7, i32 %i8, i32 %i9, i64 %s1.coerce, i64 %s2.coerce)
|
|
// CHECK: %s1 = alloca %struct.s38, align 4
|
|
// CHECK: %s2 = alloca %struct.s38, align 4
|
|
// CHECK: store i64 %s1.coerce, i64* %{{.*}}, align 4
|
|
// CHECK: store i64 %s2.coerce, i64* %{{.*}}, align 4
|
|
// CHECK: getelementptr inbounds %struct.s38, %struct.s38* %s1, i32 0, i32 0
|
|
// CHECK: getelementptr inbounds %struct.s38, %struct.s38* %s2, i32 0, i32 0
|
|
// CHECK: getelementptr inbounds %struct.s38, %struct.s38* %s1, i32 0, i32 1
|
|
// CHECK: getelementptr inbounds %struct.s38, %struct.s38* %s2, i32 0, i32 1
|
|
return s1.i + s2.i + i + i2 + i3 + i4 + i5 + i6 + i7 + i8 + i9 + s1.s + s2.s;
|
|
}
|
|
int caller38_stack() {
|
|
// CHECK: define i32 @caller38_stack()
|
|
// CHECK: %[[a:.*]] = load i64, i64* bitcast (%struct.s38* @g38 to i64*), align 4
|
|
// CHECK: %[[b:.*]] = load i64, i64* bitcast (%struct.s38* @g38_2 to i64*), align 4
|
|
// CHECK: call i32 @f38_stack(i32 1, i32 2, i32 3, i32 4, i32 5, i32 6, i32 7, i32 8, i32 9, i64 %[[a]], i64 %[[b]])
|
|
return f38_stack(1, 2, 3, 4, 5, 6, 7, 8, 9, g38, g38_2);
|
|
}
|
|
|
|
// structs with size <= 8 bytes, with alignment attribute
|
|
struct s39
|
|
{
|
|
int i;
|
|
short s;
|
|
} __attribute__((aligned(16)));
|
|
typedef struct s39 s39_with_align;
|
|
// passing aligned structs in registers
|
|
__attribute__ ((noinline))
|
|
int f39(int i, s39_with_align s1, s39_with_align s2) {
|
|
// CHECK: define i32 @f39(i32 %i, i128 %s1.coerce, i128 %s2.coerce)
|
|
// CHECK: %s1 = alloca %struct.s39, align 16
|
|
// CHECK: %s2 = alloca %struct.s39, align 16
|
|
// CHECK: store i128 %s1.coerce, i128* %{{.*}}, align 16
|
|
// CHECK: store i128 %s2.coerce, i128* %{{.*}}, align 16
|
|
// CHECK: getelementptr inbounds %struct.s39, %struct.s39* %s1, i32 0, i32 0
|
|
// CHECK: getelementptr inbounds %struct.s39, %struct.s39* %s2, i32 0, i32 0
|
|
// CHECK: getelementptr inbounds %struct.s39, %struct.s39* %s1, i32 0, i32 1
|
|
// CHECK: getelementptr inbounds %struct.s39, %struct.s39* %s2, i32 0, i32 1
|
|
return s1.i + s2.i + i + s1.s + s2.s;
|
|
}
|
|
s39_with_align g39;
|
|
s39_with_align g39_2;
|
|
int caller39() {
|
|
// CHECK: define i32 @caller39()
|
|
// CHECK: %[[a:.*]] = load i128, i128* bitcast (%struct.s39* @g39 to i128*), align 16
|
|
// CHECK: %[[b:.*]] = load i128, i128* bitcast (%struct.s39* @g39_2 to i128*), align 16
|
|
// CHECK: call i32 @f39(i32 3, i128 %[[a]], i128 %[[b]])
|
|
return f39(3, g39, g39_2);
|
|
}
|
|
// passing aligned structs on stack
|
|
__attribute__ ((noinline))
|
|
int f39_stack(int i, int i2, int i3, int i4, int i5, int i6, int i7, int i8,
|
|
int i9, s39_with_align s1, s39_with_align s2) {
|
|
// CHECK: define i32 @f39_stack(i32 %i, i32 %i2, i32 %i3, i32 %i4, i32 %i5, i32 %i6, i32 %i7, i32 %i8, i32 %i9, i128 %s1.coerce, i128 %s2.coerce)
|
|
// CHECK: %s1 = alloca %struct.s39, align 16
|
|
// CHECK: %s2 = alloca %struct.s39, align 16
|
|
// CHECK: store i128 %s1.coerce, i128* %{{.*}}, align 16
|
|
// CHECK: store i128 %s2.coerce, i128* %{{.*}}, align 16
|
|
// CHECK: getelementptr inbounds %struct.s39, %struct.s39* %s1, i32 0, i32 0
|
|
// CHECK: getelementptr inbounds %struct.s39, %struct.s39* %s2, i32 0, i32 0
|
|
// CHECK: getelementptr inbounds %struct.s39, %struct.s39* %s1, i32 0, i32 1
|
|
// CHECK: getelementptr inbounds %struct.s39, %struct.s39* %s2, i32 0, i32 1
|
|
return s1.i + s2.i + i + i2 + i3 + i4 + i5 + i6 + i7 + i8 + i9 + s1.s + s2.s;
|
|
}
|
|
int caller39_stack() {
|
|
// CHECK: define i32 @caller39_stack()
|
|
// CHECK: %[[a:.*]] = load i128, i128* bitcast (%struct.s39* @g39 to i128*), align 16
|
|
// CHECK: %[[b:.*]] = load i128, i128* bitcast (%struct.s39* @g39_2 to i128*), align 16
|
|
// CHECK: call i32 @f39_stack(i32 1, i32 2, i32 3, i32 4, i32 5, i32 6, i32 7, i32 8, i32 9, i128 %[[a]], i128 %[[b]])
|
|
return f39_stack(1, 2, 3, 4, 5, 6, 7, 8, 9, g39, g39_2);
|
|
}
|
|
|
|
// structs with size <= 16 bytes, without alignment attribute
|
|
struct s40
|
|
{
|
|
int i;
|
|
short s;
|
|
int i2;
|
|
short s2;
|
|
};
|
|
typedef struct s40 s40_no_align;
|
|
// passing structs in registers
|
|
__attribute__ ((noinline))
|
|
int f40(int i, s40_no_align s1, s40_no_align s2) {
|
|
// CHECK: define i32 @f40(i32 %i, [2 x i64] %s1.coerce, [2 x i64] %s2.coerce)
|
|
// CHECK: %s1 = alloca %struct.s40, align 4
|
|
// CHECK: %s2 = alloca %struct.s40, align 4
|
|
// CHECK: store [2 x i64] %s1.coerce, [2 x i64]* %{{.*}}, align 4
|
|
// CHECK: store [2 x i64] %s2.coerce, [2 x i64]* %{{.*}}, align 4
|
|
// CHECK: getelementptr inbounds %struct.s40, %struct.s40* %s1, i32 0, i32 0
|
|
// CHECK: getelementptr inbounds %struct.s40, %struct.s40* %s2, i32 0, i32 0
|
|
// CHECK: getelementptr inbounds %struct.s40, %struct.s40* %s1, i32 0, i32 1
|
|
// CHECK: getelementptr inbounds %struct.s40, %struct.s40* %s2, i32 0, i32 1
|
|
return s1.i + s2.i + i + s1.s + s2.s;
|
|
}
|
|
s40_no_align g40;
|
|
s40_no_align g40_2;
|
|
int caller40() {
|
|
// CHECK: define i32 @caller40()
|
|
// CHECK: %[[a:.*]] = load [2 x i64], [2 x i64]* bitcast (%struct.s40* @g40 to [2 x i64]*), align 4
|
|
// CHECK: %[[b:.*]] = load [2 x i64], [2 x i64]* bitcast (%struct.s40* @g40_2 to [2 x i64]*), align 4
|
|
// CHECK: call i32 @f40(i32 3, [2 x i64] %[[a]], [2 x i64] %[[b]])
|
|
return f40(3, g40, g40_2);
|
|
}
|
|
// passing structs on stack
|
|
__attribute__ ((noinline))
|
|
int f40_stack(int i, int i2, int i3, int i4, int i5, int i6, int i7, int i8,
|
|
int i9, s40_no_align s1, s40_no_align s2) {
|
|
// CHECK: define i32 @f40_stack(i32 %i, i32 %i2, i32 %i3, i32 %i4, i32 %i5, i32 %i6, i32 %i7, i32 %i8, i32 %i9, [2 x i64] %s1.coerce, [2 x i64] %s2.coerce)
|
|
// CHECK: %s1 = alloca %struct.s40, align 4
|
|
// CHECK: %s2 = alloca %struct.s40, align 4
|
|
// CHECK: store [2 x i64] %s1.coerce, [2 x i64]* %{{.*}}, align 4
|
|
// CHECK: store [2 x i64] %s2.coerce, [2 x i64]* %{{.*}}, align 4
|
|
// CHECK: getelementptr inbounds %struct.s40, %struct.s40* %s1, i32 0, i32 0
|
|
// CHECK: getelementptr inbounds %struct.s40, %struct.s40* %s2, i32 0, i32 0
|
|
// CHECK: getelementptr inbounds %struct.s40, %struct.s40* %s1, i32 0, i32 1
|
|
// CHECK: getelementptr inbounds %struct.s40, %struct.s40* %s2, i32 0, i32 1
|
|
return s1.i + s2.i + i + i2 + i3 + i4 + i5 + i6 + i7 + i8 + i9 + s1.s + s2.s;
|
|
}
|
|
int caller40_stack() {
|
|
// CHECK: define i32 @caller40_stack()
|
|
// CHECK: %[[a:.*]] = load [2 x i64], [2 x i64]* bitcast (%struct.s40* @g40 to [2 x i64]*), align 4
|
|
// CHECK: %[[b:.*]] = load [2 x i64], [2 x i64]* bitcast (%struct.s40* @g40_2 to [2 x i64]*), align 4
|
|
// CHECK: call i32 @f40_stack(i32 1, i32 2, i32 3, i32 4, i32 5, i32 6, i32 7, i32 8, i32 9, [2 x i64] %[[a]], [2 x i64] %[[b]])
|
|
return f40_stack(1, 2, 3, 4, 5, 6, 7, 8, 9, g40, g40_2);
|
|
}
|
|
|
|
// structs with size <= 16 bytes, with alignment attribute
|
|
struct s41
|
|
{
|
|
int i;
|
|
short s;
|
|
int i2;
|
|
short s2;
|
|
} __attribute__((aligned(16)));
|
|
typedef struct s41 s41_with_align;
|
|
// passing aligned structs in registers
|
|
__attribute__ ((noinline))
|
|
int f41(int i, s41_with_align s1, s41_with_align s2) {
|
|
// CHECK: define i32 @f41(i32 %i, i128 %s1.coerce, i128 %s2.coerce)
|
|
// CHECK: %s1 = alloca %struct.s41, align 16
|
|
// CHECK: %s2 = alloca %struct.s41, align 16
|
|
// CHECK: store i128 %s1.coerce, i128* %{{.*}}, align 16
|
|
// CHECK: store i128 %s2.coerce, i128* %{{.*}}, align 16
|
|
// CHECK: getelementptr inbounds %struct.s41, %struct.s41* %s1, i32 0, i32 0
|
|
// CHECK: getelementptr inbounds %struct.s41, %struct.s41* %s2, i32 0, i32 0
|
|
// CHECK: getelementptr inbounds %struct.s41, %struct.s41* %s1, i32 0, i32 1
|
|
// CHECK: getelementptr inbounds %struct.s41, %struct.s41* %s2, i32 0, i32 1
|
|
return s1.i + s2.i + i + s1.s + s2.s;
|
|
}
|
|
s41_with_align g41;
|
|
s41_with_align g41_2;
|
|
int caller41() {
|
|
// CHECK: define i32 @caller41()
|
|
// CHECK: %[[a:.*]] = load i128, i128* bitcast (%struct.s41* @g41 to i128*), align 16
|
|
// CHECK: %[[b:.*]] = load i128, i128* bitcast (%struct.s41* @g41_2 to i128*), align 16
|
|
// CHECK: call i32 @f41(i32 3, i128 %[[a]], i128 %[[b]])
|
|
return f41(3, g41, g41_2);
|
|
}
|
|
// passing aligned structs on stack
|
|
__attribute__ ((noinline))
|
|
int f41_stack(int i, int i2, int i3, int i4, int i5, int i6, int i7, int i8,
|
|
int i9, s41_with_align s1, s41_with_align s2) {
|
|
// CHECK: define i32 @f41_stack(i32 %i, i32 %i2, i32 %i3, i32 %i4, i32 %i5, i32 %i6, i32 %i7, i32 %i8, i32 %i9, i128 %s1.coerce, i128 %s2.coerce)
|
|
// CHECK: %s1 = alloca %struct.s41, align 16
|
|
// CHECK: %s2 = alloca %struct.s41, align 16
|
|
// CHECK: store i128 %s1.coerce, i128* %{{.*}}, align 16
|
|
// CHECK: store i128 %s2.coerce, i128* %{{.*}}, align 16
|
|
// CHECK: getelementptr inbounds %struct.s41, %struct.s41* %s1, i32 0, i32 0
|
|
// CHECK: getelementptr inbounds %struct.s41, %struct.s41* %s2, i32 0, i32 0
|
|
// CHECK: getelementptr inbounds %struct.s41, %struct.s41* %s1, i32 0, i32 1
|
|
// CHECK: getelementptr inbounds %struct.s41, %struct.s41* %s2, i32 0, i32 1
|
|
return s1.i + s2.i + i + i2 + i3 + i4 + i5 + i6 + i7 + i8 + i9 + s1.s + s2.s;
|
|
}
|
|
int caller41_stack() {
|
|
// CHECK: define i32 @caller41_stack()
|
|
// CHECK: %[[a:.*]] = load i128, i128* bitcast (%struct.s41* @g41 to i128*), align 16
|
|
// CHECK: %[[b:.*]] = load i128, i128* bitcast (%struct.s41* @g41_2 to i128*), align 16
|
|
// CHECK: call i32 @f41_stack(i32 1, i32 2, i32 3, i32 4, i32 5, i32 6, i32 7, i32 8, i32 9, i128 %[[a]], i128 %[[b]])
|
|
return f41_stack(1, 2, 3, 4, 5, 6, 7, 8, 9, g41, g41_2);
|
|
}
|
|
|
|
// structs with size > 16 bytes, without alignment attribute
|
|
struct s42
|
|
{
|
|
int i;
|
|
short s;
|
|
int i2;
|
|
short s2;
|
|
int i3;
|
|
short s3;
|
|
};
|
|
typedef struct s42 s42_no_align;
|
|
// passing structs in registers
|
|
__attribute__ ((noinline))
|
|
int f42(int i, s42_no_align s1, s42_no_align s2) {
|
|
// CHECK: define i32 @f42(i32 %i, %struct.s42* %s1, %struct.s42* %s2)
|
|
// CHECK: getelementptr inbounds %struct.s42, %struct.s42* %s1, i32 0, i32 0
|
|
// CHECK: getelementptr inbounds %struct.s42, %struct.s42* %s2, i32 0, i32 0
|
|
// CHECK: getelementptr inbounds %struct.s42, %struct.s42* %s1, i32 0, i32 1
|
|
// CHECK: getelementptr inbounds %struct.s42, %struct.s42* %s2, i32 0, i32 1
|
|
return s1.i + s2.i + i + s1.s + s2.s;
|
|
}
|
|
s42_no_align g42;
|
|
s42_no_align g42_2;
|
|
int caller42() {
|
|
// CHECK: define i32 @caller42()
|
|
// CHECK: %[[a:.*]] = alloca %struct.s42, align 4
|
|
// CHECK: %[[b:.*]] = alloca %struct.s42, align 4
|
|
// CHECK: %[[c:.*]] = bitcast %struct.s42* %[[a]] to i8*
|
|
// CHECK: call void @llvm.memcpy.p0i8.p0i8.i64
|
|
// CHECK: %[[d:.*]] = bitcast %struct.s42* %[[b]] to i8*
|
|
// CHECK: call void @llvm.memcpy.p0i8.p0i8.i64
|
|
// CHECK: call i32 @f42(i32 3, %struct.s42* %[[a]], %struct.s42* %[[b]])
|
|
return f42(3, g42, g42_2);
|
|
}
|
|
// passing structs on stack
|
|
__attribute__ ((noinline))
|
|
int f42_stack(int i, int i2, int i3, int i4, int i5, int i6, int i7, int i8,
|
|
int i9, s42_no_align s1, s42_no_align s2) {
|
|
// CHECK: define i32 @f42_stack(i32 %i, i32 %i2, i32 %i3, i32 %i4, i32 %i5, i32 %i6, i32 %i7, i32 %i8, i32 %i9, %struct.s42* %s1, %struct.s42* %s2)
|
|
// CHECK: getelementptr inbounds %struct.s42, %struct.s42* %s1, i32 0, i32 0
|
|
// CHECK: getelementptr inbounds %struct.s42, %struct.s42* %s2, i32 0, i32 0
|
|
// CHECK: getelementptr inbounds %struct.s42, %struct.s42* %s1, i32 0, i32 1
|
|
// CHECK: getelementptr inbounds %struct.s42, %struct.s42* %s2, i32 0, i32 1
|
|
return s1.i + s2.i + i + i2 + i3 + i4 + i5 + i6 + i7 + i8 + i9 + s1.s + s2.s;
|
|
}
|
|
int caller42_stack() {
|
|
// CHECK: define i32 @caller42_stack()
|
|
// CHECK: %[[a:.*]] = alloca %struct.s42, align 4
|
|
// CHECK: %[[b:.*]] = alloca %struct.s42, align 4
|
|
// CHECK: %[[c:.*]] = bitcast %struct.s42* %[[a]] to i8*
|
|
// CHECK: call void @llvm.memcpy.p0i8.p0i8.i64
|
|
// CHECK: %[[d:.*]] = bitcast %struct.s42* %[[b]] to i8*
|
|
// CHECK: call void @llvm.memcpy.p0i8.p0i8.i64
|
|
// CHECK: call i32 @f42_stack(i32 1, i32 2, i32 3, i32 4, i32 5, i32 6, i32 7, i32 8, i32 9, %struct.s42* %[[a]], %struct.s42* %[[b]])
|
|
return f42_stack(1, 2, 3, 4, 5, 6, 7, 8, 9, g42, g42_2);
|
|
}
|
|
|
|
// structs with size > 16 bytes, with alignment attribute
|
|
struct s43
|
|
{
|
|
int i;
|
|
short s;
|
|
int i2;
|
|
short s2;
|
|
int i3;
|
|
short s3;
|
|
} __attribute__((aligned(16)));
|
|
typedef struct s43 s43_with_align;
|
|
// passing aligned structs in registers
|
|
__attribute__ ((noinline))
|
|
int f43(int i, s43_with_align s1, s43_with_align s2) {
|
|
// CHECK: define i32 @f43(i32 %i, %struct.s43* %s1, %struct.s43* %s2)
|
|
// CHECK: getelementptr inbounds %struct.s43, %struct.s43* %s1, i32 0, i32 0
|
|
// CHECK: getelementptr inbounds %struct.s43, %struct.s43* %s2, i32 0, i32 0
|
|
// CHECK: getelementptr inbounds %struct.s43, %struct.s43* %s1, i32 0, i32 1
|
|
// CHECK: getelementptr inbounds %struct.s43, %struct.s43* %s2, i32 0, i32 1
|
|
return s1.i + s2.i + i + s1.s + s2.s;
|
|
}
|
|
s43_with_align g43;
|
|
s43_with_align g43_2;
|
|
int caller43() {
|
|
// CHECK: define i32 @caller43()
|
|
// CHECK: %[[a:.*]] = alloca %struct.s43, align 16
|
|
// CHECK: %[[b:.*]] = alloca %struct.s43, align 16
|
|
// CHECK: %[[c:.*]] = bitcast %struct.s43* %[[a]] to i8*
|
|
// CHECK: call void @llvm.memcpy.p0i8.p0i8.i64
|
|
// CHECK: %[[d:.*]] = bitcast %struct.s43* %[[b]] to i8*
|
|
// CHECK: call void @llvm.memcpy.p0i8.p0i8.i64
|
|
// CHECK: call i32 @f43(i32 3, %struct.s43* %[[a]], %struct.s43* %[[b]])
|
|
return f43(3, g43, g43_2);
|
|
}
|
|
// passing aligned structs on stack
|
|
__attribute__ ((noinline))
|
|
int f43_stack(int i, int i2, int i3, int i4, int i5, int i6, int i7, int i8,
|
|
int i9, s43_with_align s1, s43_with_align s2) {
|
|
// CHECK: define i32 @f43_stack(i32 %i, i32 %i2, i32 %i3, i32 %i4, i32 %i5, i32 %i6, i32 %i7, i32 %i8, i32 %i9, %struct.s43* %s1, %struct.s43* %s2)
|
|
// CHECK: getelementptr inbounds %struct.s43, %struct.s43* %s1, i32 0, i32 0
|
|
// CHECK: getelementptr inbounds %struct.s43, %struct.s43* %s2, i32 0, i32 0
|
|
// CHECK: getelementptr inbounds %struct.s43, %struct.s43* %s1, i32 0, i32 1
|
|
// CHECK: getelementptr inbounds %struct.s43, %struct.s43* %s2, i32 0, i32 1
|
|
return s1.i + s2.i + i + i2 + i3 + i4 + i5 + i6 + i7 + i8 + i9 + s1.s + s2.s;
|
|
}
|
|
int caller43_stack() {
|
|
// CHECK: define i32 @caller43_stack()
|
|
// CHECK: %[[a:.*]] = alloca %struct.s43, align 16
|
|
// CHECK: %[[b:.*]] = alloca %struct.s43, align 16
|
|
// CHECK: %[[c:.*]] = bitcast %struct.s43* %[[a]] to i8*
|
|
// CHECK: call void @llvm.memcpy.p0i8.p0i8.i64
|
|
// CHECK: %[[d:.*]] = bitcast %struct.s43* %[[b]] to i8*
|
|
// CHECK: call void @llvm.memcpy.p0i8.p0i8.i64
|
|
// CHECK: call i32 @f43_stack(i32 1, i32 2, i32 3, i32 4, i32 5, i32 6, i32 7, i32 8, i32 9, %struct.s43* %[[a]], %struct.s43* %[[b]])
|
|
return f43_stack(1, 2, 3, 4, 5, 6, 7, 8, 9, g43, g43_2);
|
|
}
|
|
|
|
// rdar://13668927
|
|
// We should not split argument s1 between registers and stack.
|
|
__attribute__ ((noinline))
|
|
int f40_split(int i, int i2, int i3, int i4, int i5, int i6, int i7,
|
|
s40_no_align s1, s40_no_align s2) {
|
|
// CHECK: define i32 @f40_split(i32 %i, i32 %i2, i32 %i3, i32 %i4, i32 %i5, i32 %i6, i32 %i7, [2 x i64] %s1.coerce, [2 x i64] %s2.coerce)
|
|
return s1.i + s2.i + i + i2 + i3 + i4 + i5 + i6 + i7 + s1.s + s2.s;
|
|
}
|
|
int caller40_split() {
|
|
// CHECK: define i32 @caller40_split()
|
|
// CHECK: call i32 @f40_split(i32 1, i32 2, i32 3, i32 4, i32 5, i32 6, i32 7, [2 x i64] %{{.*}} [2 x i64] %{{.*}})
|
|
return f40_split(1, 2, 3, 4, 5, 6, 7, g40, g40_2);
|
|
}
|
|
|
|
__attribute__ ((noinline))
|
|
int f41_split(int i, int i2, int i3, int i4, int i5, int i6, int i7,
|
|
s41_with_align s1, s41_with_align s2) {
|
|
// CHECK: define i32 @f41_split(i32 %i, i32 %i2, i32 %i3, i32 %i4, i32 %i5, i32 %i6, i32 %i7, i128 %s1.coerce, i128 %s2.coerce)
|
|
return s1.i + s2.i + i + i2 + i3 + i4 + i5 + i6 + i7 + s1.s + s2.s;
|
|
}
|
|
int caller41_split() {
|
|
// CHECK: define i32 @caller41_split()
|
|
// CHECK: call i32 @f41_split(i32 1, i32 2, i32 3, i32 4, i32 5, i32 6, i32 7, i128 %{{.*}}, i128 %{{.*}})
|
|
return f41_split(1, 2, 3, 4, 5, 6, 7, g41, g41_2);
|
|
}
|
|
|
|
// Handle homogeneous aggregates properly in variadic functions.
|
|
struct HFA {
|
|
float a, b, c, d;
|
|
};
|
|
|
|
float test_hfa(int n, ...) {
|
|
// CHECK-LABEL: define float @test_hfa(i32 %n, ...)
|
|
// CHECK: [[THELIST:%.*]] = alloca i8*
|
|
// CHECK: [[CURLIST:%.*]] = load i8*, i8** [[THELIST]]
|
|
|
|
// HFA is not indirect, so occupies its full 16 bytes on the stack.
|
|
// CHECK: [[NEXTLIST:%.*]] = getelementptr inbounds i8, i8* [[CURLIST]], i64 16
|
|
// CHECK: store i8* [[NEXTLIST]], i8** [[THELIST]]
|
|
|
|
// CHECK: bitcast i8* [[CURLIST]] to %struct.HFA*
|
|
__builtin_va_list thelist;
|
|
__builtin_va_start(thelist, n);
|
|
struct HFA h = __builtin_va_arg(thelist, struct HFA);
|
|
return h.d;
|
|
}
|
|
|
|
float test_hfa_call(struct HFA *a) {
|
|
// CHECK-LABEL: define float @test_hfa_call(%struct.HFA* %a)
|
|
// CHECK: call float (i32, ...) @test_hfa(i32 1, [4 x float] {{.*}})
|
|
test_hfa(1, *a);
|
|
}
|
|
|
|
struct TooBigHFA {
|
|
float a, b, c, d, e;
|
|
};
|
|
|
|
float test_toobig_hfa(int n, ...) {
|
|
// CHECK-LABEL: define float @test_toobig_hfa(i32 %n, ...)
|
|
// CHECK: [[THELIST:%.*]] = alloca i8*
|
|
// CHECK: [[CURLIST:%.*]] = load i8*, i8** [[THELIST]]
|
|
|
|
// TooBigHFA is not actually an HFA, so gets passed indirectly. Only 8 bytes
|
|
// of stack consumed.
|
|
// CHECK: [[NEXTLIST:%.*]] = getelementptr inbounds i8, i8* [[CURLIST]], i64 8
|
|
// CHECK: store i8* [[NEXTLIST]], i8** [[THELIST]]
|
|
|
|
// CHECK: [[HFAPTRPTR:%.*]] = bitcast i8* [[CURLIST]] to %struct.TooBigHFA**
|
|
// CHECK: [[HFAPTR:%.*]] = load %struct.TooBigHFA*, %struct.TooBigHFA** [[HFAPTRPTR]]
|
|
__builtin_va_list thelist;
|
|
__builtin_va_start(thelist, n);
|
|
struct TooBigHFA h = __builtin_va_arg(thelist, struct TooBigHFA);
|
|
return h.d;
|
|
}
|
|
|
|
struct HVA {
|
|
int32x4_t a, b;
|
|
};
|
|
|
|
int32x4_t test_hva(int n, ...) {
|
|
// CHECK-LABEL: define <4 x i32> @test_hva(i32 %n, ...)
|
|
// CHECK: [[THELIST:%.*]] = alloca i8*
|
|
// CHECK: [[CURLIST:%.*]] = load i8*, i8** [[THELIST]]
|
|
|
|
// HVA is not indirect, so occupies its full 16 bytes on the stack. but it
|
|
// must be properly aligned.
|
|
// CHECK: [[ALIGN0:%.*]] = ptrtoint i8* [[CURLIST]] to i64
|
|
// CHECK: [[ALIGN1:%.*]] = add i64 [[ALIGN0]], 15
|
|
// CHECK: [[ALIGN2:%.*]] = and i64 [[ALIGN1]], -16
|
|
// CHECK: [[ALIGNED_LIST:%.*]] = inttoptr i64 [[ALIGN2]] to i8*
|
|
|
|
// CHECK: [[NEXTLIST:%.*]] = getelementptr inbounds i8, i8* [[ALIGNED_LIST]], i64 32
|
|
// CHECK: store i8* [[NEXTLIST]], i8** [[THELIST]]
|
|
|
|
// CHECK: bitcast i8* [[ALIGNED_LIST]] to %struct.HVA*
|
|
__builtin_va_list thelist;
|
|
__builtin_va_start(thelist, n);
|
|
struct HVA h = __builtin_va_arg(thelist, struct HVA);
|
|
return h.b;
|
|
}
|
|
|
|
struct TooBigHVA {
|
|
int32x4_t a, b, c, d, e;
|
|
};
|
|
|
|
int32x4_t test_toobig_hva(int n, ...) {
|
|
// CHECK-LABEL: define <4 x i32> @test_toobig_hva(i32 %n, ...)
|
|
// CHECK: [[THELIST:%.*]] = alloca i8*
|
|
// CHECK: [[CURLIST:%.*]] = load i8*, i8** [[THELIST]]
|
|
|
|
// TooBigHVA is not actually an HVA, so gets passed indirectly. Only 8 bytes
|
|
// of stack consumed.
|
|
// CHECK: [[NEXTLIST:%.*]] = getelementptr inbounds i8, i8* [[CURLIST]], i64 8
|
|
// CHECK: store i8* [[NEXTLIST]], i8** [[THELIST]]
|
|
|
|
// CHECK: [[HVAPTRPTR:%.*]] = bitcast i8* [[CURLIST]] to %struct.TooBigHVA**
|
|
// CHECK: [[HVAPTR:%.*]] = load %struct.TooBigHVA*, %struct.TooBigHVA** [[HVAPTRPTR]]
|
|
__builtin_va_list thelist;
|
|
__builtin_va_start(thelist, n);
|
|
struct TooBigHVA h = __builtin_va_arg(thelist, struct TooBigHVA);
|
|
return h.d;
|
|
}
|
|
|
|
typedef __attribute__((__ext_vector_type__(3))) float float32x3_t;
|
|
typedef struct { float32x3_t arr[4]; } HFAv3;
|
|
|
|
float32x3_t test_hva_v3(int n, ...) {
|
|
// CHECK-LABEL: define <3 x float> @test_hva_v3(i32 %n, ...)
|
|
// CHECK: [[THELIST:%.*]] = alloca i8*
|
|
// CHECK: [[CURLIST:%.*]] = load i8*, i8** [[THELIST]]
|
|
|
|
// HVA is not indirect, so occupies its full 16 bytes on the stack. but it
|
|
// must be properly aligned.
|
|
// CHECK: [[ALIGN0:%.*]] = ptrtoint i8* [[CURLIST]] to i64
|
|
// CHECK: [[ALIGN1:%.*]] = add i64 [[ALIGN0]], 15
|
|
// CHECK: [[ALIGN2:%.*]] = and i64 [[ALIGN1]], -16
|
|
// CHECK: [[ALIGNED_LIST:%.*]] = inttoptr i64 [[ALIGN2]] to i8*
|
|
|
|
// CHECK: [[NEXTLIST:%.*]] = getelementptr inbounds i8, i8* [[ALIGNED_LIST]], i64 64
|
|
// CHECK: store i8* [[NEXTLIST]], i8** [[THELIST]]
|
|
|
|
// CHECK: bitcast i8* [[ALIGNED_LIST]] to %struct.HFAv3*
|
|
__builtin_va_list l;
|
|
__builtin_va_start(l, n);
|
|
HFAv3 r = __builtin_va_arg(l, HFAv3);
|
|
return r.arr[2];
|
|
}
|
|
|
|
float32x3_t test_hva_v3_call(HFAv3 *a) {
|
|
// CHECK-LABEL: define <3 x float> @test_hva_v3_call(%struct.HFAv3* %a)
|
|
// CHECK: call <3 x float> (i32, ...) @test_hva_v3(i32 1, [4 x <4 x float>] {{.*}})
|
|
return test_hva_v3(1, *a);
|
|
}
|