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

Change void* type for 3 intrinsics

Browse source 
- `_mm512_load_si512`
 - `_mm512_loadu_si512`
 - `_mm512_stream_si512`
This commit is contained in:
sayantn 2025-04-17 06:03:43 +05:30 • committed by Amanieu d'Antras
parent ccf36667b0
commit b10a6817d9
2 changed files with 8 additions and 8 deletions
Download patch file Download diff file Expand all files Collapse all files

14
library/stdarch/crates/core_arch/src/x86/avx512f.rs
View file

@ -29696,7 +29696,7 @@ pub unsafe fn _mm512_stream_pd(mem_addr: *mut f64, a: __m512d) {
#[unstable(feature = "stdarch_x86_avx512", issue = "111137")]
#[cfg_attr(test, assert_instr(vmovntdq))]
#[allow(clippy::cast_ptr_alignment)]
pub unsafe fn _mm512_stream_si512(mem_addr: *mut i32, a: __m512i) {
pub unsafe fn _mm512_stream_si512(mem_addr: *mut __m512i, a: __m512i) {
crate::arch::asm!(
vps!("vmovntdq", ",{a}"),
p = in(reg) mem_addr,
@ -34435,8 +34435,8 @@ pub unsafe fn _mm_storeu_epi64(mem_addr: *mut i64, a: __m128i) {
#[target_feature(enable = "avx512f")]
#[unstable(feature = "stdarch_x86_avx512", issue = "111137")]
#[cfg_attr(test, assert_instr(vmovups))] //should be vmovdqu32
pub unsafe fn _mm512_loadu_si512(mem_addr: *const i32) -> __m512i {
ptr::read_unaligned(mem_addr as *const __m512i)
pub unsafe fn _mm512_loadu_si512(mem_addr: *const __m512i) -> __m512i {
ptr::read_unaligned(mem_addr)
}
/// Store 512-bits of integer data from a into memory. mem_addr does not need to be aligned on any particular boundary.
@ -34509,8 +34509,8 @@ pub unsafe fn _mm512_storeu_ps(mem_addr: *mut f32, a: __m512) {
#[target_feature(enable = "avx512f")]
#[unstable(feature = "stdarch_x86_avx512", issue = "111137")]
#[cfg_attr(test, assert_instr(vmovaps))] //should be vmovdqa32
pub unsafe fn _mm512_load_si512(mem_addr: *const i32) -> __m512i {
ptr::read(mem_addr as *const __m512i)
pub unsafe fn _mm512_load_si512(mem_addr: *const __m512i) -> __m512i {
ptr::read(mem_addr)
}
/// Store 512-bits of integer data from a into memory. mem_addr must be aligned on a 64-byte boundary or a general-protection exception may be generated.
@ -57231,7 +57231,7 @@ mod tests {
#[simd_test(enable = "avx512f")]
unsafe fn test_mm512_loadu_si512() {
let a = &[4, 3, 2, 5, 8, 9, 64, 50, -4, -3, -2, -5, -8, -9, -64, -50];
let p = a.as_ptr();
let p = a.as_ptr().cast();
let r = _mm512_loadu_si512(black_box(p));
let e = _mm512_setr_epi32(4, 3, 2, 5, 8, 9, 64, 50, -4, -3, -2, -5, -8, -9, -64, -50);
assert_eq_m512i(r, e);
@ -57254,7 +57254,7 @@ mod tests {
let a = Align {
data: [4, 3, 2, 5, 8, 9, 64, 50, -4, -3, -2, -5, -8, -9, -64, -50],
};
let p = (a.data).as_ptr();
let p = (a.data).as_ptr().cast();
let r = _mm512_load_si512(black_box(p));
let e = _mm512_setr_epi32(4, 3, 2, 5, 8, 9, 64, 50, -4, -3, -2, -5, -8, -9, -64, -50);
assert_eq_m512i(r, e);

2
library/stdarch/crates/core_arch/src/x86/gfni.rs
View file

@ -867,7 +867,7 @@ mod tests {
#[unstable(feature = "stdarch_x86_avx512", issue = "111137")]
unsafe fn load_m512i_word<T>(data: &[T], word_index: usize) -> __m512i {
let byte_offset = word_index * 64 / size_of::<T>();
let pointer = data.as_ptr().add(byte_offset) as *const i32;
let pointer = data.as_ptr().add(byte_offset) as *const _;
_mm512_loadu_si512(black_box(pointer))
}