a5efa7386a
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
307 lines
6.8 KiB
C
307 lines
6.8 KiB
C
// RUN: %clang_cc1 -triple x86_64-unknown-unknown -emit-llvm -o - %s| FileCheck %s
|
|
#include <stdarg.h>
|
|
|
|
// CHECK: define signext i8 @f0()
|
|
char f0(void) {
|
|
return 0;
|
|
}
|
|
|
|
// CHECK: define signext i16 @f1()
|
|
short f1(void) {
|
|
return 0;
|
|
}
|
|
|
|
// CHECK: define i32 @f2()
|
|
int f2(void) {
|
|
return 0;
|
|
}
|
|
|
|
// CHECK: define float @f3()
|
|
float f3(void) {
|
|
return 0;
|
|
}
|
|
|
|
// CHECK: define double @f4()
|
|
double f4(void) {
|
|
return 0;
|
|
}
|
|
|
|
// CHECK: define x86_fp80 @f5()
|
|
long double f5(void) {
|
|
return 0;
|
|
}
|
|
|
|
// CHECK: define void @f6(i8 signext %a0, i16 signext %a1, i32 %a2, i64 %a3, i8* %a4)
|
|
void f6(char a0, short a1, int a2, long long a3, void *a4) {
|
|
}
|
|
|
|
// CHECK: define void @f7(i32 %a0)
|
|
typedef enum { A, B, C } e7;
|
|
void f7(e7 a0) {
|
|
}
|
|
|
|
// Test merging/passing of upper eightbyte with X87 class.
|
|
//
|
|
// CHECK: define void @f8_1(%union.u8* noalias sret %agg.result)
|
|
// CHECK: define void @f8_2(%union.u8* byval align 16 %a0)
|
|
union u8 {
|
|
long double a;
|
|
int b;
|
|
};
|
|
union u8 f8_1() { while (1) {} }
|
|
void f8_2(union u8 a0) {}
|
|
|
|
// CHECK: define i64 @f9()
|
|
struct s9 { int a; int b; int : 0; } f9(void) { while (1) {} }
|
|
|
|
// CHECK: define void @f10(i64 %a0.coerce)
|
|
struct s10 { int a; int b; int : 0; };
|
|
void f10(struct s10 a0) {}
|
|
|
|
// CHECK: define void @f11(%union.anon* noalias sret %agg.result)
|
|
union { long double a; float b; } f11() { while (1) {} }
|
|
|
|
// CHECK: define i32 @f12_0()
|
|
// CHECK: define void @f12_1(i32 %a0.coerce)
|
|
struct s12 { int a __attribute__((aligned(16))); };
|
|
struct s12 f12_0(void) { while (1) {} }
|
|
void f12_1(struct s12 a0) {}
|
|
|
|
// Check that sret parameter is accounted for when checking available integer
|
|
// registers.
|
|
// CHECK: define void @f13(%struct.s13_0* noalias sret %agg.result, i32 %a, i32 %b, i32 %c, i32 %d, {{.*}}* byval align 8 %e, i32 %f)
|
|
|
|
struct s13_0 { long long f0[3]; };
|
|
struct s13_1 { long long f0[2]; };
|
|
struct s13_0 f13(int a, int b, int c, int d,
|
|
struct s13_1 e, int f) { while (1) {} }
|
|
|
|
// CHECK: define void @f14({{.*}}, i8 signext %X)
|
|
void f14(int a, int b, int c, int d, int e, int f, char X) {}
|
|
|
|
// CHECK: define void @f15({{.*}}, i8* %X)
|
|
void f15(int a, int b, int c, int d, int e, int f, void *X) {}
|
|
|
|
// CHECK: define void @f16({{.*}}, float %X)
|
|
void f16(float a, float b, float c, float d, float e, float f, float g, float h,
|
|
float X) {}
|
|
|
|
// CHECK: define void @f17({{.*}}, x86_fp80 %X)
|
|
void f17(float a, float b, float c, float d, float e, float f, float g, float h,
|
|
long double X) {}
|
|
|
|
// Check for valid coercion. The struct should be passed/returned as i32, not
|
|
// as i64 for better code quality.
|
|
// rdar://8135035
|
|
// CHECK: define void @f18(i32 %a, i32 %f18_arg1.coerce)
|
|
struct f18_s0 { int f0; };
|
|
void f18(int a, struct f18_s0 f18_arg1) { while (1) {} }
|
|
|
|
// Check byval alignment.
|
|
|
|
// CHECK: define void @f19(%struct.s19* byval align 16 %x)
|
|
struct s19 {
|
|
long double a;
|
|
};
|
|
void f19(struct s19 x) {}
|
|
|
|
// CHECK: define void @f20(%struct.s20* byval align 32 %x)
|
|
struct __attribute__((aligned(32))) s20 {
|
|
int x;
|
|
int y;
|
|
};
|
|
void f20(struct s20 x) {}
|
|
|
|
struct StringRef {
|
|
long x;
|
|
const char *Ptr;
|
|
};
|
|
|
|
// rdar://7375902
|
|
// CHECK: define i8* @f21(i64 %S.coerce0, i8* %S.coerce1)
|
|
const char *f21(struct StringRef S) { return S.x+S.Ptr; }
|
|
|
|
// PR7567
|
|
typedef __attribute__ ((aligned(16))) struct f22s { unsigned long long x[2]; } L;
|
|
void f22(L x, L y) { }
|
|
// CHECK: @f22
|
|
// CHECK: %x = alloca{{.*}}, align 16
|
|
// CHECK: %y = alloca{{.*}}, align 16
|
|
|
|
|
|
|
|
// PR7714
|
|
struct f23S {
|
|
short f0;
|
|
unsigned f1;
|
|
int f2;
|
|
};
|
|
|
|
|
|
void f23(int A, struct f23S B) {
|
|
// CHECK: define void @f23(i32 %A, i64 %B.coerce0, i32 %B.coerce1)
|
|
}
|
|
|
|
struct f24s { long a; int b; };
|
|
|
|
struct f23S f24(struct f23S *X, struct f24s *P2) {
|
|
return *X;
|
|
|
|
// CHECK: define { i64, i32 } @f24(%struct.f23S* %X, %struct.f24s* %P2)
|
|
}
|
|
|
|
// rdar://8248065
|
|
typedef float v4f32 __attribute__((__vector_size__(16)));
|
|
v4f32 f25(v4f32 X) {
|
|
// CHECK: define <4 x float> @f25(<4 x float> %X)
|
|
// CHECK-NOT: alloca
|
|
// CHECK: alloca <4 x float>
|
|
// CHECK-NOT: alloca
|
|
// CHECK: store <4 x float> %X, <4 x float>*
|
|
// CHECK-NOT: store
|
|
// CHECK: ret <4 x float>
|
|
return X+X;
|
|
}
|
|
|
|
struct foo26 {
|
|
int *X;
|
|
float *Y;
|
|
};
|
|
|
|
struct foo26 f26(struct foo26 *P) {
|
|
// CHECK: define { i32*, float* } @f26(%struct.foo26* %P)
|
|
return *P;
|
|
}
|
|
|
|
|
|
struct v4f32wrapper {
|
|
v4f32 v;
|
|
};
|
|
|
|
struct v4f32wrapper f27(struct v4f32wrapper X) {
|
|
// CHECK: define <4 x float> @f27(<4 x float> %X.coerce)
|
|
return X;
|
|
}
|
|
|
|
// rdar://5711709
|
|
struct f28c {
|
|
double x;
|
|
int y;
|
|
};
|
|
void f28(struct f28c C) {
|
|
// CHECK: define void @f28(double %C.coerce0, i32 %C.coerce1)
|
|
}
|
|
|
|
struct f29a {
|
|
struct c {
|
|
double x;
|
|
int y;
|
|
} x[1];
|
|
};
|
|
|
|
void f29a(struct f29a A) {
|
|
// CHECK: define void @f29a(double %A.coerce0, i32 %A.coerce1)
|
|
}
|
|
|
|
// rdar://8249586
|
|
struct S0 { char f0[8]; char f2; char f3; char f4; };
|
|
void f30(struct S0 p_4) {
|
|
// CHECK: define void @f30(i64 %p_4.coerce0, i24 %p_4.coerce1)
|
|
}
|
|
|
|
// Pass the third element as a float when followed by tail padding.
|
|
// rdar://8251384
|
|
struct f31foo { float a, b, c; };
|
|
float f31(struct f31foo X) {
|
|
// CHECK: define float @f31(<2 x float> %X.coerce0, float %X.coerce1)
|
|
return X.c;
|
|
}
|
|
|
|
_Complex float f32(_Complex float A, _Complex float B) {
|
|
// rdar://6379669
|
|
// CHECK: define <2 x float> @f32(<2 x float> %A.coerce, <2 x float> %B.coerce)
|
|
return A+B;
|
|
}
|
|
|
|
|
|
// rdar://8357396
|
|
struct f33s { long x; float c,d; };
|
|
|
|
void f33(va_list X) {
|
|
va_arg(X, struct f33s);
|
|
}
|
|
|
|
typedef unsigned long long v1i64 __attribute__((__vector_size__(8)));
|
|
|
|
// rdar://8359248
|
|
// CHECK: define i64 @f34(i64 %arg.coerce)
|
|
v1i64 f34(v1i64 arg) { return arg; }
|
|
|
|
|
|
// rdar://8358475
|
|
// CHECK: define i64 @f35(i64 %arg.coerce)
|
|
typedef unsigned long v1i64_2 __attribute__((__vector_size__(8)));
|
|
v1i64_2 f35(v1i64_2 arg) { return arg+arg; }
|
|
|
|
// rdar://9122143
|
|
// CHECK: declare void @func(%struct._str* byval align 16)
|
|
typedef struct _str {
|
|
union {
|
|
long double a;
|
|
long c;
|
|
};
|
|
} str;
|
|
|
|
void func(str s);
|
|
str ss;
|
|
void f9122143()
|
|
{
|
|
func(ss);
|
|
}
|
|
|
|
// CHECK: define double @f36(double %arg.coerce)
|
|
typedef unsigned v2i32 __attribute((__vector_size__(8)));
|
|
v2i32 f36(v2i32 arg) { return arg; }
|
|
|
|
// CHECK: declare void @f38(<8 x float>)
|
|
// CHECK: declare void @f37(<8 x float>)
|
|
typedef float __m256 __attribute__ ((__vector_size__ (32)));
|
|
typedef struct {
|
|
__m256 m;
|
|
} s256;
|
|
|
|
s256 x38;
|
|
__m256 x37;
|
|
|
|
void f38(s256 x);
|
|
void f37(__m256 x);
|
|
void f39() { f38(x38); f37(x37); }
|
|
|
|
// The two next tests make sure that the struct below is passed
|
|
// in the same way regardless of avx being used
|
|
|
|
// CHECK: declare void @func40(%struct.t128* byval align 16)
|
|
typedef float __m128 __attribute__ ((__vector_size__ (16)));
|
|
typedef struct t128 {
|
|
__m128 m;
|
|
__m128 n;
|
|
} two128;
|
|
|
|
extern void func40(two128 s);
|
|
void func41(two128 s) {
|
|
func40(s);
|
|
}
|
|
|
|
// CHECK: declare void @func42(%struct.t128_2* byval align 16)
|
|
typedef struct xxx {
|
|
__m128 array[2];
|
|
} Atwo128;
|
|
typedef struct t128_2 {
|
|
Atwo128 x;
|
|
} SA;
|
|
|
|
extern void func42(SA s);
|
|
void func43(SA s) {
|
|
func42(s);
|
|
}
|