[Headers][X86] Allow AVX512 masked arithmetic intrinsics to be used in constexpr

[RKSimon]

These appear to be missed in earlier patches like #152313 as we didn't have mask/maskz constexpr support back then

avx512fintrin.h

_mm_mask_add_ss / _mm_maskz_add_ss
_mm_mask_add_sd / _mm_maskz_add_sd
_mm_mask_sub_ss / _mm_maskz_sub_ss
_mm_mask_sub_sd / _mm_maskz_sub_sd
_mm_mask_mul_ss / _mm_maskz_mul_ss
_mm_mask_mul_sd / _mm_maskz_mul_sd
_mm_mask_div_ss / _mm_maskz_div_ss
_mm_mask_div_sd / _mm_maskz_div_sd

_mm512_mask_add_pd / _mm512_maskz_add_pd
_mm512_mask_add_ps / _mm512_maskz_add_ps
_mm512_mask_sub_pd / _mm512_maskz_sub_pd
_mm512_mask_sub_ps / _mm512_maskz_sub_ps
_mm512_mask_mul_pd / _mm512_maskz_mul_pd
_mm512_mask_mul_ps / _mm512_maskz_mul_ps
_mm512_mask_div_pd / _mm512_maskz_div_pd
_mm512_mask_div_ps / _mm512_maskz_div_ps

_mm512_mask_mul_epi32 / _mm512_maskz_mul_epi32
_mm512_mask_mul_epu32 / _mm512_maskz_mul_epu32

avx512vlintrin.h

_mm_mask_add_pd / _mm_maskz_add_pd / _mm256_mask_add_pd / _mm256_maskz_add_pd
_mm_mask_add_ps / _mm_maskz_add_ps / _mm256_mask_add_ps / _mm256_maskz_add_ps
_mm_mask_sub_pd / _mm_maskz_sub_pd / _mm256_mask_sub_pd / _mm256_maskz_sub_pd
_mm_mask_sub_ps / _mm_maskz_sub_ps / _mm256_mask_sub_ps / _mm256_maskz_sub_ps
_mm_mask_mul_pd / _mm_maskz_mul_pd / _mm256_mask_mul_pd / _mm256_maskz_mul_pd
_mm_mask_mul_ps / _mm_maskz_mul_ps / _mm256_mask_mul_ps / _mm256_maskz_mul_ps
_mm_mask_div_pd / _mm_maskz_div_pd / _mm256_mask_div_pd / _mm256_maskz_div_pd
_mm_mask_div_ps / _mm_maskz_div_ps / _mm256_mask_div_ps / _mm256_maskz_div_ps

_mm_mask_mul_epi32 / _mm_maskz_mul_epi32 / _mm256_mask_mul_epi32 / _mm256_maskz_mul_epi32
_mm_mask_mul_epu32 / _mm_maskz_mul_epu32 / _mm256_mask_mul_epu32 / _mm256_maskz_mul_epu32

[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)

Details

These appear to be missed in earlier patches like https://github.com//issues/152313 as we didn't have mask/maskz constexpr support back then

avx512fintrin.h

_mm_mask_add_ss / _mm_maskz_add_ss
_mm_mask_add_sd / _mm_maskz_add_sd
_mm_mask_sub_ss / _mm_maskz_sub_ss
_mm_mask_sub_sd / _mm_maskz_sub_sd
_mm_mask_mul_ss / _mm_maskz_mul_ss
_mm_mask_mul_sd / _mm_maskz_mul_sd
_mm_mask_div_ss / _mm_maskz_div_ss
_mm_mask_div_sd / _mm_maskz_div_sd

_mm512_mask_add_pd / _mm512_maskz_add_pd
_mm512_mask_add_ps / _mm512_maskz_add_ps
_mm512_mask_sub_pd / _mm512_maskz_sub_pd
_mm512_mask_sub_ps / _mm512_maskz_sub_ps
_mm512_mask_mul_pd / _mm512_maskz_mul_pd
_mm512_mask_mul_ps / _mm512_maskz_mul_ps
_mm512_mask_div_pd / _mm512_maskz_div_pd
_mm512_mask_div_ps / _mm512_maskz_div_ps

_mm512_mask_mul_epi32 / _mm512_maskz_mul_epi32
_mm512_mask_mul_epu32 / _mm512_maskz_mul_epu32

avx512vlintrin.h

