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

convert _mm_i32gather_pd to const generics

Browse source
This commit is contained in:
Rémy Rakic 2021-03-06 00:58:26 +01:00 • committed by Amanieu d'Antras
parent 3da94f7f68
commit 47fc2fc7ed
1 changed files with 6 additions and 10 deletions
Download patch file Download diff file Expand all files Collapse all files

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

@ -1365,20 +1365,16 @@ pub unsafe fn _mm256_mask_i32gather_epi64<const SCALE: i32>(
/// [Intel's documentation](https://software.intel.com/sites/landingpage/IntrinsicsGuide/#text=_mm_i32gather_pd)
#[inline]
#[target_feature(enable = "avx2")]
#[cfg_attr(test, assert_instr(vgatherdpd, scale = 1))]
#[rustc_args_required_const(2)]
#[cfg_attr(test, assert_instr(vgatherdpd, SCALE = 1))]
#[rustc_legacy_const_generics(2)]
#[stable(feature = "simd_x86", since = "1.27.0")]
pub unsafe fn _mm_i32gather_pd(slice: *const f64, offsets: __m128i, scale: i32) -> __m128d {
pub unsafe fn _mm_i32gather_pd<const SCALE: i32>(slice: *const f64, offsets: __m128i) -> __m128d {
static_assert_imm8_scale!(SCALE);
let zero = _mm_setzero_pd();
let neg_one = _mm_set1_pd(-1.0);
let offsets = offsets.as_i32x4();
let slice = slice as *const i8;
macro_rules! call {
($imm8:expr) => {
pgatherdpd(zero, slice, offsets, neg_one, $imm8)
};
}
constify_imm8_gather!(scale, call)
pgatherdpd(zero, slice, offsets, neg_one, SCALE as i8)
}
/// Returns values from `slice` at offsets determined by `offsets * scale`,
@ -5708,7 +5704,7 @@ mod tests {
j += 1.0;
}
// A multiplier of 8 is word-addressing for f64s
let r = _mm_i32gather_pd(arr.as_ptr(), _mm_setr_epi32(0, 16, 0, 0), 8);
let r = _mm_i32gather_pd::<8>(arr.as_ptr(), _mm_setr_epi32(0, 16, 0, 0));
assert_eq_m128d(r, _mm_setr_pd(0.0, 16.0));
}