[Headers][X86] Allow AVX512BW masked 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

_mm_mask_set1_epi8 _mm_maskz_set1_epi8
_mm512_mask_set1_epi8 _mm512_maskz_set1_epi8 
_mm256_mask_set1_epi8 _mm256_maskz_set1_epi8
_mm_mask_set1_epi16 _mm_maskz_set1_epi16
_mm256_mask_set1_epi16 _mm256_maskz_set1_epi16
_mm512_mask_set1_epi16 _mm512_maskz_set1_epi16

_mm_mask_broadcastb_epi8 _mm_maskz_broadcastb_epi8
_mm_mask_broadcastw_epi16 _mm_maskz_broadcastw_epi16
_mm256_mask_broadcastb_epi8 _mm256_maskz_broadcastb_epi8
_mm256_mask_broadcastw_epi16 _mm256_maskz_broadcastw_epi16
_mm512_mask_broadcastb_epi8 _mm512_maskz_broadcastb_epi8
_mm512_mask_broadcastw_epi16 _mm512_maskz_broadcastw_epi16

_mm_mask_adds_epi8 _mm_maskz_adds_epi8
_mm_mask_adds_epu8 _mm_maskz_adds_epu8
_mm_mask_adds_epi16 _mm_maskz_adds_epi16
_mm_mask_adds_epu16 _mm_maskz_adds_epu16
_mm256_mask_adds_epi8 _mm256_maskz_adds_epi8
_mm256_mask_adds_epu8 _mm256_maskz_adds_epu8
_mm256_mask_adds_epi16 _mm256_maskz_adds_epi16
_mm256_mask_adds_epu16 _mm256_maskz_adds_epu16
_mm512_mask_adds_epi8 _mm512_maskz_adds_epi8
_mm512_mask_adds_epu8 _mm512_maskz_adds_epu8
_mm512_mask_adds_epi16 _mm512_maskz_adds_epi16
_mm512_mask_adds_epu16 _mm512_maskz_adds_epu16

_mm_mask_subs_epi8 _mm_maskz_subs_epi8
_mm_mask_subs_epu8 _mm_maskz_subs_epu8
_mm_mask_subs_epi16 _mm_maskz_subs_epi16
_mm_mask_subs_epu16 _mm_maskz_subs_epu16
_mm256_mask_subs_epi8 _mm256_maskz_subs_epi8
_mm256_mask_subs_epu8 _mm256_maskz_subs_epu8
_mm256_mask_subs_epi16 _mm256_maskz_subs_epi16
_mm256_mask_subs_epu16 _mm256_maskz_subs_epu16
_mm512_mask_subs_epi8 _mm512_maskz_subs_epi8
_mm512_mask_subs_epu8 _mm512_maskz_subs_epu8
_mm512_mask_subs_epi16 _mm512_maskz_subs_epi16
_mm512_mask_subs_epu16 _mm512_maskz_subs_epu16

_mm_mask_unpackhi_epi8 _mm_maskz_unpackhi_epi8
_mm_mask_unpacklo_epi8 _mm_maskz_unpacklo_epi8
_mm_mask_unpackhi_epi16 _mm_maskz_unpackhi_epi16
_mm_mask_unpacklo_epi16 _mm_maskz_unpacklo_epi16

_mm256_mask_unpackhi_epi8 _mm256_maskz_unpackhi_epi8
_mm256_mask_unpacklo_epi8 _mm256_maskz_unpacklo_epi8
_mm256_mask_unpackhi_epi16 _mm256_maskz_unpackhi_epi16
_mm256_mask_unpacklo_epi16 _mm256_maskz_unpacklo_epi16

_mm512_mask_unpackhi_epi8 _mm512_maskz_unpackhi_epi8
_mm512_mask_unpacklo_epi8 _mm512_maskz_unpacklo_epi8
_mm512_mask_unpackhi_epi16 _mm512_maskz_unpackhi_epi16
_mm512_mask_unpacklo_epi16 _mm512_maskz_unpacklo_epi16

