[Headers][X86] Allow AVX/AVX512 generic integer conversion intrinsics to be used in constexpr

[RKSimon]

Followup to #152315, these are all the remaining integer intrinsics I can locate that just wrap __builtin_convertvector/__builtin_shufflevector and can be easily used in constexpr with suitable test coverage

avx512fintrin.h
_mm512_mask_cvtepi8_epi32 _mm512_maskz_cvtepi8_epi32
_mm512_mask_cvtepi8_epi64 _mm512_maskz_cvtepi8_epi64
_mm512_mask_cvtepi16_epi32 _mm512_maskz_cvtepi16_epi32
_mm512_mask_cvtepi16_epi64 _mm512_maskz_cvtepi16_epi64
_mm512_mask_cvtepi32_epi64 _mm512_maskz_cvtepi32_epi64

_mm512_mask_cvtepu8_epi32 _mm512_maskz_cvtepu8_epi32
_mm512_mask_cvtepu8_epi64 _mm512_maskz_cvtepu8_epi64
_mm512_mask_cvtepu16_epi32 _mm512_maskz_cvtepu16_epi32
_mm512_mask_cvtepu16_epi64 _mm512_maskz_cvtepu16_epi64
_mm512_mask_cvtepu32_epi64 _mm512_maskz_cvtepu32_epi64

avx512vlintrin.h
_mm_cvtepi32_epi8 _mm_mask_cvtepi32_epi8 _mm_maskz_cvtepi32_epi8
_mm_cvtepi32_epi16 _mm_mask_cvtepi32_epi16 _mm_maskz_cvtepi32_epi16
_mm_cvtepi64_epi8 _mm_mask_cvtepi64_epi8 _mm_maskz_cvtepi64_epi8
_mm_cvtepi64_epi16 _mm_mask_cvtepi64_epi16 _mm_maskz_cvtepi64_epi16
_mm_cvtepi64_epi32 _mm_mask_cvtepi64_epi32 _mm_maskz_cvtepi64_epi32
_mm256_cvtepi32_epi8 _mm256_mask_cvtepi32_epi8 _mm256_maskz_cvtepi32_epi8
_mm256_cvtepi32_epi16 _mm256_mask_cvtepi32_epi16 _mm256_maskz_cvtepi32_epi16
_mm256_cvtepi64_epi8 _mm256_mask_cvtepi64_epi8 _mm256_maskz_cvtepi64_epi8
_mm256_cvtepi64_epi16 _mm256_mask_cvtepi64_epi16 _mm256_maskz_cvtepi64_epi16
_mm256_cvtepi64_epi32 _mm256_mask_cvtepi64_epi32 _mm256_maskz_cvtepi64_epi32

avx512bwintrin.h
_mm512_mask_cvtepi8_epi16 _mm512_maskz_cvtepi8_epi16
_mm512_mask_cvtepu8_epi16 _mm512_maskz_cvtepu8_epi16

avx512vlbwintrin.h
_mm_cvtepi16_epi8 _mm_mask_cvtepi16_epi8 _mm_maskz_cvtepi16_epi8
_mm256_cvtepi16_epi8 _mm256_mask_cvtepi16_epi8 _mm256_maskz_cvtepi16_epi8

I may have missed a few others :/

[llvmbot]

@llvm/issue-subscribers-backend-x86

Author: Simon Pilgrim (RKSimon)

Followup to #152315, these are all the remaining intrinsics I can locate that just wrap __builtin_convertvector/__builtin_shufflevector and can be easily used in constexpr with suitable test coverage

avxintrin.h
_mm256_cvtepi32_pd
_mm256_cvtepi32_ps
_mm256_cvtps_pd

avx512fintrin.h
_mm512_cvtepi32_ps _mm512_mask_cvtepi32_ps _mm512_maskz_cvtepi32_ps
_mm512_cvtepu32_ps _mm512_mask_cvtepu32_ps _mm512_maskz_cvtepu32_ps
_mm512_cvtepi32_pd _mm512_mask_cvtepi32_pd _mm512_maskz_cvtepi32_pd _mm512_cvtepi32lo_pd _mm512_mask_cvtepi32lo_pd 
_mm512_cvtepu32_pd _mm512_mask_cvtepu32_pd _mm512_maskz_cvtepu32_pd _mm512_cvtepu32lo_pd _mm512_mask_cvtepu32lo_pd

_mm512_cvtps_pd _mm512_mask_cvtps_pd _mm512_maskz_cvtps_pd _mm512_cvtpslo_pd _mm512_mask_cvtpslo_pd

