From f89f15eebd3cfb8f0c0ab03d3da1783381674795 Mon Sep 17 00:00:00 2001 From: Jason Volk Date: Sun, 9 Aug 2020 06:33:50 -0700 Subject: [PATCH] ircd::simd: Minor typedef cleanup. [ci skip] --- include/ircd/simd/type.h | 45 +++++++++++++++++++++------------------- 1 file changed, 24 insertions(+), 21 deletions(-) diff --git a/include/ircd/simd/type.h b/include/ircd/simd/type.h index 073316959..095b1ffc0 100644 --- a/include/ircd/simd/type.h +++ b/include/ircd/simd/type.h @@ -30,7 +30,6 @@ NAME \ __attribute__((packed)) \ __attribute__((aligned(1))) - // // scalar // @@ -71,13 +70,14 @@ namespace ircd typedef __v8du u64x8; // [ typedef __v4du u64x4; // [____0____|____1____|____2____|____3____| typedef __v2du u64x2; // [____0____|____1____| - typedef __m128i u128x1; // [________0________| - typedef __m256i u256x1; // [________________0________________| - typedef __m512i u512x1; // [_______________________________0________________________________| - IRCD_SIMD_TYPEDEF_UNALIGNED(__m128i, u128x1_u); - IRCD_SIMD_TYPEDEF_UNALIGNED(__m256i, u256x1_u); + typedef __m512i u512x1; // [_______________________________0________________________________| + typedef __m256i u256x1; // [________________0________________| + typedef __m128i u128x1; // [________0________| + IRCD_SIMD_TYPEDEF_UNALIGNED(__m512i, u512x1_u); + IRCD_SIMD_TYPEDEF_UNALIGNED(__m256i, u256x1_u); + IRCD_SIMD_TYPEDEF_UNALIGNED(__m128i, u128x1_u); } #endif @@ -100,13 +100,14 @@ namespace ircd typedef __v8di i64x8; // [ typedef __v4di i64x4; // [____0____|____1____|____2____|____3____| typedef __v2di i64x2; // [____0____|____1____| - typedef __m128i i128x1; // [________0________] - typedef __m256i i256x1; // [________________0________________| - typedef __m512i i512x1; // [_______________________________0________________________________| - IRCD_SIMD_TYPEDEF_UNALIGNED(__m128i, i128x1_u); - IRCD_SIMD_TYPEDEF_UNALIGNED(__m256i, i256x1_u); + typedef __m512i i512x1; // [_______________________________0________________________________| + typedef __m256i i256x1; // [________________0________________| + typedef __m128i i128x1; // [________0________| + IRCD_SIMD_TYPEDEF_UNALIGNED(__m512i, i512x1_u); + IRCD_SIMD_TYPEDEF_UNALIGNED(__m256i, i256x1_u); + IRCD_SIMD_TYPEDEF_UNALIGNED(__m128i, i128x1_u); } #endif @@ -121,13 +122,14 @@ namespace ircd typedef __v16sf f32x16; // [ typedef __v8sf f32x8; // [__0__|__1__|__2__|__3__|__4__|__5__|__6__|__7__| typedef __v4sf f32x4; // [__0__|__1__|__2__|__3__| - typedef __m128 f128x1; // [____|____0____|____| - typedef __m256 f256x1; // [________________0________________| - typedef __m512 f512x1; // [_______________________________0________________________________| - IRCD_SIMD_TYPEDEF_UNALIGNED(__m128, f128x1_u); - IRCD_SIMD_TYPEDEF_UNALIGNED(__m256, f256x1_u); + typedef __m512 f512x1; // [_______________________________0________________________________| + typedef __m256 f256x1; // [________________0________________| + typedef __m128 f128x1; // [____|____0____|____| + IRCD_SIMD_TYPEDEF_UNALIGNED(__m512, f512x1_u); + IRCD_SIMD_TYPEDEF_UNALIGNED(__m256, f256x1_u); + IRCD_SIMD_TYPEDEF_UNALIGNED(__m128, f128x1_u); } #endif @@ -141,13 +143,14 @@ namespace ircd typedef __v8df f64x8; // [ typedef __v4df f64x4; // [____0____|____1____|____2____|____3____| typedef __v2df f64x2; // [____0____|____1____| - typedef __m128d d128x1; // [________0________] - typedef __m256d d256x1; // [________________0________________| - typedef __m512d d512x1; // [_______________________________0________________________________| - IRCD_SIMD_TYPEDEF_UNALIGNED(__m128d, d128x1_u); - IRCD_SIMD_TYPEDEF_UNALIGNED(__m256d, d256x1_u); + typedef __m512d d512x1; // [_______________________________0________________________________| + typedef __m256d d256x1; // [________________0________________| + typedef __m128d d128x1; // [________0________] + IRCD_SIMD_TYPEDEF_UNALIGNED(__m512d, d512x1_u); + IRCD_SIMD_TYPEDEF_UNALIGNED(__m256d, d256x1_u); + IRCD_SIMD_TYPEDEF_UNALIGNED(__m128d, d128x1_u); } #endif