diff --git a/src/simd/simd_f16_ignore_nan.rs b/src/simd/simd_f16_ignore_nan.rs index edd6ff9..1908e88 100644 --- a/src/simd/simd_f16_ignore_nan.rs +++ b/src/simd/simd_f16_ignore_nan.rs @@ -423,7 +423,7 @@ mod avx512_ignore_nan { #[inline(always)] unsafe fn _mm_loadu(data: *const f16) -> __m512i { - _f16_as_m521i_to_i16ord(_mm512_loadu_epi16(data as *const i16)) + _f16_as_m521i_to_i16ord(_mm512_loadu_si512(data as *const i32)) } #[inline(always)] diff --git a/src/simd/simd_f16_return_nan.rs b/src/simd/simd_f16_return_nan.rs index 28eb849..0968cfb 100644 --- a/src/simd/simd_f16_return_nan.rs +++ b/src/simd/simd_f16_return_nan.rs @@ -394,7 +394,7 @@ mod avx512 { #[inline(always)] unsafe fn _mm_loadu(data: *const f16) -> __m512i { - _f16_as_m521i_to_i16ord(_mm512_loadu_epi16(data as *const i16)) + _f16_as_m521i_to_i16ord(_mm512_loadu_si512(data as *const i32)) } #[inline(always)] diff --git a/src/simd/simd_i16.rs b/src/simd/simd_i16.rs index 78f2b89..9f82bbe 100644 --- a/src/simd/simd_i16.rs +++ b/src/simd/simd_i16.rs @@ -283,7 +283,7 @@ mod avx512 { #[inline(always)] unsafe fn _mm_loadu(data: *const i16) -> __m512i { - _mm512_loadu_epi16(data as *const i16) + _mm512_loadu_si512(data as *const i32) } #[inline(always)] diff --git a/src/simd/simd_i8.rs b/src/simd/simd_i8.rs index ddcbc39..7088059 100644 --- a/src/simd/simd_i8.rs +++ b/src/simd/simd_i8.rs @@ -297,7 +297,7 @@ mod avx512 { #[inline(always)] unsafe fn _mm_loadu(data: *const i8) -> __m512i { - _mm512_loadu_epi8(data as *const i8) + _mm512_loadu_si512(data as *const i32) } #[inline(always)] diff --git a/src/simd/simd_u16.rs b/src/simd/simd_u16.rs index 7d5179b..2bd0b29 100644 --- a/src/simd/simd_u16.rs +++ b/src/simd/simd_u16.rs @@ -353,7 +353,7 @@ mod avx512 { #[inline(always)] unsafe fn _mm_loadu(data: *const u16) -> __m512i { - _u16_as_m512i_to_i16ord(_mm512_loadu_epi16(data as *const i16)) + _u16_as_m512i_to_i16ord(_mm512_loadu_si512(data as *const i32)) } #[inline(always)] diff --git a/src/simd/simd_u8.rs b/src/simd/simd_u8.rs index c378130..0777aff 100644 --- a/src/simd/simd_u8.rs +++ b/src/simd/simd_u8.rs @@ -368,7 +368,7 @@ mod avx512 { #[inline(always)] unsafe fn _mm_loadu(data: *const u8) -> __m512i { - _u8_as_m512i_to_i8ord(_mm512_loadu_epi8(data as *const i8)) + _u8_as_m512i_to_i8ord(_mm512_loadu_si512(data as *const i32)) } #[inline(always)]