avx512vbmi2 (rust-lang#979)

CPerezz · Jan 11, 2021 · 3447076 · 3447076
1 parent 0000457
commit 3447076
Show file tree

Hide file tree

Showing 6 changed files with 3,639 additions and 5 deletions.
diff --git a/.github/workflows/main.yml b/.github/workflows/main.yml
@@ -77,7 +77,7 @@ jobs:
         - mips64-unknown-linux-gnuabi64
         - mips64el-unknown-linux-gnuabi64
         - s390x-unknown-linux-gnu
-        - wasm32-wasi
+        #- wasm32-wasi
         - i586-unknown-linux-gnu
         - x86_64-linux-android
         - arm-linux-androideabi
@@ -130,8 +130,8 @@ jobs:
           disable_assert_instr: true
         - target: s390x-unknown-linux-gnu
           os: ubuntu-latest
-        - target: wasm32-wasi
-          os: ubuntu-latest
+        #- target: wasm32-wasi
+        #  os: ubuntu-latest
         - target: aarch64-unknown-linux-gnu
           os: ubuntu-latest
         - target: x86_64-apple-darwin

diff --git a/crates/core_arch/avx512vbmi2.md b/crates/core_arch/avx512vbmi2.md
@@ -0,0 +1,153 @@
+<summary>["AVX512_VBMI2"]</summary><p>
+
+  * [x] [`_mm_mask_compress_epi16`]
+  * [x] [`_mm_maskz_compress_epi16`]
+  * [x] [`_mm256_mask_compress_epi16`]
+  * [x] [`_mm256_maskz_compress_epi16`]
+  * [x] [`_mm512_mask_compress_epi16`]
+  * [x] [`_mm512_maskz_compress_epi16`]
+  * [x] [`_mm_mask_compress_epi8`]
+  * [x] [`_mm_maskz_compress_epi8`]
+  * [x] [`_mm256_mask_compress_epi8`]
+  * [x] [`_mm256_maskz_compress_epi8`]
+  * [x] [`_mm512_mask_compress_epi8`]
+  * [x] [`_mm512_maskz_compress_epi8`]
+  * [_] [`_mm_mask_compressstoreu_epi16`]
+  * [_] [`_mm256_mask_compressstoreu_epi16`]
+  * [_] [`_mm512_mask_compressstoreu_epi16`]
+  * [_] [`_mm_mask_compressstoreu_epi8`]
+  * [_] [`_mm256_mask_compressstoreu_epi8`]
+  * [_] [`_mm512_mask_compressstoreu_epi8`]
+  * [x] [`_mm_mask_expand_epi16`]
+  * [x] [`_mm_maskz_expand_epi16`]
+  * [x] [`_mm256_mask_expand_epi16`]
+  * [x] [`_mm256_maskz_expand_epi16`]
+  * [x] [`_mm512_mask_expand_epi16`]
+  * [x] [`_mm512_maskz_expand_epi16`]
+  * [x] [`_mm_mask_expand_epi8`]
+  * [x] [`_mm_maskz_expand_epi8`]
+  * [x] [`_mm256_mask_expand_epi8`]
+  * [x] [`_mm256_maskz_expand_epi8`]
+  * [x] [`_mm512_mask_expand_epi8`]
+  * [x] [`_mm512_maskz_expand_epi8`]
+  * [_] [`_mm_mask_expandloadu_epi16`]
+  * [_] [`_mm_maskz_expandloadu_epi16`]
+  * [_] [`_mm256_mask_expandloadu_epi16`]
+  * [_] [`_mm256_maskz_expandloadu_epi16`]
+  * [_] [`_mm512_mask_expandloadu_epi16`]
+  * [_] [`_mm512_maskz_expandloadu_epi16`]
+  * [_] [`_mm_mask_expandloadu_epi8`]
+  * [_] [`_mm_maskz_expandloadu_epi8`]
+  * [_] [`_mm256_mask_expandloadu_epi8`]
+  * [_] [`_mm256_maskz_expandloadu_epi8`]
+  * [_] [`_mm512_mask_expandloadu_epi8`]
+  * [_] [`_mm512_maskz_expandloadu_epi8`]
+  * [x] [`_mm_mask_shldi_epi16`]
+  * [x] [`_mm_maskz_shldi_epi16`]
+  * [x] [`_mm_shldi_epi16`]
+  * [x] [`_mm256_mask_shldi_epi16`]
+  * [x] [`_mm256_maskz_shldi_epi16`]
+  * [x] [`_mm256_shldi_epi16`]
+  * [x] [`_mm512_mask_shldi_epi16`]
+  * [x] [`_mm512_maskz_shldi_epi16`]
+  * [x] [`_mm512_shldi_epi16`]
+  * [x] [`_mm_mask_shldi_epi32`]
+  * [x] [`_mm_maskz_shldi_epi32`]
+  * [x] [`_mm_shldi_epi32`]
+  * [x] [`_mm256_mask_shldi_epi32`]
+  * [x] [`_mm256_maskz_shldi_epi32`]
+  * [x] [`_mm256_shldi_epi32`]
+  * [x] [`_mm512_mask_shldi_epi32`]
+  * [x] [`_mm512_maskz_shldi_epi32`]
+  * [x] [`_mm512_shldi_epi32`]
+  * [x] [`_mm_mask_shldi_epi64`]
+  * [x] [`_mm_maskz_shldi_epi64`]
+  * [x] [`_mm_shldi_epi64`]
+  * [x] [`_mm256_mask_shldi_epi64`]
+  * [x] [`_mm256_maskz_shldi_epi64`]
+  * [x] [`_mm256_shldi_epi64`]
+  * [x] [`_mm512_mask_shldi_epi64`]
+  * [x] [`_mm512_maskz_shldi_epi64`]
+  * [x] [`_mm512_shldi_epi64`]
+  * [x] [`_mm_mask_shldv_epi16`]
+  * [x] [`_mm_maskz_shldv_epi16`]
+  * [x] [`_mm_shldv_epi16`]
+  * [x] [`_mm256_mask_shldv_epi16`]
+  * [x] [`_mm256_maskz_shldv_epi16`]
+  * [x] [`_mm256_shldv_epi16`]
+  * [x] [`_mm512_mask_shldv_epi16`]
+  * [x] [`_mm512_maskz_shldv_epi16`]
+  * [x] [`_mm512_shldv_epi16`]
+  * [x] [`_mm_mask_shldv_epi32`]
+  * [x] [`_mm_maskz_shldv_epi32`]
+  * [x] [`_mm_shldv_epi32`]
+  * [x] [`_mm256_mask_shldv_epi32`]
+  * [x] [`_mm256_maskz_shldv_epi32`]
+  * [x] [`_mm256_shldv_epi32`]
+  * [x] [`_mm512_mask_shldv_epi32`]
+  * [x] [`_mm512_maskz_shldv_epi32`]
+  * [x] [`_mm512_shldv_epi32`]
+  * [x] [`_mm_mask_shldv_epi64`]
+  * [x] [`_mm_maskz_shldv_epi64`]
+  * [x] [`_mm_shldv_epi64`]
+  * [x] [`_mm256_mask_shldv_epi64`]
+  * [x] [`_mm256_maskz_shldv_epi64`]
+  * [x] [`_mm256_shldv_epi64`]
+  * [x] [`_mm512_mask_shldv_epi64`]
+  * [x] [`_mm512_maskz_shldv_epi64`]
+  * [x] [`_mm512_shldv_epi64`]
+  * [x] [`_mm_mask_shrdi_epi16`]
+  * [x] [`_mm_maskz_shrdi_epi16`]
+  * [x] [`_mm_shrdi_epi16`]
+  * [x] [`_mm256_mask_shrdi_epi16`]
+  * [x] [`_mm256_maskz_shrdi_epi16`]
+  * [x] [`_mm256_shrdi_epi16`]
+  * [x] [`_mm512_mask_shrdi_epi16`]
+  * [x] [`_mm512_maskz_shrdi_epi16`]
+  * [x] [`_mm512_shrdi_epi16`]
+  * [x] [`_mm_mask_shrdi_epi32`]
+  * [x] [`_mm_maskz_shrdi_epi32`]
+  * [x] [`_mm_shrdi_epi32`]
+  * [x] [`_mm256_mask_shrdi_epi32`]
+  * [x] [`_mm256_maskz_shrdi_epi32`]
+  * [x] [`_mm256_shrdi_epi32`]
+  * [x] [`_mm512_mask_shrdi_epi32`]
+  * [x] [`_mm512_maskz_shrdi_epi32`]
+  * [x] [`_mm512_shrdi_epi32`]
+  * [x] [`_mm_mask_shrdi_epi64`]
+  * [x] [`_mm_maskz_shrdi_epi64`]
+  * [x] [`_mm_shrdi_epi64`]
+  * [x] [`_mm256_mask_shrdi_epi64`]
+  * [x] [`_mm256_maskz_shrdi_epi64`]
+  * [x] [`_mm256_shrdi_epi64`]
+  * [x] [`_mm512_mask_shrdi_epi64`]
+  * [x] [`_mm512_maskz_shrdi_epi64`]
+  * [x] [`_mm512_shrdi_epi64`]
+  * [x] [`_mm_mask_shrdv_epi16`]
+  * [x] [`_mm_maskz_shrdv_epi16`]
+  * [x] [`_mm_shrdv_epi16`]
+  * [x] [`_mm256_mask_shrdv_epi16`]
+  * [x] [`_mm256_maskz_shrdv_epi16`]
+  * [x] [`_mm256_shrdv_epi16`]
+  * [x] [`_mm512_mask_shrdv_epi16`]
+  * [x] [`_mm512_maskz_shrdv_epi16`]
+  * [x] [`_mm512_shrdv_epi16`]
+  * [x] [`_mm_mask_shrdv_epi32`]
+  * [x] [`_mm_maskz_shrdv_epi32`]
+  * [x] [`_mm_shrdv_epi32`]
+  * [x] [`_mm256_mask_shrdv_epi32`]
+  * [x] [`_mm256_maskz_shrdv_epi32`]
+  * [x] [`_mm256_shrdv_epi32`]
+  * [x] [`_mm512_mask_shrdv_epi32`]
+  * [x] [`_mm512_maskz_shrdv_epi32`]
+  * [x] [`_mm512_shrdv_epi32`]
+  * [x] [`_mm_mask_shrdv_epi64`]
+  * [x] [`_mm_maskz_shrdv_epi64`]
+  * [x] [`_mm_shrdv_epi64`]
+  * [x] [`_mm256_mask_shrdv_epi64`]
+  * [x] [`_mm256_maskz_shrdv_epi64`]
+  * [x] [`_mm256_shrdv_epi64`]
+  * [x] [`_mm512_mask_shrdv_epi64`]
+  * [x] [`_mm512_maskz_shrdv_epi64`]
+  * [x] [`_mm512_shrdv_epi64`]
+</p>
diff --git a/crates/core_arch/src/x86/avx512vbmi.rs b/crates/core_arch/src/x86/avx512vbmi.rs
@@ -438,8 +438,6 @@ mod tests {
     use stdarch_test::simd_test;
 
     use crate::core_arch::x86::*;
-    //use crate::hint::black_box;
-    //use crate::mem::{self};
 
     #[simd_test(enable = "avx512vbmi")]
     unsafe fn test_mm512_permutex2var_epi8() {