_mm_mask_packs_epi16 _mm_maskz_packs_epi16
_mm_mask_packs_epi32 _mm_maskz_packs_epi32
_mm256_mask_packs_epi16 _mm256_maskz_packs_epi16
_mm256_mask_packs_epi32 _mm256_maskz_packs_epi32
_mm512_mask_packs_epi16 _mm512_maskz_packs_epi16
_mm512_mask_packs_epi32 _mm512_maskz_packs_epi32

_mm_mask_packus_epi16 _mm_maskz_packus_epi16
_mm_mask_packus_epi32 _mm_maskz_packus_epi32
_mm256_mask_packus_epi16 _mm256_maskz_packus_epi16
_mm256_mask_packus_epi32 _mm256_maskz_packus_epi32
_mm512_mask_packus_epi16 _mm512_maskz_packus_epi16
_mm512_mask_packus_epi32 _mm512_maskz_packus_epi32

_mm_mask_cvtepi8_epi16 _mm_maskz_cvtepi8_epi16
_mm_mask_cvtepu8_epi16 _mm_maskz_cvtepu8_epi16
_mm256_mask_cvtepi8_epi16 _mm256_maskz_cvtepi8_epi16
_mm256_mask_cvtepu8_epi16 _mm256_maskz_cvtepu8_epi16

_mm_mask_slli_epi16 _mm_mask_slli_epi16
_mm256_mask_slli_epi16 _mm256_mask_slli_epi16

_mm512_mask_mov_epi8 _mm512_maskz_mov_epi8
_mm512_mask_mov_epi16 _mm512_maskz_mov_epi16

These should just fixes to the headers along with adding test coverage to avx512bw-builtins.c and avx512vlbw-builtins.c

[llvmbot]

@llvm/issue-subscribers-backend-x86

Author: Simon Pilgrim (RKSimon)

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

_mm_mask_set1_epi8 _mm_maskz_set1_epi8
_mm512_mask_set1_epi8 _mm512_maskz_set1_epi8 
_mm256_mask_set1_epi8 _mm256_maskz_set1_epi8
_mm_mask_set1_epi16 _mm_maskz_set1_epi16
_mm256_mask_set1_epi16 _mm256_maskz_set1_epi16
_mm512_mask_set1_epi16 _mm512_maskz_set1_epi16

_mm_mask_broadcastb_epi8 _mm_maskz_broadcastb_epi8
_mm_mask_broadcastw_epi16 _mm_maskz_broadcastw_epi16
_mm256_mask_broadcastb_epi8 _mm256_maskz_broadcastb_epi8
_mm256_mask_broadcastw_epi16 _mm256_maskz_broadcastw_epi16
_mm512_mask_broadcastb_epi8 _mm512_maskz_broadcastb_epi8
_mm512_mask_broadcastw_epi16 _mm512_maskz_broadcastw_epi16

_mm_mask_adds_epi8 _mm_maskz_adds_epi8
_mm_mask_adds_epu8 _mm_maskz_adds_epu8
_mm_mask_adds_epi16 _mm_maskz_adds_epi16
_mm_mask_adds_epu16 _mm_maskz_adds_epu16
_mm256_mask_adds_epi8 _mm256_maskz_adds_epi8
_mm256_mask_adds_epu8 _mm256_maskz_adds_epu8
_mm256_mask_adds_epi16 _mm256_maskz_adds_epi16
_mm256_mask_adds_epu16 _mm256_maskz_adds_epu16
_mm512_mask_adds_epi8 _mm512_maskz_adds_epi8
_mm512_mask_adds_epu8 _mm512_maskz_adds_epu8
_mm512_mask_adds_epi16 _mm512_maskz_adds_epi16
_mm512_mask_adds_epu16 _mm512_maskz_adds_epu16