_mm512_mask_cvtepi8_epi32 _mm512_maskz_cvtepi8_epi32
_mm512_mask_cvtepi8_epi64 _mm512_maskz_cvtepi8_epi64
_mm512_mask_cvtepi16_epi32 _mm512_maskz_cvtepi16_epi32
_mm512_mask_cvtepi16_epi64 _mm512_maskz_cvtepi16_epi64
_mm512_mask_cvtepi32_epi64 _mm512_maskz_cvtepi32_epi64

_mm512_mask_cvtepu8_epi32 _mm512_maskz_cvtepu8_epi32
_mm512_mask_cvtepu8_epi64 _mm512_maskz_cvtepu8_epi64
_mm512_mask_cvtepu16_epi32 _mm512_maskz_cvtepu16_epi32
_mm512_mask_cvtepu16_epi64 _mm512_maskz_cvtepu16_epi64
_mm512_mask_cvtepu32_epi64 _mm512_maskz_cvtepu32_epi64

avx512vlintrin.h
_mm_mask_cvtepi32_pd _mm_maskz_cvtepi32_pd
_mm_mask_cvtepi32_ps _mm_maskz_cvtepi32_ps
_mm_cvtepu32_pd _mm_mask_cvtepu32_pd _mm_maskz_cvtepu32_pd
_mm_cvtepu32_ps _mm_mask_cvtepu32_ps _mm_maskz_cvtepu32_ps
_mm256_mask_cvtepi32_pd _mm256_maskz_cvtepi32_pd
_mm256_mask_cvtepi32_ps _mm256_maskz_cvtepi32_ps
_mm256_cvtepu32_pd _mm256_mask_cvtepu32_pd _mm256_maskz_cvtepu32_pd
_mm256_cvtepu32_ps _mm256_mask_cvtepu32_ps _mm256_maskz_cvtepu32_ps

_mm_cvtepi32_epi8 _mm_mask_cvtepi32_epi8 _mm_maskz_cvtepi32_epi8
_mm_cvtepi32_epi16 _mm_mask_cvtepi32_epi16 _mm_maskz_cvtepi32_epi16
_mm_cvtepi64_epi8 _mm_mask_cvtepi64_epi8 _mm_maskz_cvtepi64_epi8
_mm_cvtepi64_epi16 _mm_mask_cvtepi64_epi16 _mm_maskz_cvtepi64_epi16
_mm_cvtepi64_epi32 _mm_mask_cvtepi64_epi32 _mm_maskz_cvtepi64_epi32
_mm256_cvtepi32_epi8 _mm256_mask_cvtepi32_epi8 _mm256_maskz_cvtepi32_epi8
_mm256_cvtepi32_epi16 _mm256_mask_cvtepi32_epi16 _mm256_maskz_cvtepi32_epi16
_mm256_cvtepi64_epi8 _mm256_mask_cvtepi64_epi8 _mm256_maskz_cvtepi64_epi8
_mm256_cvtepi64_epi16 _mm256_mask_cvtepi64_epi16 _mm256_maskz_cvtepi64_epi16
_mm256_cvtepi64_epi32 _mm256_mask_cvtepi64_epi32 _mm256_maskz_cvtepi64_epi32

avx512dqintrin.h
_mm512_cvtepi64_pd _mm512_mask_cvtepi64_pd _mm512_maskz_cvtepi64_pd
_mm512_cvtepu64_pd _mm512_mask_cvtepu64_pd _mm512_maskz_cvtepu64_pd

avx512vldqintrin.h
_mm_cvtepi64_pd _mm_mask_cvtepi64_pd _mm_maskz_cvtepi64_pd
_mm_cvtepu64_pd _mm_mask_cvtepu64_pd _mm_maskz_cvtepu64_pd
_mm_cvtepi64_ps _mm_mask_cvtepi64_ps _mm_maskz_cvtepi64_ps
_mm_cvtepu64_ps _mm_mask_cvtepu64_ps _mm_maskz_cvtepu64_ps
_mm256_cvtepi64_pd _mm256_mask_cvtepi64_pd _mm256_maskz_cvtepi64_pd
_mm256_cvtepu64_pd _mm256_mask_cvtepu64_pd _mm256_maskz_cvtepu64_pd
_mm256_cvtepi64_ps _mm256_mask_cvtepi64_ps _mm256_maskz_cvtepi64_ps
_mm256_cvtepu64_ps _mm256_mask_cvtepu64_ps _mm256_maskz_cvtepu64_ps

avx512bwintrin.h
_mm512_mask_cvtepi8_epi16 _mm512_maskz_cvtepi8_epi16
_mm512_mask_cvtepu8_epi16 _mm512_maskz_cvtepu8_epi16

