1f4a2713aSLionel Sambuc // RUN: %clang_cc1 -triple i386-apple-darwin9 -verify %s
2*0a6a1f1dSLionel Sambuc // RUN: %clang_cc1 -triple i386-apple-darwin9 -target-feature +avx -verify %s
3*0a6a1f1dSLionel Sambuc
4f4a2713aSLionel Sambuc // <rdar://problem/12415959>
5*0a6a1f1dSLionel Sambuc // rdar://problem/11846140
6*0a6a1f1dSLionel Sambuc // rdar://problem/17476970
7f4a2713aSLionel Sambuc
8f4a2713aSLionel Sambuc typedef unsigned int u_int32_t;
9f4a2713aSLionel Sambuc typedef u_int32_t uint32_t;
10f4a2713aSLionel Sambuc
11f4a2713aSLionel Sambuc typedef unsigned long long u_int64_t;
12f4a2713aSLionel Sambuc typedef u_int64_t uint64_t;
13f4a2713aSLionel Sambuc
14*0a6a1f1dSLionel Sambuc typedef float __m128 __attribute__ ((vector_size (16)));
15*0a6a1f1dSLionel Sambuc typedef float __m256 __attribute__ ((vector_size (32)));
16*0a6a1f1dSLionel Sambuc typedef float __m512 __attribute__ ((vector_size (64)));
17*0a6a1f1dSLionel Sambuc
18*0a6a1f1dSLionel Sambuc __m128 val128;
19*0a6a1f1dSLionel Sambuc __m256 val256;
20*0a6a1f1dSLionel Sambuc __m512 val512;
21*0a6a1f1dSLionel Sambuc
func1()22f4a2713aSLionel Sambuc int func1() {
23f4a2713aSLionel Sambuc // Error out if size is > 32-bits.
24f4a2713aSLionel Sambuc uint32_t msr = 0x8b;
25f4a2713aSLionel Sambuc uint64_t val = 0;
26f4a2713aSLionel Sambuc __asm__ volatile("wrmsr"
27f4a2713aSLionel Sambuc :
28f4a2713aSLionel Sambuc : "c" (msr),
29f4a2713aSLionel Sambuc "a" ((val & 0xFFFFFFFFUL)), // expected-error {{invalid input size for constraint 'a'}}
30f4a2713aSLionel Sambuc "d" (((val >> 32) & 0xFFFFFFFFUL)));
31f4a2713aSLionel Sambuc
32f4a2713aSLionel Sambuc // Don't error out if the size of the destination is <= 32 bits.
33f4a2713aSLionel Sambuc unsigned char data;
34f4a2713aSLionel Sambuc unsigned int port;
35f4a2713aSLionel Sambuc __asm__ volatile("outb %0, %w1" : : "a" (data), "Nd" (port)); // No error expected.
36*0a6a1f1dSLionel Sambuc
37*0a6a1f1dSLionel Sambuc __asm__ volatile("outb %0, %w1" : : "R" (val), "Nd" (port)); // expected-error {{invalid input size for constraint 'R'}}
38*0a6a1f1dSLionel Sambuc __asm__ volatile("outb %0, %w1" : : "q" (val), "Nd" (port)); // expected-error {{invalid input size for constraint 'q'}}
39*0a6a1f1dSLionel Sambuc __asm__ volatile("outb %0, %w1" : : "Q" (val), "Nd" (port)); // expected-error {{invalid input size for constraint 'Q'}}
40*0a6a1f1dSLionel Sambuc __asm__ volatile("outb %0, %w1" : : "b" (val), "Nd" (port)); // expected-error {{invalid input size for constraint 'b'}}
41*0a6a1f1dSLionel Sambuc __asm__ volatile("outb %0, %w1" : : "c" (val), "Nd" (port)); // expected-error {{invalid input size for constraint 'c'}}
42*0a6a1f1dSLionel Sambuc __asm__ volatile("outb %0, %w1" : : "d" (val), "Nd" (port)); // expected-error {{invalid input size for constraint 'd'}}
43*0a6a1f1dSLionel Sambuc __asm__ volatile("outb %0, %w1" : : "S" (val), "Nd" (port)); // expected-error {{invalid input size for constraint 'S'}}
44*0a6a1f1dSLionel Sambuc __asm__ volatile("outb %0, %w1" : : "D" (val), "Nd" (port)); // expected-error {{invalid input size for constraint 'D'}}
45*0a6a1f1dSLionel Sambuc __asm__ volatile("foo1 %0" : : "A" (val128)); // expected-error {{invalid input size for constraint 'A'}}
46*0a6a1f1dSLionel Sambuc __asm__ volatile("foo1 %0" : : "f" (val256)); // expected-error {{invalid input size for constraint 'f'}}
47*0a6a1f1dSLionel Sambuc __asm__ volatile("foo1 %0" : : "t" (val256)); // expected-error {{invalid input size for constraint 't'}}
48*0a6a1f1dSLionel Sambuc __asm__ volatile("foo1 %0" : : "u" (val256)); // expected-error {{invalid input size for constraint 'u'}}
49*0a6a1f1dSLionel Sambuc __asm__ volatile("foo1 %0" : : "x" (val512)); // expected-error {{invalid input size for constraint 'x'}}
50*0a6a1f1dSLionel Sambuc
51*0a6a1f1dSLionel Sambuc __asm__ volatile("foo1 %0" : "=R" (val)); // expected-error {{invalid output size for constraint '=R'}}
52*0a6a1f1dSLionel Sambuc __asm__ volatile("foo1 %0" : "=q" (val)); // expected-error {{invalid output size for constraint '=q'}}
53*0a6a1f1dSLionel Sambuc __asm__ volatile("foo1 %0" : "=Q" (val)); // expected-error {{invalid output size for constraint '=Q'}}
54*0a6a1f1dSLionel Sambuc __asm__ volatile("foo1 %0" : "=a" (val)); // expected-error {{invalid output size for constraint '=a'}}
55*0a6a1f1dSLionel Sambuc __asm__ volatile("foo1 %0" : "=b" (val)); // expected-error {{invalid output size for constraint '=b'}}
56*0a6a1f1dSLionel Sambuc __asm__ volatile("foo1 %0" : "=c" (val)); // expected-error {{invalid output size for constraint '=c'}}
57*0a6a1f1dSLionel Sambuc __asm__ volatile("foo1 %0" : "=d" (val)); // expected-error {{invalid output size for constraint '=d'}}
58*0a6a1f1dSLionel Sambuc __asm__ volatile("foo1 %0" : "=S" (val)); // expected-error {{invalid output size for constraint '=S'}}
59*0a6a1f1dSLionel Sambuc __asm__ volatile("foo1 %0" : "=D" (val)); // expected-error {{invalid output size for constraint '=D'}}
60*0a6a1f1dSLionel Sambuc __asm__ volatile("foo1 %0" : "=A" (val128)); // expected-error {{invalid output size for constraint '=A'}}
61*0a6a1f1dSLionel Sambuc __asm__ volatile("foo1 %0" : "=t" (val256)); // expected-error {{invalid output size for constraint '=t'}}
62*0a6a1f1dSLionel Sambuc __asm__ volatile("foo1 %0" : "=u" (val256)); // expected-error {{invalid output size for constraint '=u'}}
63*0a6a1f1dSLionel Sambuc __asm__ volatile("foo1 %0" : "=x" (val512)); // expected-error {{invalid output size for constraint '=x'}}
64*0a6a1f1dSLionel Sambuc
65*0a6a1f1dSLionel Sambuc #ifdef __AVX__
66*0a6a1f1dSLionel Sambuc __asm__ volatile("foo1 %0" : : "x" (val256)); // No error.
67*0a6a1f1dSLionel Sambuc __asm__ volatile("foo1 %0" : "=x" (val256)); // No error.
68*0a6a1f1dSLionel Sambuc #else
69*0a6a1f1dSLionel Sambuc __asm__ volatile("foo1 %0" : : "x" (val256)); // expected-error {{invalid input size for constraint 'x'}}
70*0a6a1f1dSLionel Sambuc __asm__ volatile("foo1 %0" : "=x" (val256)); // expected-error {{invalid output size for constraint '=x'}}
71*0a6a1f1dSLionel Sambuc #endif
72f4a2713aSLionel Sambuc }
73