user0/rust
1
0
Fork 0
Code Issues Pull requests Projects Releases Packages Wiki Activity Actions

Convert _mm256_insert_epi8 to const generics

Browse source
This commit is contained in:
Rémy Rakic 2021-03-01 21:23:57 +01:00 • committed by Amanieu d'Antras
parent cadf5ceedc
commit 2200894df3
2 changed files with 10 additions and 15 deletions
Download patch file Download diff file Expand all files Collapse all files

15
library/stdarch/crates/core_arch/src/x86/avx.rs
View file

@ -1470,16 +1470,11 @@ pub unsafe fn _mm256_insertf128_si256(a: __m256i, b: __m128i, imm8: i32) -> __m2
#[inline]
#[target_feature(enable = "avx")]
// This intrinsic has no corresponding instruction.
#[rustc_args_required_const(2)]
#[rustc_legacy_const_generics(2)]
#[stable(feature = "simd_x86", since = "1.27.0")]
pub unsafe fn _mm256_insert_epi8(a: __m256i, i: i8, index: i32) -> __m256i {
let a = a.as_i8x32();
macro_rules! call {
($index:expr) => {
simd_insert(a, $index, i)
};
}
transmute(constify_imm5!(index, call))
pub unsafe fn _mm256_insert_epi8<const INDEX: i32>(a: __m256i, i: i8) -> __m256i {
static_assert_imm5!(INDEX);
transmute(simd_insert(a.as_i8x32(), INDEX as u32, i))
}
/// Copies `a` to result, and inserts the 16-bit integer `i` into result
@ -3931,7 +3926,7 @@ mod tests {
17, 18, 19, 20, 21, 22, 23, 24,
25, 26, 27, 28, 29, 30, 31, 32,
);
let r = _mm256_insert_epi8(a, 0, 31);
let r = _mm256_insert_epi8::<31>(a, 0);
#[rustfmt::skip]
let e = _mm256_setr_epi8(
1, 2, 3, 4, 5, 6, 7, 8,

10
library/stdarch/crates/core_arch/src/x86/avx2.rs
View file

@ -4384,8 +4384,8 @@ mod tests {
#[simd_test(enable = "avx2")]
unsafe fn test_mm256_blendv_epi8() {
let (a, b) = (_mm256_set1_epi8(4), _mm256_set1_epi8(2));
let mask = _mm256_insert_epi8(_mm256_set1_epi8(0), -1, 2);
let e = _mm256_insert_epi8(_mm256_set1_epi8(4), 2, 2);
let mask = _mm256_insert_epi8::<2>(_mm256_set1_epi8(0), -1);
let e = _mm256_insert_epi8::<2>(_mm256_set1_epi8(4), 2);
let r = _mm256_blendv_epi8(a, b, mask);
assert_eq_m256i(r, e);
}
@ -4504,7 +4504,7 @@ mod tests {
7, 6, 5, 4, 3, 2, 1, 0,
);
let r = _mm256_cmpeq_epi8(a, b);
assert_eq_m256i(r, _mm256_insert_epi8(_mm256_set1_epi8(0), !0, 2));
assert_eq_m256i(r, _mm256_insert_epi8::<2>(_mm256_set1_epi8(0), !0));
}
#[simd_test(enable = "avx2")]
@ -4543,10 +4543,10 @@ mod tests {
#[simd_test(enable = "avx2")]
unsafe fn test_mm256_cmpgt_epi8() {
let a = _mm256_insert_epi8(_mm256_set1_epi8(0), 5, 0);
let a = _mm256_insert_epi8::<0>(_mm256_set1_epi8(0), 5);
let b = _mm256_set1_epi8(0);
let r = _mm256_cmpgt_epi8(a, b);
assert_eq_m256i(r, _mm256_insert_epi8(_mm256_set1_epi8(0), !0, 0));
assert_eq_m256i(r, _mm256_insert_epi8::<0>(_mm256_set1_epi8(0), !0));
}
#[simd_test(enable = "avx2")]