avx512vlbwintrin.h
_mm_cvtepi16_epi8 _mm_mask_cvtepi16_epi8 _mm_maskz_cvtepi16_epi8
_mm256_cvtepi16_epi8 _mm256_mask_cvtepi16_epi8 _mm256_maskz_cvtepi16_epi8

avx512vlfp16intrin.h
_mm_cvtepi16_ph _mm_mask_cvtepi16_ph _mm_maskz_cvtepi16_ph
_mm_cvtepu16_ph _mm_mask_cvtepu16_ph _mm_maskz_cvtepu16_ph
_mm256_cvtepi16_ph _mm256_mask_cvtepi16_ph _mm256_maskz_cvtepi16_ph
_mm256_cvtepu16_ph _mm256_mask_cvtepu16_ph _mm256_maskz_cvtepu16_ph
_mm256_cvtepi32_ph _mm256_mask_cvtepi32_ph _mm256_maskz_cvtepi32_ph
_mm256_cvtepu32_ph _mm256_mask_cvtepu32_ph _mm256_maskz_cvtepu32_ph

I may have missed a few others :/

[llvmbot]

Hi!

This issue may be a good introductory issue for people new to working on LLVM. If you would like to work on this issue, your first steps are:

1. Check that no other contributor is working on this issue. If someone is assigned to the issue or claimed to be working on it, ping the person. After one week without a response, the assignee may be changed.
2. Leave a comment indicating that you are working on the issue, or just create a pull request after following the steps below. Mention this issue in the description of the pull request.
3. Fix the issue locally.
4. Run the test suite locally. Remember that the subdirectories under test/ create fine-grained testing targets, so you can e.g. use make check-clang-ast to only run Clang's AST tests.
5. Create a Git commit.
6. Run git clang-format HEAD~1 to format your changes.
7. Open a pull request to the upstream repository on GitHub. Detailed instructions can be found in GitHub's documentation. Mention this issue in the description of the pull request.

If you have any further questions about this issue, don't hesitate to ask via a comment in the thread below.

[llvmbot]

@llvm/issue-subscribers-good-first-issue

Author: Simon Pilgrim (RKSimon)

Followup to #152315, these are all the remaining intrinsics I can locate that just wrap __builtin_convertvector/__builtin_shufflevector and can be easily used in constexpr with suitable test coverage

avxintrin.h
_mm256_cvtepi32_pd
_mm256_cvtepi32_ps
_mm256_cvtps_pd

avx512fintrin.h
_mm512_cvtepi32_ps _mm512_mask_cvtepi32_ps _mm512_maskz_cvtepi32_ps
_mm512_cvtepu32_ps _mm512_mask_cvtepu32_ps _mm512_maskz_cvtepu32_ps
_mm512_cvtepi32_pd _mm512_mask_cvtepi32_pd _mm512_maskz_cvtepi32_pd _mm512_cvtepi32lo_pd _mm512_mask_cvtepi32lo_pd 
_mm512_cvtepu32_pd _mm512_mask_cvtepu32_pd _mm512_maskz_cvtepu32_pd _mm512_cvtepu32lo_pd _mm512_mask_cvtepu32lo_pd

_mm512_cvtps_pd _mm512_mask_cvtps_pd _mm512_maskz_cvtps_pd _mm512_cvtpslo_pd _mm512_mask_cvtpslo_pd

_mm512_mask_cvtepi8_epi32 _mm512_maskz_cvtepi8_epi32
_mm512_mask_cvtepi8_epi64 _mm512_maskz_cvtepi8_epi64
_mm512_mask_cvtepi16_epi32 _mm512_maskz_cvtepi16_epi32
_mm512_mask_cvtepi16_epi64 _mm512_maskz_cvtepi16_epi64
_mm512_mask_cvtepi32_epi64 _mm512_maskz_cvtepi32_epi64

_mm512_mask_cvtepu8_epi32 _mm512_maskz_cvtepu8_epi32
_mm512_mask_cvtepu8_epi64 _mm512_maskz_cvtepu8_epi64
_mm512_mask_cvtepu16_epi32 _mm512_maskz_cvtepu16_epi32
_mm512_mask_cvtepu16_epi64 _mm512_maskz_cvtepu16_epi64
_mm512_mask_cvtepu32_epi64 _mm512_maskz_cvtepu32_epi64

