[Headers][X86] Allow AVX512 masked shuffles 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, most just need a header tweak and test coverage:

_mm_mask_set1_epi32 _mm_maskz_set1_epi32
_mm_mask_set1_epi64 _mm_maskz_set1_epi64
_mm256_mask_set1_epi32 _mm256_maskz_set1_epi32
_mm256_mask_set1_epi64 _mm256_maskz_set1_epi64
_mm512_mask_set1_epi32 _mm512_maskz_set1_epi32
_mm512_mask_set1_epi64 _mm512_maskz_set1_epi64

_mm_mask_broadcast_i32x2 _mm_mask_broadcast_i32x2
_mm256_mask_broadcast_f32x2 _mm256_maskz_broadcast_f32x2
_mm256_mask_broadcast_f64x2 _mm256_maskx_broadcast_f64x2
_mm256_mask_broadcast_i32x2 _mm256_maskz_broadcast_i32x2
_mm256_mask_broadcast_i64x2 _mm256_maskz_broadcast_i64x2

_mm512_mask_broadcast_f32x2 _mm512_maskz_broadcast_f32x2
_mm512_mask_broadcast_f32x8 _mm512_maskz_broadcast_f32x8
_mm512_mask_broadcast_f64x2 _mm512_maskz_broadcast_f64x2
_mm512_mask_broadcast_i32x2 _mm512_maskz_broadcast_i32x2
_mm512_mask_broadcast_i32x8 _mm512_maskz_broadcast_i32x8
_mm512_mask_broadcast_i64x2 _mm512_maskz_broadcast_i64x2
_mm256_mask_broadcast_i32x4 _mm256_maskz_broadcast_i32x4
_mm256_mask_broadcast_f32x4 _mm256_maskz_broadcast_f32x4

_mm_mask_broadcastss_ps _mm_maskz_broadcastss_ps
_mm256_mask_broadcastsd_pd _mm256_maskz_broadcastsd_pd
_mm256_mask_broadcastss_ps _mm256_maskz_broadcastss_ps
_mm_mask_broadcastd_epi32 _mm_maskz_broadcastd_epi32
_mm_mask_broadcastq_epi64 _mm_maskz_broadcastq_epi64
_mm256_mask_broadcastd_epi32 _mm256_maskz_broadcastd_epi32
_mm256_mask_broadcastq_epi64 _mm256_maskz_broadcastq_epi64
_mm512_mask_broadcastd_epi32 / _mm512_maskz_broadcastd_epi32
_mm512_mask_broadcastq_epi64 / _mm512_maskz_broadcastq_epi64

_mm_mask_movehdup_ps / _mm_maskz_movehdup_ps
_mm_mask_moveldup_ps / _mm_maskz_moveldup_ps
_mm_mask_unpackhi_pd / _mm_maskz_unpackhi_pd
_mm_mask_unpacklo_pd / _mm_maskz_unpacklo_pd
_mm_mask_unpackhi_ps / _mm_maskz_unpackhi_ps
_mm_mask_unpacklo_ps / _mm_maskz_unpacklo_ps
_mm_mask_unpackhi_epi64 / _mm_maskz_unpackhi_epi64
_mm_mask_unpacklo_epi64 / _mm_maskz_unpacklo_epi64
_mm_mask_unpackhi_epi32 / _mm_maskz_unpackhi_epi32
_mm_mask_unpacklo_epi32 / _mm_maskz_unpacklo_epi32

_mm256_mask_movehdup_ps / _mm256_maskz_movehdup_ps
_mm256_mask_moveldup_ps / _mm256_maskz_moveldup_ps
_mm256_mask_unpackhi_pd / _mm256_maskz_unpackhi_pd
_mm256_mask_unpacklo_pd / _mm256_maskz_unpacklo_pd
_mm256_mask_unpackhi_ps / _mm256_maskz_unpackhi_ps
_mm256_mask_unpacklo_ps / _mm256_maskz_unpacklo_ps
_mm256_mask_unpackhi_epi64 / _mm256_maskz_unpackhi_epi64
_mm256_mask_unpacklo_epi64 / _mm256_maskz_unpacklo_epi64
_mm256_mask_unpackhi_epi32 / _mm256_maskz_unpackhi_epi32
_mm256_mask_unpacklo_epi32 / _mm256_maskz_unpacklo_epi32

