Fix interface to be consistent

Author: Daniel Smith

crates/core_arch/src/x86/avx512f.rs

@@ -93,9 +93,10 @@ pub unsafe fn _mm512_setr_epi32(
 #[inline]
 #[target_feature(enable = "avx512f")]
 #[cfg_attr(test, assert_instr(vpgatherdq))]
-pub unsafe fn _mm512_i32gather_epi64(offsets: __m256i, slice: *const i8, scale: i32) -> __m512i {
+pub unsafe fn _mm512_i32gather_epi64(offsets: __m256i, slice: *const u8, scale: i32) -> __m512i {
     let zero = _mm512_setzero_si512().as_i64x8();
     let neg_one = -1;
+    let slice = slice as *const i8;
     let offsets = offsets.as_i32x8();
     macro_rules! call {
         ($imm8:expr) => {

crates/core_arch/src/x86_64/avx512f.rs

@@ -237,15 +237,15 @@ mod tests {
 
     // _mm512_i32gather_epi64(offsets: __m256i, slice: *const i64, scale: i32)
     #[simd_test(enable = "avx512f")]
-    unsafe fn test_mm512_mask_i32gather_epi64() {
+    unsafe fn test_mm512_i32gather_epi64() {
         let mut arr = [0i64; 128];
         for i in 0..128i64 {
             arr[i as usize] = i;
         }
         // A multiplier of 8 is word-addressing
         #[rustfmt::skip]
         let index = _mm256_setr_epi32(0, 16, 32, 48, 64, 80, 96, 112);
-        let r = _mm512_i32gather_epi64(index, arr.as_ptr(), 8);
+        let r = _mm512_i32gather_epi64(index, arr.as_ptr() as *const u8, 8);
         assert_eq_m512i(r, _mm512_setr_epi64(0, 16, 32, 48, 64, 80, 96, 112));
     }
 }