122fd4baf2eba2103e2b41e463f1a5f6486c398fbChris Lattner// RUN: %clang_cc1 -triple x86_64-unknown-unknown -emit-llvm -o - %s| FileCheck %s 2ee1ad99f1ced9ffee436466ef674d4541c37864eEli Friedman// RUN: %clang_cc1 -triple x86_64-unknown-unknown -emit-llvm -o - %s -target-feature +avx | FileCheck %s -check-prefix=AVX 3a8b7a7d3eaa51dd200cba1e5541f2542d24d7a6eChris Lattner#include <stdarg.h> 4644f4c3fe4130c7be75d6191340ba8d857ba0730Daniel Dunbar 50aa1cba02fb3d08500217a46fa1287e43fdae2e1Daniel Dunbar// CHECK: define signext i8 @f0() 6644f4c3fe4130c7be75d6191340ba8d857ba0730Daniel Dunbarchar f0(void) { 7c36541e7bfa69cc63e2668a986bc99117559c545Mike Stump return 0; 8644f4c3fe4130c7be75d6191340ba8d857ba0730Daniel Dunbar} 9644f4c3fe4130c7be75d6191340ba8d857ba0730Daniel Dunbar 100aa1cba02fb3d08500217a46fa1287e43fdae2e1Daniel Dunbar// CHECK: define signext i16 @f1() 11644f4c3fe4130c7be75d6191340ba8d857ba0730Daniel Dunbarshort f1(void) { 12c36541e7bfa69cc63e2668a986bc99117559c545Mike Stump return 0; 13644f4c3fe4130c7be75d6191340ba8d857ba0730Daniel Dunbar} 14644f4c3fe4130c7be75d6191340ba8d857ba0730Daniel Dunbar 150aa1cba02fb3d08500217a46fa1287e43fdae2e1Daniel Dunbar// CHECK: define i32 @f2() 16644f4c3fe4130c7be75d6191340ba8d857ba0730Daniel Dunbarint f2(void) { 17c36541e7bfa69cc63e2668a986bc99117559c545Mike Stump return 0; 18644f4c3fe4130c7be75d6191340ba8d857ba0730Daniel Dunbar} 19644f4c3fe4130c7be75d6191340ba8d857ba0730Daniel Dunbar 200aa1cba02fb3d08500217a46fa1287e43fdae2e1Daniel Dunbar// CHECK: define float @f3() 21644f4c3fe4130c7be75d6191340ba8d857ba0730Daniel Dunbarfloat f3(void) { 22c36541e7bfa69cc63e2668a986bc99117559c545Mike Stump return 0; 23644f4c3fe4130c7be75d6191340ba8d857ba0730Daniel Dunbar} 24644f4c3fe4130c7be75d6191340ba8d857ba0730Daniel Dunbar 250aa1cba02fb3d08500217a46fa1287e43fdae2e1Daniel Dunbar// CHECK: define double @f4() 26644f4c3fe4130c7be75d6191340ba8d857ba0730Daniel Dunbardouble f4(void) { 27c36541e7bfa69cc63e2668a986bc99117559c545Mike Stump return 0; 28644f4c3fe4130c7be75d6191340ba8d857ba0730Daniel Dunbar} 29644f4c3fe4130c7be75d6191340ba8d857ba0730Daniel Dunbar 300aa1cba02fb3d08500217a46fa1287e43fdae2e1Daniel Dunbar// CHECK: define x86_fp80 @f5() 31644f4c3fe4130c7be75d6191340ba8d857ba0730Daniel Dunbarlong double f5(void) { 32c36541e7bfa69cc63e2668a986bc99117559c545Mike Stump return 0; 33644f4c3fe4130c7be75d6191340ba8d857ba0730Daniel Dunbar} 34644f4c3fe4130c7be75d6191340ba8d857ba0730Daniel Dunbar 350aa1cba02fb3d08500217a46fa1287e43fdae2e1Daniel Dunbar// CHECK: define void @f6(i8 signext %a0, i16 signext %a1, i32 %a2, i64 %a3, i8* %a4) 36644f4c3fe4130c7be75d6191340ba8d857ba0730Daniel Dunbarvoid f6(char a0, short a1, int a2, long long a3, void *a4) { 37644f4c3fe4130c7be75d6191340ba8d857ba0730Daniel Dunbar} 38730f909e146b0ac5dbcf9b8be65cb8f82c68d883Anders Carlsson 390aa1cba02fb3d08500217a46fa1287e43fdae2e1Daniel Dunbar// CHECK: define void @f7(i32 %a0) 400aa1cba02fb3d08500217a46fa1287e43fdae2e1Daniel Dunbartypedef enum { A, B, C } e7; 410aa1cba02fb3d08500217a46fa1287e43fdae2e1Daniel Dunbarvoid f7(e7 a0) { 424b87142aba52c76ff9ed7c9c2fe0067bd935a2f4Mike Stump} 43100f402451da96f74ea58b1f49fc53b4fa149a57Daniel Dunbar 44100f402451da96f74ea58b1f49fc53b4fa149a57Daniel Dunbar// Test merging/passing of upper eightbyte with X87 class. 450aa1cba02fb3d08500217a46fa1287e43fdae2e1Daniel Dunbar// 465e31474b9c8348e8d0404264ae6a8775e34df6acBill Wendling// CHECK: define void @f8_1(%union.u8* noalias sret %agg.result) 47c1ea4b96adca4767991bb0a7b21052cef4db059cBill Wendling// CHECK: define void @f8_2(%union.u8* byval align 16 %a0) 48100f402451da96f74ea58b1f49fc53b4fa149a57Daniel Dunbarunion u8 { 49100f402451da96f74ea58b1f49fc53b4fa149a57Daniel Dunbar long double a; 50100f402451da96f74ea58b1f49fc53b4fa149a57Daniel Dunbar int b; 51100f402451da96f74ea58b1f49fc53b4fa149a57Daniel Dunbar}; 52c36541e7bfa69cc63e2668a986bc99117559c545Mike Stumpunion u8 f8_1() { while (1) {} } 53100f402451da96f74ea58b1f49fc53b4fa149a57Daniel Dunbarvoid f8_2(union u8 a0) {} 548236bf1800641d1c296579e25218f68f74c5caacDaniel Dunbar 550aa1cba02fb3d08500217a46fa1287e43fdae2e1Daniel Dunbar// CHECK: define i64 @f9() 56c36541e7bfa69cc63e2668a986bc99117559c545Mike Stumpstruct s9 { int a; int b; int : 0; } f9(void) { while (1) {} } 578236bf1800641d1c296579e25218f68f74c5caacDaniel Dunbar 58225e286110bcc8b7b1ff8b35f0d51a10a158b18cChris Lattner// CHECK: define void @f10(i64 %a0.coerce) 598236bf1800641d1c296579e25218f68f74c5caacDaniel Dunbarstruct s10 { int a; int b; int : 0; }; 608236bf1800641d1c296579e25218f68f74c5caacDaniel Dunbarvoid f10(struct s10 a0) {} 618236bf1800641d1c296579e25218f68f74c5caacDaniel Dunbar 625e31474b9c8348e8d0404264ae6a8775e34df6acBill Wendling// CHECK: define void @f11(%union.anon* noalias sret %agg.result) 63c36541e7bfa69cc63e2668a986bc99117559c545Mike Stumpunion { long double a; float b; } f11() { while (1) {} } 6420e95c5eb400c864bbd4421624fdf7b25ce70f56Daniel Dunbar 65e2962be11e8894329d37985eccaa4f4a12dea402Chris Lattner// CHECK: define i32 @f12_0() 66e2962be11e8894329d37985eccaa4f4a12dea402Chris Lattner// CHECK: define void @f12_1(i32 %a0.coerce) 677ef455be9beb7a755d815bfbdc38d55d1ce59b86Daniel Dunbarstruct s12 { int a __attribute__((aligned(16))); }; 68c36541e7bfa69cc63e2668a986bc99117559c545Mike Stumpstruct s12 f12_0(void) { while (1) {} } 697ef455be9beb7a755d815bfbdc38d55d1ce59b86Daniel Dunbarvoid f12_1(struct s12 a0) {} 707ef455be9beb7a755d815bfbdc38d55d1ce59b86Daniel Dunbar 713a5f5c57e0a262207f7cb721a60df3676ab5209fDaniel Dunbar// Check that sret parameter is accounted for when checking available integer 723a5f5c57e0a262207f7cb721a60df3676ab5209fDaniel Dunbar// registers. 73c1ea4b96adca4767991bb0a7b21052cef4db059cBill Wendling// 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) 743a5f5c57e0a262207f7cb721a60df3676ab5209fDaniel Dunbar 753a5f5c57e0a262207f7cb721a60df3676ab5209fDaniel Dunbarstruct s13_0 { long long f0[3]; }; 7655a759b8bb52e9d74c92e17543780751c5e5c5ecDaniel Dunbarstruct s13_1 { long long f0[2]; }; 770aa1cba02fb3d08500217a46fa1287e43fdae2e1Daniel Dunbarstruct s13_0 f13(int a, int b, int c, int d, 7855a759b8bb52e9d74c92e17543780751c5e5c5ecDaniel Dunbar struct s13_1 e, int f) { while (1) {} } 793a5f5c57e0a262207f7cb721a60df3676ab5209fDaniel Dunbar 800aa1cba02fb3d08500217a46fa1287e43fdae2e1Daniel Dunbar// CHECK: define void @f14({{.*}}, i8 signext %X) 810aa1cba02fb3d08500217a46fa1287e43fdae2e1Daniel Dunbarvoid f14(int a, int b, int c, int d, int e, int f, char X) {} 820aa1cba02fb3d08500217a46fa1287e43fdae2e1Daniel Dunbar 830aa1cba02fb3d08500217a46fa1287e43fdae2e1Daniel Dunbar// CHECK: define void @f15({{.*}}, i8* %X) 840aa1cba02fb3d08500217a46fa1287e43fdae2e1Daniel Dunbarvoid f15(int a, int b, int c, int d, int e, int f, void *X) {} 850aa1cba02fb3d08500217a46fa1287e43fdae2e1Daniel Dunbar 860aa1cba02fb3d08500217a46fa1287e43fdae2e1Daniel Dunbar// CHECK: define void @f16({{.*}}, float %X) 8786e13eeb65397f7b64173523a40c742b2702364bDaniel Dunbarvoid f16(float a, float b, float c, float d, float e, float f, float g, float h, 8886e13eeb65397f7b64173523a40c742b2702364bDaniel Dunbar float X) {} 890aa1cba02fb3d08500217a46fa1287e43fdae2e1Daniel Dunbar 900aa1cba02fb3d08500217a46fa1287e43fdae2e1Daniel Dunbar// CHECK: define void @f17({{.*}}, x86_fp80 %X) 9186e13eeb65397f7b64173523a40c742b2702364bDaniel Dunbarvoid f17(float a, float b, float c, float d, float e, float f, float g, float h, 9286e13eeb65397f7b64173523a40c742b2702364bDaniel Dunbar long double X) {} 9386e13eeb65397f7b64173523a40c742b2702364bDaniel Dunbar 94faf23b72f171ef997d48c453a5a4783c5759f8feChris Lattner// Check for valid coercion. The struct should be passed/returned as i32, not 95faf23b72f171ef997d48c453a5a4783c5759f8feChris Lattner// as i64 for better code quality. 96faf23b72f171ef997d48c453a5a4783c5759f8feChris Lattner// rdar://8135035 97225e286110bcc8b7b1ff8b35f0d51a10a158b18cChris Lattner// CHECK: define void @f18(i32 %a, i32 %f18_arg1.coerce) 9855a759b8bb52e9d74c92e17543780751c5e5c5ecDaniel Dunbarstruct f18_s0 { int f0; }; 9955a759b8bb52e9d74c92e17543780751c5e5c5ecDaniel Dunbarvoid f18(int a, struct f18_s0 f18_arg1) { while (1) {} } 100fdf4986c4c75514df428ed71d5942252f18e129bDaniel Dunbar 10146c54fb8ec45765a475b7b709b9aee7f94c490c2Daniel Dunbar// Check byval alignment. 10246c54fb8ec45765a475b7b709b9aee7f94c490c2Daniel Dunbar 103c1ea4b96adca4767991bb0a7b21052cef4db059cBill Wendling// CHECK: define void @f19(%struct.s19* byval align 16 %x) 10446c54fb8ec45765a475b7b709b9aee7f94c490c2Daniel Dunbarstruct s19 { 10546c54fb8ec45765a475b7b709b9aee7f94c490c2Daniel Dunbar long double a; 10646c54fb8ec45765a475b7b709b9aee7f94c490c2Daniel Dunbar}; 10746c54fb8ec45765a475b7b709b9aee7f94c490c2Daniel Dunbarvoid f19(struct s19 x) {} 10846c54fb8ec45765a475b7b709b9aee7f94c490c2Daniel Dunbar 109c1ea4b96adca4767991bb0a7b21052cef4db059cBill Wendling// CHECK: define void @f20(%struct.s20* byval align 32 %x) 11046c54fb8ec45765a475b7b709b9aee7f94c490c2Daniel Dunbarstruct __attribute__((aligned(32))) s20 { 11146c54fb8ec45765a475b7b709b9aee7f94c490c2Daniel Dunbar int x; 11246c54fb8ec45765a475b7b709b9aee7f94c490c2Daniel Dunbar int y; 11346c54fb8ec45765a475b7b709b9aee7f94c490c2Daniel Dunbar}; 11446c54fb8ec45765a475b7b709b9aee7f94c490c2Daniel Dunbarvoid f20(struct s20 x) {} 1159c254f0415bef9a0bafe5b5026ddb54b727597b1Chris Lattner 1169c254f0415bef9a0bafe5b5026ddb54b727597b1Chris Lattnerstruct StringRef { 1179c254f0415bef9a0bafe5b5026ddb54b727597b1Chris Lattner long x; 1189c254f0415bef9a0bafe5b5026ddb54b727597b1Chris Lattner const char *Ptr; 1199c254f0415bef9a0bafe5b5026ddb54b727597b1Chris Lattner}; 1209c254f0415bef9a0bafe5b5026ddb54b727597b1Chris Lattner 1219c254f0415bef9a0bafe5b5026ddb54b727597b1Chris Lattner// rdar://7375902 1229c254f0415bef9a0bafe5b5026ddb54b727597b1Chris Lattner// CHECK: define i8* @f21(i64 %S.coerce0, i8* %S.coerce1) 1239c254f0415bef9a0bafe5b5026ddb54b727597b1Chris Lattnerconst char *f21(struct StringRef S) { return S.x+S.Ptr; } 1249c254f0415bef9a0bafe5b5026ddb54b727597b1Chris Lattner 125121b3facb4e0585d23766f9c1e4fdf9018a4b217Chris Lattner// PR7567 126121b3facb4e0585d23766f9c1e4fdf9018a4b217Chris Lattnertypedef __attribute__ ((aligned(16))) struct f22s { unsigned long long x[2]; } L; 127121b3facb4e0585d23766f9c1e4fdf9018a4b217Chris Lattnervoid f22(L x, L y) { } 128121b3facb4e0585d23766f9c1e4fdf9018a4b217Chris Lattner// CHECK: @f22 129121b3facb4e0585d23766f9c1e4fdf9018a4b217Chris Lattner// CHECK: %x = alloca{{.*}}, align 16 130121b3facb4e0585d23766f9c1e4fdf9018a4b217Chris Lattner// CHECK: %y = alloca{{.*}}, align 16 131121b3facb4e0585d23766f9c1e4fdf9018a4b217Chris Lattner 132121b3facb4e0585d23766f9c1e4fdf9018a4b217Chris Lattner 1331daf808a48d26328dd31a3275ce599cee326c957Chris Lattner 1341daf808a48d26328dd31a3275ce599cee326c957Chris Lattner// PR7714 1351daf808a48d26328dd31a3275ce599cee326c957Chris Lattnerstruct f23S { 1361daf808a48d26328dd31a3275ce599cee326c957Chris Lattner short f0; 1371daf808a48d26328dd31a3275ce599cee326c957Chris Lattner unsigned f1; 1381daf808a48d26328dd31a3275ce599cee326c957Chris Lattner int f2; 1391daf808a48d26328dd31a3275ce599cee326c957Chris Lattner}; 1401daf808a48d26328dd31a3275ce599cee326c957Chris Lattner 141519f68cd26777c755763a644a7f7ed7ac389beb9Chris Lattner 1421daf808a48d26328dd31a3275ce599cee326c957Chris Lattnervoid f23(int A, struct f23S B) { 1431daf808a48d26328dd31a3275ce599cee326c957Chris Lattner // CHECK: define void @f23(i32 %A, i64 %B.coerce0, i32 %B.coerce1) 1441daf808a48d26328dd31a3275ce599cee326c957Chris Lattner} 1451daf808a48d26328dd31a3275ce599cee326c957Chris Lattner 146519f68cd26777c755763a644a7f7ed7ac389beb9Chris Lattnerstruct f24s { long a; int b; }; 1471daf808a48d26328dd31a3275ce599cee326c957Chris Lattner 148519f68cd26777c755763a644a7f7ed7ac389beb9Chris Lattnerstruct f23S f24(struct f23S *X, struct f24s *P2) { 149519f68cd26777c755763a644a7f7ed7ac389beb9Chris Lattner return *X; 150519f68cd26777c755763a644a7f7ed7ac389beb9Chris Lattner 1519cbe4f0ba01ec304e1e3d071c071f7bca33631c0Chris Lattner // CHECK: define { i64, i32 } @f24(%struct.f23S* %X, %struct.f24s* %P2) 152519f68cd26777c755763a644a7f7ed7ac389beb9Chris Lattner} 1531daf808a48d26328dd31a3275ce599cee326c957Chris Lattner 154800588fd230d2c37ddce8fbf4a3881352715d700Chris Lattner// rdar://8248065 155ab5722e67794b3954c874a369086fc5f41ac46a5Chris Lattnertypedef float v4f32 __attribute__((__vector_size__(16))); 156ab5722e67794b3954c874a369086fc5f41ac46a5Chris Lattnerv4f32 f25(v4f32 X) { 157800588fd230d2c37ddce8fbf4a3881352715d700Chris Lattner // CHECK: define <4 x float> @f25(<4 x float> %X) 158800588fd230d2c37ddce8fbf4a3881352715d700Chris Lattner // CHECK-NOT: alloca 159c10ab19fcbc70e3d3897f3c8dbacf6f89a3dfa8cChris Lattner // CHECK: alloca <4 x float> 160800588fd230d2c37ddce8fbf4a3881352715d700Chris Lattner // CHECK-NOT: alloca 161c10ab19fcbc70e3d3897f3c8dbacf6f89a3dfa8cChris Lattner // CHECK: store <4 x float> %X, <4 x float>* 162800588fd230d2c37ddce8fbf4a3881352715d700Chris Lattner // CHECK-NOT: store 163800588fd230d2c37ddce8fbf4a3881352715d700Chris Lattner // CHECK: ret <4 x float> 164ab5722e67794b3954c874a369086fc5f41ac46a5Chris Lattner return X+X; 165ab5722e67794b3954c874a369086fc5f41ac46a5Chris Lattner} 166ab5722e67794b3954c874a369086fc5f41ac46a5Chris Lattner 1674711cb065922d46bfe80383b2001ae681f74780aChris Lattnerstruct foo26 { 1684711cb065922d46bfe80383b2001ae681f74780aChris Lattner int *X; 1694711cb065922d46bfe80383b2001ae681f74780aChris Lattner float *Y; 1704711cb065922d46bfe80383b2001ae681f74780aChris Lattner}; 171ab5722e67794b3954c874a369086fc5f41ac46a5Chris Lattner 1724711cb065922d46bfe80383b2001ae681f74780aChris Lattnerstruct foo26 f26(struct foo26 *P) { 1739cbe4f0ba01ec304e1e3d071c071f7bca33631c0Chris Lattner // CHECK: define { i32*, float* } @f26(%struct.foo26* %P) 1744711cb065922d46bfe80383b2001ae681f74780aChris Lattner return *P; 1754711cb065922d46bfe80383b2001ae681f74780aChris Lattner} 17615842bd05bd6d3b7450385ac8f73aaee5f807e19Chris Lattner 17715842bd05bd6d3b7450385ac8f73aaee5f807e19Chris Lattner 17815842bd05bd6d3b7450385ac8f73aaee5f807e19Chris Lattnerstruct v4f32wrapper { 17915842bd05bd6d3b7450385ac8f73aaee5f807e19Chris Lattner v4f32 v; 18015842bd05bd6d3b7450385ac8f73aaee5f807e19Chris Lattner}; 18115842bd05bd6d3b7450385ac8f73aaee5f807e19Chris Lattner 18215842bd05bd6d3b7450385ac8f73aaee5f807e19Chris Lattnerstruct v4f32wrapper f27(struct v4f32wrapper X) { 18315842bd05bd6d3b7450385ac8f73aaee5f807e19Chris Lattner // CHECK: define <4 x float> @f27(<4 x float> %X.coerce) 18415842bd05bd6d3b7450385ac8f73aaee5f807e19Chris Lattner return X; 185e2962be11e8894329d37985eccaa4f4a12dea402Chris Lattner} 186e2962be11e8894329d37985eccaa4f4a12dea402Chris Lattner 187e2962be11e8894329d37985eccaa4f4a12dea402Chris Lattner// rdar://5711709 188e2962be11e8894329d37985eccaa4f4a12dea402Chris Lattnerstruct f28c { 189e2962be11e8894329d37985eccaa4f4a12dea402Chris Lattner double x; 190e2962be11e8894329d37985eccaa4f4a12dea402Chris Lattner int y; 191e2962be11e8894329d37985eccaa4f4a12dea402Chris Lattner}; 192e2962be11e8894329d37985eccaa4f4a12dea402Chris Lattnervoid f28(struct f28c C) { 193e2962be11e8894329d37985eccaa4f4a12dea402Chris Lattner // CHECK: define void @f28(double %C.coerce0, i32 %C.coerce1) 194e2962be11e8894329d37985eccaa4f4a12dea402Chris Lattner} 195e2962be11e8894329d37985eccaa4f4a12dea402Chris Lattner 196021c3a349d4f55cc2c7970268758bcf37b924493Chris Lattnerstruct f29a { 197021c3a349d4f55cc2c7970268758bcf37b924493Chris Lattner struct c { 198021c3a349d4f55cc2c7970268758bcf37b924493Chris Lattner double x; 199021c3a349d4f55cc2c7970268758bcf37b924493Chris Lattner int y; 200021c3a349d4f55cc2c7970268758bcf37b924493Chris Lattner } x[1]; 201021c3a349d4f55cc2c7970268758bcf37b924493Chris Lattner}; 202021c3a349d4f55cc2c7970268758bcf37b924493Chris Lattner 203021c3a349d4f55cc2c7970268758bcf37b924493Chris Lattnervoid f29a(struct f29a A) { 204021c3a349d4f55cc2c7970268758bcf37b924493Chris Lattner // CHECK: define void @f29a(double %A.coerce0, i32 %A.coerce1) 205021c3a349d4f55cc2c7970268758bcf37b924493Chris Lattner} 2069e45a3de3f462785a86bba77dee168ab354d9704Chris Lattner 2079e45a3de3f462785a86bba77dee168ab354d9704Chris Lattner// rdar://8249586 2089e45a3de3f462785a86bba77dee168ab354d9704Chris Lattnerstruct S0 { char f0[8]; char f2; char f3; char f4; }; 2099e45a3de3f462785a86bba77dee168ab354d9704Chris Lattnervoid f30(struct S0 p_4) { 2109e45a3de3f462785a86bba77dee168ab354d9704Chris Lattner // CHECK: define void @f30(i64 %p_4.coerce0, i24 %p_4.coerce1) 2119e45a3de3f462785a86bba77dee168ab354d9704Chris Lattner} 212f47c944b5710a545d564b4d4b641a2f8bac96af3Chris Lattner 213f47c944b5710a545d564b4d4b641a2f8bac96af3Chris Lattner// Pass the third element as a float when followed by tail padding. 214f47c944b5710a545d564b4d4b641a2f8bac96af3Chris Lattner// rdar://8251384 215f47c944b5710a545d564b4d4b641a2f8bac96af3Chris Lattnerstruct f31foo { float a, b, c; }; 216f47c944b5710a545d564b4d4b641a2f8bac96af3Chris Lattnerfloat f31(struct f31foo X) { 21722fd4baf2eba2103e2b41e463f1a5f6486c398fbChris Lattner // CHECK: define float @f31(<2 x float> %X.coerce0, float %X.coerce1) 218f47c944b5710a545d564b4d4b641a2f8bac96af3Chris Lattner return X.c; 219f47c944b5710a545d564b4d4b641a2f8bac96af3Chris Lattner} 220f47c944b5710a545d564b4d4b641a2f8bac96af3Chris Lattner 22122fd4baf2eba2103e2b41e463f1a5f6486c398fbChris Lattner_Complex float f32(_Complex float A, _Complex float B) { 22222fd4baf2eba2103e2b41e463f1a5f6486c398fbChris Lattner // rdar://6379669 22322fd4baf2eba2103e2b41e463f1a5f6486c398fbChris Lattner // CHECK: define <2 x float> @f32(<2 x float> %A.coerce, <2 x float> %B.coerce) 22422fd4baf2eba2103e2b41e463f1a5f6486c398fbChris Lattner return A+B; 22522fd4baf2eba2103e2b41e463f1a5f6486c398fbChris Lattner} 22622fd4baf2eba2103e2b41e463f1a5f6486c398fbChris Lattner 227f47c944b5710a545d564b4d4b641a2f8bac96af3Chris Lattner 228a8b7a7d3eaa51dd200cba1e5541f2542d24d7a6eChris Lattner// rdar://8357396 229a8b7a7d3eaa51dd200cba1e5541f2542d24d7a6eChris Lattnerstruct f33s { long x; float c,d; }; 230a8b7a7d3eaa51dd200cba1e5541f2542d24d7a6eChris Lattner 231a8b7a7d3eaa51dd200cba1e5541f2542d24d7a6eChris Lattnervoid f33(va_list X) { 232a8b7a7d3eaa51dd200cba1e5541f2542d24d7a6eChris Lattner va_arg(X, struct f33s); 233a8b7a7d3eaa51dd200cba1e5541f2542d24d7a6eChris Lattner} 234a8b7a7d3eaa51dd200cba1e5541f2542d24d7a6eChris Lattner 235473f8e723be93d84bd5fd15b094f4184802d4676Chris Lattnertypedef unsigned long long v1i64 __attribute__((__vector_size__(8))); 236473f8e723be93d84bd5fd15b094f4184802d4676Chris Lattner 237473f8e723be93d84bd5fd15b094f4184802d4676Chris Lattner// rdar://8359248 238473f8e723be93d84bd5fd15b094f4184802d4676Chris Lattner// CHECK: define i64 @f34(i64 %arg.coerce) 239473f8e723be93d84bd5fd15b094f4184802d4676Chris Lattnerv1i64 f34(v1i64 arg) { return arg; } 240a8b7a7d3eaa51dd200cba1e5541f2542d24d7a6eChris Lattner 2410fefa4175b0c9101564946f6a975ee9946c16d4bChris Lattner 2420fefa4175b0c9101564946f6a975ee9946c16d4bChris Lattner// rdar://8358475 2430fefa4175b0c9101564946f6a975ee9946c16d4bChris Lattner// CHECK: define i64 @f35(i64 %arg.coerce) 2440fefa4175b0c9101564946f6a975ee9946c16d4bChris Lattnertypedef unsigned long v1i64_2 __attribute__((__vector_size__(8))); 2450fefa4175b0c9101564946f6a975ee9946c16d4bChris Lattnerv1i64_2 f35(v1i64_2 arg) { return arg+arg; } 2460fefa4175b0c9101564946f6a975ee9946c16d4bChris Lattner 24767a5773ba529aebcad03fa5e7cc95555d133e93dJohn McCall// rdar://9122143 248c1ea4b96adca4767991bb0a7b21052cef4db059cBill Wendling// CHECK: declare void @func(%struct._str* byval align 16) 24967a5773ba529aebcad03fa5e7cc95555d133e93dJohn McCalltypedef struct _str { 25067a5773ba529aebcad03fa5e7cc95555d133e93dJohn McCall union { 25167a5773ba529aebcad03fa5e7cc95555d133e93dJohn McCall long double a; 25267a5773ba529aebcad03fa5e7cc95555d133e93dJohn McCall long c; 25367a5773ba529aebcad03fa5e7cc95555d133e93dJohn McCall }; 25467a5773ba529aebcad03fa5e7cc95555d133e93dJohn McCall} str; 25567a5773ba529aebcad03fa5e7cc95555d133e93dJohn McCall 25667a5773ba529aebcad03fa5e7cc95555d133e93dJohn McCallvoid func(str s); 25767a5773ba529aebcad03fa5e7cc95555d133e93dJohn McCallstr ss; 25867a5773ba529aebcad03fa5e7cc95555d133e93dJohn McCallvoid f9122143() 25967a5773ba529aebcad03fa5e7cc95555d133e93dJohn McCall{ 26067a5773ba529aebcad03fa5e7cc95555d133e93dJohn McCall func(ss); 26167a5773ba529aebcad03fa5e7cc95555d133e93dJohn McCall} 26267a5773ba529aebcad03fa5e7cc95555d133e93dJohn McCall 26314508ff0bffee0fdfe5d336946c6db0e709099c8Eli Friedman// CHECK: define double @f36(double %arg.coerce) 26414508ff0bffee0fdfe5d336946c6db0e709099c8Eli Friedmantypedef unsigned v2i32 __attribute((__vector_size__(8))); 26514508ff0bffee0fdfe5d336946c6db0e709099c8Eli Friedmanv2i32 f36(v2i32 arg) { return arg; } 2664943c15df59fdec444656a48c16e72a2077ab61fBruno Cardoso Lopes 267ee1ad99f1ced9ffee436466ef674d4541c37864eEli Friedman// AVX: declare void @f38(<8 x float>) 268ee1ad99f1ced9ffee436466ef674d4541c37864eEli Friedman// AVX: declare void @f37(<8 x float>) 269c1ea4b96adca4767991bb0a7b21052cef4db059cBill Wendling// CHECK: declare void @f38(%struct.s256* byval align 32) 270c1ea4b96adca4767991bb0a7b21052cef4db059cBill Wendling// CHECK: declare void @f37(<8 x float>* byval align 32) 2714943c15df59fdec444656a48c16e72a2077ab61fBruno Cardoso Lopestypedef float __m256 __attribute__ ((__vector_size__ (32))); 2724943c15df59fdec444656a48c16e72a2077ab61fBruno Cardoso Lopestypedef struct { 2734943c15df59fdec444656a48c16e72a2077ab61fBruno Cardoso Lopes __m256 m; 2744943c15df59fdec444656a48c16e72a2077ab61fBruno Cardoso Lopes} s256; 2754943c15df59fdec444656a48c16e72a2077ab61fBruno Cardoso Lopes 2764943c15df59fdec444656a48c16e72a2077ab61fBruno Cardoso Lopess256 x38; 2774943c15df59fdec444656a48c16e72a2077ab61fBruno Cardoso Lopes__m256 x37; 2784943c15df59fdec444656a48c16e72a2077ab61fBruno Cardoso Lopes 2794943c15df59fdec444656a48c16e72a2077ab61fBruno Cardoso Lopesvoid f38(s256 x); 2804943c15df59fdec444656a48c16e72a2077ab61fBruno Cardoso Lopesvoid f37(__m256 x); 2814943c15df59fdec444656a48c16e72a2077ab61fBruno Cardoso Lopesvoid f39() { f38(x38); f37(x37); } 2824943c15df59fdec444656a48c16e72a2077ab61fBruno Cardoso Lopes 283089d8927abe73fe6a806987937d9b54b1a7a8659Bruno Cardoso Lopes// The two next tests make sure that the struct below is passed 284089d8927abe73fe6a806987937d9b54b1a7a8659Bruno Cardoso Lopes// in the same way regardless of avx being used 285089d8927abe73fe6a806987937d9b54b1a7a8659Bruno Cardoso Lopes 286c1ea4b96adca4767991bb0a7b21052cef4db059cBill Wendling// CHECK: declare void @func40(%struct.t128* byval align 16) 2874943c15df59fdec444656a48c16e72a2077ab61fBruno Cardoso Lopestypedef float __m128 __attribute__ ((__vector_size__ (16))); 288ccafadb68f5a8132a4ee23f441cf5d6976a4133bBruno Cardoso Lopestypedef struct t128 { 2894943c15df59fdec444656a48c16e72a2077ab61fBruno Cardoso Lopes __m128 m; 2904943c15df59fdec444656a48c16e72a2077ab61fBruno Cardoso Lopes __m128 n; 2914943c15df59fdec444656a48c16e72a2077ab61fBruno Cardoso Lopes} two128; 2924943c15df59fdec444656a48c16e72a2077ab61fBruno Cardoso Lopes 2934943c15df59fdec444656a48c16e72a2077ab61fBruno Cardoso Lopesextern void func40(two128 s); 2944943c15df59fdec444656a48c16e72a2077ab61fBruno Cardoso Lopesvoid func41(two128 s) { 2954943c15df59fdec444656a48c16e72a2077ab61fBruno Cardoso Lopes func40(s); 2964943c15df59fdec444656a48c16e72a2077ab61fBruno Cardoso Lopes} 2974943c15df59fdec444656a48c16e72a2077ab61fBruno Cardoso Lopes 298c1ea4b96adca4767991bb0a7b21052cef4db059cBill Wendling// CHECK: declare void @func42(%struct.t128_2* byval align 16) 299089d8927abe73fe6a806987937d9b54b1a7a8659Bruno Cardoso Lopestypedef struct xxx { 300089d8927abe73fe6a806987937d9b54b1a7a8659Bruno Cardoso Lopes __m128 array[2]; 301089d8927abe73fe6a806987937d9b54b1a7a8659Bruno Cardoso Lopes} Atwo128; 302089d8927abe73fe6a806987937d9b54b1a7a8659Bruno Cardoso Lopestypedef struct t128_2 { 303089d8927abe73fe6a806987937d9b54b1a7a8659Bruno Cardoso Lopes Atwo128 x; 304089d8927abe73fe6a806987937d9b54b1a7a8659Bruno Cardoso Lopes} SA; 305089d8927abe73fe6a806987937d9b54b1a7a8659Bruno Cardoso Lopes 306089d8927abe73fe6a806987937d9b54b1a7a8659Bruno Cardoso Lopesextern void func42(SA s); 307089d8927abe73fe6a806987937d9b54b1a7a8659Bruno Cardoso Lopesvoid func43(SA s) { 308089d8927abe73fe6a806987937d9b54b1a7a8659Bruno Cardoso Lopes func42(s); 309089d8927abe73fe6a806987937d9b54b1a7a8659Bruno Cardoso Lopes} 3108d2fe42417fcc861b3324d585dc29ac4da59bee0Eli Friedman 3118d2fe42417fcc861b3324d585dc29ac4da59bee0Eli Friedman// CHECK: define i32 @f44 3128d2fe42417fcc861b3324d585dc29ac4da59bee0Eli Friedman// CHECK: ptrtoint 3138d2fe42417fcc861b3324d585dc29ac4da59bee0Eli Friedman// CHECK-NEXT: and {{.*}}, -32 3148d2fe42417fcc861b3324d585dc29ac4da59bee0Eli Friedman// CHECK-NEXT: inttoptr 3158d2fe42417fcc861b3324d585dc29ac4da59bee0Eli Friedmantypedef int T44 __attribute((vector_size(32))); 3168d2fe42417fcc861b3324d585dc29ac4da59bee0Eli Friedmanstruct s44 { T44 x; int y; }; 3178d2fe42417fcc861b3324d585dc29ac4da59bee0Eli Friedmanint f44(int i, ...) { 3188d2fe42417fcc861b3324d585dc29ac4da59bee0Eli Friedman __builtin_va_list ap; 3198d2fe42417fcc861b3324d585dc29ac4da59bee0Eli Friedman __builtin_va_start(ap, i); 3208d2fe42417fcc861b3324d585dc29ac4da59bee0Eli Friedman struct s44 s = __builtin_va_arg(ap, struct s44); 3218d2fe42417fcc861b3324d585dc29ac4da59bee0Eli Friedman __builtin_va_end(ap); 3228d2fe42417fcc861b3324d585dc29ac4da59bee0Eli Friedman return s.y; 3238d2fe42417fcc861b3324d585dc29ac4da59bee0Eli Friedman} 324ce275675d33142c235d7027db16abe43da616ee4Tanya Lattner 325ce275675d33142c235d7027db16abe43da616ee4Tanya Lattner// Text that vec3 returns the correct LLVM IR type. 326ee1ad99f1ced9ffee436466ef674d4541c37864eEli Friedman// AVX: define i32 @foo(<3 x i64> %X) 327ce275675d33142c235d7027db16abe43da616ee4Tanya Lattnertypedef long long3 __attribute((ext_vector_type(3))); 328ce275675d33142c235d7027db16abe43da616ee4Tanya Lattnerint foo(long3 X) 329ce275675d33142c235d7027db16abe43da616ee4Tanya Lattner{ 330ce275675d33142c235d7027db16abe43da616ee4Tanya Lattner return 0; 331ce275675d33142c235d7027db16abe43da616ee4Tanya Lattner} 3323ed7903d27f0e7e0cd3a61c165d39eca70f3cff5Eli Friedman 3333ed7903d27f0e7e0cd3a61c165d39eca70f3cff5Eli Friedman// Make sure we don't use a varargs convention for a function without a 3343ed7903d27f0e7e0cd3a61c165d39eca70f3cff5Eli Friedman// prototype where AVX types are involved. 335ee1ad99f1ced9ffee436466ef674d4541c37864eEli Friedman// AVX: @test45 336ee1ad99f1ced9ffee436466ef674d4541c37864eEli Friedman// AVX: call i32 bitcast (i32 (...)* @f45 to i32 (<8 x float>)*) 3373ed7903d27f0e7e0cd3a61c165d39eca70f3cff5Eli Friedmanint f45(); 3383ed7903d27f0e7e0cd3a61c165d39eca70f3cff5Eli Friedman__m256 x45; 3393ed7903d27f0e7e0cd3a61c165d39eca70f3cff5Eli Friedmanvoid test45() { f45(x45); } 340ee1ad99f1ced9ffee436466ef674d4541c37864eEli Friedman 341ee1ad99f1ced9ffee436466ef674d4541c37864eEli Friedman// Make sure we use byval to pass 64-bit vectors in memory; the LLVM call 342ee1ad99f1ced9ffee436466ef674d4541c37864eEli Friedman// lowering can't handle this case correctly because it runs after legalization. 343ee1ad99f1ced9ffee436466ef674d4541c37864eEli Friedman// CHECK: @test46 344c1ea4b96adca4767991bb0a7b21052cef4db059cBill Wendling// CHECK: call void @f46({{.*}}<2 x float>* byval align 8 {{.*}}, <2 x float>* byval align 8 {{.*}}) 345ee1ad99f1ced9ffee436466ef674d4541c37864eEli Friedmantypedef float v46 __attribute((vector_size(8))); 346ee1ad99f1ced9ffee436466ef674d4541c37864eEli Friedmanvoid f46(v46,v46,v46,v46,v46,v46,v46,v46,v46,v46); 347ee1ad99f1ced9ffee436466ef674d4541c37864eEli Friedmanvoid test46() { v46 x = {1,2}; f46(x,x,x,x,x,x,x,x,x,x); } 348edfac0302490d84419eb958c812c533b8df29785Daniel Dunbar 349edfac0302490d84419eb958c812c533b8df29785Daniel Dunbar// Check that we pass the struct below without using byval, which helps out 350edfac0302490d84419eb958c812c533b8df29785Daniel Dunbar// codegen. 351edfac0302490d84419eb958c812c533b8df29785Daniel Dunbar// 352edfac0302490d84419eb958c812c533b8df29785Daniel Dunbar// CHECK: @test47 353edfac0302490d84419eb958c812c533b8df29785Daniel Dunbar// CHECK: call void @f47(i32 {{.*}}, i32 {{.*}}, i32 {{.*}}, i32 {{.*}}, i32 {{.*}}, i32 {{.*}}, i32 {{.*}}) 354edfac0302490d84419eb958c812c533b8df29785Daniel Dunbarstruct s47 { unsigned a; }; 355edfac0302490d84419eb958c812c533b8df29785Daniel Dunbarvoid f47(int,int,int,int,int,int,struct s47); 356edfac0302490d84419eb958c812c533b8df29785Daniel Dunbarvoid test47(int a, struct s47 b) { f47(a, a, a, a, a, a, b); } 357f51c61c78e8487061b6a434286488fa3e5b919e5Manman Ren 358f51c61c78e8487061b6a434286488fa3e5b919e5Manman Ren// rdar://12723368 359f51c61c78e8487061b6a434286488fa3e5b919e5Manman Ren// In the following example, there are holes in T4 at the 3rd byte and the 4th 360f51c61c78e8487061b6a434286488fa3e5b919e5Manman Ren// byte, however, T2 does not have those holes. T4 is chosen to be the 361f51c61c78e8487061b6a434286488fa3e5b919e5Manman Ren// representing type for union T1, but we can't use load or store of T4 since 362f51c61c78e8487061b6a434286488fa3e5b919e5Manman Ren// it will skip the 3rd byte and the 4th byte. 363f51c61c78e8487061b6a434286488fa3e5b919e5Manman Ren// In general, Since we don't accurately represent the data fields of a union, 364f51c61c78e8487061b6a434286488fa3e5b919e5Manman Ren// do not use load or store of the representing llvm type for the union. 365f51c61c78e8487061b6a434286488fa3e5b919e5Manman Rentypedef _Complex int T2; 366f51c61c78e8487061b6a434286488fa3e5b919e5Manman Rentypedef _Complex char T5; 367f51c61c78e8487061b6a434286488fa3e5b919e5Manman Rentypedef _Complex int T7; 368f51c61c78e8487061b6a434286488fa3e5b919e5Manman Rentypedef struct T4 { T5 field0; T7 field1; } T4; 369f51c61c78e8487061b6a434286488fa3e5b919e5Manman Rentypedef union T1 { T2 field0; T4 field1; } T1; 370f51c61c78e8487061b6a434286488fa3e5b919e5Manman Renextern T1 T1_retval; 371f51c61c78e8487061b6a434286488fa3e5b919e5Manman RenT1 test48(void) { 372f51c61c78e8487061b6a434286488fa3e5b919e5Manman Ren// CHECK: @test48 373060f34d6d12a851faa9463da522f7dff1104d0e1Manman Ren// CHECK: memcpy 374060f34d6d12a851faa9463da522f7dff1104d0e1Manman Ren// CHECK: memcpy 375f51c61c78e8487061b6a434286488fa3e5b919e5Manman Ren return T1_retval; 376f51c61c78e8487061b6a434286488fa3e5b919e5Manman Ren} 377e56bb36e8eea89bae7dfe6eb6ea0455af126bf4aJohn McCall 378e56bb36e8eea89bae7dfe6eb6ea0455af126bf4aJohn McCallvoid test49_helper(double, ...); 379e56bb36e8eea89bae7dfe6eb6ea0455af126bf4aJohn McCallvoid test49(double d, double e) { 380e56bb36e8eea89bae7dfe6eb6ea0455af126bf4aJohn McCall test49_helper(d, e); 381e56bb36e8eea89bae7dfe6eb6ea0455af126bf4aJohn McCall} 382e56bb36e8eea89bae7dfe6eb6ea0455af126bf4aJohn McCall// CHECK: define void @test49( 383e56bb36e8eea89bae7dfe6eb6ea0455af126bf4aJohn McCall// CHECK: [[T0:%.*]] = load double* 384e56bb36e8eea89bae7dfe6eb6ea0455af126bf4aJohn McCall// CHECK-NEXT: [[T1:%.*]] = load double* 385e56bb36e8eea89bae7dfe6eb6ea0455af126bf4aJohn McCall// CHECK-NEXT: call void (double, ...)* @test49_helper(double [[T0]], double [[T1]]) 386e56bb36e8eea89bae7dfe6eb6ea0455af126bf4aJohn McCall 387e56bb36e8eea89bae7dfe6eb6ea0455af126bf4aJohn McCallvoid test50_helper(); 388e56bb36e8eea89bae7dfe6eb6ea0455af126bf4aJohn McCallvoid test50(double d, double e) { 389e56bb36e8eea89bae7dfe6eb6ea0455af126bf4aJohn McCall test50_helper(d, e); 390e56bb36e8eea89bae7dfe6eb6ea0455af126bf4aJohn McCall} 391e56bb36e8eea89bae7dfe6eb6ea0455af126bf4aJohn McCall// CHECK: define void @test50( 392e56bb36e8eea89bae7dfe6eb6ea0455af126bf4aJohn McCall// CHECK: [[T0:%.*]] = load double* 393e56bb36e8eea89bae7dfe6eb6ea0455af126bf4aJohn McCall// CHECK-NEXT: [[T1:%.*]] = load double* 394e56bb36e8eea89bae7dfe6eb6ea0455af126bf4aJohn McCall// CHECK-NEXT: call void (double, double, ...)* bitcast (void (...)* @test50_helper to void (double, double, ...)*)(double [[T0]], double [[T1]]) 395eeb00624413d4a4856e66809b84c558d2cdce17fEli Friedman 396eeb00624413d4a4856e66809b84c558d2cdce17fEli Friedmanstruct test51_s { __uint128_t intval; }; 397eeb00624413d4a4856e66809b84c558d2cdce17fEli Friedmanvoid test51(struct test51_s *s, __builtin_va_list argList) { 398eeb00624413d4a4856e66809b84c558d2cdce17fEli Friedman *s = __builtin_va_arg(argList, struct test51_s); 399eeb00624413d4a4856e66809b84c558d2cdce17fEli Friedman} 400eeb00624413d4a4856e66809b84c558d2cdce17fEli Friedman 401eeb00624413d4a4856e66809b84c558d2cdce17fEli Friedman// CHECK: define void @test51 402939d83efba53994af07c7dc82b88873132a18c0dEli Friedman// CHECK: [[TMP_ADDR:%.*]] = alloca [[STRUCT_TEST51:%.*]], align 16 403939d83efba53994af07c7dc82b88873132a18c0dEli Friedman// CHECK: br i1 404939d83efba53994af07c7dc82b88873132a18c0dEli Friedman// CHECK: [[REG_SAVE_AREA_PTR:%.*]] = getelementptr inbounds {{.*}}, i32 0, i32 3 405939d83efba53994af07c7dc82b88873132a18c0dEli Friedman// CHECK-NEXT: [[REG_SAVE_AREA:%.*]] = load i8** [[REG_SAVE_AREA_PTR]] 406939d83efba53994af07c7dc82b88873132a18c0dEli Friedman// CHECK-NEXT: [[VALUE_ADDR:%.*]] = getelementptr i8* [[REG_SAVE_AREA]], i32 {{.*}} 407939d83efba53994af07c7dc82b88873132a18c0dEli Friedman// CHECK-NEXT: [[CASTED_VALUE_ADDR:%.*]] = bitcast i8* [[VALUE_ADDR]] to [[STRUCT_TEST51]] 408939d83efba53994af07c7dc82b88873132a18c0dEli Friedman// CHECK-NEXT: [[CASTED_TMP_ADDR:%.*]] = bitcast [[STRUCT_TEST51]]* [[TMP_ADDR]] to i8* 409939d83efba53994af07c7dc82b88873132a18c0dEli Friedman// CHECK-NEXT: [[RECASTED_VALUE_ADDR:%.*]] = bitcast [[STRUCT_TEST51]]* [[CASTED_VALUE_ADDR]] to i8* 410939d83efba53994af07c7dc82b88873132a18c0dEli Friedman// CHECK-NEXT: call void @llvm.memcpy.p0i8.p0i8.i64(i8* [[CASTED_TMP_ADDR]], i8* [[RECASTED_VALUE_ADDR]], i64 16, i32 8, i1 false) 411939d83efba53994af07c7dc82b88873132a18c0dEli Friedman// CHECK-NEXT: add i32 {{.*}}, 16 412939d83efba53994af07c7dc82b88873132a18c0dEli Friedman// CHECK-NEXT: store i32 {{.*}}, i32* {{.*}} 413939d83efba53994af07c7dc82b88873132a18c0dEli Friedman// CHECK-NEXT: br label 4147a1b586a383622e3287a5f3d82736ec513032744Eli Friedman 4157a1b586a383622e3287a5f3d82736ec513032744Eli Friedmanvoid test52_helper(int, ...); 4167a1b586a383622e3287a5f3d82736ec513032744Eli Friedman__m256 x52; 4177a1b586a383622e3287a5f3d82736ec513032744Eli Friedmanvoid test52() { 4187a1b586a383622e3287a5f3d82736ec513032744Eli Friedman test52_helper(0, x52, 1.0, 1.0, 1.0, 1.0, 1.0, 1.0, 1.0i); 4197a1b586a383622e3287a5f3d82736ec513032744Eli Friedman} 4207a1b586a383622e3287a5f3d82736ec513032744Eli Friedman// AVX: @test52_helper(i32 0, <8 x float> {{%[a-zA-Z0-9]+}}, double 1.000000e+00, double 1.000000e+00, double 1.000000e+00, double 1.000000e+00, double 1.000000e+00, double 1.000000e+00, double {{%[a-zA-Z0-9]+}}, double {{%[a-zA-Z0-9]+}}) 4217a1b586a383622e3287a5f3d82736ec513032744Eli Friedman 4227a1b586a383622e3287a5f3d82736ec513032744Eli Friedmanvoid test53(__m256 *m, __builtin_va_list argList) { 4237a1b586a383622e3287a5f3d82736ec513032744Eli Friedman *m = __builtin_va_arg(argList, __m256); 4247a1b586a383622e3287a5f3d82736ec513032744Eli Friedman} 4257a1b586a383622e3287a5f3d82736ec513032744Eli Friedman// AVX: define void @test53 4267a1b586a383622e3287a5f3d82736ec513032744Eli Friedman// AVX-NOT: br i1 4277a1b586a383622e3287a5f3d82736ec513032744Eli Friedman// AVX: ret void 4287a1b586a383622e3287a5f3d82736ec513032744Eli Friedman 4297a1b586a383622e3287a5f3d82736ec513032744Eli Friedmanvoid test54_helper(__m256, ...); 4307a1b586a383622e3287a5f3d82736ec513032744Eli Friedman__m256 x54; 4317a1b586a383622e3287a5f3d82736ec513032744Eli Friedmanvoid test54() { 4327a1b586a383622e3287a5f3d82736ec513032744Eli Friedman test54_helper(x54, x54, 1.0, 1.0, 1.0, 1.0, 1.0, 1.0i); 4337a1b586a383622e3287a5f3d82736ec513032744Eli Friedman test54_helper(x54, x54, 1.0, 1.0, 1.0, 1.0, 1.0, 1.0, 1.0i); 4347a1b586a383622e3287a5f3d82736ec513032744Eli Friedman} 4357a1b586a383622e3287a5f3d82736ec513032744Eli Friedman// AVX: @test54_helper(<8 x float> {{%[a-zA-Z0-9]+}}, <8 x float> {{%[a-zA-Z0-9]+}}, double 1.000000e+00, double 1.000000e+00, double 1.000000e+00, double 1.000000e+00, double 1.000000e+00, double {{%[a-zA-Z0-9]+}}, double {{%[a-zA-Z0-9]+}}) 4367a1b586a383622e3287a5f3d82736ec513032744Eli Friedman// AVX: @test54_helper(<8 x float> {{%[a-zA-Z0-9]+}}, <8 x float> {{%[a-zA-Z0-9]+}}, double 1.000000e+00, double 1.000000e+00, double 1.000000e+00, double 1.000000e+00, double 1.000000e+00, double 1.000000e+00, { double, double }* byval align 8 {{%[a-zA-Z0-9]+}}) 437