Fix incorrect tmop fp8 definition and formatting of tmop and mop4 intrinsics (#393)

Author: Lukacma

main/acle.md

@@ -10917,17 +10917,17 @@ Replacing `_hor` with `_ver` gives the associated vertical forms.
   //   _za32[_s8_s8]
   //   _za32[_u8_u8]
   void svtmopa_lane_za32[_f32_f32](uint64_t tile, svfloat32x2_t zn, svfloat32_t zm, 
-                              svuint8_t zk, uint64_t imm_idx)
+                                   svuint8_t zk, uint64_t imm_idx)
     __arm_streaming __arm_inout("za");
 
   // Only if __ARM_FEATURE_SME_TMOP != 0 && __ARM_FEATURE_SME_F8F16 != 0
-  void svtmopa_lane_za16[_mf8_mf8]_fpm(uint64_t tile, svfloat32x2_t zn, svfloat32_t zm, 
-                            svuint8_t zk, uint64_t imm_idx, fpm_t fpm)
+  void svtmopa_lane_za16[_mf8_mf8]_fpm(uint64_t tile, svmfloat8x2_t zn, svmfloat8_t zm, 
+                                       svuint8_t zk, uint64_t imm_idx, fpm_t fpm)
     __arm_streaming __arm_inout("za");
 
   // Only if __ARM_FEATURE_SME_TMOP != 0 && __ARM_FEATURE_SME_F8F32 != 0
-  void svtmopa_lane_za32[_mf8_mf8]_fpm(uint64_t tile, svfloat32x2_t zn, svfloat32_t zm, 
-                              svuint8_t zk, uint64_t imm_idx, fpm_t fpm)
+  void svtmopa_lane_za32[_mf8_mf8]_fpm(uint64_t tile, svmfloat8x2_t zn, svmfloat8_t zm, 
+                                       svuint8_t zk, uint64_t imm_idx, fpm_t fpm)
     __arm_streaming __arm_inout("za");
 ```
 
@@ -10936,12 +10936,12 @@ Replacing `_hor` with `_ver` gives the associated vertical forms.
 ``` c
   // Only if __ARM_FEATURE_SME_TMOP != 0
   void svtmopa_lane_za32[_s8_u8](uint64_t tile, svint8x2_t zn, svuint8_t zm, 
-                            svuint8_t zk, uint64_t imm_idx)
+                                 svuint8_t zk, uint64_t imm_idx)
     __arm_streaming __arm_inout("za");
 
   // Only if __ARM_FEATURE_SME_TMOP != 0
   void svtmopa_lane_za32[_u8_s8](uint64_t tile, svuint8x2_t zn, svint8_t zm, 
-                            svuint8_t zk, uint64_t imm_idx)
+                                 svuint8_t zk, uint64_t imm_idx)
     __arm_streaming __arm_inout("za");
 ```
 
@@ -13838,7 +13838,7 @@ non-overloaded names to indicate which vector argument is a vector register pair
   //   _za64[_s16_s16] (only if __ARM_FEATURE_SME_I16I64 != 0)
   //   _za64[_u16_u16] (only if __ARM_FEATURE_SME_I16I64 != 0)
   void svmop4a[_1x1]_za32[_f32_f32](uint64_t tile, svfloat32_t zn, 
-                             svfloat32_t zm)
+                                    svfloat32_t zm)
     __arm_streaming __arm_inout("za");
 
   // Variants are also available for:
@@ -13854,7 +13854,7 @@ non-overloaded names to indicate which vector argument is a vector register pair
   //   _za64[_s16_s16] (only if __ARM_FEATURE_SME_I16I64 != 0)
   //   _za64[_u16_u16] (only if __ARM_FEATURE_SME_I16I64 != 0)
   void svmop4a[_2x2]_za32[_f32_f32](uint64_t tile, svfloat32x2_t zn, 
-                             svfloat32x2_t zm)
+                                    svfloat32x2_t zm)
     __arm_streaming __arm_inout("za");
 
   // Variants are also available for:
@@ -13870,7 +13870,7 @@ non-overloaded names to indicate which vector argument is a vector register pair
   //   _za64[_s16_s16] (only if __ARM_FEATURE_SME_I16I64 != 0)
   //   _za64[_u16_u16] (only if __ARM_FEATURE_SME_I16I64 != 0)
   void svmop4a[_2x1]_za32[_f32_f32](uint64_t tile, svfloat32x2_t zn, 
-                                      svfloat32_t zm)
+                                    svfloat32_t zm)
     __arm_streaming __arm_inout("za");
 
   // Variants are also available for:
@@ -13886,7 +13886,7 @@ non-overloaded names to indicate which vector argument is a vector register pair
   //   _za64[_s16_s16] (only if __ARM_FEATURE_SME_I16I64 != 0)
   //   _za64[_u16_u16] (only if __ARM_FEATURE_SME_I16I64 != 0)
   void svmop4a[_1x2]_za32[_f32_f32](uint64_t tile, svfloat32_t zn, 
-                                      svfloat32x2_t zm)
+                                    svfloat32x2_t zm)
     __arm_streaming __arm_inout("za");
   ```
 