avx512vlintrin.h
_mm_mask_cvtepi32_pd _mm_maskz_cvtepi32_pd
_mm_mask_cvtepi32_ps _mm_maskz_cvtepi32_ps
_mm_cvtepu32_pd _mm_mask_cvtepu32_pd _mm_maskz_cvtepu32_pd
_mm_cvtepu32_ps _mm_mask_cvtepu32_ps _mm_maskz_cvtepu32_ps
_mm256_mask_cvtepi32_pd _mm256_maskz_cvtepi32_pd
_mm256_mask_cvtepi32_ps _mm256_maskz_cvtepi32_ps
_mm256_cvtepu32_pd _mm256_mask_cvtepu32_pd _mm256_maskz_cvtepu32_pd
_mm256_cvtepu32_ps _mm256_mask_cvtepu32_ps _mm256_maskz_cvtepu32_ps

_mm_cvtepi32_epi8 _mm_mask_cvtepi32_epi8 _mm_maskz_cvtepi32_epi8
_mm_cvtepi32_epi16 _mm_mask_cvtepi32_epi16 _mm_maskz_cvtepi32_epi16
_mm_cvtepi64_epi8 _mm_mask_cvtepi64_epi8 _mm_maskz_cvtepi64_epi8
_mm_cvtepi64_epi16 _mm_mask_cvtepi64_epi16 _mm_maskz_cvtepi64_epi16
_mm_cvtepi64_epi32 _mm_mask_cvtepi64_epi32 _mm_maskz_cvtepi64_epi32
_mm256_cvtepi32_epi8 _mm256_mask_cvtepi32_epi8 _mm256_maskz_cvtepi32_epi8
_mm256_cvtepi32_epi16 _mm256_mask_cvtepi32_epi16 _mm256_maskz_cvtepi32_epi16
_mm256_cvtepi64_epi8 _mm256_mask_cvtepi64_epi8 _mm256_maskz_cvtepi64_epi8
_mm256_cvtepi64_epi16 _mm256_mask_cvtepi64_epi16 _mm256_maskz_cvtepi64_epi16
_mm256_cvtepi64_epi32 _mm256_mask_cvtepi64_epi32 _mm256_maskz_cvtepi64_epi32

avx512dqintrin.h
_mm512_cvtepi64_pd _mm512_mask_cvtepi64_pd _mm512_maskz_cvtepi64_pd
_mm512_cvtepu64_pd _mm512_mask_cvtepu64_pd _mm512_maskz_cvtepu64_pd

avx512vldqintrin.h
_mm_cvtepi64_pd _mm_mask_cvtepi64_pd _mm_maskz_cvtepi64_pd
_mm_cvtepu64_pd _mm_mask_cvtepu64_pd _mm_maskz_cvtepu64_pd
_mm_cvtepi64_ps _mm_mask_cvtepi64_ps _mm_maskz_cvtepi64_ps
_mm_cvtepu64_ps _mm_mask_cvtepu64_ps _mm_maskz_cvtepu64_ps
_mm256_cvtepi64_pd _mm256_mask_cvtepi64_pd _mm256_maskz_cvtepi64_pd
_mm256_cvtepu64_pd _mm256_mask_cvtepu64_pd _mm256_maskz_cvtepu64_pd
_mm256_cvtepi64_ps _mm256_mask_cvtepi64_ps _mm256_maskz_cvtepi64_ps
_mm256_cvtepu64_ps _mm256_mask_cvtepu64_ps _mm256_maskz_cvtepu64_ps

avx512bwintrin.h
_mm512_mask_cvtepi8_epi16 _mm512_maskz_cvtepi8_epi16
_mm512_mask_cvtepu8_epi16 _mm512_maskz_cvtepu8_epi16

avx512vlbwintrin.h
_mm_cvtepi16_epi8 _mm_mask_cvtepi16_epi8 _mm_maskz_cvtepi16_epi8
_mm256_cvtepi16_epi8 _mm256_mask_cvtepi16_epi8 _mm256_maskz_cvtepi16_epi8

avx512vlfp16intrin.h
_mm_cvtepi16_ph _mm_mask_cvtepi16_ph _mm_maskz_cvtepi16_ph
_mm_cvtepu16_ph _mm_mask_cvtepu16_ph _mm_maskz_cvtepu16_ph
_mm256_cvtepi16_ph _mm256_mask_cvtepi16_ph _mm256_maskz_cvtepi16_ph
_mm256_cvtepu16_ph _mm256_mask_cvtepu16_ph _mm256_maskz_cvtepu16_ph
_mm256_cvtepi32_ph _mm256_mask_cvtepi32_ph _mm256_maskz_cvtepi32_ph
_mm256_cvtepu32_ph _mm256_mask_cvtepu32_ph _mm256_maskz_cvtepu32_ph

I may have missed a few others :/

[ckoparkar]

@RKSimon can you assign this to me?

[RKSimon]

CC @sivk-kex and @vso42

[RKSimon]

To reduce the scope of each task, I've split off the fp conversions here: #155798