_mm512_mask_movehdup_ps / _mm512_maskz_movehdup_ps
_mm512_mask_moveldup_ps / _mm512_maskz_moveldup_ps
_mm512_mask_unpackhi_pd / _mm512_maskz_unpackhi_pd
_mm512_mask_unpacklo_pd / _mm512_maskz_unpacklo_pd
_mm512_mask_unpackhi_ps / _mm512_maskz_unpackhi_ps
_mm512_mask_unpacklo_ps / _mm512_maskz_unpacklo_ps
_mm512_mask_unpackhi_epi64 / _mm512_maskz_unpackhi_epi64
_mm512_mask_unpacklo_epi64 / _mm512_maskz_unpacklo_epi64
_mm512_mask_unpackhi_epi32 / _mm512_maskz_unpackhi_epi32
_mm512_mask_unpacklo_epi32 / _mm512_maskz_unpacklo_epi32

_mm_mask_move_ss / _mm_maskz_move_ss
_mm_mask_move_sd / _mm_maskz_move_sd

(I may have missed some shuffle cases from avx512fintrin.h / avx512vlintrin.h)

[llvmbot]

@llvm/issue-subscribers-backend-x86

Author: Simon Pilgrim (RKSimon)

These appear to be missed in earlier patches like #152313 as we didn't have mask/maskz constexpr support back then, most just need a header tweak and test coverage: ``` _mm_mask_set1_epi32 _mm_maskz_set1_epi32 _mm_mask_set1_epi64 _mm_maskz_set1_epi64 _mm256_mask_set1_epi32 _mm256_maskz_set1_epi32 _mm256_mask_set1_epi64 _mm256_maskz_set1_epi64 _mm512_mask_set1_epi32 _mm512_maskz_set1_epi32 _mm512_mask_set1_epi64 _mm512_maskz_set1_epi64

_mm_mask_broadcast_i32x2 _mm_mask_broadcast_i32x2
_mm256_mask_broadcast_f32x2 _mm256_maskz_broadcast_f32x2
_mm256_mask_broadcast_f64x2 _mm256_maskx_broadcast_f64x2
_mm256_mask_broadcast_i32x2 _mm256_maskz_broadcast_i32x2
_mm256_mask_broadcast_i64x2 _mm256_maskz_broadcast_i64x2

_mm512_mask_broadcast_f32x2 _mm512_maskz_broadcast_f32x2
_mm512_mask_broadcast_f32x8 _mm512_maskz_broadcast_f32x8
_mm512_mask_broadcast_f64x2 _mm512_maskz_broadcast_f64x2
_mm512_mask_broadcast_i32x2 _mm512_maskz_broadcast_i32x2
_mm512_mask_broadcast_i32x8 _mm512_maskz_broadcast_i32x8
_mm512_mask_broadcast_i64x2 _mm512_maskz_broadcast_i64x2
_mm256_mask_broadcast_i32x4 _mm256_maskz_broadcast_i32x4
_mm256_mask_broadcast_f32x4 _mm256_maskz_broadcast_f32x4

_mm_mask_broadcastss_ps _mm_maskz_broadcastss_ps
_mm256_mask_broadcastsd_pd _mm256_maskz_broadcastsd_pd
_mm256_mask_broadcastss_ps _mm256_maskz_broadcastss_ps
_mm_mask_broadcastd_epi32 _mm_maskz_broadcastd_epi32
_mm_mask_broadcastq_epi64 _mm_maskz_broadcastq_epi64
_mm256_mask_broadcastd_epi32 _mm256_maskz_broadcastd_epi32
_mm256_mask_broadcastq_epi64 _mm256_maskz_broadcastq_epi64
_mm512_mask_broadcastd_epi32 / _mm512_maskz_broadcastd_epi32
_mm512_mask_broadcastq_epi64 / _mm512_maskz_broadcastq_epi64