@@ -13906,7 +13906,7 @@ non-overloaded names to indicate which vector argument is a vector register pair
   //   _za64[_s16_s16] (only if __ARM_FEATURE_SME_I16I64 != 0)
   //   _za64[_u16_u16] (only if __ARM_FEATURE_SME_I16I64 != 0)
   void svmop4s[_1x1]_za32[_f32_f32](uint64_t tile, svfloat32_t zn, 
-                             svfloat32_t zm)
+                                    svfloat32_t zm)
     __arm_streaming __arm_inout("za");
 
   // Variants are also available for:
@@ -13922,7 +13922,7 @@ non-overloaded names to indicate which vector argument is a vector register pair
   //   _za64[_s16_s16] (only if __ARM_FEATURE_SME_I16I64 != 0)
   //   _za64[_s16_s16] (only if __ARM_FEATURE_SME_I16I64 != 0)
   void svmop4s[_2x2]_za32[_f32_f32](uint64_t tile, svfloat32x2_t zn, 
-                             svfloat32x2_t zm)
+                                    svfloat32x2_t zm)
     __arm_streaming __arm_inout("za");
 
   // Variants are also available for:
@@ -13938,7 +13938,7 @@ non-overloaded names to indicate which vector argument is a vector register pair
   //   _za64[_s16_s16] (only if __ARM_FEATURE_SME_I16I64 != 0)
   //   _za64[_u16_u16] (only if __ARM_FEATURE_SME_I16I64 != 0)
   void svmop4s[_2x1]_za32[_f32_f32](uint64_t tile, svfloat32x2_t zn, 
-                                      svfloat32_t zm)
+                                    svfloat32_t zm)
     __arm_streaming __arm_inout("za");
 
   // Variants are also available for:
@@ -13954,7 +13954,7 @@ non-overloaded names to indicate which vector argument is a vector register pair
   //   _za64[_s16_s16] (only if __ARM_FEATURE_SME_I16I64 != 0)
   //   _za64[_u16_u16] (only if __ARM_FEATURE_SME_I16I64 != 0)
   void svmop4s[_1x2]_za32[_f32_f32](uint64_t tile, svfloat32_t zn, 
-                                      svfloat32x2_t zm)
+                                    svfloat32x2_t zm)
     __arm_streaming __arm_inout("za");
 ```
 
@@ -13964,25 +13964,25 @@ non-overloaded names to indicate which vector argument is a vector register pair
   // Variants are also available for:
   //   _za64[_s16_u16] (only if __ARM_FEATURE_SME_I16I64 != 0)
   void svmop4a[_1x1]_za32[_s8_u8](uint64_t tile, svint8_t zn, 
-                           svuint8_t zm)
+                                  svuint8_t zm)
     __arm_streaming __arm_inout("za");
 
   // Variants are also available for:
   //   _za64[_s16_u16] (only if __ARM_FEATURE_SME_I16I64 != 0)
   void svmop4a[_2x2]_za32[_s8_u8](uint64_t tile, svint8x2_t zn, 
-                           svuint8x2_t zm)
+                                  svuint8x2_t zm)
     __arm_streaming __arm_inout("za");
 
   // Variants are also available for:
   //   _za64[_s16_u16] (only if __ARM_FEATURE_SME_I16I64 != 0)
   void svmop4a[_2x1]_za32[_s8_u8](uint64_t tile, svint8x2_t zn, 
-                                    svuint8__t zm)
+                                  svuint8_t zm)
     __arm_streaming __arm_inout("za");
 
   // Variants are also available for:
   //   _za64[_s16_u16] (only if __ARM_FEATURE_SME_I16I64 != 0)
   void svmop4a[_1x2]_za32[_s8_u8](uint64_t tile, svint8_t zn, 
-                                    svuint8x2_t zm)
+                                  svuint8x2_t zm)
     __arm_streaming __arm_inout("za");
 ```
 
