137 lines · c
1// RUN: %clang_cc1 -triple i386-unknown-unknown -fsyntax-only -ffreestanding -Wcast-qual %s -verify2// RUN: %clang_cc1 -triple x86_64-unknown-unknown -fsyntax-only -ffreestanding -Wcast-qual %s -verify3// RUN: %clang_cc1 -triple i386-unknown-unknown -fsyntax-only -ffreestanding -flax-vector-conversions=none -Wcast-qual %s -verify4// RUN: %clang_cc1 -triple x86_64-unknown-unknown -fsyntax-only -ffreestanding -flax-vector-conversions=none -Wcast-qual %s -verify5// RUN: %clang_cc1 -triple i386-unknown-unknown -fsyntax-only -ffreestanding -Wcast-qual -x c++ %s -verify6// RUN: %clang_cc1 -triple x86_64-unknown-unknown -fsyntax-only -ffreestanding -Wcast-qual -x c++ %s -verify7// expected-no-diagnostics8 9// Include the metaheader that includes all x86 intrinsic headers.10#include <x86intrin.h>11 12void __attribute__((__target__("mmx"))) mm_empty_wrap(void) {13 _mm_empty();14}15 16__m128 __attribute__((__target__("sse"))) mm_add_ss_wrap(__m128 a, __m128 b) {17 return _mm_add_ss(a, b);18}19 20void __attribute__((__target__("sse"))) mm_prefetch_wrap(const void *p) {21 _mm_prefetch(p, 0x3);22}23 24__m128d __attribute__((__target__("sse2"))) mm_sqrt_sd_wrap(__m128d a, __m128d b) {25 return _mm_sqrt_sd(a, b);26}27 28void __attribute__((__target__("sse3"))) mm_mwait_wrap(int a) {29 _mm_mwait(0, 0);30}31 32__m64 __attribute__((__target__("ssse3"))) mm_abs_pi8_wrap(__m64 a) {33 return _mm_abs_pi8(a);34}35 36__m128i __attribute__((__target__("sse4.1"))) mm_minpos_epu16_wrap(__m128i v) {37 return _mm_minpos_epu16(v);38}39 40unsigned int __attribute__((__target__("sse4.2"))) mm_crc32_u8_wrap(unsigned int c, unsigned char d) {41 return _mm_crc32_u8(c, d);42}43 44__m128i __attribute__((__target__("aes"))) mm_aesenc_si128_wrap(__m128i v, __m128i r) {45 return _mm_aesenc_si128(v, r);46}47 48__m256d __attribute__((__target__("avx"))) mm256_add_pd_wrap(__m256d a, __m256d b) {49 return _mm256_add_pd(a, b);50}51 52__m256i __attribute__((__target__("avx2"))) mm256_abs_epi8_wrap(__m256i a) {53 return _mm256_abs_epi8(a);54}55 56unsigned short __attribute__((__target__("bmi"))) tzcnt_u16_wrap(unsigned short x) {57 return __tzcnt_u16(x);58}59 60unsigned int __attribute__((__target__("bmi2"))) bzhi_u32_wrap(unsigned int x, unsigned int y) {61 return _bzhi_u32(x, y);62}63 64unsigned short __attribute__((__target__("lzcnt"))) lzcnt16_wrap(unsigned short x) {65 return __lzcnt16(x);66}67 68__m256d __attribute__((__target__("fma"))) mm256_fmsubadd_pd_wrap(__m256d a, __m256d b, __m256d c) {69 return _mm256_fmsubadd_pd(a, b, c);70}71 72__m512i __attribute__((__target__("avx512f"))) mm512_setzero_si512_wrap(void) {73 return _mm512_setzero_si512();74}75 76__mmask8 __attribute__((__target__("avx512vl"))) mm_cmpeq_epi32_mask_wrap(__m128i a, __m128i b) {77 return _mm_cmpeq_epi32_mask(a, b);78}79 80__m512i __attribute__((__target__("avx512dq"))) mm512_mullo_epi64_wrap(__m512i a, __m512i b) {81 return _mm512_mullo_epi64(a, b);82}83 84__mmask16 __attribute__((__target__("avx512vl,avx512bw"))) mm_cmpeq_epi8_mask_wrap(__m128i a, __m128i b) {85 return _mm_cmpeq_epi8_mask(a, b);86}87 88__m256i __attribute__((__target__("avx512vl,avx512dq"))) mm256_mullo_epi64_wrap(__m256i a, __m256i b) {89 return _mm256_mullo_epi64(a, b);90}91 92int __attribute__((__target__("rdrnd"))) rdrand16_step_wrap(unsigned short *p) {93 return _rdrand16_step(p);94}95 96#if defined(__x86_64__)97unsigned int __attribute__((__target__("fsgsbase"))) readfsbase_u32_wrap(void) {98 return _readfsbase_u32();99}100#endif101 102unsigned int __attribute__((__target__("rtm"))) xbegin_wrap(void) {103 return _xbegin();104}105 106__m128i __attribute__((__target__("sha"))) mm_sha1nexte_epu32_wrap(__m128i x, __m128i y) {107 return _mm_sha1nexte_epu32(x, y);108}109 110int __attribute__((__target__("rdseed"))) rdseed16_step_wrap(unsigned short *p) {111 return _rdseed16_step(p);112}113 114__m128i __attribute__((__target__("sse4a"))) mm_extract_si64_wrap(__m128i x, __m128i y) {115 return _mm_extract_si64(x, y);116}117 118__m128 __attribute__((__target__("fma4"))) mm_macc_ps_wrap(__m128 a, __m128 b, __m128 c) {119 return _mm_macc_ps(a, b, c);120}121 122__m256 __attribute__((__target__("xop"))) mm256_frcz_ps_wrap(__m256 a) {123 return _mm256_frcz_ps(a);124}125 126unsigned int __attribute__((__target__("tbm"))) blcfill_u32_wrap(unsigned int a) {127 return __blcfill_u32(a);128}129 130__m128 __attribute__((__target__("f16c"))) mm_cvtph_ps_wrap(__m128i a) {131 return _mm_cvtph_ps(a);132}133 134int __attribute__((__target__("rtm"))) xtest_wrap(void) {135 return _xtest();136}137