From e417600a606b1216b30ab46738c9b8f7734f5089 Mon Sep 17 00:00:00 2001 From: Swapnil Gaikwad Date: Wed, 26 Jun 2024 11:29:23 +0100 Subject: [PATCH] Incorporate review comments --- src/coreclr/jit/hwintrinsiclistarm64sve.h | 2 +- .../src/System/Runtime/Intrinsics/Arm/Sve.cs | 20 +++++++++---------- 2 files changed, 11 insertions(+), 11 deletions(-) diff --git a/src/coreclr/jit/hwintrinsiclistarm64sve.h b/src/coreclr/jit/hwintrinsiclistarm64sve.h index 45fd7e57bbe73..e7af2383674f7 100644 --- a/src/coreclr/jit/hwintrinsiclistarm64sve.h +++ b/src/coreclr/jit/hwintrinsiclistarm64sve.h @@ -213,7 +213,7 @@ HARDWARE_INTRINSIC(Sve, TransposeEven, HARDWARE_INTRINSIC(Sve, TransposeOdd, -1, 2, true, {INS_sve_trn2, INS_sve_trn2, INS_sve_trn2, INS_sve_trn2, INS_sve_trn2, INS_sve_trn2, INS_sve_trn2, INS_sve_trn2, INS_sve_trn2, INS_sve_trn2}, HW_Category_SIMD, HW_Flag_Scalable|HW_Flag_SpecialCodeGen) HARDWARE_INTRINSIC(Sve, UnzipEven, -1, 2, true, {INS_sve_uzp1, INS_sve_uzp1, INS_sve_uzp1, INS_sve_uzp1, INS_sve_uzp1, INS_sve_uzp1, INS_sve_uzp1, INS_sve_uzp1, INS_sve_uzp1, INS_sve_uzp1}, HW_Category_SIMD, HW_Flag_Scalable|HW_Flag_SpecialCodeGen) HARDWARE_INTRINSIC(Sve, UnzipOdd, -1, 2, true, {INS_sve_uzp2, INS_sve_uzp2, INS_sve_uzp2, INS_sve_uzp2, INS_sve_uzp2, INS_sve_uzp2, INS_sve_uzp2, INS_sve_uzp2, INS_sve_uzp2, INS_sve_uzp2}, HW_Category_SIMD, HW_Flag_Scalable|HW_Flag_SpecialCodeGen) -HARDWARE_INTRINSIC(Sve, VectorTableLookup, -1, 2, true, {INS_sve_tbl, INS_sve_tbl, INS_sve_tbl, INS_sve_tbl, INS_sve_tbl, INS_sve_tbl, INS_sve_tbl, INS_sve_tbl, INS_sve_tbl, INS_sve_tbl}, HW_Category_SIMD, HW_Flag_Scalable|HW_Flag_BaseTypeFromSecondArg) +HARDWARE_INTRINSIC(Sve, VectorTableLookup, -1, 2, true, {INS_sve_tbl, INS_sve_tbl, INS_sve_tbl, INS_sve_tbl, INS_sve_tbl, INS_sve_tbl, INS_sve_tbl, INS_sve_tbl, INS_sve_tbl, INS_sve_tbl}, HW_Category_SIMD, HW_Flag_Scalable) HARDWARE_INTRINSIC(Sve, Xor, -1, -1, false, {INS_sve_eor, INS_sve_eor, INS_sve_eor, INS_sve_eor, INS_sve_eor, INS_sve_eor, INS_sve_eor, INS_sve_eor, INS_invalid, INS_invalid}, HW_Category_SIMD, HW_Flag_Scalable|HW_Flag_OptionalEmbeddedMaskedOperation|HW_Flag_HasRMWSemantics|HW_Flag_LowMaskedOperation) HARDWARE_INTRINSIC(Sve, XorAcross, -1, -1, false, {INS_sve_eorv, INS_sve_eorv, INS_sve_eorv, INS_sve_eorv, INS_sve_eorv, INS_sve_eorv, INS_sve_eorv, INS_sve_eorv, INS_invalid, INS_invalid}, HW_Category_SIMD, HW_Flag_Scalable|HW_Flag_EmbeddedMaskedOperation|HW_Flag_LowMaskedOperation) HARDWARE_INTRINSIC(Sve, ZeroExtend16, -1, -1, false, {INS_invalid, INS_invalid, INS_invalid, INS_invalid, INS_invalid, INS_sve_uxth, INS_invalid, INS_sve_uxth, INS_invalid, INS_invalid}, HW_Category_SIMD, HW_Flag_Scalable|HW_Flag_EmbeddedMaskedOperation|HW_Flag_LowMaskedOperation) diff --git a/src/libraries/System.Private.CoreLib/src/System/Runtime/Intrinsics/Arm/Sve.cs b/src/libraries/System.Private.CoreLib/src/System/Runtime/Intrinsics/Arm/Sve.cs index ea74cf934b105..8f712b8ca8bbd 100644 --- a/src/libraries/System.Private.CoreLib/src/System/Runtime/Intrinsics/Arm/Sve.cs +++ b/src/libraries/System.Private.CoreLib/src/System/Runtime/Intrinsics/Arm/Sve.cs @@ -6698,61 +6698,61 @@ internal Arm64() { } /// /// svuint8_t svtbl[_u8](svuint8_t data, svuint8_t indices) - /// TBL Zresult.B, Zdata.B, Zindices.B + /// TBL Zresult.B, {Zdata.B}, Zindices.B /// public static unsafe Vector VectorTableLookup(Vector data, Vector indices) => VectorTableLookup(data, indices); /// /// svfloat64_t svtbl[_f64](svfloat64_t data, svuint64_t indices) - /// TBL Zresult.D, Zdata.D, Zindices.D + /// TBL Zresult.D, {Zdata.D}, Zindices.D /// public static unsafe Vector VectorTableLookup(Vector data, Vector indices) => VectorTableLookup(data, indices); /// /// svint16_t svtbl[_s16](svint16_t data, svuint16_t indices) - /// TBL Zresult.H, Zdata.H, Zindices.H + /// TBL Zresult.H, {Zdata.H}, Zindices.H /// public static unsafe Vector VectorTableLookup(Vector data, Vector indices) => VectorTableLookup(data, indices); /// /// svint32_t svtbl[_s32](svint32_t data, svuint32_t indices) - /// TBL Zresult.S, Zdata.S, Zindices.S + /// TBL Zresult.S, {Zdata.S}, Zindices.S /// public static unsafe Vector VectorTableLookup(Vector data, Vector indices) => VectorTableLookup(data, indices); /// /// svint64_t svtbl[_s64](svint64_t data, svuint64_t indices) - /// TBL Zresult.D, Zdata.D, Zindices.D + /// TBL Zresult.D, {Zdata.D}, Zindices.D /// public static unsafe Vector VectorTableLookup(Vector data, Vector indices) => VectorTableLookup(data, indices); /// /// svint8_t svtbl[_s8](svint8_t data, svuint8_t indices) - /// TBL Zresult.B, Zdata.B, Zindices.B + /// TBL Zresult.B, {Zdata.B}, Zindices.B /// public static unsafe Vector VectorTableLookup(Vector data, Vector indices) => VectorTableLookup(data, indices); /// /// svfloat32_t svtbl[_f32](svfloat32_t data, svuint32_t indices) - /// TBL Zresult.S, Zdata.S, Zindices.S + /// TBL Zresult.S, {Zdata.S}, Zindices.S /// public static unsafe Vector VectorTableLookup(Vector data, Vector indices) => VectorTableLookup(data, indices); /// /// svuint16_t svtbl[_u16](svuint16_t data, svuint16_t indices) - /// TBL Zresult.H, Zdata.H, Zindices.H + /// TBL Zresult.H, {Zdata.H}, Zindices.H /// public static unsafe Vector VectorTableLookup(Vector data, Vector indices) => VectorTableLookup(data, indices); /// /// svuint32_t svtbl[_u32](svuint32_t data, svuint32_t indices) - /// TBL Zresult.S, Zdata.S, Zindices.S + /// TBL Zresult.S, {Zdata.S}, Zindices.S /// public static unsafe Vector VectorTableLookup(Vector data, Vector indices) => VectorTableLookup(data, indices); /// /// svuint64_t svtbl[_u64](svuint64_t data, svuint64_t indices) - /// TBL Zresult.D, Zdata.D, Zindices.D + /// TBL Zresult.D, {Zdata.D}, Zindices.D /// public static unsafe Vector VectorTableLookup(Vector data, Vector indices) => VectorTableLookup(data, indices);