@@ -13992,25 +13992,25 @@ non-overloaded names to indicate which vector argument is a vector register pair
   // Variants are also available for:
   //   _za64[_s16_u16] (only if __ARM_FEATURE_SME_I16I64 != 0)
   void svmop4s[_1x1]_za32[_s8_u8](uint64_t tile, svint8_t zn, 
-                           svuint8_t zm)
+                                  svuint8_t zm)
     __arm_streaming __arm_inout("za");
 
   // Variants are also available for:
   //   _za64[_s16_u16] (only if __ARM_FEATURE_SME_I16I64 != 0)
   void svmop4s[_2x2]_za32[_s8_u8](uint64_t tile, svint8x2_t zn, 
-                           svuint8x2_t zm)
+                                  svuint8x2_t zm)
     __arm_streaming __arm_inout("za");
 
   // Variants are also available for:
   //   _za64[_s16_u16] (only if __ARM_FEATURE_SME_I16I64 != 0)
   void svmop4s[_2x1]_za32[_s8_u8](uint64_t tile, svint8x2_t zn, 
-                                    svuint8__t zm)
+                                  svuint8_t zm)
     __arm_streaming __arm_inout("za");
 
   // Variants are also available for:
   //   _za64[_s16_u16] (only if __ARM_FEATURE_SME_I16I64 != 0)
   void svmop4s[_1x2]_za32[_s8_u8](uint64_t tile, svint8_t zn, 
-                                    svuint8x2_t zm)
+                                  svuint8x2_t zm)
     __arm_streaming __arm_inout("za");
 ```
 
@@ -14020,25 +14020,25 @@ non-overloaded names to indicate which vector argument is a vector register pair
   // Variants are also available for:
   //   _za64[_u16_s16] (only if __ARM_FEATURE_SME_I16I64 != 0)
   void svmop4a[_1x1]_za32[_u8_s8](uint64_t tile, svuint8_t zn, 
-                           svint8_t zm)
+                                  svint8_t zm)
     __arm_streaming __arm_inout("za");
 
   // Variants are also available for:
   //   _za64[_u16_s16] (only if __ARM_FEATURE_SME_I16I64 != 0)
   void svmop4a[_2x2]_za32[_u8_s8](uint64_t tile, svuint8x2_t zn, 
-                           svint8x2_t zm)
+                                  svint8x2_t zm)
     __arm_streaming __arm_inout("za");
 
   // Variants are also available for:
   //   _za64[_u16_s16] (only if __ARM_FEATURE_SME_I16I64 != 0)
   void svmop4a[_2x1]_za32[_u8_s8](uint64_t tile, svuint8x2_t zn, 
-                                    svint8__t zm)
+                                  svint8_t zm)
     __arm_streaming __arm_inout("za");
 
   // Variants are also available for:
   //   _za64[_u16_s16] (only if __ARM_FEATURE_SME_I16I64 != 0)
   void svmop4a[_1x2]_za32[_u8_s8](uint64_t tile, svuint8_t zn, 
-                                    svint8x2_t zm)
+                                  svint8x2_t zm)
     __arm_streaming __arm_inout("za");
 ```
 
