Add const tests for fma

Author: sayantn

crates/core_arch/src/x86/fma.rs

@@ -553,13 +553,14 @@ pub const fn _mm_fnmsub_ss(a: __m128, b: __m128, c: __m128) -> __m128 {
 
 #[cfg(test)]
 mod tests {
+    use crate::core_arch::assert_eq_const as assert_eq;
 
     use stdarch_test::simd_test;
 
     use crate::core_arch::x86::*;
 
     #[simd_test(enable = "fma")]
-    unsafe fn test_mm_fmadd_pd() {
+    const unsafe fn test_mm_fmadd_pd() {
         let a = _mm_setr_pd(1., 2.);
         let b = _mm_setr_pd(5., 3.);
         let c = _mm_setr_pd(4., 9.);
@@ -568,7 +569,7 @@ mod tests {
     }
 
     #[simd_test(enable = "fma")]
-    unsafe fn test_mm256_fmadd_pd() {
+    const unsafe fn test_mm256_fmadd_pd() {
         let a = _mm256_setr_pd(1., 2., 3., 4.);
         let b = _mm256_setr_pd(5., 3., 7., 2.);
         let c = _mm256_setr_pd(4., 9., 1., 7.);
@@ -577,7 +578,7 @@ mod tests {
     }
 
     #[simd_test(enable = "fma")]
-    unsafe fn test_mm_fmadd_ps() {
+    const unsafe fn test_mm_fmadd_ps() {
         let a = _mm_setr_ps(1., 2., 3., 4.);
         let b = _mm_setr_ps(5., 3., 7., 2.);
         let c = _mm_setr_ps(4., 9., 1., 7.);
@@ -586,7 +587,7 @@ mod tests {
     }
 
     #[simd_test(enable = "fma")]
-    unsafe fn test_mm256_fmadd_ps() {
+    const unsafe fn test_mm256_fmadd_ps() {
         let a = _mm256_setr_ps(1., 2., 3., 4., 0., 10., -1., -2.);
         let b = _mm256_setr_ps(5., 3., 7., 2., 4., -6., 0., 14.);
         let c = _mm256_setr_ps(4., 9., 1., 7., -5., 11., -2., -3.);
@@ -595,7 +596,7 @@ mod tests {
     }
 
     #[simd_test(enable = "fma")]
-    unsafe fn test_mm_fmadd_sd() {
+    const unsafe fn test_mm_fmadd_sd() {
         let a = _mm_setr_pd(1., 2.);
         let b = _mm_setr_pd(5., 3.);
         let c = _mm_setr_pd(4., 9.);
@@ -604,7 +605,7 @@ mod tests {
     }
 
     #[simd_test(enable = "fma")]
-    unsafe fn test_mm_fmadd_ss() {
+    const unsafe fn test_mm_fmadd_ss() {
         let a = _mm_setr_ps(1., 2., 3., 4.);
         let b = _mm_setr_ps(5., 3., 7., 2.);
         let c = _mm_setr_ps(4., 9., 1., 7.);
@@ -613,7 +614,7 @@ mod tests {
     }
 
     #[simd_test(enable = "fma")]
-    unsafe fn test_mm_fmaddsub_pd() {
+    const unsafe fn test_mm_fmaddsub_pd() {
         let a = _mm_setr_pd(1., 2.);
         let b = _mm_setr_pd(5., 3.);
         let c = _mm_setr_pd(4., 9.);
@@ -622,7 +623,7 @@ mod tests {
     }
 
     #[simd_test(enable = "fma")]
-    unsafe fn test_mm256_fmaddsub_pd() {
+    const unsafe fn test_mm256_fmaddsub_pd() {
         let a = _mm256_setr_pd(1., 2., 3., 4.);
         let b = _mm256_setr_pd(5., 3., 7., 2.);
         let c = _mm256_setr_pd(4., 9., 1., 7.);
@@ -631,7 +632,7 @@ mod tests {
     }
 
     #[simd_test(enable = "fma")]
-    unsafe fn test_mm_fmaddsub_ps() {
+    const unsafe fn test_mm_fmaddsub_ps() {
         let a = _mm_setr_ps(1., 2., 3., 4.);
         let b = _mm_setr_ps(5., 3., 7., 2.);
         let c = _mm_setr_ps(4., 9., 1., 7.);
@@ -640,7 +641,7 @@ mod tests {
     }
 
     #[simd_test(enable = "fma")]
-    unsafe fn test_mm256_fmaddsub_ps() {
+    const unsafe fn test_mm256_fmaddsub_ps() {
         let a = _mm256_setr_ps(1., 2., 3., 4., 0., 10., -1., -2.);
         let b = _mm256_setr_ps(5., 3., 7., 2., 4., -6., 0., 14.);
         let c = _mm256_setr_ps(4., 9., 1., 7., -5., 11., -2., -3.);
@@ -649,7 +650,7 @@ mod tests {
     }
 
     #[simd_test(enable = "fma")]
-    unsafe fn test_mm_fmsub_pd() {
+    const unsafe fn test_mm_fmsub_pd() {
         let a = _mm_setr_pd(1., 2.);
         let b = _mm_setr_pd(5., 3.);
         let c = _mm_setr_pd(4., 9.);
@@ -658,7 +659,7 @@ mod tests {
     }
 
     #[simd_test(enable = "fma")]
-    unsafe fn test_mm256_fmsub_pd() {
+    const unsafe fn test_mm256_fmsub_pd() {
         let a = _mm256_setr_pd(1., 2., 3., 4.);
         let b = _mm256_setr_pd(5., 3., 7., 2.);
         let c = _mm256_setr_pd(4., 9., 1., 7.);
@@ -667,7 +668,7 @@ mod tests {
     }
 
     #[simd_test(enable = "fma")]
-    unsafe fn test_mm_fmsub_ps() {
+    const unsafe fn test_mm_fmsub_ps() {
         let a = _mm_setr_ps(1., 2., 3., 4.);
         let b = _mm_setr_ps(5., 3., 7., 2.);
         let c = _mm_setr_ps(4., 9., 1., 7.);
@@ -676,7 +677,7 @@ mod tests {
     }
 
     #[simd_test(enable = "fma")]
-    unsafe fn test_mm256_fmsub_ps() {
+    const unsafe fn test_mm256_fmsub_ps() {
         let a = _mm256_setr_ps(1., 2., 3., 4., 0., 10., -1., -2.);
         let b = _mm256_setr_ps(5., 3., 7., 2., 4., -6., 0., 14.);
         let c = _mm256_setr_ps(4., 9., 1., 7., -5., 11., -2., -3.);
@@ -685,7 +686,7 @@ mod tests {
     }
 
     #[simd_test(enable = "fma")]
-    unsafe fn test_mm_fmsub_sd() {
+    const unsafe fn test_mm_fmsub_sd() {
         let a = _mm_setr_pd(1., 2.);
         let b = _mm_setr_pd(5., 3.);
         let c = _mm_setr_pd(4., 9.);
@@ -694,7 +695,7 @@ mod tests {
     }
 
     #[simd_test(enable = "fma")]
-    unsafe fn test_mm_fmsub_ss() {
+    const unsafe fn test_mm_fmsub_ss() {
         let a = _mm_setr_ps(1., 2., 3., 4.);
         let b = _mm_setr_ps(5., 3., 7., 2.);
         let c = _mm_setr_ps(4., 9., 1., 7.);
@@ -703,7 +704,7 @@ mod tests {
     }
 
     #[simd_test(enable = "fma")]
-    unsafe fn test_mm_fmsubadd_pd() {
+    const unsafe fn test_mm_fmsubadd_pd() {
         let a = _mm_setr_pd(1., 2.);
         let b = _mm_setr_pd(5., 3.);
         let c = _mm_setr_pd(4., 9.);
@@ -712,7 +713,7 @@ mod tests {
     }
 
     #[simd_test(enable = "fma")]
-    unsafe fn test_mm256_fmsubadd_pd() {
+    const unsafe fn test_mm256_fmsubadd_pd() {
         let a = _mm256_setr_pd(1., 2., 3., 4.);
         let b = _mm256_setr_pd(5., 3., 7., 2.);
         let c = _mm256_setr_pd(4., 9., 1., 7.);
@@ -721,7 +722,7 @@ mod tests {
     }
 
     #[simd_test(enable = "fma")]
-    unsafe fn test_mm_fmsubadd_ps() {
+    const unsafe fn test_mm_fmsubadd_ps() {
         let a = _mm_setr_ps(1., 2., 3., 4.);
         let b = _mm_setr_ps(5., 3., 7., 2.);
         let c = _mm_setr_ps(4., 9., 1., 7.);
@@ -730,7 +731,7 @@ mod tests {
     }
 
     #[simd_test(enable = "fma")]
-    unsafe fn test_mm256_fmsubadd_ps() {
+    const unsafe fn test_mm256_fmsubadd_ps() {
         let a = _mm256_setr_ps(1., 2., 3., 4., 0., 10., -1., -2.);
         let b = _mm256_setr_ps(5., 3., 7., 2., 4., -6., 0., 14.);
         let c = _mm256_setr_ps(4., 9., 1., 7., -5., 11., -2., -3.);
@@ -739,7 +740,7 @@ mod tests {
     }
 
     #[simd_test(enable = "fma")]
-    unsafe fn test_mm_fnmadd_pd() {
+    const unsafe fn test_mm_fnmadd_pd() {
         let a = _mm_setr_pd(1., 2.);
         let b = _mm_setr_pd(5., 3.);
         let c = _mm_setr_pd(4., 9.);
@@ -748,7 +749,7 @@ mod tests {
     }
 
     #[simd_test(enable = "fma")]
-    unsafe fn test_mm256_fnmadd_pd() {
+    const unsafe fn test_mm256_fnmadd_pd() {
         let a = _mm256_setr_pd(1., 2., 3., 4.);
         let b = _mm256_setr_pd(5., 3., 7., 2.);
         let c = _mm256_setr_pd(4., 9., 1., 7.);
@@ -757,7 +758,7 @@ mod tests {
     }
 
     #[simd_test(enable = "fma")]
-    unsafe fn test_mm_fnmadd_ps() {
+    const unsafe fn test_mm_fnmadd_ps() {
         let a = _mm_setr_ps(1., 2., 3., 4.);
         let b = _mm_setr_ps(5., 3., 7., 2.);
         let c = _mm_setr_ps(4., 9., 1., 7.);
@@ -766,7 +767,7 @@ mod tests {
     }
 
     #[simd_test(enable = "fma")]
-    unsafe fn test_mm256_fnmadd_ps() {
+    const unsafe fn test_mm256_fnmadd_ps() {
         let a = _mm256_setr_ps(1., 2., 3., 4., 0., 10., -1., -2.);
         let b = _mm256_setr_ps(5., 3., 7., 2., 4., -6., 0., 14.);
         let c = _mm256_setr_ps(4., 9., 1., 7., -5., 11., -2., -3.);
@@ -775,7 +776,7 @@ mod tests {
     }
 
     #[simd_test(enable = "fma")]
-    unsafe fn test_mm_fnmadd_sd() {
+    const unsafe fn test_mm_fnmadd_sd() {
         let a = _mm_setr_pd(1., 2.);
         let b = _mm_setr_pd(5., 3.);
         let c = _mm_setr_pd(4., 9.);
@@ -784,7 +785,7 @@ mod tests {
     }
 
     #[simd_test(enable = "fma")]
-    unsafe fn test_mm_fnmadd_ss() {
+    const unsafe fn test_mm_fnmadd_ss() {
         let a = _mm_setr_ps(1., 2., 3., 4.);
         let b = _mm_setr_ps(5., 3., 7., 2.);
         let c = _mm_setr_ps(4., 9., 1., 7.);
@@ -793,7 +794,7 @@ mod tests {
     }
 
     #[simd_test(enable = "fma")]
-    unsafe fn test_mm_fnmsub_pd() {
+    const unsafe fn test_mm_fnmsub_pd() {
         let a = _mm_setr_pd(1., 2.);
         let b = _mm_setr_pd(5., 3.);
         let c = _mm_setr_pd(4., 9.);
@@ -802,7 +803,7 @@ mod tests {
     }
 
     #[simd_test(enable = "fma")]
-    unsafe fn test_mm256_fnmsub_pd() {
+    const unsafe fn test_mm256_fnmsub_pd() {
         let a = _mm256_setr_pd(1., 2., 3., 4.);
         let b = _mm256_setr_pd(5., 3., 7., 2.);
         let c = _mm256_setr_pd(4., 9., 1., 7.);
@@ -811,7 +812,7 @@ mod tests {
     }
 
     #[simd_test(enable = "fma")]
-    unsafe fn test_mm_fnmsub_ps() {
+    const unsafe fn test_mm_fnmsub_ps() {
         let a = _mm_setr_ps(1., 2., 3., 4.);
         let b = _mm_setr_ps(5., 3., 7., 2.);
         let c = _mm_setr_ps(4., 9., 1., 7.);
@@ -820,7 +821,7 @@ mod tests {
     }
 
     #[simd_test(enable = "fma")]
-    unsafe fn test_mm256_fnmsub_ps() {
+    const unsafe fn test_mm256_fnmsub_ps() {
         let a = _mm256_setr_ps(1., 2., 3., 4., 0., 10., -1., -2.);
         let b = _mm256_setr_ps(5., 3., 7., 2., 4., -6., 0., 14.);
         let c = _mm256_setr_ps(4., 9., 1., 7., -5., 11., -2., -3.);
@@ -829,7 +830,7 @@ mod tests {
     }
 
     #[simd_test(enable = "fma")]
-    unsafe fn test_mm_fnmsub_sd() {
+    const unsafe fn test_mm_fnmsub_sd() {
         let a = _mm_setr_pd(1., 2.);
         let b = _mm_setr_pd(5., 3.);
         let c = _mm_setr_pd(4., 9.);
@@ -838,7 +839,7 @@ mod tests {
     }
 
     #[simd_test(enable = "fma")]
-    unsafe fn test_mm_fnmsub_ss() {
+    const unsafe fn test_mm_fnmsub_ss() {
         let a = _mm_setr_ps(1., 2., 3., 4.);
         let b = _mm_setr_ps(5., 3., 7., 2.);
         let c = _mm_setr_ps(4., 9., 1., 7.);