r360918 - [X86] Update doxygen comments for AVX512BF16 to not refer to masks as 'immediates'. Refer to parameter names instead of 'src', 'src1', 'src2'. NFC
Craig Topper via cfe-commits
cfe-commits at lists.llvm.org
Thu May 16 10:34:36 PDT 2019
Author: ctopper
Date: Thu May 16 10:34:35 2019
New Revision: 360918
URL: http://llvm.org/viewvc/llvm-project?rev=360918&view=rev
Log:
[X86] Update doxygen comments for AVX512BF16 to not refer to masks as 'immediates'. Refer to parameter names instead of 'src', 'src1', 'src2'. NFC
Modified:
cfe/trunk/lib/Headers/avx512bf16intrin.h
cfe/trunk/lib/Headers/avx512vlbf16intrin.h
Modified: cfe/trunk/lib/Headers/avx512bf16intrin.h
URL: http://llvm.org/viewvc/llvm-project/cfe/trunk/lib/Headers/avx512bf16intrin.h?rev=360918&r1=360917&r2=360918&view=diff
==============================================================================
--- cfe/trunk/lib/Headers/avx512bf16intrin.h (original)
+++ cfe/trunk/lib/Headers/avx512bf16intrin.h Thu May 16 10:34:35 2019
@@ -31,7 +31,7 @@ typedef short __m256bh __attribute__((__
/// \param __B
/// A 512-bit vector of [16 x float].
/// \returns A 512-bit vector of [32 x bfloat] whose lower 256 bits come from
-/// convertion of src2, and higher 256 bits come from conversion of src1.
+/// conversion of __B, and higher 256 bits come from conversion of __A.
static __inline__ __m512bh __DEFAULT_FN_ATTRS512
_mm512_cvtne2ps_pbh(__m512 __A, __m512 __B) {
return (__m512bh)__builtin_ia32_cvtne2ps2bf16_512((__v16sf) __A,
@@ -51,10 +51,10 @@ _mm512_cvtne2ps_pbh(__m512 __A, __m512 _
/// \param __W
/// A 512-bit vector of [32 x bfloat].
/// \param __U
-/// An immediate value containing an 32-bit value specifying which element
-/// is choosed. 1 means __A or __B, 0 means __W.
+/// A 32-bit mask value specifying what is chosen for each element.
+/// A 1 means conversion of __A or __B. A 0 means element from __W.
/// \returns A 512-bit vector of [32 x bfloat] whose lower 256 bits come from
-/// convertion of src2, and higher 256 bits come from conversion of src1.
+/// conversion of __B, and higher 256 bits come from conversion of __A.
static __inline__ __m512bh __DEFAULT_FN_ATTRS512
_mm512_mask_cvtne2ps_pbh(__m512bh __W, __mmask32 __U, __m512 __A, __m512 __B) {
return (__m512bh)__builtin_ia32_selectw_512((__mmask32)__U,
@@ -73,10 +73,10 @@ _mm512_mask_cvtne2ps_pbh(__m512bh __W, _
/// \param __B
/// A 512-bit vector of [16 x float].
/// \param __U
-/// An immediate value containing an 32-bit value specifying which element
-/// is choosed. 1 means __A or __B, 0 means zero.
+/// A 32-bit mask value specifying what is chosen for each element.
+/// A 1 means conversion of __A or __B. A 0 means element is zero.
/// \returns A 512-bit vector of [32 x bfloat] whose lower 256 bits come from
-/// convertion of src2, and higher 256 bits come from conversion of src1.
+/// conversion of __B, and higher 256 bits come from conversion of __A.
static __inline__ __m512bh __DEFAULT_FN_ATTRS512
_mm512_maskz_cvtne2ps_pbh(__mmask32 __U, __m512 __A, __m512 __B) {
return (__m512bh)__builtin_ia32_selectw_512((__mmask32)__U,
@@ -92,7 +92,7 @@ _mm512_maskz_cvtne2ps_pbh(__mmask32 __U,
///
/// \param __A
/// A 512-bit vector of [16 x float].
-/// \returns A 256-bit vector of [16 x bfloat] come from convertion of src
+/// \returns A 256-bit vector of [16 x bfloat] come from conversion of __A.
static __inline__ __m256bh __DEFAULT_FN_ATTRS512
_mm512_cvtneps_pbh(__m512 __A) {
return (__m256bh)__builtin_ia32_cvtneps2bf16_512((__v16sf) __A);
@@ -109,9 +109,9 @@ _mm512_cvtneps_pbh(__m512 __A) {
/// \param __W
/// A 256-bit vector of [16 x bfloat].
/// \param __U
-/// An immediate value containing an 16-bit value specifying which element
-/// is choosed. 1 means __A, 0 means __W.
-/// \returns A 256-bit vector of [16 x bfloat] come from convertion of src
+/// A 16-bit mask value specifying what is chosen for each element.
+/// A 1 means conversion of __A. A 0 means element from __W.
+/// \returns A 256-bit vector of [16 x bfloat] come from conversion of __A.
static __inline__ __m256bh __DEFAULT_FN_ATTRS512
_mm512_mask_cvtneps_pbh(__m256bh __W, __mmask16 __U, __m512 __A) {
return (__m256bh)__builtin_ia32_selectw_256((__mmask16)__U,
@@ -128,9 +128,9 @@ _mm512_mask_cvtneps_pbh(__m256bh __W, __
/// \param __A
/// A 512-bit vector of [16 x float].
/// \param __U
-/// An immediate value containing an 16-bit value specifying which element
-/// is choosed. 1 means __A, 0 means zero.
-/// \returns A 256-bit vector of [16 x bfloat] come from convertion of src
+/// A 16-bit mask value specifying what is chosen for each element.
+/// A 1 means conversion of __A. A 0 means element is zero.
+/// \returns A 256-bit vector of [16 x bfloat] come from conversion of __A.
static __inline__ __m256bh __DEFAULT_FN_ATTRS512
_mm512_maskz_cvtneps_pbh(__mmask16 __U, __m512 __A) {
return (__m256bh)__builtin_ia32_selectw_256((__mmask16)__U,
@@ -172,8 +172,8 @@ _mm512_dpbf16_ps(__m512 __D, __m512bh __
/// \param __D
/// A 512-bit vector of [16 x float].
/// \param __U
-/// An immediate value containing an 16-bit value specifying which element
-/// is choosed. 1 means __A and __B's dot product, 0 means __D.
+/// A 16-bit mask value specifying what is chosen for each element.
+/// A 1 means __A and __B's dot product accumulated with __D. A 0 means __D.
/// \returns A 512-bit vector of [16 x float] comes from Dot Product of
/// __A, __B and __D
static __inline__ __m512 __DEFAULT_FN_ATTRS512
@@ -196,8 +196,8 @@ _mm512_mask_dpbf16_ps(__m512 __D, __mmas
/// \param __D
/// A 512-bit vector of [16 x float].
/// \param __U
-/// An immediate value containing an 16-bit value specifying which element
-/// is choosed. 1 means __A and __B's dot product, 0 means 0.
+/// A 16-bit mask value specifying what is chosen for each element.
+/// A 1 means __A and __B's dot product accumulated with __D. A 0 means 0.
/// \returns A 512-bit vector of [16 x float] comes from Dot Product of
/// __A, __B and __D
static __inline__ __m512 __DEFAULT_FN_ATTRS512
Modified: cfe/trunk/lib/Headers/avx512vlbf16intrin.h
URL: http://llvm.org/viewvc/llvm-project/cfe/trunk/lib/Headers/avx512vlbf16intrin.h?rev=360918&r1=360917&r2=360918&view=diff
==============================================================================
--- cfe/trunk/lib/Headers/avx512vlbf16intrin.h (original)
+++ cfe/trunk/lib/Headers/avx512vlbf16intrin.h Thu May 16 10:34:35 2019
@@ -33,7 +33,7 @@ typedef short __m128bh __attribute__((__
/// \param __B
/// A 128-bit vector of [4 x float].
/// \returns A 128-bit vector of [8 x bfloat] whose lower 64 bits come from
-/// convertion of src2, and higher 64 bits come from conversion of src1.
+/// conversion of __B, and higher 64 bits come from conversion of __A.
static __inline__ __m128bh __DEFAULT_FN_ATTRS128
_mm_cvtne2ps_pbh(__m128 __A, __m128 __B) {
return (__m128bh)__builtin_ia32_cvtne2ps2bf16_128((__v4sf) __A,
@@ -53,10 +53,10 @@ _mm_cvtne2ps_pbh(__m128 __A, __m128 __B)
/// \param __W
/// A 128-bit vector of [8 x bfloat].
/// \param __U
-/// An immediate value containing an 8-bit value specifying which element
-/// is choosed. 1 means __A or __B, 0 means __W.
+/// A 8-bit mask value specifying what is chosen for each element.
+/// A 1 means conversion of __A or __B. A 0 means element from __W.
/// \returns A 128-bit vector of [8 x bfloat] whose lower 64 bits come from
-/// convertion of src2, and higher 64 bits come from conversion of src1.
+/// conversion of __B, and higher 64 bits come from conversion of __A.
static __inline__ __m128bh __DEFAULT_FN_ATTRS128
_mm_mask_cvtne2ps_pbh(__m128bh __W, __mmask8 __U, __m128 __A, __m128 __B) {
return (__m128bh)__builtin_ia32_selectw_128((__mmask8)__U,
@@ -75,10 +75,10 @@ _mm_mask_cvtne2ps_pbh(__m128bh __W, __mm
/// \param __B
/// A 128-bit vector of [4 x float].
/// \param __U
-/// An immediate value containing an 8-bit value specifying which element
-/// is choosed. 1 means __A or __B, 0 means zero.
+/// A 8-bit mask value specifying what is chosen for each element.
+/// A 1 means conversion of __A or __B. A 0 means element is zero.
/// \returns A 128-bit vector of [8 x bfloat] whose lower 64 bits come from
-/// convertion of src2, and higher 64 bits come from conversion of src1.
+/// conversion of __B, and higher 64 bits come from conversion of __A.
static __inline__ __m128bh __DEFAULT_FN_ATTRS128
_mm_maskz_cvtne2ps_pbh(__mmask8 __U, __m128 __A, __m128 __B) {
return (__m128bh)__builtin_ia32_selectw_128((__mmask8)__U,
@@ -97,7 +97,7 @@ _mm_maskz_cvtne2ps_pbh(__mmask8 __U, __m
/// \param __B
/// A 256-bit vector of [8 x float].
/// \returns A 256-bit vector of [16 x bfloat] whose lower 128 bits come from
-/// convertion of src2, and higher 128 bits come from conversion of src1.
+/// conversion of __B, and higher 128 bits come from conversion of __A.
static __inline__ __m256bh __DEFAULT_FN_ATTRS256
_mm256_cvtne2ps_pbh(__m256 __A, __m256 __B) {
return (__m256bh)__builtin_ia32_cvtne2ps2bf16_256((__v8sf) __A,
@@ -117,10 +117,10 @@ _mm256_cvtne2ps_pbh(__m256 __A, __m256 _
/// \param __W
/// A 256-bit vector of [16 x bfloat].
/// \param __U
-/// An immediate value containing an 16-bit value specifying which element
-/// is choosed. 1 means __A or __B, 0 means __W.
+/// A 16-bit mask value specifying what is chosen for each element.
+/// A 1 means conversion of __A or __B. A 0 means element from __W.
/// \returns A 256-bit vector of [16 x bfloat] whose lower 128 bits come from
-/// convertion of src2, and higher 128 bits come from conversion of src1.
+/// conversion of __B, and higher 128 bits come from conversion of __A.
static __inline__ __m256bh __DEFAULT_FN_ATTRS256
_mm256_mask_cvtne2ps_pbh(__m256bh __W, __mmask16 __U, __m256 __A, __m256 __B) {
return (__m256bh)__builtin_ia32_selectw_256((__mmask16)__U,
@@ -139,10 +139,10 @@ _mm256_mask_cvtne2ps_pbh(__m256bh __W, _
/// \param __B
/// A 256-bit vector of [8 x float].
/// \param __U
-/// An immediate value containing an 16-bit value specifying which element
-/// is choosed. 1 means __A or __B, 0 means zero.
+/// A 16-bit mask value specifying what is chosen for each element.
+/// A 1 means conversion of __A or __B. A 0 means element is zero.
/// \returns A 256-bit vector of [16 x bfloat] whose lower 128 bits come from
-/// convertion of src2, and higher 128 bits come from conversion of src1.
+/// conversion of __B, and higher 128 bits come from conversion of __A.
static __inline__ __m256bh __DEFAULT_FN_ATTRS256
_mm256_maskz_cvtne2ps_pbh(__mmask16 __U, __m256 __A, __m256 __B) {
return (__m256bh)__builtin_ia32_selectw_256((__mmask16)__U,
@@ -159,7 +159,7 @@ _mm256_maskz_cvtne2ps_pbh(__mmask16 __U,
/// \param __A
/// A 128-bit vector of [4 x float].
/// \returns A 128-bit vector of [8 x bfloat] whose lower 64 bits come from
-/// convertion of src, and higher 64 bits are 0.
+/// conversion of __A, and higher 64 bits are 0.
static __inline__ __m128bh __DEFAULT_FN_ATTRS128
_mm_cvtneps_pbh(__m128 __A) {
return (__m128bh)__builtin_ia32_cvtneps2bf16_128_mask((__v4sf) __A,
@@ -178,10 +178,10 @@ _mm_cvtneps_pbh(__m128 __A) {
/// \param __W
/// A 128-bit vector of [8 x bfloat].
/// \param __U
-/// An immediate value containing an 8-bit value specifying which element
-/// is choosed. 1 means __A, 0 means __W.
+/// A 4-bit mask value specifying what is chosen for each element.
+/// A 1 means conversion of __A. A 0 means element from __W.
/// \returns A 128-bit vector of [8 x bfloat] whose lower 64 bits come from
-/// convertion of src, and higher 64 bits are 0.
+/// conversion of __A, and higher 64 bits are 0.
static __inline__ __m128bh __DEFAULT_FN_ATTRS128
_mm_mask_cvtneps_pbh(__m128bh __W, __mmask8 __U, __m128 __A) {
return (__m128bh)__builtin_ia32_cvtneps2bf16_128_mask((__v4sf) __A,
@@ -198,10 +198,10 @@ _mm_mask_cvtneps_pbh(__m128bh __W, __mma
/// \param __A
/// A 128-bit vector of [4 x float].
/// \param __U
-/// An immediate value containing an 8-bit value specifying which element
-/// is choosed. 1 means __A, 0 means 0.
+/// A 4-bit mask value specifying what is chosen for each element.
+/// A 1 means conversion of __A. A 0 means element is zero.
/// \returns A 128-bit vector of [8 x bfloat] whose lower 64 bits come from
-/// convertion of src, and higher 64 bits are 0.
+/// conversion of __A, and higher 64 bits are 0.
static __inline__ __m128bh __DEFAULT_FN_ATTRS128
_mm_maskz_cvtneps_pbh(__mmask8 __U, __m128 __A) {
return (__m128bh)__builtin_ia32_cvtneps2bf16_128_mask((__v4sf) __A,
@@ -217,7 +217,7 @@ _mm_maskz_cvtneps_pbh(__mmask8 __U, __m1
///
/// \param __A
/// A 256-bit vector of [8 x float].
-/// \returns A 128-bit vector of [8 x bfloat] comes from convertion of src.
+/// \returns A 128-bit vector of [8 x bfloat] comes from conversion of __A.
static __inline__ __m128bh __DEFAULT_FN_ATTRS256
_mm256_cvtneps_pbh(__m256 __A) {
return (__m128bh)__builtin_ia32_cvtneps2bf16_256((__v8sf)__A);
@@ -234,9 +234,9 @@ _mm256_cvtneps_pbh(__m256 __A) {
/// \param __W
/// A 256-bit vector of [8 x bfloat].
/// \param __U
-/// An immediate value containing an 8-bit value specifying which element
-/// is choosed. 1 means __A, 0 means __W.
-/// \returns A 128-bit vector of [8 x bfloat] comes from convertion of src.
+/// A 8-bit mask value specifying what is chosen for each element.
+/// A 1 means conversion of __A. A 0 means element from __W.
+/// \returns A 128-bit vector of [8 x bfloat] comes from conversion of __A.
static __inline__ __m128bh __DEFAULT_FN_ATTRS256
_mm256_mask_cvtneps_pbh(__m128bh __W, __mmask8 __U, __m256 __A) {
return (__m128bh)__builtin_ia32_selectw_128((__mmask8)__U,
@@ -253,9 +253,9 @@ _mm256_mask_cvtneps_pbh(__m128bh __W, __
/// \param __A
/// A 256-bit vector of [8 x float].
/// \param __U
-/// An immediate value containing an 8-bit value specifying which element
-/// is choosed. 1 means __A, 0 means __W.
-/// \returns A 128-bit vector of [8 x bfloat] comes from convertion of src.
+/// A 8-bit mask value specifying what is chosen for each element.
+/// A 1 means conversion of __A. A 0 means element is zero.
+/// \returns A 128-bit vector of [8 x bfloat] comes from conversion of __A.
static __inline__ __m128bh __DEFAULT_FN_ATTRS256
_mm256_maskz_cvtneps_pbh(__mmask8 __U, __m256 __A) {
return (__m128bh)__builtin_ia32_selectw_128((__mmask8)__U,
@@ -297,8 +297,8 @@ _mm_dpbf16_ps(__m128 __D, __m128bh __A,
/// \param __D
/// A 128-bit vector of [4 x float].
/// \param __U
-/// An immediate value containing an 8-bit value specifying which element
-/// is choosed. 1 means __A and __B's dot product, 0 means __D.
+/// A 8-bit mask value specifying what is chosen for each element.
+/// A 1 means __A and __B's dot product accumulated with __D. A 0 means __D.
/// \returns A 128-bit vector of [4 x float] comes from Dot Product of
/// __A, __B and __D
static __inline__ __m128 __DEFAULT_FN_ATTRS128
@@ -321,8 +321,8 @@ _mm_mask_dpbf16_ps(__m128 __D, __mmask8
/// \param __D
/// A 128-bit vector of [4 x float].
/// \param __U
-/// An immediate value containing an 8-bit value specifying which element
-/// is choosed. 1 means __A and __B's dot product, 0 means 0.
+/// A 8-bit mask value specifying what is chosen for each element.
+/// A 1 means __A and __B's dot product accumulated with __D. A 0 means 0.
/// \returns A 128-bit vector of [4 x float] comes from Dot Product of
/// __A, __B and __D
static __inline__ __m128 __DEFAULT_FN_ATTRS128
@@ -366,8 +366,8 @@ _mm256_dpbf16_ps(__m256 __D, __m256bh __
/// \param __D
/// A 256-bit vector of [8 x float].
/// \param __U
-/// An immediate value containing an 8-bit value specifying which element
-/// is choosed. 1 means __A and __B's dot product, 0 means __D.
+/// A 16-bit mask value specifying what is chosen for each element.
+/// A 1 means __A and __B's dot product accumulated with __D. A 0 means __D.
/// \returns A 256-bit vector of [8 x float] comes from Dot Product of
/// __A, __B and __D
static __inline__ __m256 __DEFAULT_FN_ATTRS256
@@ -390,8 +390,8 @@ _mm256_mask_dpbf16_ps(__m256 __D, __mmas
/// \param __D
/// A 256-bit vector of [8 x float].
/// \param __U
-/// An immediate value containing an 8-bit value specifying which element
-/// is choosed. 1 means __A and __B's dot product, 0 means 0.
+/// A 8-bit mask value specifying what is chosen for each element.
+/// A 1 means __A and __B's dot product accumulated with __D. A 0 means 0.
/// \returns A 256-bit vector of [8 x float] comes from Dot Product of
/// __A, __B and __D
static __inline__ __m256 __DEFAULT_FN_ATTRS256
@@ -400,6 +400,7 @@ _mm256_maskz_dpbf16_ps(__mmask8 __U, __m
(__v8sf)_mm256_dpbf16_ps(__D, __A, __B),
(__v8sf)_mm256_setzero_si256());
}
+
#undef __DEFAULT_FN_ATTRS128
#undef __DEFAULT_FN_ATTRS256
More information about the cfe-commits
mailing list