[Clang][AVX512][Builtin] Adding intrinsics of vpmovus{d|q}{b|w|d}{128|256|512} instruction set

Differential Revision: http://reviews.llvm.org/D19050

llvm-svn: 266278

1 files changed, 120 insertions, 0 deletions

diff --git a/clang/test/CodeGen/avx512f-builtins.c b/clang/test/CodeGen/avx512f-builtins.c
index a13d92e9816..cde81e47ae1 100644
--- a/clang/test/CodeGen/avx512f-builtins.c
+++ b/clang/test/CodeGen/avx512f-builtins.c
@@ -3819,3 +3819,123 @@ void test_mm512_mask_cvtsepi64_storeu_epi16(void * __P, __mmask8 __M, __m512i __
   // CHECK: @llvm.x86.avx512.mask.pmovs.qw.mem.512
   return _mm512_mask_cvtsepi64_storeu_epi16(__P, __M, __A); 
 }
+
+__m128i test_mm512_cvtusepi32_epi8(__m512i __A) {
+  // CHECK-LABEL: @test_mm512_cvtusepi32_epi8
+  // CHECK: @llvm.x86.avx512.mask.pmovus.db.512
+  return _mm512_cvtusepi32_epi8(__A); 
+}
+
+__m128i test_mm512_mask_cvtusepi32_epi8(__m128i __O, __mmask16 __M, __m512i __A) {
+  // CHECK-LABEL: @test_mm512_mask_cvtusepi32_epi8
+  // CHECK: @llvm.x86.avx512.mask.pmovus.db.512
+  return _mm512_mask_cvtusepi32_epi8(__O, __M, __A); 
+}
+
+__m128i test_mm512_maskz_cvtusepi32_epi8(__mmask16 __M, __m512i __A) {
+  // CHECK-LABEL: @test_mm512_maskz_cvtusepi32_epi8
+  // CHECK: @llvm.x86.avx512.mask.pmovus.db.512
+  return _mm512_maskz_cvtusepi32_epi8(__M, __A); 
+}
+
+void test_mm512_mask_cvtusepi32_storeu_epi8(void * __P, __mmask16 __M, __m512i __A) {
+  // CHECK-LABEL: @test_mm512_mask_cvtusepi32_storeu_epi8
+  // CHECK: @llvm.x86.avx512.mask.pmovus.db.mem.512
+  return _mm512_mask_cvtusepi32_storeu_epi8(__P, __M, __A); 
+}
+
+__m256i test_mm512_cvtusepi32_epi16(__m512i __A) {
+  // CHECK-LABEL: @test_mm512_cvtusepi32_epi16
+  // CHECK: @llvm.x86.avx512.mask.pmovus.dw.512
+  return _mm512_cvtusepi32_epi16(__A); 
+}
+
+__m256i test_mm512_mask_cvtusepi32_epi16(__m256i __O, __mmask16 __M, __m512i __A) {
+  // CHECK-LABEL: @test_mm512_mask_cvtusepi32_epi16
+  // CHECK: @llvm.x86.avx512.mask.pmovus.dw.512
+  return _mm512_mask_cvtusepi32_epi16(__O, __M, __A); 
+}
+
+__m256i test_mm512_maskz_cvtusepi32_epi16(__mmask16 __M, __m512i __A) {
+  // CHECK-LABEL: @test_mm512_maskz_cvtusepi32_epi16
+  // CHECK: @llvm.x86.avx512.mask.pmovus.dw.512
+  return _mm512_maskz_cvtusepi32_epi16(__M, __A); 
+}
+
+void test_mm512_mask_cvtusepi32_storeu_epi16(void *__P, __mmask16 __M, __m512i __A) {
+  // CHECK-LABEL: @test_mm512_mask_cvtusepi32_storeu_epi16
+  // CHECK: @llvm.x86.avx512.mask.pmovus.dw.mem.512
+  return _mm512_mask_cvtusepi32_storeu_epi16(__P, __M, __A); 
+}
+
+__m128i test_mm512_cvtusepi64_epi8(__m512i __A) {
+  // CHECK-LABEL: @test_mm512_cvtusepi64_epi8
+  // CHECK: @llvm.x86.avx512.mask.pmovus.qb.512
+  return _mm512_cvtusepi64_epi8(__A); 
+}
+
+__m128i test_mm512_mask_cvtusepi64_epi8(__m128i __O, __mmask8 __M, __m512i __A) {
+  // CHECK-LABEL: @test_mm512_mask_cvtusepi64_epi8
+  // CHECK: @llvm.x86.avx512.mask.pmovus.qb.512
+  return _mm512_mask_cvtusepi64_epi8(__O, __M, __A); 
+}
+
+__m128i test_mm512_maskz_cvtusepi64_epi8(__mmask8 __M, __m512i __A) {
+  // CHECK-LABEL: @test_mm512_maskz_cvtusepi64_epi8
+  // CHECK: @llvm.x86.avx512.mask.pmovus.qb.512
+  return _mm512_maskz_cvtusepi64_epi8(__M, __A); 
+}
+
+void test_mm512_mask_cvtusepi64_storeu_epi8(void * __P, __mmask8 __M, __m512i __A) {
+  // CHECK-LABEL: @test_mm512_mask_cvtusepi64_storeu_epi8
+  // CHECK: @llvm.x86.avx512.mask.pmovus.qb.mem.512
+  return _mm512_mask_cvtusepi64_storeu_epi8(__P, __M, __A); 
+}
+
+__m256i test_mm512_cvtusepi64_epi32(__m512i __A) {
+  // CHECK-LABEL: @test_mm512_cvtusepi64_epi32
+  // CHECK: @llvm.x86.avx512.mask.pmovus.qd.512
+  return _mm512_cvtusepi64_epi32(__A); 
+}
+
+__m256i test_mm512_mask_cvtusepi64_epi32(__m256i __O, __mmask8 __M, __m512i __A) {
+  // CHECK-LABEL: @test_mm512_mask_cvtusepi64_epi32
+  // CHECK: @llvm.x86.avx512.mask.pmovus.qd.512
+  return _mm512_mask_cvtusepi64_epi32(__O, __M, __A); 
+}
+
+__m256i test_mm512_maskz_cvtusepi64_epi32(__mmask8 __M, __m512i __A) {
+  // CHECK-LABEL: @test_mm512_maskz_cvtusepi64_epi32
+  // CHECK: @llvm.x86.avx512.mask.pmovus.qd.512
+  return _mm512_maskz_cvtusepi64_epi32(__M, __A); 
+}
+
+void test_mm512_mask_cvtusepi64_storeu_epi32(void* __P, __mmask8 __M, __m512i __A) {
+  // CHECK-LABEL: @test_mm512_mask_cvtusepi64_storeu_epi32
+  // CHECK: @llvm.x86.avx512.mask.pmovus.qd.mem.512
+  return _mm512_mask_cvtusepi64_storeu_epi32(__P, __M, __A); 
+}
+
+__m128i test_mm512_cvtusepi64_epi16(__m512i __A) {
+  // CHECK-LABEL: @test_mm512_cvtusepi64_epi16
+  // CHECK: @llvm.x86.avx512.mask.pmovus.qw.512
+  return _mm512_cvtusepi64_epi16(__A); 
+}
+
+__m128i test_mm512_mask_cvtusepi64_epi16(__m128i __O, __mmask8 __M, __m512i __A) {
+  // CHECK-LABEL: @test_mm512_mask_cvtusepi64_epi16
+  // CHECK: @llvm.x86.avx512.mask.pmovus.qw.512
+  return _mm512_mask_cvtusepi64_epi16(__O, __M, __A); 
+}
+
+__m128i test_mm512_maskz_cvtusepi64_epi16(__mmask8 __M, __m512i __A) {
+  // CHECK-LABEL: @test_mm512_maskz_cvtusepi64_epi16
+  // CHECK: @llvm.x86.avx512.mask.pmovus.qw.512
+  return _mm512_maskz_cvtusepi64_epi16(__M, __A); 
+}
+
+void test_mm512_mask_cvtusepi64_storeu_epi16(void *__P, __mmask8 __M, __m512i __A) {
+  // CHECK-LABEL: @test_mm512_mask_cvtusepi64_storeu_epi16
+  // CHECK: @llvm.x86.avx512.mask.pmovus.qw.mem.512
+  return _mm512_mask_cvtusepi64_storeu_epi16(__P, __M, __A); 
+}