xref: /aosp_15_r20/external/clang/test/CodeGen/asm.c (revision 67e74705e28f6214e480b399dd47ea732279e315)
1*67e74705SXin Li // RUN: %clang_cc1 -triple i386-unknown-unknown -emit-llvm %s -o - | FileCheck %s
2*67e74705SXin Li 
3*67e74705SXin Li // PR10415
4*67e74705SXin Li __asm__ ("foo1");
5*67e74705SXin Li __asm__ ("foo2");
6*67e74705SXin Li __asm__ ("foo3");
7*67e74705SXin Li // CHECK: module asm "foo1"
8*67e74705SXin Li // CHECK-NEXT: module asm "foo2"
9*67e74705SXin Li // CHECK-NEXT: module asm "foo3"
10*67e74705SXin Li 
t1(int len)11*67e74705SXin Li void t1(int len) {
12*67e74705SXin Li   __asm__ volatile("" : "=&r"(len), "+&r"(len));
13*67e74705SXin Li }
14*67e74705SXin Li 
t2(unsigned long long t)15*67e74705SXin Li void t2(unsigned long long t)  {
16*67e74705SXin Li   __asm__ volatile("" : "+m"(t));
17*67e74705SXin Li }
18*67e74705SXin Li 
t3(unsigned char * src,unsigned long long temp)19*67e74705SXin Li void t3(unsigned char *src, unsigned long long temp) {
20*67e74705SXin Li   __asm__ volatile("" : "+m"(temp), "+r"(src));
21*67e74705SXin Li }
22*67e74705SXin Li 
t4()23*67e74705SXin Li void t4() {
24*67e74705SXin Li   unsigned long long a;
25*67e74705SXin Li   struct reg { unsigned long long a, b; } b;
26*67e74705SXin Li 
27*67e74705SXin Li   __asm__ volatile ("":: "m"(a), "m"(b));
28*67e74705SXin Li }
29*67e74705SXin Li 
30*67e74705SXin Li // PR3417
t5(int i)31*67e74705SXin Li void t5(int i) {
32*67e74705SXin Li   asm("nop" : "=r"(i) : "0"(t5));
33*67e74705SXin Li }
34*67e74705SXin Li 
35*67e74705SXin Li // PR3641
t6(void)36*67e74705SXin Li void t6(void) {
37*67e74705SXin Li   __asm__ volatile("" : : "i" (t6));
38*67e74705SXin Li }
39*67e74705SXin Li 
t7(int a)40*67e74705SXin Li void t7(int a) {
41*67e74705SXin Li   __asm__ volatile("T7 NAMED: %[input]" : "+r"(a): [input] "i" (4));
42*67e74705SXin Li   // CHECK: @t7(i32
43*67e74705SXin Li   // CHECK: T7 NAMED: $1
44*67e74705SXin Li }
45*67e74705SXin Li 
t8()46*67e74705SXin Li void t8() {
47*67e74705SXin Li   __asm__ volatile("T8 NAMED MODIFIER: %c[input]" :: [input] "i" (4));
48*67e74705SXin Li   // CHECK: @t8()
49*67e74705SXin Li   // CHECK: T8 NAMED MODIFIER: ${0:c}
50*67e74705SXin Li }
51*67e74705SXin Li 
52*67e74705SXin Li // PR3682
t9(unsigned int a)53*67e74705SXin Li unsigned t9(unsigned int a) {
54*67e74705SXin Li   asm("bswap %0 %1" : "+r" (a));
55*67e74705SXin Li   return a;
56*67e74705SXin Li }
57*67e74705SXin Li 
58*67e74705SXin Li // PR3908
t10(int r)59*67e74705SXin Li void t10(int r) {
60*67e74705SXin Li   __asm__("PR3908 %[lf] %[xx] %[li] %[r]" : [r] "+r" (r) : [lf] "mx" (0), [li] "mr" (0), [xx] "x" ((double)(0)));
61*67e74705SXin Li 
62*67e74705SXin Li // CHECK: @t10(
63*67e74705SXin Li // CHECK:PR3908 $1 $3 $2 $0
64*67e74705SXin Li }
65*67e74705SXin Li 
66*67e74705SXin Li // PR3373
t11(signed char input)67*67e74705SXin Li unsigned t11(signed char input) {
68*67e74705SXin Li   unsigned  output;
69*67e74705SXin Li   __asm__("xyz"
70*67e74705SXin Li           : "=a" (output)
71*67e74705SXin Li           : "0" (input));
72*67e74705SXin Li   return output;
73*67e74705SXin Li }
74*67e74705SXin Li 
75*67e74705SXin Li // PR3373
t12(unsigned input)76*67e74705SXin Li unsigned char t12(unsigned input) {
77*67e74705SXin Li   unsigned char output;
78*67e74705SXin Li   __asm__("xyz"
79*67e74705SXin Li           : "=a" (output)
80*67e74705SXin Li           : "0" (input));
81*67e74705SXin Li   return output;
82*67e74705SXin Li }
83*67e74705SXin Li 
t13(unsigned input)84*67e74705SXin Li unsigned char t13(unsigned input) {
85*67e74705SXin Li   unsigned char output;
86*67e74705SXin Li   __asm__("xyz %1"
87*67e74705SXin Li           : "=a" (output)
88*67e74705SXin Li           : "0" (input));
89*67e74705SXin Li   return output;
90*67e74705SXin Li }
91*67e74705SXin Li 
92*67e74705SXin Li struct large {
93*67e74705SXin Li   int x[1000];
94*67e74705SXin Li };
95*67e74705SXin Li 
t15(int x,struct large * P)96*67e74705SXin Li unsigned long t15(int x, struct large *P) {
97*67e74705SXin Li   __asm__("xyz "
98*67e74705SXin Li           : "=r" (x)
99*67e74705SXin Li           : "m" (*P), "0" (x));
100*67e74705SXin Li   return x;
101*67e74705SXin Li }
102*67e74705SXin Li 
103*67e74705SXin Li // bitfield destination of an asm.
104*67e74705SXin Li struct S {
105*67e74705SXin Li   int a : 4;
106*67e74705SXin Li };
107*67e74705SXin Li 
t14(struct S * P)108*67e74705SXin Li void t14(struct S *P) {
109*67e74705SXin Li   __asm__("abc %0" : "=r"(P->a) );
110*67e74705SXin Li }
111*67e74705SXin Li 
112*67e74705SXin Li // PR4938
t16()113*67e74705SXin Li int t16() {
114*67e74705SXin Li   int a,b;
115*67e74705SXin Li   asm ( "nop;"
116*67e74705SXin Li        :"=%c" (a)
117*67e74705SXin Li        : "r" (b)
118*67e74705SXin Li        );
119*67e74705SXin Li   return 0;
120*67e74705SXin Li }
121*67e74705SXin Li 
122*67e74705SXin Li // PR6475
t17()123*67e74705SXin Li void t17() {
124*67e74705SXin Li   int i;
125*67e74705SXin Li   __asm__ ( "nop": "=m"(i));
126*67e74705SXin Li 
127*67e74705SXin Li // CHECK: @t17()
128*67e74705SXin Li // CHECK: call void asm "nop", "=*m,
129*67e74705SXin Li }
130*67e74705SXin Li 
131*67e74705SXin Li // <rdar://problem/6841383>
t18(unsigned data)132*67e74705SXin Li int t18(unsigned data) {
133*67e74705SXin Li   int a, b;
134*67e74705SXin Li 
135*67e74705SXin Li   asm("xyz" :"=a"(a), "=d"(b) : "a"(data));
136*67e74705SXin Li   return a + b;
137*67e74705SXin Li // CHECK: t18(i32
138*67e74705SXin Li // CHECK: = call {{.*}}asm "xyz"
139*67e74705SXin Li // CHECK-NEXT: extractvalue
140*67e74705SXin Li // CHECK-NEXT: extractvalue
141*67e74705SXin Li }
142*67e74705SXin Li 
143*67e74705SXin Li // PR6780
t19(unsigned data)144*67e74705SXin Li int t19(unsigned data) {
145*67e74705SXin Li   int a, b;
146*67e74705SXin Li 
147*67e74705SXin Li   asm("x{abc|def|ghi}z" :"=r"(a): "r"(data));
148*67e74705SXin Li   return a + b;
149*67e74705SXin Li   // CHECK: t19(i32
150*67e74705SXin Li   // CHECK: = call {{.*}}asm "x$(abc$|def$|ghi$)z"
151*67e74705SXin Li }
152*67e74705SXin Li 
153*67e74705SXin Li // PR6845 - Mismatching source/dest fp types.
t20(double x)154*67e74705SXin Li double t20(double x) {
155*67e74705SXin Li   register long double result;
156*67e74705SXin Li   __asm __volatile ("frndint"  : "=t" (result) : "0" (x));
157*67e74705SXin Li   return result;
158*67e74705SXin Li 
159*67e74705SXin Li   // CHECK: @t20
160*67e74705SXin Li   // CHECK: fpext double {{.*}} to x86_fp80
161*67e74705SXin Li   // CHECK-NEXT: call x86_fp80 asm sideeffect "frndint"
162*67e74705SXin Li   // CHECK: fptrunc x86_fp80 {{.*}} to double
163*67e74705SXin Li }
164*67e74705SXin Li 
t21(long double x)165*67e74705SXin Li float t21(long double x) {
166*67e74705SXin Li   register float result;
167*67e74705SXin Li   __asm __volatile ("frndint"  : "=t" (result) : "0" (x));
168*67e74705SXin Li   return result;
169*67e74705SXin Li   // CHECK: @t21
170*67e74705SXin Li   // CHECK: call x86_fp80 asm sideeffect "frndint"
171*67e74705SXin Li   // CHECK-NEXT: fptrunc x86_fp80 {{.*}} to float
172*67e74705SXin Li }
173*67e74705SXin Li 
174*67e74705SXin Li // <rdar://problem/8348447> - accept 'l' constraint
t22(unsigned char a,unsigned char b)175*67e74705SXin Li unsigned char t22(unsigned char a, unsigned char b) {
176*67e74705SXin Li   unsigned int la = a;
177*67e74705SXin Li   unsigned int lb = b;
178*67e74705SXin Li   unsigned int bigres;
179*67e74705SXin Li   unsigned char res;
180*67e74705SXin Li   __asm__ ("0:\n1:\n" : [bigres] "=la"(bigres) : [la] "0"(la), [lb] "c"(lb) :
181*67e74705SXin Li                         "edx", "cc");
182*67e74705SXin Li   res = bigres;
183*67e74705SXin Li   return res;
184*67e74705SXin Li }
185*67e74705SXin Li 
186*67e74705SXin Li // <rdar://problem/8348447> - accept 'l' constraint
t23(unsigned char a,unsigned char b)187*67e74705SXin Li unsigned char t23(unsigned char a, unsigned char b) {
188*67e74705SXin Li   unsigned int la = a;
189*67e74705SXin Li   unsigned int lb = b;
190*67e74705SXin Li   unsigned char res;
191*67e74705SXin Li   __asm__ ("0:\n1:\n" : [res] "=la"(res) : [la] "0"(la), [lb] "c"(lb) :
192*67e74705SXin Li                         "edx", "cc");
193*67e74705SXin Li   return res;
194*67e74705SXin Li }
195*67e74705SXin Li 
t24(char c)196*67e74705SXin Li void *t24(char c) {
197*67e74705SXin Li   void *addr;
198*67e74705SXin Li   // CHECK: @t24
199*67e74705SXin Li   // CHECK: zext i8 {{.*}} to i32
200*67e74705SXin Li   // CHECK-NEXT: call i8* asm "foobar"
201*67e74705SXin Li   __asm__ ("foobar" : "=a" (addr) : "0" (c));
202*67e74705SXin Li   return addr;
203*67e74705SXin Li }
204*67e74705SXin Li 
205*67e74705SXin Li // PR10299 - fpsr, fpcr
t25(void)206*67e74705SXin Li void t25(void)
207*67e74705SXin Li {
208*67e74705SXin Li   __asm__ __volatile__(					   \
209*67e74705SXin Li 		       "finit"				   \
210*67e74705SXin Li 		       :				   \
211*67e74705SXin Li 		       :				   \
212*67e74705SXin Li 		       :"st","st(1)","st(2)","st(3)",	   \
213*67e74705SXin Li 			"st(4)","st(5)","st(6)","st(7)",   \
214*67e74705SXin Li 			"fpsr","fpcr"			   \
215*67e74705SXin Li 							   );
216*67e74705SXin Li }
217*67e74705SXin Li 
218*67e74705SXin Li // rdar://10510405 - AVX registers
219*67e74705SXin Li typedef long long __m256i __attribute__((__vector_size__(32)));
t26(__m256i * p)220*67e74705SXin Li void t26 (__m256i *p) {
221*67e74705SXin Li   __asm__ volatile("vmovaps  %0, %%ymm0" :: "m" (*(__m256i*)p) : "ymm0");
222*67e74705SXin Li }
223*67e74705SXin Li 
224*67e74705SXin Li // Check to make sure the inline asm non-standard dialect attribute _not_ is
225*67e74705SXin Li // emitted.
t27(void)226*67e74705SXin Li void t27(void) {
227*67e74705SXin Li   asm volatile("nop");
228*67e74705SXin Li // CHECK: @t27
229*67e74705SXin Li // CHECK: call void asm sideeffect "nop"
230*67e74705SXin Li // CHECK-NOT: ia_nsdialect
231*67e74705SXin Li // CHECK: ret void
232*67e74705SXin Li }
233*67e74705SXin Li 
234*67e74705SXin Li // Check handling of '*' and '#' constraint modifiers.
t28(void)235*67e74705SXin Li void t28(void)
236*67e74705SXin Li {
237*67e74705SXin Li   asm volatile ("/* %0 */" : : "i#*X,*r" (1));
238*67e74705SXin Li // CHECK: @t28
239*67e74705SXin Li // CHECK: call void asm sideeffect "/* $0 */", "i|r,~{dirflag},~{fpsr},~{flags}"(i32 1)
240*67e74705SXin Li }
241*67e74705SXin Li 
242*67e74705SXin Li static unsigned t29_var[1];
243*67e74705SXin Li 
t29(void)244*67e74705SXin Li void t29(void) {
245*67e74705SXin Li   asm volatile("movl %%eax, %0"
246*67e74705SXin Li                :
247*67e74705SXin Li                : "m"(t29_var));
248*67e74705SXin Li   // CHECK: @t29
249*67e74705SXin Li   // CHECK: call void asm sideeffect "movl %eax, $0", "*m,~{dirflag},~{fpsr},~{flags}"([1 x i32]* @t29_var)
250*67e74705SXin Li }
251*67e74705SXin Li 
t30(int len)252*67e74705SXin Li void t30(int len) {
253*67e74705SXin Li   __asm__ volatile(""
254*67e74705SXin Li                    : "+&&rm"(len));
255*67e74705SXin Li   // CHECK: @t30
256*67e74705SXin Li   // CHECK: call void asm sideeffect "", "=*&rm,0,~{dirflag},~{fpsr},~{flags}"
257*67e74705SXin Li }
258*67e74705SXin Li 
t31(int len)259*67e74705SXin Li void t31(int len) {
260*67e74705SXin Li   __asm__ volatile(""
261*67e74705SXin Li                    : "+%%rm"(len), "+rm"(len));
262*67e74705SXin Li   // CHECK: @t31
263*67e74705SXin Li   // CHECK: call void asm sideeffect "", "=*%rm,=*rm,0,1,~{dirflag},~{fpsr},~{flags}"
264*67e74705SXin Li }
265