replica
/
hanchenye-llvm-project
2
0
Fork 0
Code Issues Pull Requests Projects Releases Wiki Activity

[Clang][AVX512][Builtin] Adding intrinsics for vcvttpd2udq instruction set 

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

llvm-svn: 268373
This commit is contained in:
Michael Zuckerman 2016-05-03 11:05:24 +00:00
parent 708e759b86
commit 138fc5b5a8
2 changed files with 84 additions and 0 deletions
Show Stats Download Patch File Download Diff File Expand all files Collapse all files

48
clang/lib/Headers/avx512fintrin.h
View File

@ -5229,6 +5229,54 @@ _mm512_mask_testn_epi64_mask (__mmask8 __U, __m512i __A, __m512i __B)
(__v8di) __B, __U);
}
#define _mm512_cvtt_roundpd_epu32( __A, __R) __extension__ ({ \
__builtin_ia32_cvttpd2udq512_mask ((__v8df)( __A),\
(__v8si)\
_mm256_undefined_si256 (),\
(__mmask8) -1,( __R));\
})
#define _mm512_mask_cvtt_roundpd_epu32( __W, __U, __A, __R) __extension__ ({ \
__builtin_ia32_cvttpd2udq512_mask ((__v8df)( __A),\
(__v8si)( __W),\
(__mmask8)( __U),( __R));\
})
#define _mm512_maskz_cvtt_roundpd_epu32( __U, __A, __R) __extension__ ({ \
__builtin_ia32_cvttpd2udq512_mask ((__v8df)( __A),\
(__v8si)\
_mm256_setzero_si256 (),\
(__mmask8)( __U),( __R));\
})
static __inline__ __m256i __DEFAULT_FN_ATTRS
_mm512_cvttpd_epu32 (__m512d __A)
{
return (__m256i) __builtin_ia32_cvttpd2udq512_mask ((__v8df) __A,
(__v8si)
_mm256_undefined_si256 (),
(__mmask8) -1,
_MM_FROUND_CUR_DIRECTION);
}
static __inline__ __m256i __DEFAULT_FN_ATTRS
_mm512_mask_cvttpd_epu32 (__m256i __W, __mmask8 __U, __m512d __A)
{
return (__m256i) __builtin_ia32_cvttpd2udq512_mask ((__v8df) __A,
(__v8si) __W,
(__mmask8) __U,
_MM_FROUND_CUR_DIRECTION);
}
static __inline__ __m256i __DEFAULT_FN_ATTRS
_mm512_maskz_cvttpd_epu32 (__mmask8 __U, __m512d __A)
{
return (__m256i) __builtin_ia32_cvttpd2udq512_mask ((__v8df) __A,
(__v8si)
_mm256_setzero_si256 (),
(__mmask8) __U,
_MM_FROUND_CUR_DIRECTION);
}
static __inline__ __m512i __DEFAULT_FN_ATTRS
_mm512_mask_unpackhi_epi32 (__m512i __W, __mmask16 __U, __m512i __A,

36
clang/test/CodeGen/avx512f-builtins.c
View File

@ -5552,3 +5552,39 @@ void test_mm512_mask_compressstoreu_epi32(void *__P, __mmask16 __U, __m512i __A)
// CHECK: @llvm.x86.avx512.mask.compress.store.d.512
return _mm512_mask_compressstoreu_epi32(__P, __U, __A);
}
__m256i test_mm512_cvtt_roundpd_epu32(__m512d __A) {
// CHECK-LABEL: @test_mm512_cvtt_roundpd_epu32
// CHECK: @llvm.x86.avx512.mask.cvttpd2udq.512
return _mm512_cvtt_roundpd_epu32(__A, _MM_FROUND_CUR_DIRECTION);
}
__m256i test_mm512_mask_cvtt_roundpd_epu32(__m256i __W, __mmask8 __U, __m512d __A) {
// CHECK-LABEL: @test_mm512_mask_cvtt_roundpd_epu32
// CHECK: @llvm.x86.avx512.mask.cvttpd2udq.512
return _mm512_mask_cvtt_roundpd_epu32(__W, __U, __A, _MM_FROUND_CUR_DIRECTION);
}
__m256i test_mm512_maskz_cvtt_roundpd_epu32(__mmask8 __U, __m512d __A) {
// CHECK-LABEL: @test_mm512_maskz_cvtt_roundpd_epu32
// CHECK: @llvm.x86.avx512.mask.cvttpd2udq.512
return _mm512_maskz_cvtt_roundpd_epu32(__U, __A, _MM_FROUND_CUR_DIRECTION);
}
__m256i test_mm512_cvttpd_epu32(__m512d __A) {
// CHECK-LABEL: @test_mm512_cvttpd_epu32
// CHECK: @llvm.x86.avx512.mask.cvttpd2udq.512
return _mm512_cvttpd_epu32(__A);
}
__m256i test_mm512_mask_cvttpd_epu32(__m256i __W, __mmask8 __U, __m512d __A) {
// CHECK-LABEL: @test_mm512_mask_cvttpd_epu32
// CHECK: @llvm.x86.avx512.mask.cvttpd2udq.512
return _mm512_mask_cvttpd_epu32(__W, __U, __A);
}
__m256i test_mm512_maskz_cvttpd_epu32(__mmask8 __U, __m512d __A) {
// CHECK-LABEL: @test_mm512_maskz_cvttpd_epu32
// CHECK: @llvm.x86.avx512.mask.cvttpd2udq.512
return _mm512_maskz_cvttpd_epu32(__U, __A);
}