mlir::gpu::index_lowering::OpLowering< Op, XOp, YOp, ZOp > Struct Template Reference
#include "Conversion/GPUCommon/IndexIntrinsicsOpLowering.h"
Inheritance diagram for mlir::gpu::index_lowering::OpLowering< Op, XOp, YOp, ZOp >:
Public Member Functions | |
| OpLowering (const LLVMTypeConverter &typeConverter, PatternBenefit benefit=1) | |
| OpLowering (const LLVMTypeConverter &typeConverter, IndexKind indexKind, IntrType intrType, PatternBenefit benefit=1) | |
| LogicalResult | matchAndRewrite (Op op, typename Op::Adaptor adaptor, ConversionPatternRewriter &rewriter) const override |
| Public Member Functions inherited from mlir::ConvertOpToLLVMPattern< Op > | |
| ConvertOpToLLVMPattern (const LLVMTypeConverter &typeConverter, PatternBenefit benefit=1) | |
| LogicalResult | matchAndRewrite (Operation *op, ArrayRef< Value > operands, ConversionPatternRewriter &rewriter) const final |
| Wrappers around the RewritePattern methods that pass the derived op type. | |
| Public Member Functions inherited from mlir::ConvertToLLVMPattern | |
| ConvertToLLVMPattern (StringRef rootOpName, MLIRContext *context, const LLVMTypeConverter &typeConverter, PatternBenefit benefit=1) | |
Additional Inherited Members | |
| Public Types inherited from mlir::ConvertOpToLLVMPattern< Op > | |
| using | OpAdaptor |
| using | OneToNOpAdaptor |
| Protected Member Functions inherited from mlir::ConvertToLLVMPattern | |
| LLVM::LLVMDialect & | getDialect () const |
| Returns the LLVM dialect. | |
| const LLVMTypeConverter * | getTypeConverter () const |
| Type | getIndexType () const |
| Gets the MLIR type wrapping the LLVM integer type whose bit width is defined by the used type converter. | |
| Type | getIntPtrType (unsigned addressSpace=0) const |
| Gets the MLIR type wrapping the LLVM integer type whose bit width corresponds to that of a LLVM pointer type. | |
| Type | getVoidType () const |
| Gets the MLIR type wrapping the LLVM void type. | |
| Type | getVoidPtrType () const |
| Get the MLIR type wrapping the LLVM i8* type. | |
| Type | getPtrType (unsigned addressSpace=0) const |
| Get the MLIR type wrapping the LLVM ptr type. | |
| Value | getStridedElementPtr (ConversionPatternRewriter &rewriter, Location loc, MemRefType type, Value memRefDesc, ValueRange indices, LLVM::GEPNoWrapFlags noWrapFlags=LLVM::GEPNoWrapFlags::none) const |
| Convenience wrapper for the corresponding helper utility. | |
| bool | isConvertibleAndHasIdentityMaps (MemRefType type) const |
| Returns if the given memref type is convertible to LLVM and has an identity layout map. | |
| Type | getElementPtrType (MemRefType type) const |
| Returns the type of a pointer to an element of the memref. | |
| void | getMemRefDescriptorSizes (Location loc, MemRefType memRefType, ValueRange dynamicSizes, ConversionPatternRewriter &rewriter, SmallVectorImpl< Value > &sizes, SmallVectorImpl< Value > &strides, Value &size, bool sizeInBytes=true) const |
| Computes sizes, strides and buffer size of memRefType with identity layout. | |
| Value | getSizeInBytes (Location loc, Type type, ConversionPatternRewriter &rewriter) const |
| Computes the size of type in bytes. | |
| Value | getNumElements (Location loc, MemRefType memRefType, ValueRange dynamicSizes, ConversionPatternRewriter &rewriter) const |
| Computes total number of elements for the given MemRef and dynamicSizes. | |
| MemRefDescriptor | createMemRefDescriptor (Location loc, MemRefType memRefType, Value allocatedPtr, Value alignedPtr, ArrayRef< Value > sizes, ArrayRef< Value > strides, ConversionPatternRewriter &rewriter) const |
| Creates and populates a canonical memref descriptor struct. | |
| Value | copyUnrankedDescriptor (OpBuilder &builder, Location loc, UnrankedMemRefType memRefType, Value operand, bool toDynamic) const |
| Copies the given unranked memory descriptor to heap-allocated memory (if toDynamic is true) or to stack-allocated memory (otherwise) and returns the new descriptor. | |
| LogicalResult | copyUnrankedDescriptors (OpBuilder &builder, Location loc, TypeRange origTypes, SmallVectorImpl< Value > &operands, bool toDynamic) const |
| Copies the memory descriptor for any operands that were unranked descriptors originally to heap-allocated memory (if toDynamic is true) or to stack-allocated memory (otherwise). | |
| Static Protected Member Functions inherited from mlir::ConvertToLLVMPattern | |
| static Value | createIndexAttrConstant (OpBuilder &builder, Location loc, Type resultType, int64_t value) |
| Create a constant Op producing a value of resultType from an index-typed integer attribute. | |
Detailed Description
template<typename Op, typename XOp, typename YOp, typename ZOp>
struct mlir::gpu::index_lowering::OpLowering< Op, XOp, YOp, ZOp >
struct mlir::gpu::index_lowering::OpLowering< Op, XOp, YOp, ZOp >
Definition at line 33 of file IndexIntrinsicsOpLowering.h.
Constructor & Destructor Documentation
◆ OpLowering() [1/2]
template<typename Op, typename XOp, typename YOp, typename ZOp>
|
inlineexplicit |
Definition at line 40 of file IndexIntrinsicsOpLowering.h.
References mlir::ConvertOpToLLVMPattern< Op >::ConvertOpToLLVMPattern(), mlir::gpu::index_lowering::None, and mlir::gpu::index_lowering::Other.
◆ OpLowering() [2/2]
template<typename Op, typename XOp, typename YOp, typename ZOp>
|
inlineexplicit |
Definition at line 46 of file IndexIntrinsicsOpLowering.h.
References mlir::ConvertOpToLLVMPattern< Op >::ConvertOpToLLVMPattern().
Member Function Documentation
◆ matchAndRewrite()
template<typename Op, typename XOp, typename YOp, typename ZOp>
|
inlineoverride |
Definition at line 55 of file IndexIntrinsicsOpLowering.h.
References mlir::detail::DenseArrayAttrImpl< T >::asArrayRef(), mlir::gpu::index_lowering::Block, mlir::gpu::index_lowering::Dim, mlir::OpState::getContext(), mlir::OpState::getLoc(), mlir::Operation::getResult(), mlir::Operation::getResults(), mlir::gpu::index_lowering::Grid, mlir::gpu::index_lowering::Id, max(), min(), mlir::gpu::index_lowering::None, mlir::gpu::index_lowering::Other, mlir::Operation::setAttr(), and success().
The documentation for this struct was generated from the following file:
- lib/Conversion/GPUCommon/IndexIntrinsicsOpLowering.h
Generated on for MLIR by
1.14.0