_mm_mask_movehdup_ps / _mm_maskz_movehdup_ps
_mm_mask_moveldup_ps / _mm_maskz_moveldup_ps
_mm_mask_unpackhi_pd / _mm_maskz_unpackhi_pd
_mm_mask_unpacklo_pd / _mm_maskz_unpacklo_pd
_mm_mask_unpackhi_ps / _mm_maskz_unpackhi_ps
_mm_mask_unpacklo_ps / _mm_maskz_unpacklo_ps
_mm_mask_unpackhi_epi64 / _mm_maskz_unpackhi_epi64
_mm_mask_unpacklo_epi64 / _mm_maskz_unpacklo_epi64
_mm_mask_unpackhi_epi32 / _mm_maskz_unpackhi_epi32
_mm_mask_unpacklo_epi32 / _mm_maskz_unpacklo_epi32

_mm256_mask_movehdup_ps / _mm256_maskz_movehdup_ps
_mm256_mask_moveldup_ps / _mm256_maskz_moveldup_ps
_mm256_mask_unpackhi_pd / _mm256_maskz_unpackhi_pd
_mm256_mask_unpacklo_pd / _mm256_maskz_unpacklo_pd
_mm256_mask_unpackhi_ps / _mm256_maskz_unpackhi_ps
_mm256_mask_unpacklo_ps / _mm256_maskz_unpacklo_ps
_mm256_mask_unpackhi_epi64 / _mm256_maskz_unpackhi_epi64
_mm256_mask_unpacklo_epi64 / _mm256_maskz_unpacklo_epi64
_mm256_mask_unpackhi_epi32 / _mm256_maskz_unpackhi_epi32
_mm256_mask_unpacklo_epi32 / _mm256_maskz_unpacklo_epi32

_mm512_mask_movehdup_ps / _mm512_maskz_movehdup_ps
_mm512_mask_moveldup_ps / _mm512_maskz_moveldup_ps
_mm512_mask_unpackhi_pd / _mm512_maskz_unpackhi_pd
_mm512_mask_unpacklo_pd / _mm512_maskz_unpacklo_pd
_mm512_mask_unpackhi_ps / _mm512_maskz_unpackhi_ps
_mm512_mask_unpacklo_ps / _mm512_maskz_unpacklo_ps
_mm512_mask_unpackhi_epi64 / _mm512_maskz_unpackhi_epi64
_mm512_mask_unpacklo_epi64 / _mm512_maskz_unpacklo_epi64
_mm512_mask_unpackhi_epi32 / _mm512_maskz_unpackhi_epi32
_mm512_mask_unpacklo_epi32 / _mm512_maskz_unpacklo_epi32

_mm_mask_move_ss / _mm_maskz_move_ss
_mm_mask_move_sd / _mm_maskz_move_sd

(I may have missed some shuffle cases from avx512fintrin.h / avx512vlintrin.h)
</details>

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

These appear to be missed in earlier patches like #152313 as we didn't have mask/maskz constexpr support back then, most just need a header tweak and test coverage: ``` _mm_mask_set1_epi32 _mm_maskz_set1_epi32 _mm_mask_set1_epi64 _mm_maskz_set1_epi64 _mm256_mask_set1_epi32 _mm256_maskz_set1_epi32 _mm256_mask_set1_epi64 _mm256_maskz_set1_epi64 _mm512_mask_set1_epi32 _mm512_maskz_set1_epi32 _mm512_mask_set1_epi64 _mm512_maskz_set1_epi64

_mm_mask_broadcast_i32x2 _mm_mask_broadcast_i32x2
_mm256_mask_broadcast_f32x2 _mm256_maskz_broadcast_f32x2
_mm256_mask_broadcast_f64x2 _mm256_maskx_broadcast_f64x2
_mm256_mask_broadcast_i32x2 _mm256_maskz_broadcast_i32x2
_mm256_mask_broadcast_i64x2 _mm256_maskz_broadcast_i64x2

