Skip to content

Commit 5e76227

Browse files
committed
Address review comments
1 parent 86f82f6 commit 5e76227

File tree

4 files changed

+12
-12
lines changed

4 files changed

+12
-12
lines changed

clang/lib/CodeGen/CGBuiltin.cpp

Lines changed: 1 addition & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -17040,7 +17040,7 @@ Value *CodeGenFunction::EmitX86BuiltinExpr(unsigned BuiltinID,
1704017040
Value *Store = Builder.CreateDefaultAlignedStore(VecT1, Ops[4]);
1704117041

1704217042
// Note: Here we escape directly use x86_tilestored64_internal to store
17043-
// the results due to it can't make sure the Mem writen scope. This may
17043+
// the results due to it can't make sure the Mem written scope. This may
1704417044
// cause shapes reloads after first amx intrinsic, which current amx reg-
1704517045
// ister allocation has no ability to handle it.
1704617046

clang/lib/Headers/amxtransposeintrin.h

Lines changed: 3 additions & 3 deletions
Original file line numberDiff line numberDiff line change
@@ -32,15 +32,15 @@
3232
/// \headerfile <immintrin.h>
3333
///
3434
/// \code
35-
/// void __tile_transposed(__tile dst, __tile src);
35+
/// void _tile_transposed(__tile dst, __tile src);
3636
/// \endcode
3737
///
3838
/// This intrinsic corresponds to the <c> TTRANSPOSED </c> instruction.
3939
///
4040
/// \param dst
4141
/// The destination tile. Max size is 1024 Bytes.
4242
/// \param src
43-
/// The 1st source tile. Max size is 1024 Bytes.
43+
/// The source tile. Max size is 1024 Bytes.
4444
///
4545
/// \code{.operation}
4646
///
@@ -238,7 +238,7 @@ static void __tile_2rpntlvwz1t1(__tile1024i *dst0, __tile1024i *dst1,
238238
/// \param dst
239239
/// The destination tile. Max size is 1024 Bytes.
240240
/// \param src
241-
/// The 1st source tile. Max size is 1024 Bytes.
241+
/// The source tile. Max size is 1024 Bytes.
242242
__DEFAULT_FN_ATTRS_TRANSPOSE
243243
static void __tile_transposed(__tile1024i *dst, __tile1024i src) {
244244
dst->tile = _tile_transposed_internal(dst->row, dst->col, src.tile);

llvm/include/llvm/CodeGen/TileShapeInfo.h

Lines changed: 3 additions & 3 deletions
Original file line numberDiff line numberDiff line change
@@ -34,14 +34,14 @@ class ShapeT {
3434
if (MRI)
3535
deduceImm(MRI);
3636
}
37-
// When ShapeT has mult shapes, we only use Shapes (never use Row and Col)
37+
// When ShapeT has multiple shapes, we only use Shapes (never use Row and Col)
3838
// and ImmShapes. Due to the most case is only one shape (just simply use
3939
// Shape.Row or Shape.Col), so here we don't merge Row and Col into vector
4040
// Shapes to keep the speed and code simplicity.
4141
// TODO: The upper solution is a temporary way to minimize current tile
4242
// register allocation code changes. It can not handle both Reg shape and
4343
// Imm shape for different shapes (e.g. shape 1 is reg shape while shape 2
44-
// is imm shape). Refine me when we have more mult-tile shape instructions!
44+
// is imm shape). Refine me when we have more multi-tile shape instructions!
4545
ShapeT(ArrayRef<MachineOperand *> ShapesOperands,
4646
const MachineRegisterInfo *MRI = nullptr)
4747
: Row(nullptr), Col(nullptr), RowImm(InvalidImmShape),
@@ -57,7 +57,7 @@ class ShapeT {
5757
ShapeT()
5858
: Row(nullptr), Col(nullptr), RowImm(InvalidImmShape),
5959
ColImm(InvalidImmShape) {}
60-
// TODO: We need to extern cmp operator for muti-shapes if
60+
// TODO: We need to extern cmp operator for multi-shapes if
6161
// we have requirement in the future.
6262
bool operator==(const ShapeT &Shape) const {
6363
MachineOperand *R = Shape.Row;

llvm/lib/Target/X86/X86LowerAMXType.cpp

Lines changed: 5 additions & 5 deletions
Original file line numberDiff line numberDiff line change
@@ -551,7 +551,7 @@ static Instruction *createTileStore(Instruction *TileDef, Value *Ptr) {
551551
assert(TileDef->getType()->isX86_AMXTy() && "Not define tile!");
552552
auto *II = dyn_cast<IntrinsicInst>(TileDef);
553553
unsigned Idx = 0;
554-
// Extract tile from mult tiles' def.
554+
// Extract tile from multiple tiles' def.
555555
if (auto *Extr = dyn_cast<ExtractValueInst>(TileDef)) {
556556
assert(Extr->hasIndices() && "Tile extract miss index!");
557557
Idx = Extr->getIndices()[0];
@@ -584,7 +584,7 @@ static void replaceWithTileLoad(Use &U, Value *Ptr, bool IsPHI = false) {
584584
Value *PhiOp = cast<PHINode>(V)->getIncomingValue(0);
585585
II = cast<IntrinsicInst>(PhiOp);
586586
} else if (auto *Extr = dyn_cast<ExtractValueInst>(V)) {
587-
// Extract tile from mult tiles' def.
587+
// Extract tile from multiple tiles' def.
588588
assert(Extr->hasIndices() && "Tile extract miss index!");
589589
Idx = Extr->getIndices()[0];
590590
II = cast<IntrinsicInst>(Extr->getOperand(0));
@@ -1040,7 +1040,7 @@ bool X86LowerAMXCast::combineCastStore(IntrinsicInst *Cast, StoreInst *ST) {
10401040

10411041
assert(Tile->getType()->isX86_AMXTy() && "Not Tile Operand!");
10421042

1043-
// TODO: Specially handle the mult-use case.
1043+
// TODO: Specially handle the multi-use case.
10441044
if (Tile->getNumUses() != 1)
10451045
return false;
10461046

@@ -1057,8 +1057,8 @@ bool X86LowerAMXCast::combineCastStore(IntrinsicInst *Cast, StoreInst *ST) {
10571057
Row = II->getOperand(0);
10581058
Col = II->getOperand(1);
10591059
} else {
1060-
// Now we supported mult-tiles value in structure, so we may get tile
1061-
// from extracting mult-tiles structure.
1060+
// Now we supported multi-tiles value in structure, so we may get tile
1061+
// from extracting multi-tiles structure.
10621062
// For example:
10631063
// %6 = call { x86_amx, x86_amx } @llvm.x86.t2rpntlvwz0.internal(i16 %1,
10641064
// i16 %2, i16 %3, i8* %4, i64 %5)

0 commit comments

Comments
 (0)