Skip to content

Commit b6db22d

Browse files
sayantnsayantn
committed
Make avx512bitalg functions const
1 parent 2792ab5 commit b6db22d

File tree

1 file changed

+55
-36
lines changed

1 file changed

+55
-36
lines changed

‎crates/core_arch/src/x86/avx512bitalg.rs‎

Lines changed: 55 additions & 36 deletions
Original file line numberDiff line numberDiff line change
@@ -43,7 +43,8 @@ unsafe extern "C" {
4343
#[target_feature(enable = "avx512bitalg")]
4444
#[stable(feature = "stdarch_x86_avx512", since = "1.89")]
4545
#[cfg_attr(test, assert_instr(vpopcntw))]
46-
pub fn _mm512_popcnt_epi16(a: __m512i) -> __m512i {
46+
#[rustc_const_unstable(feature = "stdarch_const_x86", issue = "149298")]
47+
pub const fn _mm512_popcnt_epi16(a: __m512i) -> __m512i {
4748
unsafe { transmute(simd_ctpop(a.as_i16x32())) }
4849
}
4950

@@ -57,7 +58,8 @@ pub fn _mm512_popcnt_epi16(a: __m512i) -> __m512i {
5758
#[target_feature(enable = "avx512bitalg")]
5859
#[stable(feature = "stdarch_x86_avx512", since = "1.89")]
5960
#[cfg_attr(test, assert_instr(vpopcntw))]
60-
pub fn _mm512_maskz_popcnt_epi16(k: __mmask32, a: __m512i) -> __m512i {
61+
#[rustc_const_unstable(feature = "stdarch_const_x86", issue = "149298")]
62+
pub const fn _mm512_maskz_popcnt_epi16(k: __mmask32, a: __m512i) -> __m512i {
6163
unsafe {
6264
transmute(simd_select_bitmask(
6365
k,
@@ -77,7 +79,8 @@ pub fn _mm512_maskz_popcnt_epi16(k: __mmask32, a: __m512i) -> __m512i {
7779
#[target_feature(enable = "avx512bitalg")]
7880
#[stable(feature = "stdarch_x86_avx512", since = "1.89")]
7981
#[cfg_attr(test, assert_instr(vpopcntw))]
80-
pub fn _mm512_mask_popcnt_epi16(src: __m512i, k: __mmask32, a: __m512i) -> __m512i {
82+
#[rustc_const_unstable(feature = "stdarch_const_x86", issue = "149298")]
83+
pub const fn _mm512_mask_popcnt_epi16(src: __m512i, k: __mmask32, a: __m512i) -> __m512i {
8184
unsafe {
8285
transmute(simd_select_bitmask(
8386
k,
@@ -94,7 +97,8 @@ pub fn _mm512_mask_popcnt_epi16(src: __m512i, k: __mmask32, a: __m512i) -> __m51
9497
#[target_feature(enable = "avx512bitalg,avx512vl")]
9598
#[stable(feature = "stdarch_x86_avx512", since = "1.89")]
9699
#[cfg_attr(test, assert_instr(vpopcntw))]
97-
pub fn _mm256_popcnt_epi16(a: __m256i) -> __m256i {
100+
#[rustc_const_unstable(feature = "stdarch_const_x86", issue = "149298")]
101+
pub const fn _mm256_popcnt_epi16(a: __m256i) -> __m256i {
98102
unsafe { transmute(simd_ctpop(a.as_i16x16())) }
99103
}
100104

@@ -108,7 +112,8 @@ pub fn _mm256_popcnt_epi16(a: __m256i) -> __m256i {
108112
#[target_feature(enable = "avx512bitalg,avx512vl")]
109113
#[stable(feature = "stdarch_x86_avx512", since = "1.89")]
110114
#[cfg_attr(test, assert_instr(vpopcntw))]
111-
pub fn _mm256_maskz_popcnt_epi16(k: __mmask16, a: __m256i) -> __m256i {
115+
#[rustc_const_unstable(feature = "stdarch_const_x86", issue = "149298")]
116+
pub const fn _mm256_maskz_popcnt_epi16(k: __mmask16, a: __m256i) -> __m256i {
112117
unsafe {
113118
transmute(simd_select_bitmask(
114119
k,
@@ -128,7 +133,8 @@ pub fn _mm256_maskz_popcnt_epi16(k: __mmask16, a: __m256i) -> __m256i {
128133
#[target_feature(enable = "avx512bitalg,avx512vl")]
129134
#[stable(feature = "stdarch_x86_avx512", since = "1.89")]
130135
#[cfg_attr(test, assert_instr(vpopcntw))]
131-
pub fn _mm256_mask_popcnt_epi16(src: __m256i, k: __mmask16, a: __m256i) -> __m256i {
136+
#[rustc_const_unstable(feature = "stdarch_const_x86", issue = "149298")]
137+
pub const fn _mm256_mask_popcnt_epi16(src: __m256i, k: __mmask16, a: __m256i) -> __m256i {
132138
unsafe {
133139
transmute(simd_select_bitmask(
134140
k,
@@ -145,7 +151,8 @@ pub fn _mm256_mask_popcnt_epi16(src: __m256i, k: __mmask16, a: __m256i) -> __m25
145151
#[target_feature(enable = "avx512bitalg,avx512vl")]
146152
#[stable(feature = "stdarch_x86_avx512", since = "1.89")]
147153
#[cfg_attr(test, assert_instr(vpopcntw))]
148-
pub fn _mm_popcnt_epi16(a: __m128i) -> __m128i {
154+
#[rustc_const_unstable(feature = "stdarch_const_x86", issue = "149298")]
155+
pub const fn _mm_popcnt_epi16(a: __m128i) -> __m128i {
149156
unsafe { transmute(simd_ctpop(a.as_i16x8())) }
150157
}
151158

@@ -159,7 +166,8 @@ pub fn _mm_popcnt_epi16(a: __m128i) -> __m128i {
159166
#[target_feature(enable = "avx512bitalg,avx512vl")]
160167
#[stable(feature = "stdarch_x86_avx512", since = "1.89")]
161168
#[cfg_attr(test, assert_instr(vpopcntw))]
162-
pub fn _mm_maskz_popcnt_epi16(k: __mmask8, a: __m128i) -> __m128i {
169+
#[rustc_const_unstable(feature = "stdarch_const_x86", issue = "149298")]
170+
pub const fn _mm_maskz_popcnt_epi16(k: __mmask8, a: __m128i) -> __m128i {
163171
unsafe {
164172
transmute(simd_select_bitmask(
165173
k,
@@ -179,7 +187,8 @@ pub fn _mm_maskz_popcnt_epi16(k: __mmask8, a: __m128i) -> __m128i {
179187
#[target_feature(enable = "avx512bitalg,avx512vl")]
180188
#[stable(feature = "stdarch_x86_avx512", since = "1.89")]
181189
#[cfg_attr(test, assert_instr(vpopcntw))]
182-
pub fn _mm_mask_popcnt_epi16(src: __m128i, k: __mmask8, a: __m128i) -> __m128i {
190+
#[rustc_const_unstable(feature = "stdarch_const_x86", issue = "149298")]
191+
pub const fn _mm_mask_popcnt_epi16(src: __m128i, k: __mmask8, a: __m128i) -> __m128i {
183192
unsafe {
184193
transmute(simd_select_bitmask(
185194
k,
@@ -196,7 +205,8 @@ pub fn _mm_mask_popcnt_epi16(src: __m128i, k: __mmask8, a: __m128i) -> __m128i {
196205
#[target_feature(enable = "avx512bitalg")]
197206
#[stable(feature = "stdarch_x86_avx512", since = "1.89")]
198207
#[cfg_attr(test, assert_instr(vpopcntb))]
199-
pub fn _mm512_popcnt_epi8(a: __m512i) -> __m512i {
208+
#[rustc_const_unstable(feature = "stdarch_const_x86", issue = "149298")]
209+
pub const fn _mm512_popcnt_epi8(a: __m512i) -> __m512i {
200210
unsafe { transmute(simd_ctpop(a.as_i8x64())) }
201211
}
202212

@@ -210,7 +220,8 @@ pub fn _mm512_popcnt_epi8(a: __m512i) -> __m512i {
210220
#[target_feature(enable = "avx512bitalg")]
211221
#[stable(feature = "stdarch_x86_avx512", since = "1.89")]
212222
#[cfg_attr(test, assert_instr(vpopcntb))]
213-
pub fn _mm512_maskz_popcnt_epi8(k: __mmask64, a: __m512i) -> __m512i {
223+
#[rustc_const_unstable(feature = "stdarch_const_x86", issue = "149298")]
224+
pub const fn _mm512_maskz_popcnt_epi8(k: __mmask64, a: __m512i) -> __m512i {
214225
unsafe {
215226
transmute(simd_select_bitmask(
216227
k,
@@ -230,7 +241,8 @@ pub fn _mm512_maskz_popcnt_epi8(k: __mmask64, a: __m512i) -> __m512i {
230241
#[target_feature(enable = "avx512bitalg")]
231242
#[stable(feature = "stdarch_x86_avx512", since = "1.89")]
232243
#[cfg_attr(test, assert_instr(vpopcntb))]
233-
pub fn _mm512_mask_popcnt_epi8(src: __m512i, k: __mmask64, a: __m512i) -> __m512i {
244+
#[rustc_const_unstable(feature = "stdarch_const_x86", issue = "149298")]
245+
pub const fn _mm512_mask_popcnt_epi8(src: __m512i, k: __mmask64, a: __m512i) -> __m512i {
234246
unsafe {
235247
transmute(simd_select_bitmask(
236248
k,
@@ -247,7 +259,8 @@ pub fn _mm512_mask_popcnt_epi8(src: __m512i, k: __mmask64, a: __m512i) -> __m512
247259
#[target_feature(enable = "avx512bitalg,avx512vl")]
248260
#[stable(feature = "stdarch_x86_avx512", since = "1.89")]
249261
#[cfg_attr(test, assert_instr(vpopcntb))]
250-
pub fn _mm256_popcnt_epi8(a: __m256i) -> __m256i {
262+
#[rustc_const_unstable(feature = "stdarch_const_x86", issue = "149298")]
263+
pub const fn _mm256_popcnt_epi8(a: __m256i) -> __m256i {
251264
unsafe { transmute(simd_ctpop(a.as_i8x32())) }
252265
}
253266

@@ -261,7 +274,8 @@ pub fn _mm256_popcnt_epi8(a: __m256i) -> __m256i {
261274
#[target_feature(enable = "avx512bitalg,avx512vl")]
262275
#[stable(feature = "stdarch_x86_avx512", since = "1.89")]
263276
#[cfg_attr(test, assert_instr(vpopcntb))]
264-
pub fn _mm256_maskz_popcnt_epi8(k: __mmask32, a: __m256i) -> __m256i {
277+
#[rustc_const_unstable(feature = "stdarch_const_x86", issue = "149298")]
278+
pub const fn _mm256_maskz_popcnt_epi8(k: __mmask32, a: __m256i) -> __m256i {
265279
unsafe {
266280
transmute(simd_select_bitmask(
267281
k,
@@ -281,7 +295,8 @@ pub fn _mm256_maskz_popcnt_epi8(k: __mmask32, a: __m256i) -> __m256i {
281295
#[target_feature(enable = "avx512bitalg,avx512vl")]
282296
#[stable(feature = "stdarch_x86_avx512", since = "1.89")]
283297
#[cfg_attr(test, assert_instr(vpopcntb))]
284-
pub fn _mm256_mask_popcnt_epi8(src: __m256i, k: __mmask32, a: __m256i) -> __m256i {
298+
#[rustc_const_unstable(feature = "stdarch_const_x86", issue = "149298")]
299+
pub const fn _mm256_mask_popcnt_epi8(src: __m256i, k: __mmask32, a: __m256i) -> __m256i {
285300
unsafe {
286301
transmute(simd_select_bitmask(
287302
k,
@@ -298,7 +313,8 @@ pub fn _mm256_mask_popcnt_epi8(src: __m256i, k: __mmask32, a: __m256i) -> __m256
298313
#[target_feature(enable = "avx512bitalg,avx512vl")]
299314
#[stable(feature = "stdarch_x86_avx512", since = "1.89")]
300315
#[cfg_attr(test, assert_instr(vpopcntb))]
301-
pub fn _mm_popcnt_epi8(a: __m128i) -> __m128i {
316+
#[rustc_const_unstable(feature = "stdarch_const_x86", issue = "149298")]
317+
pub const fn _mm_popcnt_epi8(a: __m128i) -> __m128i {
302318
unsafe { transmute(simd_ctpop(a.as_i8x16())) }
303319
}
304320

@@ -312,7 +328,8 @@ pub fn _mm_popcnt_epi8(a: __m128i) -> __m128i {
312328
#[target_feature(enable = "avx512bitalg,avx512vl")]
313329
#[stable(feature = "stdarch_x86_avx512", since = "1.89")]
314330
#[cfg_attr(test, assert_instr(vpopcntb))]
315-
pub fn _mm_maskz_popcnt_epi8(k: __mmask16, a: __m128i) -> __m128i {
331+
#[rustc_const_unstable(feature = "stdarch_const_x86", issue = "149298")]
332+
pub const fn _mm_maskz_popcnt_epi8(k: __mmask16, a: __m128i) -> __m128i {
316333
unsafe {
317334
transmute(simd_select_bitmask(
318335
k,
@@ -332,7 +349,8 @@ pub fn _mm_maskz_popcnt_epi8(k: __mmask16, a: __m128i) -> __m128i {
332349
#[target_feature(enable = "avx512bitalg,avx512vl")]
333350
#[stable(feature = "stdarch_x86_avx512", since = "1.89")]
334351
#[cfg_attr(test, assert_instr(vpopcntb))]
335-
pub fn _mm_mask_popcnt_epi8(src: __m128i, k: __mmask16, a: __m128i) -> __m128i {
352+
#[rustc_const_unstable(feature = "stdarch_const_x86", issue = "149298")]
353+
pub const fn _mm_mask_popcnt_epi8(src: __m128i, k: __mmask16, a: __m128i) -> __m128i {
336354
unsafe {
337355
transmute(simd_select_bitmask(
338356
k,
@@ -436,12 +454,13 @@ mod tests {
436454
// __mXXXi happens to be defined in terms of signed integers.
437455
#![allow(overflowing_literals)]
438456

457+
use crate::core_arch::assert_eq_const as assert_eq;
439458
use stdarch_test::simd_test;
440459

441460
use crate::core_arch::x86::*;
442461

443462
#[simd_test(enable = "avx512bitalg,avx512f")]
444-
unsafe fn test_mm512_popcnt_epi16() {
463+
const unsafe fn test_mm512_popcnt_epi16() {
445464
let test_data = _mm512_set_epi16(
446465
0, 1, 3, 7, 0xF, 0x1F, 0x3F, 0x7F, 0xFF, 0x1_FF, 0x3_FF, 0x7_FF, 0xF_FF, 0x1F_FF,
447466
0x3F_FF, 0x7F_FF, 0xFF_FF, -1, -100, 255, 256, 2, 4, 8, 16, 32, 64, 128, 256, 512,
@@ -456,7 +475,7 @@ mod tests {
456475
}
457476

458477
#[simd_test(enable = "avx512bitalg,avx512f")]
459-
unsafe fn test_mm512_maskz_popcnt_epi16() {
478+
const unsafe fn test_mm512_maskz_popcnt_epi16() {
460479
let test_data = _mm512_set_epi16(
461480
0, 1, 3, 7, 0xF, 0x1F, 0x3F, 0x7F, 0xFF, 0x1_FF, 0x3_FF, 0x7_FF, 0xF_FF, 0x1F_FF,
462481
0x3F_FF, 0x7F_FF, 0xFF_FF, -1, -100, 255, 256, 2, 4, 8, 16, 32, 64, 128, 256, 512,
@@ -472,7 +491,7 @@ mod tests {
472491
}
473492

474493
#[simd_test(enable = "avx512bitalg,avx512f")]
475-
unsafe fn test_mm512_mask_popcnt_epi16() {
494+
const unsafe fn test_mm512_mask_popcnt_epi16() {
476495
let test_data = _mm512_set_epi16(
477496
0, 1, 3, 7, 0xF, 0x1F, 0x3F, 0x7F, 0xFF, 0x1_FF, 0x3_FF, 0x7_FF, 0xF_FF, 0x1F_FF,
478497
0x3F_FF, 0x7F_FF, 0xFF_FF, -1, -100, 255, 256, 2, 4, 8, 16, 32, 64, 128, 256, 512,
@@ -488,7 +507,7 @@ mod tests {
488507
}
489508

490509
#[simd_test(enable = "avx512bitalg,avx512f,avx512vl")]
491-
unsafe fn test_mm256_popcnt_epi16() {
510+
const unsafe fn test_mm256_popcnt_epi16() {
492511
let test_data = _mm256_set_epi16(
493512
0, 1, 3, 7, 0xF, 0x1F, 0x3F, 0x7F, 0xFF, 0x1_FF, 0x3_FF, 0x7_FF, 0xF_FF, 0x1F_FF,
494513
0x3F_FF, 0x7F_FF,
@@ -500,7 +519,7 @@ mod tests {
500519
}
501520

502521
#[simd_test(enable = "avx512bitalg,avx512f,avx512vl")]
503-
unsafe fn test_mm256_maskz_popcnt_epi16() {
522+
const unsafe fn test_mm256_maskz_popcnt_epi16() {
504523
let test_data = _mm256_set_epi16(
505524
0, 1, 3, 7, 0xF, 0x1F, 0x3F, 0x7F, 0xFF, 0x1_FF, 0x3_FF, 0x7_FF, 0xF_FF, 0x1F_FF,
506525
0x3F_FF, 0x7F_FF,
@@ -512,7 +531,7 @@ mod tests {
512531
}
513532

514533
#[simd_test(enable = "avx512bitalg,avx512f,avx512vl")]
515-
unsafe fn test_mm256_mask_popcnt_epi16() {
534+
const unsafe fn test_mm256_mask_popcnt_epi16() {
516535
let test_data = _mm256_set_epi16(
517536
0, 1, 3, 7, 0xF, 0x1F, 0x3F, 0x7F, 0xFF, 0x1_FF, 0x3_FF, 0x7_FF, 0xF_FF, 0x1F_FF,
518537
0x3F_FF, 0x7F_FF,
@@ -526,15 +545,15 @@ mod tests {
526545
}
527546

528547
#[simd_test(enable = "avx512bitalg,avx512f,avx512vl")]
529-
unsafe fn test_mm_popcnt_epi16() {
548+
const unsafe fn test_mm_popcnt_epi16() {
530549
let test_data = _mm_set_epi16(0, 1, 3, 7, 0xF, 0x1F, 0x3F, 0x7F);
531550
let actual_result = _mm_popcnt_epi16(test_data);
532551
let reference_result = _mm_set_epi16(0, 1, 2, 3, 4, 5, 6, 7);
533552
assert_eq_m128i(actual_result, reference_result);
534553
}
535554

536555
#[simd_test(enable = "avx512bitalg,avx512f,avx512vl")]
537-
unsafe fn test_mm_maskz_popcnt_epi16() {
556+
const unsafe fn test_mm_maskz_popcnt_epi16() {
538557
let test_data = _mm_set_epi16(0, 1, 3, 7, 0xF, 0x1F, 0x3F, 0x7F);
539558
let mask = 0xF0;
540559
let actual_result = _mm_maskz_popcnt_epi16(mask, test_data);
@@ -543,7 +562,7 @@ mod tests {
543562
}
544563

545564
#[simd_test(enable = "avx512bitalg,avx512f,avx512vl")]
546-
unsafe fn test_mm_mask_popcnt_epi16() {
565+
const unsafe fn test_mm_mask_popcnt_epi16() {
547566
let test_data = _mm_set_epi16(0, 1, 3, 7, 0xF, 0x1F, 0x3F, 0x7F);
548567
let mask = 0xF0;
549568
let actual_result = _mm_mask_popcnt_epi16(test_data, mask, test_data);
@@ -552,7 +571,7 @@ mod tests {
552571
}
553572

554573
#[simd_test(enable = "avx512bitalg,avx512f")]
555-
unsafe fn test_mm512_popcnt_epi8() {
574+
const unsafe fn test_mm512_popcnt_epi8() {
556575
let test_data = _mm512_set_epi8(
557576
0, 1, 3, 7, 0xF, 0x1F, 0x3F, 0x7F, 0xFF, -1, 2, 4, 8, 16, 32, 64, 128, 171, 206, 100,
558577
217, 109, 253, 190, 177, 254, 179, 215, 230, 68, 201, 172, 183, 154, 84, 56, 227, 189,
@@ -569,7 +588,7 @@ mod tests {
569588
}
570589

571590
#[simd_test(enable = "avx512bitalg,avx512f")]
572-
unsafe fn test_mm512_maskz_popcnt_epi8() {
591+
const unsafe fn test_mm512_maskz_popcnt_epi8() {
573592
let test_data = _mm512_set_epi8(
574593
0, 1, 3, 7, 0xF, 0x1F, 0x3F, 0x7F, 0xFF, -1, 2, 4, 8, 16, 32, 64, 128, 171, 206, 100,
575594
217, 109, 253, 190, 177, 254, 179, 215, 230, 68, 201, 172, 183, 154, 84, 56, 227, 189,
@@ -587,7 +606,7 @@ mod tests {
587606
}
588607

589608
#[simd_test(enable = "avx512bitalg,avx512f")]
590-
unsafe fn test_mm512_mask_popcnt_epi8() {
609+
const unsafe fn test_mm512_mask_popcnt_epi8() {
591610
let test_data = _mm512_set_epi8(
592611
0, 1, 3, 7, 0xF, 0x1F, 0x3F, 0x7F, 0xFF, -1, 2, 4, 8, 16, 32, 64, 128, 171, 206, 100,
593612
217, 109, 253, 190, 177, 254, 179, 215, 230, 68, 201, 172, 183, 154, 84, 56, 227, 189,
@@ -605,7 +624,7 @@ mod tests {
605624
}
606625

607626
#[simd_test(enable = "avx512bitalg,avx512f,avx512vl")]
608-
unsafe fn test_mm256_popcnt_epi8() {
627+
const unsafe fn test_mm256_popcnt_epi8() {
609628
let test_data = _mm256_set_epi8(
610629
0, 1, 3, 7, 0xF, 0x1F, 0x3F, 0x7F, 0xFF, -1, 2, 4, 8, 16, 32, 64, 128, 171, 206, 100,
611630
217, 109, 253, 190, 177, 254, 179, 215, 230, 68, 201, 172,
@@ -619,7 +638,7 @@ mod tests {
619638
}
620639

621640
#[simd_test(enable = "avx512bitalg,avx512f,avx512vl")]
622-
unsafe fn test_mm256_maskz_popcnt_epi8() {
641+
const unsafe fn test_mm256_maskz_popcnt_epi8() {
623642
let test_data = _mm256_set_epi8(
624643
0, 1, 3, 7, 0xF, 0x1F, 0x3F, 0x7F, 0xFF, -1, 2, 4, 8, 16, 32, 64, 251, 73, 121, 143,
625644
145, 85, 91, 137, 90, 225, 21, 249, 211, 155, 228, 70,
@@ -634,7 +653,7 @@ mod tests {
634653
}
635654

636655
#[simd_test(enable = "avx512bitalg,avx512f,avx512vl")]
637-
unsafe fn test_mm256_mask_popcnt_epi8() {
656+
const unsafe fn test_mm256_mask_popcnt_epi8() {
638657
let test_data = _mm256_set_epi8(
639658
0, 1, 3, 7, 0xF, 0x1F, 0x3F, 0x7F, 0xFF, -1, 2, 4, 8, 16, 32, 64, 251, 73, 121, 143,
640659
145, 85, 91, 137, 90, 225, 21, 249, 211, 155, 228, 70,
@@ -649,7 +668,7 @@ mod tests {
649668
}
650669

651670
#[simd_test(enable = "avx512bitalg,avx512f,avx512vl")]
652-
unsafe fn test_mm_popcnt_epi8() {
671+
const unsafe fn test_mm_popcnt_epi8() {
653672
let test_data = _mm_set_epi8(
654673
0, 1, 3, 7, 0xF, 0x1F, 0x3F, 0x7F, 0xFF, -1, 2, 4, 8, 16, 32, 64,
655674
);
@@ -659,7 +678,7 @@ mod tests {
659678
}
660679

661680
#[simd_test(enable = "avx512bitalg,avx512f,avx512vl")]
662-
unsafe fn test_mm_maskz_popcnt_epi8() {
681+
const unsafe fn test_mm_maskz_popcnt_epi8() {
663682
let test_data = _mm_set_epi8(
664683
0, 1, 3, 7, 0xF, 0x1F, 0x3F, 0x7F, 90, 225, 21, 249, 211, 155, 228, 70,
665684
);
@@ -670,7 +689,7 @@ mod tests {
670689
}
671690

672691
#[simd_test(enable = "avx512bitalg,avx512f,avx512vl")]
673-
unsafe fn test_mm_mask_popcnt_epi8() {
692+
const unsafe fn test_mm_mask_popcnt_epi8() {
674693
let test_data = _mm_set_epi8(
675694
0, 1, 3, 7, 0xF, 0x1F, 0x3F, 0x7F, 90, 225, 21, 249, 211, 155, 228, 70,
676695
);

0 commit comments

Comments
 (0)