Author: ctopper
Date: Sun Jan 20 15:49:50 2019
New Revision: 351708
URL: http://llvm.org/viewvc/llvm-project?rev=351708&view=rev
Log:
[X86] Add missing test cases for some int/fp->fp conversion intrinsics with
rounding mode. Use non-default rounding mode on some tests.
For some reason we were missing tests for several unmasked conversion
intrinsics, but had their mask form.
Also use a non-default rounding mode on some tests to provide better coverage
for a future patch.
Modified:
cfe/trunk/test/CodeGen/avx512f-builtins.c
Modified: cfe/trunk/test/CodeGen/avx512f-builtins.c
URL:
http://llvm.org/viewvc/llvm-project/cfe/trunk/test/CodeGen/avx512f-builtins.c?rev=351708&r1=351707&r2=351708&view=diff
==============================================================================
--- cfe/trunk/test/CodeGen/avx512f-builtins.c (original)
+++ cfe/trunk/test/CodeGen/avx512f-builtins.c Sun Jan 20 15:49:50 2019
@@ -5019,137 +5019,193 @@ __m512 test_mm512_maskz_cvt_roundph_ps(_
return _mm512_maskz_cvt_roundph_ps(__U, __A, _MM_FROUND_CUR_DIRECTION);
}
+__m512 test_mm512_cvt_roundepi32_ps( __m512i __A)
+{
+ // CHECK-LABEL: @test_mm512_cvt_roundepi32_ps
+ // CHECK: @llvm.x86.avx512.mask.cvtdq2ps.512
+ return _mm512_cvt_roundepi32_ps(__A, _MM_FROUND_TO_NEAREST_INT |
_MM_FROUND_NO_EXC);
+}
+
__m512 test_mm512_mask_cvt_roundepi32_ps(__m512 __W, __mmask16 __U, __m512i
__A)
{
// CHECK-LABEL: @test_mm512_mask_cvt_roundepi32_ps
// CHECK: @llvm.x86.avx512.mask.cvtdq2ps.512
- return _mm512_mask_cvt_roundepi32_ps(__W,__U,__A,4);
+ return _mm512_mask_cvt_roundepi32_ps(__W,__U,__A, _MM_FROUND_TO_NEAREST_INT
| _MM_FROUND_NO_EXC);
}
__m512 test_mm512_maskz_cvt_roundepi32_ps(__mmask16 __U, __m512i __A)
{
// CHECK-LABEL: @test_mm512_maskz_cvt_roundepi32_ps
// CHECK: @llvm.x86.avx512.mask.cvtdq2ps.512
- return _mm512_maskz_cvt_roundepi32_ps(__U,__A,4);
+ return _mm512_maskz_cvt_roundepi32_ps(__U,__A, _MM_FROUND_TO_NEAREST_INT |
_MM_FROUND_NO_EXC);
+}
+
+__m512 test_mm512_cvt_roundepu32_ps(__m512i __A)
+{
+ // CHECK-LABEL: @test_mm512_cvt_roundepu32_ps
+ // CHECK: @llvm.x86.avx512.mask.cvtudq2ps.512
+ return _mm512_cvt_roundepu32_ps(__A, _MM_FROUND_TO_NEAREST_INT |
_MM_FROUND_NO_EXC);
}
__m512 test_mm512_mask_cvt_roundepu32_ps(__m512 __W, __mmask16 __U,__m512i __A)
{
// CHECK-LABEL: @test_mm512_mask_cvt_roundepu32_ps
// CHECK: @llvm.x86.avx512.mask.cvtudq2ps.512
- return _mm512_mask_cvt_roundepu32_ps(__W,__U,__A,4);
+ return _mm512_mask_cvt_roundepu32_ps(__W,__U,__A, _MM_FROUND_TO_NEAREST_INT
| _MM_FROUND_NO_EXC);
}
__m512 test_mm512_maskz_cvt_roundepu32_ps(__mmask16 __U,__m512i __A)
{
// CHECK-LABEL: @test_mm512_maskz_cvt_roundepu32_ps
// CHECK: @llvm.x86.avx512.mask.cvtudq2ps.512
- return _mm512_maskz_cvt_roundepu32_ps(__U,__A,4);
+ return _mm512_maskz_cvt_roundepu32_ps(__U,__A, _MM_FROUND_TO_NEAREST_INT |
_MM_FROUND_NO_EXC);
+}
+
+__m256 test_mm512_cvt_roundpd_ps(__m512d A)
+{
+ // CHECK-LABEL: @test_mm512_cvt_roundpd_ps
+ // CHECK: @llvm.x86.avx512.mask.cvtpd2ps.512
+ return _mm512_cvt_roundpd_ps(A, _MM_FROUND_TO_NEAREST_INT |
_MM_FROUND_NO_EXC);
}
__m256 test_mm512_mask_cvt_roundpd_ps(__m256 W, __mmask8 U,__m512d A)
{
// CHECK-LABEL: @test_mm512_mask_cvt_roundpd_ps
// CHECK: @llvm.x86.avx512.mask.cvtpd2ps.512
- return _mm512_mask_cvt_roundpd_ps(W,U,A,4);
+ return _mm512_mask_cvt_roundpd_ps(W,U,A,_MM_FROUND_TO_NEAREST_INT |
_MM_FROUND_NO_EXC);
}
__m256 test_mm512_maskz_cvt_roundpd_ps(__mmask8 U, __m512d A)
{
// CHECK-LABEL: @test_mm512_maskz_cvt_roundpd_ps
// CHECK: @llvm.x86.avx512.mask.cvtpd2ps.512
- return _mm512_maskz_cvt_roundpd_ps(U,A,4);
+ return _mm512_maskz_cvt_roundpd_ps(U,A,_MM_FROUND_TO_NEAREST_INT |
_MM_FROUND_NO_EXC);
}
__m256i test_mm512_cvtt_roundpd_epi32(__m512d A)
{
// CHECK-LABEL: @test_mm512_cvtt_roundpd_epi32
// CHECK: @llvm.x86.avx512.mask.cvttpd2dq.512
- return _mm512_cvtt_roundpd_epi32(A,4);
+ return _mm512_cvtt_roundpd_epi32(A,_MM_FROUND_TO_NEAREST_INT |
_MM_FROUND_NO_EXC);
}
__m256i test_mm512_mask_cvtt_roundpd_epi32(__m256i W, __mmask8 U, __m512d A)
{
// CHECK-LABEL: @test_mm512_mask_cvtt_roundpd_epi32
// CHECK: @llvm.x86.avx512.mask.cvttpd2dq.512
- return _mm512_mask_cvtt_roundpd_epi32(W,U,A,4);
+ return _mm512_mask_cvtt_roundpd_epi32(W,U,A,_MM_FROUND_TO_NEAREST_INT |
_MM_FROUND_NO_EXC);
}
__m256i test_mm512_maskz_cvtt_roundpd_epi32(__mmask8 U, __m512d A)
{
// CHECK-LABEL: @test_mm512_maskz_cvtt_roundpd_epi32
// CHECK: @llvm.x86.avx512.mask.cvttpd2dq.512
- return _mm512_maskz_cvtt_roundpd_epi32(U,A,4);
+ return _mm512_maskz_cvtt_roundpd_epi32(U,A,_MM_FROUND_TO_NEAREST_INT |
_MM_FROUND_NO_EXC);
+}
+
+__m512i test_mm512_cvtt_roundps_epi32(__m512 A)
+{
+ // CHECK-LABEL: @test_mm512_cvtt_roundps_epi32
+ // CHECK: @llvm.x86.avx512.mask.cvttps2dq.512
+ return _mm512_cvtt_roundps_epi32(A,_MM_FROUND_TO_NEAREST_INT |
_MM_FROUND_NO_EXC);
}
__m512i test_mm512_mask_cvtt_roundps_epi32(__m512i W,__mmask16 U, __m512 A)
{
// CHECK-LABEL: @test_mm512_mask_cvtt_roundps_epi32
// CHECK: @llvm.x86.avx512.mask.cvttps2dq.512
- return _mm512_mask_cvtt_roundps_epi32(W,U,A,4);
+ return _mm512_mask_cvtt_roundps_epi32(W,U,A,_MM_FROUND_TO_NEAREST_INT |
_MM_FROUND_NO_EXC);
}
__m512i test_mm512_maskz_cvtt_roundps_epi32(__mmask16 U, __m512 A)
{
// CHECK-LABEL: @test_mm512_maskz_cvtt_roundps_epi32
// CHECK: @llvm.x86.avx512.mask.cvttps2dq.512
- return _mm512_maskz_cvtt_roundps_epi32(U,A,4);
+ return _mm512_maskz_cvtt_roundps_epi32(U,A,_MM_FROUND_TO_NEAREST_INT |
_MM_FROUND_NO_EXC);
+}
+
+__m512i test_mm512_cvt_roundps_epi32(__m512 __A)
+{
+ // CHECK-LABEL: @test_mm512_cvt_roundps_epi32
+ // CHECK: @llvm.x86.avx512.mask.cvtps2dq.512
+ return _mm512_cvt_roundps_epi32(__A,_MM_FROUND_TO_NEAREST_INT |
_MM_FROUND_NO_EXC);
}
__m512i test_mm512_mask_cvt_roundps_epi32(__m512i __W,__mmask16 __U,__m512 __A)
{
// CHECK-LABEL: @test_mm512_mask_cvt_roundps_epi32
// CHECK: @llvm.x86.avx512.mask.cvtps2dq.512
- return _mm512_mask_cvt_roundps_epi32(__W,__U,__A,4);
+ return _mm512_mask_cvt_roundps_epi32(__W,__U,__A,_MM_FROUND_TO_NEAREST_INT |
_MM_FROUND_NO_EXC);
}
__m512i test_mm512_maskz_cvt_roundps_epi32(__mmask16 __U, __m512 __A)
{
// CHECK-LABEL: @test_mm512_maskz_cvt_roundps_epi32
// CHECK: @llvm.x86.avx512.mask.cvtps2dq.512
- return _mm512_maskz_cvt_roundps_epi32(__U,__A,4);
+ return _mm512_maskz_cvt_roundps_epi32(__U,__A,_MM_FROUND_TO_NEAREST_INT |
_MM_FROUND_NO_EXC);
+}
+
+__m256i test_mm512_cvt_roundpd_epi32(__m512d A)
+{
+ // CHECK-LABEL: @test_mm512_cvt_roundpd_epi32
+ // CHECK: @llvm.x86.avx512.mask.cvtpd2dq.512
+ return _mm512_cvt_roundpd_epi32(A,_MM_FROUND_TO_NEAREST_INT |
_MM_FROUND_NO_EXC);
}
__m256i test_mm512_mask_cvt_roundpd_epi32(__m256i W,__mmask8 U,__m512d A)
{
// CHECK-LABEL: @test_mm512_mask_cvt_roundpd_epi32
// CHECK: @llvm.x86.avx512.mask.cvtpd2dq.512
- return _mm512_mask_cvt_roundpd_epi32(W,U,A,4);
+ return _mm512_mask_cvt_roundpd_epi32(W,U,A,_MM_FROUND_TO_NEAREST_INT |
_MM_FROUND_NO_EXC);
}
__m256i test_mm512_maskz_cvt_roundpd_epi32(__mmask8 U, __m512d A)
{
// CHECK-LABEL: @test_mm512_maskz_cvt_roundpd_epi32
// CHECK: @llvm.x86.avx512.mask.cvtpd2dq.512
- return _mm512_maskz_cvt_roundpd_epi32(U,A,4);
+ return _mm512_maskz_cvt_roundpd_epi32(U,A,_MM_FROUND_TO_NEAREST_INT |
_MM_FROUND_NO_EXC);
+}
+
+__m512i test_mm512_cvt_roundps_epu32(__m512 __A)
+{
+ // CHECK-LABEL: @test_mm512_cvt_roundps_epu32
+ // CHECK: @llvm.x86.avx512.mask.cvtps2udq.512
+ return _mm512_cvt_roundps_epu32(__A,_MM_FROUND_TO_NEAREST_INT |
_MM_FROUND_NO_EXC);
}
__m512i test_mm512_mask_cvt_roundps_epu32(__m512i __W,__mmask16 __U,__m512 __A)
{
// CHECK-LABEL: @test_mm512_mask_cvt_roundps_epu32
// CHECK: @llvm.x86.avx512.mask.cvtps2udq.512
- return _mm512_mask_cvt_roundps_epu32(__W,__U,__A,4);
+ return _mm512_mask_cvt_roundps_epu32(__W,__U,__A,_MM_FROUND_TO_NEAREST_INT |
_MM_FROUND_NO_EXC);
}
__m512i test_mm512_maskz_cvt_roundps_epu32(__mmask16 __U,__m512 __A)
{
// CHECK-LABEL: @test_mm512_maskz_cvt_roundps_epu32
// CHECK: @llvm.x86.avx512.mask.cvtps2udq.512
- return _mm512_maskz_cvt_roundps_epu32(__U,__A, 4);
+ return _mm512_maskz_cvt_roundps_epu32(__U,__A, _MM_FROUND_TO_NEAREST_INT |
_MM_FROUND_NO_EXC);
+}
+
+__m256i test_mm512_cvt_roundpd_epu32(__m512d A)
+{
+ // CHECK-LABEL: @test_mm512_cvt_roundpd_epu32
+ // CHECK: @llvm.x86.avx512.mask.cvtpd2udq.512
+ return _mm512_cvt_roundpd_epu32(A,_MM_FROUND_TO_NEAREST_INT |
_MM_FROUND_NO_EXC);
}
__m256i test_mm512_mask_cvt_roundpd_epu32(__m256i W, __mmask8 U, __m512d A)
{
// CHECK-LABEL: @test_mm512_mask_cvt_roundpd_epu32
// CHECK: @llvm.x86.avx512.mask.cvtpd2udq.512
- return _mm512_mask_cvt_roundpd_epu32(W,U,A,4);
+ return _mm512_mask_cvt_roundpd_epu32(W,U,A,_MM_FROUND_TO_NEAREST_INT |
_MM_FROUND_NO_EXC);
}
__m256i test_mm512_maskz_cvt_roundpd_epu32(__mmask8 U, __m512d A)
{
// CHECK-LABEL: @test_mm512_maskz_cvt_roundpd_epu32
// CHECK: @llvm.x86.avx512.mask.cvtpd2udq.512
- return _mm512_maskz_cvt_roundpd_epu32(U, A, 4);
+ return _mm512_maskz_cvt_roundpd_epu32(U, A, _MM_FROUND_TO_NEAREST_INT |
_MM_FROUND_NO_EXC);
}
__m512 test_mm512_mask2_permutex2var_ps(__m512 __A, __m512i __I, __mmask16
__U, __m512 __B) {
_______________________________________________
cfe-commits mailing list
cfe-commits@lists.llvm.org
http://lists.llvm.org/cgi-bin/mailman/listinfo/cfe-commits