@@ -14048,25 +14048,25 @@ non-overloaded names to indicate which vector argument is a vector register pair
   // Variants are also available for:
   //   _za64[_u16_s16] (only if __ARM_FEATURE_SME_I16I64 != 0)
   void svmop4s[_1x1]_za32[_u8_s8](uint64_t tile, svuint8_t zn, 
-                           svint8_t zm)
+                                  svint8_t zm)
     __arm_streaming __arm_inout("za");
 
   // Variants are also available for:
   //   _za64[_u16_s16] (only if __ARM_FEATURE_SME_I16I64 != 0)
   void svmop4s[_2x2]_za32[_u8_s8](uint64_t tile, svuint8x2_t zn, 
-                           svint8x2_t zm)
+                                  svint8x2_t zm)
     __arm_streaming __arm_inout("za");
 
   // Variants are also available for:
   //   _za64[_u16_s16] (only if __ARM_FEATURE_SME_I16I64 != 0)
   void svmop4s[_2x1]_za32[_u8_s8](uint64_t tile, svuint8x2_t zn, 
-                                    svint8__t zm)
+                                  svint8_t zm)
     __arm_streaming __arm_inout("za");
 
   // Variants are also available for:
   //   _za64[_u16_s16] (only if __ARM_FEATURE_SME_I16I64 != 0)
   void svmop4s[_1x2]_za32[_u8_s8](uint64_t tile, svuint8_t zn, 
-                                    svint8x2_t zm)
+                                  svint8x2_t zm)
     __arm_streaming __arm_inout("za");
 ```
 
@@ -14077,28 +14077,28 @@ non-overloaded names to indicate which vector argument is a vector register pair
   //   _za16[_mf8_mf8] (only if __ARM_FEATURE_SME_F8F16 != 0)
   //   _za32[_mf8_mf8] (only if __ARM_FEATURE_SME_F8F32 != 0)
   void svmop4a[_1x1]_za32[_mf8_mf8]_fpm(uint64_t tile, svmfloat8_t zn, 
-                        svmfloat8_t zm, fpm_t fpm)
+                                        svmfloat8_t zm, fpm_t fpm)
     __arm_streaming __arm_inout("za");
 
   // Variants are also available for:
   //   _za16[_mf8_mf8] (only if __ARM_FEATURE_SME_F8F16 != 0)
   //   _za32[_mf8_mf8] (only if __ARM_FEATURE_SME_F8F32 != 0)
   void svmop4a[_2x2]_za32[_mf8_mf8]_fpm(uint64_t tile, svmfloat8x2_t zn, 
-                        svmfloat8x2_t zm, fpm_t fpm)
+                                        svmfloat8x2_t zm, fpm_t fpm)
     __arm_streaming __arm_inout("za");
 
   // Variants are also available for:
   //   _za16[_mf8_mf8] (only if __ARM_FEATURE_SME_F8F16 != 0)
   //   _za32[_mf8_mf8] (only if __ARM_FEATURE_SME_F8F32 != 0)
   void svmop4a[_2x1]_za32[_mf8_mf8]_fpm(uint64_t tile, svmfloat8x2_t zn,
-                                 svmfloat8_t zm, fpm_t fpm)
+                                        svmfloat8_t zm, fpm_t fpm)
     __arm_streaming __arm_inout("za");
 
   // Variants are also available for:
   //   _za16[_mf8_mf8] (only if __ARM_FEATURE_SME_F8F16 != 0)
   //   _za32[_mf8_mf8] (only if __ARM_FEATURE_SME_F8F32 != 0)
   void svmop4a[_1x2]_za32[_mf8_mf8]_fpm(uint64_t tile, svmfloat8_t zn,
-                                 svmfloat8x2_t zm, fpm_t fpm)
+                                        svmfloat8x2_t zm, fpm_t fpm)
     __arm_streaming __arm_inout("za");
 ```