101 lines · c
1// RUN: %clang_cc1 -triple i386-apple-darwin9 -verify %s2// RUN: %clang_cc1 -triple i386-apple-darwin9 -target-feature +avx -verify %s3 4typedef unsigned int u_int32_t;5typedef u_int32_t uint32_t;6 7typedef unsigned long long u_int64_t;8typedef u_int64_t uint64_t;9 10typedef float __m128 __attribute__ ((vector_size (16)));11typedef float __m256 __attribute__ ((vector_size (32)));12typedef float __m512 __attribute__ ((vector_size (64)));13 14__m128 val128;15__m256 val256;16__m512 val512;17 18int func1(void) {19 // Error out if size is > 32-bits.20 uint32_t msr = 0x8b;21 uint64_t val = 0;22 __asm__ volatile("wrmsr"23 :24 : "c" (msr),25 "a" ((val & 0xFFFFFFFFUL)), // expected-error {{invalid input size for constraint 'a'}}26 "d" (((val >> 32) & 0xFFFFFFFFUL)));27 28 // Don't error out if the size of the destination is <= 32 bits.29 unsigned char data;30 unsigned int port;31 __asm__ volatile("outb %0, %w1" : : "a" (data), "Nd" (port)); // No error expected.32 33 __asm__ volatile("outb %0, %w1" : : "R" (val), "Nd" (port)); // expected-error {{invalid input size for constraint 'R'}}34 __asm__ volatile("outb %0, %w1" : : "q" (val), "Nd" (port)); // expected-error {{invalid input size for constraint 'q'}}35 __asm__ volatile("outb %0, %w1" : : "Q" (val), "Nd" (port)); // expected-error {{invalid input size for constraint 'Q'}}36 __asm__ volatile("outb %0, %w1" : : "b" (val), "Nd" (port)); // expected-error {{invalid input size for constraint 'b'}}37 __asm__ volatile("outb %0, %w1" : : "c" (val), "Nd" (port)); // expected-error {{invalid input size for constraint 'c'}}38 __asm__ volatile("outb %0, %w1" : : "d" (val), "Nd" (port)); // expected-error {{invalid input size for constraint 'd'}}39 __asm__ volatile("outb %0, %w1" : : "S" (val), "Nd" (port)); // expected-error {{invalid input size for constraint 'S'}}40 __asm__ volatile("outb %0, %w1" : : "D" (val), "Nd" (port)); // expected-error {{invalid input size for constraint 'D'}}41 __asm__ volatile("foo1 %0" : : "A" (val128)); // expected-error {{invalid input size for constraint 'A'}}42 __asm__ volatile("foo1 %0" : : "f" (val256)); // expected-error {{invalid input size for constraint 'f'}}43 __asm__ volatile("foo1 %0" : : "t" (val256)); // expected-error {{invalid input size for constraint 't'}}44 __asm__ volatile("foo1 %0" : : "u" (val256)); // expected-error {{invalid input size for constraint 'u'}}45 __asm__ volatile("foo1 %0" : : "x" (val512)); // expected-error {{invalid input size for constraint 'x'}}46 47 __asm__ volatile("foo1 %0" : "=R" (val)); // expected-error {{invalid output size for constraint '=R'}}48 __asm__ volatile("foo1 %0" : "=q" (val)); // expected-error {{invalid output size for constraint '=q'}}49 __asm__ volatile("foo1 %0" : "=Q" (val)); // expected-error {{invalid output size for constraint '=Q'}}50 __asm__ volatile("foo1 %0" : "=a" (val)); // expected-error {{invalid output size for constraint '=a'}}51 __asm__ volatile("foo1 %0" : "=b" (val)); // expected-error {{invalid output size for constraint '=b'}}52 __asm__ volatile("foo1 %0" : "=c" (val)); // expected-error {{invalid output size for constraint '=c'}}53 __asm__ volatile("foo1 %0" : "=d" (val)); // expected-error {{invalid output size for constraint '=d'}}54 __asm__ volatile("foo1 %0" : "=S" (val)); // expected-error {{invalid output size for constraint '=S'}}55 __asm__ volatile("foo1 %0" : "=D" (val)); // expected-error {{invalid output size for constraint '=D'}}56 __asm__ volatile("foo1 %0" : "=A" (val128)); // expected-error {{invalid output size for constraint '=A'}}57 __asm__ volatile("foo1 %0" : "=t" (val256)); // expected-error {{invalid output size for constraint '=t'}}58 __asm__ volatile("foo1 %0" : "=u" (val256)); // expected-error {{invalid output size for constraint '=u'}}59 __asm__ volatile("foo1 %0" : "=x" (val512)); // expected-error {{invalid output size for constraint '=x'}}60 61#ifdef __AVX__62 __asm__ volatile("foo1 %0" : : "x" (val256)); // No error.63 __asm__ volatile("foo1 %0" : "=x" (val256)); // No error.64#else65 __asm__ volatile("foo1 %0" : : "x" (val256)); // expected-error {{invalid input size for constraint 'x'}}66 __asm__ volatile("foo1 %0" : "=x" (val256)); // expected-error {{invalid output size for constraint '=x'}}67#endif68}69 70int __attribute__((__target__("sse"))) _func2(void) {71 __asm__ volatile("foo1 %0" : : "x" (val128)); // No error.72 __asm__ volatile("foo1 %0" : "=x" (val128)); // No error.73#ifdef __AVX__74 __asm__ volatile("foo1 %0" : : "x" (val256)); // No error.75 __asm__ volatile("foo1 %0" : "=x" (val256)); // No error.76#else77 __asm__ volatile("foo1 %0" : : "x" (val256)); // expected-error {{invalid input size for constraint 'x'}}78 __asm__ volatile("foo1 %0" : "=x" (val256)); // expected-error {{invalid output size for constraint '=x'}}79#endif80 __asm__ volatile("foo1 %0" : : "x" (val512)); // expected-error {{invalid input size for constraint 'x'}}81 __asm__ volatile("foo1 %0" : "=x" (val512)); // expected-error {{invalid output size for constraint '=x'}}82}83 84int __attribute__((__target__("avx"))) _func3(void) {85 __asm__ volatile("foo1 %0" : : "x" (val128)); // No error.86 __asm__ volatile("foo1 %0" : "=x" (val128)); // No error.87 __asm__ volatile("foo1 %0" : : "x" (val256)); // No error.88 __asm__ volatile("foo1 %0" : "=x" (val256)); // No error.89 __asm__ volatile("foo1 %0" : : "x" (val512)); // expected-error {{invalid input size for constraint 'x'}}90 __asm__ volatile("foo1 %0" : "=x" (val512)); // expected-error {{invalid output size for constraint '=x'}}91}92 93int __attribute__((__target__("avx512f"))) _func4(void) {94 __asm__ volatile("foo1 %0" : : "x" (val128)); // No error.95 __asm__ volatile("foo1 %0" : "=x" (val128)); // No error.96 __asm__ volatile("foo1 %0" : : "x" (val256)); // No error.97 __asm__ volatile("foo1 %0" : "=x" (val256)); // No error.98 __asm__ volatile("foo1 %0" : : "x" (val512)); // No error.99 __asm__ volatile("foo1 %0" : "=x" (val512)); // No error.100}101