_mm512_mask_broadcast_f32x2 _mm512_maskz_broadcast_f32x2
_mm512_mask_broadcast_f32x8 _mm512_maskz_broadcast_f32x8
_mm512_mask_broadcast_f64x2 _mm512_maskz_broadcast_f64x2
_mm512_mask_broadcast_i32x2 _mm512_maskz_broadcast_i32x2
_mm512_mask_broadcast_i32x8 _mm512_maskz_broadcast_i32x8
_mm512_mask_broadcast_i64x2 _mm512_maskz_broadcast_i64x2
_mm256_mask_broadcast_i32x4 _mm256_maskz_broadcast_i32x4
_mm256_mask_broadcast_f32x4 _mm256_maskz_broadcast_f32x4

_mm_mask_broadcastss_ps _mm_maskz_broadcastss_ps
_mm256_mask_broadcastsd_pd _mm256_maskz_broadcastsd_pd
_mm256_mask_broadcastss_ps _mm256_maskz_broadcastss_ps
_mm_mask_broadcastd_epi32 _mm_maskz_broadcastd_epi32
_mm_mask_broadcastq_epi64 _mm_maskz_broadcastq_epi64
_mm256_mask_broadcastd_epi32 _mm256_maskz_broadcastd_epi32
_mm256_mask_broadcastq_epi64 _mm256_maskz_broadcastq_epi64
_mm512_mask_broadcastd_epi32 / _mm512_maskz_broadcastd_epi32
_mm512_mask_broadcastq_epi64 / _mm512_maskz_broadcastq_epi64

_mm_mask_movehdup_ps / _mm_maskz_movehdup_ps
_mm_mask_moveldup_ps / _mm_maskz_moveldup_ps
_mm_mask_unpackhi_pd / _mm_maskz_unpackhi_pd
_mm_mask_unpacklo_pd / _mm_maskz_unpacklo_pd
_mm_mask_unpackhi_ps / _mm_maskz_unpackhi_ps
_mm_mask_unpacklo_ps / _mm_maskz_unpacklo_ps
_mm_mask_unpackhi_epi64 / _mm_maskz_unpackhi_epi64
_mm_mask_unpacklo_epi64 / _mm_maskz_unpacklo_epi64
_mm_mask_unpackhi_epi32 / _mm_maskz_unpackhi_epi32
_mm_mask_unpacklo_epi32 / _mm_maskz_unpacklo_epi32

_mm256_mask_movehdup_ps / _mm256_maskz_movehdup_ps
_mm256_mask_moveldup_ps / _mm256_maskz_moveldup_ps
_mm256_mask_unpackhi_pd / _mm256_maskz_unpackhi_pd
_mm256_mask_unpacklo_pd / _mm256_maskz_unpacklo_pd
_mm256_mask_unpackhi_ps / _mm256_maskz_unpackhi_ps
_mm256_mask_unpacklo_ps / _mm256_maskz_unpacklo_ps
_mm256_mask_unpackhi_epi64 / _mm256_maskz_unpackhi_epi64
_mm256_mask_unpacklo_epi64 / _mm256_maskz_unpacklo_epi64
_mm256_mask_unpackhi_epi32 / _mm256_maskz_unpackhi_epi32
_mm256_mask_unpacklo_epi32 / _mm256_maskz_unpacklo_epi32

_mm512_mask_movehdup_ps / _mm512_maskz_movehdup_ps
_mm512_mask_moveldup_ps / _mm512_maskz_moveldup_ps
_mm512_mask_unpackhi_pd / _mm512_maskz_unpackhi_pd
_mm512_mask_unpacklo_pd / _mm512_maskz_unpacklo_pd
_mm512_mask_unpackhi_ps / _mm512_maskz_unpackhi_ps
_mm512_mask_unpacklo_ps / _mm512_maskz_unpacklo_ps
_mm512_mask_unpackhi_epi64 / _mm512_maskz_unpackhi_epi64
_mm512_mask_unpacklo_epi64 / _mm512_maskz_unpacklo_epi64
_mm512_mask_unpackhi_epi32 / _mm512_maskz_unpackhi_epi32
_mm512_mask_unpacklo_epi32 / _mm512_maskz_unpacklo_epi32

_mm_mask_move_ss / _mm_maskz_move_ss
_mm_mask_move_sd / _mm_maskz_move_sd

(I may have missed some shuffle cases from avx512fintrin.h / avx512vlintrin.h)
</details>