_mm_mask_subs_epi8 _mm_maskz_subs_epi8
_mm_mask_subs_epu8 _mm_maskz_subs_epu8
_mm_mask_subs_epi16 _mm_maskz_subs_epi16
_mm_mask_subs_epu16 _mm_maskz_subs_epu16
_mm256_mask_subs_epi8 _mm256_maskz_subs_epi8
_mm256_mask_subs_epu8 _mm256_maskz_subs_epu8
_mm256_mask_subs_epi16 _mm256_maskz_subs_epi16
_mm256_mask_subs_epu16 _mm256_maskz_subs_epu16
_mm512_mask_subs_epi8 _mm512_maskz_subs_epi8
_mm512_mask_subs_epu8 _mm512_maskz_subs_epu8
_mm512_mask_subs_epi16 _mm512_maskz_subs_epi16
_mm512_mask_subs_epu16 _mm512_maskz_subs_epu16

_mm_mask_unpackhi_epi8 _mm_maskz_unpackhi_epi8
_mm_mask_unpacklo_epi8 _mm_maskz_unpacklo_epi8
_mm_mask_unpackhi_epi16 _mm_maskz_unpackhi_epi16
_mm_mask_unpacklo_epi16 _mm_maskz_unpacklo_epi16

_mm256_mask_unpackhi_epi8 _mm256_maskz_unpackhi_epi8
_mm256_mask_unpacklo_epi8 _mm256_maskz_unpacklo_epi8
_mm256_mask_unpackhi_epi16 _mm256_maskz_unpackhi_epi16
_mm256_mask_unpacklo_epi16 _mm256_maskz_unpacklo_epi16

_mm512_mask_unpackhi_epi8 _mm512_maskz_unpackhi_epi8
_mm512_mask_unpacklo_epi8 _mm512_maskz_unpacklo_epi8
_mm512_mask_unpackhi_epi16 _mm512_maskz_unpackhi_epi16
_mm512_mask_unpacklo_epi16 _mm512_maskz_unpacklo_epi16

_mm_mask_packs_epi16 _mm_maskz_packs_epi16
_mm_mask_packs_epi32 _mm_maskz_packs_epi32
_mm256_mask_packs_epi16 _mm256_maskz_packs_epi16
_mm256_mask_packs_epi32 _mm256_maskz_packs_epi32
_mm512_mask_packs_epi16 _mm512_maskz_packs_epi16
_mm512_mask_packs_epi32 _mm512_maskz_packs_epi32

_mm_mask_packus_epi16 _mm_maskz_packus_epi16
_mm_mask_packus_epi32 _mm_maskz_packus_epi32
_mm256_mask_packus_epi16 _mm256_maskz_packus_epi16
_mm256_mask_packus_epi32 _mm256_maskz_packus_epi32
_mm512_mask_packus_epi16 _mm512_maskz_packus_epi16
_mm512_mask_packus_epi32 _mm512_maskz_packus_epi32

_mm_mask_cvtepi8_epi16 _mm_maskz_cvtepi8_epi16
_mm_mask_cvtepu8_epi16 _mm_maskz_cvtepu8_epi16
_mm256_mask_cvtepi8_epi16 _mm256_maskz_cvtepi8_epi16
_mm256_mask_cvtepu8_epi16 _mm256_maskz_cvtepu8_epi16

_mm_mask_slli_epi16 _mm_mask_slli_epi16
_mm256_mask_slli_epi16 _mm256_mask_slli_epi16

These should just fixes to the headers along with adding test coverage to avx512bw-builtins.c and avx512vlbw-builtins.c

