Forgot files from previous check-in.

Author: ChipKerchner

kernel/riscv64/sgemm_kernel_16x8_zvl256b.c

@@ -2214,67 +2214,37 @@ int CNAME(BLASLONG M, BLASLONG N, BLASLONG K, FLOAT alpha, FLOAT* A, FLOAT* B, F
 
             FLOAT *C2 = C;
 
-            vfloat32m2_t c00;
-            c00 = __riscv_vle32_v_f32m2(C, 16); C += ldc;
-            vfloat32m1_t c0 = __riscv_vget_v_f32m2_f32m1(c00, 0);
-            vfloat32m1_t c1 = __riscv_vget_v_f32m2_f32m1(c00, 1);
-            c00 = __riscv_vle32_v_f32m2(C, 16); C += ldc;
-            vfloat32m1_t c2 = __riscv_vget_v_f32m2_f32m1(c00, 0);
-            vfloat32m1_t c3 = __riscv_vget_v_f32m2_f32m1(c00, 1);
-            c00 = __riscv_vle32_v_f32m2(C, 16); C += ldc;
-            vfloat32m1_t c4 = __riscv_vget_v_f32m2_f32m1(c00, 0);
-            vfloat32m1_t c5 = __riscv_vget_v_f32m2_f32m1(c00, 1);
-            c00 = __riscv_vle32_v_f32m2(C, 16); C += ldc;
-            vfloat32m1_t c6 = __riscv_vget_v_f32m2_f32m1(c00, 0);
-            vfloat32m1_t c7 = __riscv_vget_v_f32m2_f32m1(c00, 1);
-            c00 = __riscv_vle32_v_f32m2(C, 16); C += ldc;
-            vfloat32m1_t c8 = __riscv_vget_v_f32m2_f32m1(c00, 0);
-            vfloat32m1_t c9 = __riscv_vget_v_f32m2_f32m1(c00, 1);
-            c00 = __riscv_vle32_v_f32m2(C, 16); C += ldc;
-            vfloat32m1_t c10 = __riscv_vget_v_f32m2_f32m1(c00, 0);
-            vfloat32m1_t c11 = __riscv_vget_v_f32m2_f32m1(c00, 1);
-            c00 = __riscv_vle32_v_f32m2(C, 16); C += ldc;
-            vfloat32m1_t c12 = __riscv_vget_v_f32m2_f32m1(c00, 0);
-            vfloat32m1_t c13 = __riscv_vget_v_f32m2_f32m1(c00, 1);
-            c00 = __riscv_vle32_v_f32m2(C, 16);
-            vfloat32m1_t c14 = __riscv_vget_v_f32m2_f32m1(c00, 0);
-            vfloat32m1_t c15 = __riscv_vget_v_f32m2_f32m1(c00, 1);
-
-            c0 = __riscv_vfmacc_vf_f32m1( c0, alpha, result0, 8 );
-            c1 = __riscv_vfmacc_vf_f32m1( c1, alpha, result1, 8 );
-            c2 = __riscv_vfmacc_vf_f32m1( c2, alpha, result2, 8 );
-            c3 = __riscv_vfmacc_vf_f32m1( c3, alpha, result3, 8 );
-            c4 = __riscv_vfmacc_vf_f32m1( c4, alpha, result4, 8 );
-            c5 = __riscv_vfmacc_vf_f32m1( c5, alpha, result5, 8 );
-            c6 = __riscv_vfmacc_vf_f32m1( c6, alpha, result6, 8 );
-            c7 = __riscv_vfmacc_vf_f32m1( c7, alpha, result7, 8 );
-            c8 = __riscv_vfmacc_vf_f32m1( c8, alpha, result8, 8 );
-            c9 = __riscv_vfmacc_vf_f32m1( c9, alpha, result9, 8 );
-            c10 = __riscv_vfmacc_vf_f32m1( c10, alpha, result10, 8 );
-            c11 = __riscv_vfmacc_vf_f32m1( c11, alpha, result11, 8 );
-            c12 = __riscv_vfmacc_vf_f32m1( c12, alpha, result12, 8 );
-            c13 = __riscv_vfmacc_vf_f32m1( c13, alpha, result13, 8 );
-            c14 = __riscv_vfmacc_vf_f32m1( c14, alpha, result14, 8 );
-            c15 = __riscv_vfmacc_vf_f32m1( c15, alpha, result15, 8 );
+            vfloat32m2_t c01 = __riscv_vle32_v_f32m2(C, 16); C += ldc;
+            vfloat32m2_t c23 = __riscv_vle32_v_f32m2(C, 16); C += ldc;
+            vfloat32m2_t c45 = __riscv_vle32_v_f32m2(C, 16); C += ldc;
+            vfloat32m2_t c67 = __riscv_vle32_v_f32m2(C, 16); C += ldc;
+
+            c01 = __riscv_vfmacc_vf_f32m2( c01, alpha, result01, 16 );
+            c23 = __riscv_vfmacc_vf_f32m2( c23, alpha, result23, 16 );
+            c45 = __riscv_vfmacc_vf_f32m2( c45, alpha, result45, 16 );
+            c67 = __riscv_vfmacc_vf_f32m2( c67, alpha, result67, 16 );
+
+            vfloat32m2_t c89 = __riscv_vle32_v_f32m2(C, 16); C += ldc;
+            vfloat32m2_t cAB = __riscv_vle32_v_f32m2(C, 16); C += ldc;
+            vfloat32m2_t cCD = __riscv_vle32_v_f32m2(C, 16); C += ldc;
+            vfloat32m2_t cEF = __riscv_vle32_v_f32m2(C, 16);
+
+            c89 = __riscv_vfmacc_vf_f32m2( c89, alpha, result89, 16 );
+            cAB = __riscv_vfmacc_vf_f32m2( cAB, alpha, resultAB, 16 );
+            cCD = __riscv_vfmacc_vf_f32m2( cCD, alpha, resultCD, 16 );
+            cEF = __riscv_vfmacc_vf_f32m2( cEF, alpha, resultEF, 16 );
 
             C = C2;
 
-            c00 = __riscv_vcreate_v_f32m1_f32m2(c0, c1);
-            __riscv_vse32_v_f32m2(C, c00, 16); C += ldc;
-            c00 = __riscv_vcreate_v_f32m1_f32m2(c2, c3);
-            __riscv_vse32_v_f32m2(C, c00, 16); C += ldc;
-            c00 = __riscv_vcreate_v_f32m1_f32m2(c4, c5);
-            __riscv_vse32_v_f32m2(C, c00, 16); C += ldc;
-            c00 = __riscv_vcreate_v_f32m1_f32m2(c6, c7);
-            __riscv_vse32_v_f32m2(C, c00, 16); C += ldc;
-            c00 = __riscv_vcreate_v_f32m1_f32m2(c8, c9);
-            __riscv_vse32_v_f32m2(C, c00, 16); C += ldc;
-            c00 = __riscv_vcreate_v_f32m1_f32m2(c10, c11);
-            __riscv_vse32_v_f32m2(C, c00, 16); C += ldc;
-            c00 = __riscv_vcreate_v_f32m1_f32m2(c12, c13);
-            __riscv_vse32_v_f32m2(C, c00, 16); C += ldc;
-            c00 = __riscv_vcreate_v_f32m1_f32m2(c14, c15);
-            __riscv_vse32_v_f32m2(C, c00, 16);
+            __riscv_vse32_v_f32m2(C, c01, 16); C += ldc;
+            __riscv_vse32_v_f32m2(C, c23, 16); C += ldc;
+            __riscv_vse32_v_f32m2(C, c45, 16); C += ldc;
+            __riscv_vse32_v_f32m2(C, c67, 16); C += ldc;
+            __riscv_vse32_v_f32m2(C, c89, 16); C += ldc;
+            __riscv_vse32_v_f32m2(C, cAB, 16); C += ldc;
+            __riscv_vse32_v_f32m2(C, cCD, 16); C += ldc;
+            __riscv_vse32_v_f32m2(C, cEF, 16);
+
             C = C2 + 16;
         }