_mm_mask_add_pd / _mm_maskz_add_pd / _mm256_mask_add_pd / _mm256_maskz_add_pd
_mm_mask_add_ps / _mm_maskz_add_ps / _mm256_mask_add_ps / _mm256_maskz_add_ps
_mm_mask_sub_pd / _mm_maskz_sub_pd / _mm256_mask_sub_pd / _mm256_maskz_sub_pd
_mm_mask_sub_ps / _mm_maskz_sub_ps / _mm256_mask_sub_ps / _mm256_maskz_sub_ps
_mm_mask_mul_pd / _mm_maskz_mul_pd / _mm256_mask_mul_pd / _mm256_maskz_mul_pd
_mm_mask_mul_ps / _mm_maskz_mul_ps / _mm256_mask_mul_ps / _mm256_maskz_mul_ps
_mm_mask_div_pd / _mm_maskz_div_pd / _mm256_mask_div_pd / _mm256_maskz_div_pd
_mm_mask_div_ps / _mm_maskz_div_ps / _mm256_mask_div_ps / _mm256_maskz_div_ps

_mm_mask_mul_epi32 / _mm_maskz_mul_epi32 / _mm256_mask_mul_epi32 / _mm256_maskz_mul_epi32
_mm_mask_mul_epu32 / _mm_maskz_mul_epu32 / _mm256_mask_mul_epu32 / _mm256_maskz_mul_epu32

[llvmbot]

@llvm/issue-subscribers-backend-x86

Author: Simon Pilgrim (RKSimon)

Details

These appear to be missed in earlier patches like https://github.com//issues/152313 as we didn't have mask/maskz constexpr support back then

avx512fintrin.h

_mm_mask_add_ss / _mm_maskz_add_ss
_mm_mask_add_sd / _mm_maskz_add_sd
_mm_mask_sub_ss / _mm_maskz_sub_ss
_mm_mask_sub_sd / _mm_maskz_sub_sd
_mm_mask_mul_ss / _mm_maskz_mul_ss
_mm_mask_mul_sd / _mm_maskz_mul_sd
_mm_mask_div_ss / _mm_maskz_div_ss
_mm_mask_div_sd / _mm_maskz_div_sd

_mm512_mask_add_pd / _mm512_maskz_add_pd
_mm512_mask_add_ps / _mm512_maskz_add_ps
_mm512_mask_sub_pd / _mm512_maskz_sub_pd
_mm512_mask_sub_ps / _mm512_maskz_sub_ps
_mm512_mask_mul_pd / _mm512_maskz_mul_pd
_mm512_mask_mul_ps / _mm512_maskz_mul_ps
_mm512_mask_div_pd / _mm512_maskz_div_pd
_mm512_mask_div_ps / _mm512_maskz_div_ps

_mm512_mask_mul_epi32 / _mm512_maskz_mul_epi32
_mm512_mask_mul_epu32 / _mm512_maskz_mul_epu32

avx512vlintrin.h

_mm_mask_add_pd / _mm_maskz_add_pd / _mm256_mask_add_pd / _mm256_maskz_add_pd
_mm_mask_add_ps / _mm_maskz_add_ps / _mm256_mask_add_ps / _mm256_maskz_add_ps
_mm_mask_sub_pd / _mm_maskz_sub_pd / _mm256_mask_sub_pd / _mm256_maskz_sub_pd
_mm_mask_sub_ps / _mm_maskz_sub_ps / _mm256_mask_sub_ps / _mm256_maskz_sub_ps
_mm_mask_mul_pd / _mm_maskz_mul_pd / _mm256_mask_mul_pd / _mm256_maskz_mul_pd
_mm_mask_mul_ps / _mm_maskz_mul_ps / _mm256_mask_mul_ps / _mm256_maskz_mul_ps
_mm_mask_div_pd / _mm_maskz_div_pd / _mm256_mask_div_pd / _mm256_maskz_div_pd
_mm_mask_div_ps / _mm_maskz_div_ps / _mm256_mask_div_ps / _mm256_maskz_div_ps

_mm_mask_mul_epi32 / _mm_maskz_mul_epi32 / _mm256_mask_mul_epi32 / _mm256_maskz_mul_epi32
_mm_mask_mul_epu32 / _mm_maskz_mul_epu32 / _mm256_mask_mul_epu32 / _mm256_maskz_mul_epu32

[woruyu]

I'm happy to work on this!