[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 https://github.com//issues/152313 as we didn't have mask/maskz constexpr support back then

_mm_mask_set1_epi8 _mm_maskz_set1_epi8
_mm512_mask_set1_epi8 _mm512_maskz_set1_epi8 
_mm256_mask_set1_epi8 _mm256_maskz_set1_epi8
_mm_mask_set1_epi16 _mm_maskz_set1_epi16
_mm256_mask_set1_epi16 _mm256_maskz_set1_epi16
_mm512_mask_set1_epi16 _mm512_maskz_set1_epi16

_mm_mask_broadcastb_epi8 _mm_maskz_broadcastb_epi8
_mm_mask_broadcastw_epi16 _mm_maskz_broadcastw_epi16
_mm256_mask_broadcastb_epi8 _mm256_maskz_broadcastb_epi8
_mm256_mask_broadcastw_epi16 _mm256_maskz_broadcastw_epi16
_mm512_mask_broadcastb_epi8 _mm512_maskz_broadcastb_epi8
_mm512_mask_broadcastw_epi16 _mm512_maskz_broadcastw_epi16

_mm_mask_adds_epi8 _mm_maskz_adds_epi8
_mm_mask_adds_epu8 _mm_maskz_adds_epu8
_mm_mask_adds_epi16 _mm_maskz_adds_epi16
_mm_mask_adds_epu16 _mm_maskz_adds_epu16
_mm256_mask_adds_epi8 _mm256_maskz_adds_epi8
_mm256_mask_adds_epu8 _mm256_maskz_adds_epu8
_mm256_mask_adds_epi16 _mm256_maskz_adds_epi16
_mm256_mask_adds_epu16 _mm256_maskz_adds_epu16
_mm512_mask_adds_epi8 _mm512_maskz_adds_epi8
_mm512_mask_adds_epu8 _mm512_maskz_adds_epu8
_mm512_mask_adds_epi16 _mm512_maskz_adds_epi16
_mm512_mask_adds_epu16 _mm512_maskz_adds_epu16

_mm_mask_subs_epi8 _mm_maskz_subs_epi8
_mm_mask_subs_epu8 _mm_maskz_subs_epu8
_mm_mask_subs_epi16 _mm_maskz_subs_epi16
_mm_mask_subs_epu16 _mm_maskz_subs_epu16
_mm256_mask_subs_epi8 _mm256_maskz_subs_epi8
_mm256_mask_subs_epu8 _mm256_maskz_subs_epu8
_mm256_mask_subs_epi16 _mm256_maskz_subs_epi16
_mm256_mask_subs_epu16 _mm256_maskz_subs_epu16
_mm512_mask_subs_epi8 _mm512_maskz_subs_epi8
_mm512_mask_subs_epu8 _mm512_maskz_subs_epu8
_mm512_mask_subs_epi16 _mm512_maskz_subs_epi16
_mm512_mask_subs_epu16 _mm512_maskz_subs_epu16

_mm_mask_unpackhi_epi8 _mm_maskz_unpackhi_epi8
_mm_mask_unpacklo_epi8 _mm_maskz_unpacklo_epi8
_mm_mask_unpackhi_epi16 _mm_maskz_unpackhi_epi16
_mm_mask_unpacklo_epi16 _mm_maskz_unpacklo_epi16

_mm256_mask_unpackhi_epi8 _mm256_maskz_unpackhi_epi8
_mm256_mask_unpacklo_epi8 _mm256_maskz_unpacklo_epi8
_mm256_mask_unpackhi_epi16 _mm256_maskz_unpackhi_epi16
_mm256_mask_unpacklo_epi16 _mm256_maskz_unpacklo_epi16

_mm512_mask_unpackhi_epi8 _mm512_maskz_unpackhi_epi8
_mm512_mask_unpacklo_epi8 _mm512_maskz_unpacklo_epi8
_mm512_mask_unpackhi_epi16 _mm512_maskz_unpackhi_epi16
_mm512_mask_unpacklo_epi16 _mm512_maskz_unpacklo_epi16

_mm_mask_packs_epi16 _mm_maskz_packs_epi16
_mm_mask_packs_epi32 _mm_maskz_packs_epi32
_mm256_mask_packs_epi16 _mm256_maskz_packs_epi16
_mm256_mask_packs_epi32 _mm256_maskz_packs_epi32
_mm512_mask_packs_epi16 _mm512_maskz_packs_epi16
_mm512_mask_packs_epi32 _mm512_maskz_packs_epi32

_mm_mask_packus_epi16 _mm_maskz_packus_epi16
_mm_mask_packus_epi32 _mm_maskz_packus_epi32
_mm256_mask_packus_epi16 _mm256_maskz_packus_epi16
_mm256_mask_packus_epi32 _mm256_maskz_packus_epi32
_mm512_mask_packus_epi16 _mm512_maskz_packus_epi16
_mm512_mask_packus_epi32 _mm512_maskz_packus_epi32

_mm_mask_cvtepi8_epi16 _mm_maskz_cvtepi8_epi16
_mm_mask_cvtepu8_epi16 _mm_maskz_cvtepu8_epi16
_mm256_mask_cvtepi8_epi16 _mm256_maskz_cvtepi8_epi16
_mm256_mask_cvtepu8_epi16 _mm256_maskz_cvtepu8_epi16

_mm_mask_slli_epi16 _mm_mask_slli_epi16
_mm256_mask_slli_epi16 _mm256_mask_slli_epi16

These should just fixes to the headers along with adding test coverage to avx512bw-builtins.c and avx512vlbw-builtins.c

[GrumpyPigSkin]

Hi, can I be assigned to this one? I see there are a number of similar issues so I will have a look at others also :)

[RKSimon]

Hi, can I be assigned to this one? I see there are a number of similar issues so I will have a look at others also :)

Most of this work will be adding TEST_CONSTEXPR test coverage - take a look at some of the other sub-issues from #30794

[GrumpyPigSkin]

Is there any methodology that wants applying to the tests? I have just been doing along the lines of what I've copied in but thought it is worth checking if there is anything more elaborate that needs doing:

TEST_CONSTEXPR(
  match_v64qi(
    _mm512_mask_subs_epu8(
      (__m512i)(__v64qu){
         1,   2,  3,  4,  5,  6,  7,  8,
         9,  10, 11, 12, 13, 14, 15, 16,
         17, 18, 19, 20, 21, 22, 23, 24,
         25, 26, 27, 28, 29, 30, 31, 32,
         33, 34, 35, 36, 37, 38, 39, 40,
         41, 42, 43, 44, 45, 46, 47, 48,
         49, 50, 51, 52, 53, 54, 55, 56,
         57, 58, 59, 60, 61, 62, 63, 64
      },
      (__mmask64)0xAAAAAAAAAAAAAAAAu,
      (__m512i)(__v64qu){
         1,  100,  3,  4,  5,  6,  7,  8,
         9,  100, 11, 12, 13, 14, 15, 16,
         17, 100, 19, 20, 21, 22, 23, 24,
         25, 100, 27, 28, 29, 30, 31, 32,
         33, 100, 35, 36, 37, 38, 39, 40,
         41, 100, 43, 44, 45, 46, 47, 48,
         49, 100, 51, 52, 53, 54, 55, 56,
         57, 100, 59, 60, 61, 62, 63, 64
      },
      (__m512i)(__v64qu){
         1,   200,  3,  4,  5,  6,  7,  8,
         9,   200, 11, 12, 13, 14, 15, 16,
         17,  200, 19, 20, 21, 22, 23, 24,
         25,  200, 27, 28, 29, 30, 31, 32,
         33,  200, 35, 36, 37, 38, 39, 40,
         41,  200, 43, 44, 45, 46, 47, 48,
         49,  200, 51, 52, 53, 54, 55, 56,
         57,  200, 59, 60, 61, 62, 63, 64
      }
    ),
         1,  0,  3, 0,  5,  0,  7, 0,
         9,  0, 11, 0, 13,  0, 15, 0,
         17, 0, 19, 0, 21,  0, 23, 0,
         25, 0, 27, 0, 29,  0, 31, 0,
         33, 0, 35, 0, 37,  0, 39, 0,
         41, 0, 43, 0, 45,  0, 47, 0,
         49, 0, 51, 0, 53,  0, 55, 0,
         57, 0, 59, 0, 61,  0, 63, 0
  )
);