Inheritance diagram for mlir::impl::ConvertGpuOpsToROCDLOpsBase< DerivedT >:

Public Types
using	Base = ConvertGpuOpsToROCDLOpsBase

Public Member Functions
	ConvertGpuOpsToROCDLOpsBase ()
	ConvertGpuOpsToROCDLOpsBase (const ConvertGpuOpsToROCDLOpsBase &other)
ConvertGpuOpsToROCDLOpsBase &	operator= (const ConvertGpuOpsToROCDLOpsBase &)=delete
	ConvertGpuOpsToROCDLOpsBase (ConvertGpuOpsToROCDLOpsBase &&)=delete
ConvertGpuOpsToROCDLOpsBase &	operator= (ConvertGpuOpsToROCDLOpsBase &&)=delete
	~ConvertGpuOpsToROCDLOpsBase ()=default
::llvm::StringRef	getArgument () const override
	Return the command line argument used when registering this pass.
::llvm::StringRef	getDescription () const override
	Return the command line description used when registering this pass.
::llvm::StringRef	getName () const override
	Returns the derived pass name.
std::unique_ptr<::mlir::Pass >	clonePass () const override
	A clone method to create a copy of this pass.
void	getDependentDialects (::mlir::DialectRegistry &registry) const override
	Return the dialect that must be loaded in the context before this pass.
	ConvertGpuOpsToROCDLOpsBase (ConvertGpuOpsToROCDLOpsOptions options)
	Explicitly declare the TypeID for this class.
Public Member Functions inherited from mlir::OperationPass< gpu::GPUModuleOp >
	~OperationPass () override=default
Public Member Functions inherited from mlir::Pass
virtual	~Pass ()=default
TypeID	getTypeID () const
	Returns the unique identifier that corresponds to this pass.
const PassInfo *	lookupPassInfo () const
	Returns the pass info for this pass, or null if unknown.
virtual void	getDependentDialects (DialectRegistry &registry) const
	Register dependent dialects for the current pass.
std::optional< StringRef >	getOpName () const
	Returns the name of the operation that this pass operates on, or std::nullopt if this is a generic OperationPass.
virtual LogicalResult	initializeOptions (StringRef options, function_ref< LogicalResult(const Twine &)> errorHandler)
	Attempt to initialize the options of this pass from the given string.
void	printAsTextualPipeline (raw_ostream &os, bool pretty=false)
	Prints out the pass in the textual representation of pipelines.
ArrayRef< Statistic * >	getStatistics () const
	Returns the main statistics for this pass instance.
MutableArrayRef< Statistic * >	getStatistics ()
const Pass *	getThreadingSibling () const
	Returns the thread sibling of this pass.
const Pass *	getThreadingSiblingOrThis () const
	Returns the thread sibling of this pass, or the pass itself it has no sibling.

Static Public Member Functions
static constexpr ::llvm::StringLiteral	getArgumentName ()
	Returns the command-line argument attached to this pass.
static constexpr ::llvm::StringLiteral	getPassName ()
	Returns the derived pass name.
static bool	classof (const ::mlir::Pass *pass)
	Support isa/dyn_cast functionality for the derived pass class.

Protected Attributes
::mlir::Pass::Option< std::string >	arch {*this, "arch", ::llvm::cl::desc(R"PO(Target architecture, as in Clang, with optional target-ID modifiers. New-style triples such as amdgpu9.42-amd-amdhsa are preferred, and can be extended to a full target ID like amdgpu9.42-amd-amdhsa--gfx942:xnack+:sramecc-. Bare chip names like gfx1250 or gfx942:xnack- are also supported. Defaults to an invalid target so that one must be given explicitly)PO"), ::llvm::cl::init("invalid")}
::mlir::Pass::Option< std::string >	chipset {*this, "chipset", ::llvm::cl::desc(R"PO(Deprecated alias for 'arch'.)PO"), ::llvm::cl::init("")}
::mlir::Pass::Option< unsigned >	waveSize {*this, "wavesize", ::llvm::cl::desc(R"PO(Wavefront size (32 or 64) for targets that run at either, or 0 to use the architecture's default)PO"), ::llvm::cl::init(0)}
::mlir::Pass::Option< unsigned >	indexBitwidth {*this, "index-bitwidth", ::llvm::cl::desc(R"PO(Bitwidth of the index type, 0 to use size of machine word)PO"), ::llvm::cl::init(0)}
::mlir::Pass::Option< bool >	useBarePtrCallConv {*this, "use-bare-ptr-memref-call-conv", ::llvm::cl::desc(R"PO(Replace memref arguments in GPU functions with bare pointers.All memrefs must have static shape)PO"), ::llvm::cl::init(false)}
::mlir::Pass::Option<::mlir::gpu::amd::Runtime >	runtime
::mlir::Pass::ListOption< std::string >	allowedDialects {*this, "allowed-dialects", ::llvm::cl::desc(R"PO(Run conversion patterns of only the specified dialects)PO")}

Friends
std::unique_ptr<::mlir::Pass >	createConvertGpuOpsToROCDLOps ()
std::unique_ptr<::mlir::Pass >	createConvertGpuOpsToROCDLOps (ConvertGpuOpsToROCDLOpsOptions options)

Additional Inherited Members
Protected Member Functions inherited from mlir::OperationPass< gpu::GPUModuleOp >
	OperationPass (TypeID passID)
OperationPass &	operator= (const OperationPass &)=delete
bool	canScheduleOn (RegisteredOperationName opName) const final
	Indicate if the current pass can be scheduled on the given operation type.
gpu::GPUModuleOp	getOperation ()
	Return the current operation being transformed.
AnalysisT &	getAnalysis ()
	Query an analysis for the current operation of the specific derived operation type.
Protected Member Functions inherited from mlir::Pass
	Pass (TypeID passID, std::optional< StringRef > opName=std::nullopt)
	Pass (const Pass &other)
Pass &	operator= (const Pass &)=delete
	Pass (Pass &&)=delete
Pass &	operator= (Pass &&)=delete
detail::PassExecutionState &	getPassState ()
	Returns the current pass state.
MLIRContext &	getContext ()
	Return the MLIR context for the current operation being transformed.
virtual void	runOnOperation ()=0
	The polymorphic API that runs the pass over the currently held operation.
virtual LogicalResult	initialize (MLIRContext *context)
	Initialize any complex state necessary for running this pass.
virtual bool	canScheduleOn (Operation *op) const
LogicalResult	runPipeline (OpPassManager &pipeline, Operation *op)
	Schedule an arbitrary pass pipeline on the provided operation.
std::unique_ptr< Pass >	clone () const
	A clone method to create a copy of this pass.
Operation *	getOperation ()
	Return the current operation being transformed.
void	signalPassFailure ()
	Signal that some invariant was broken when running.
template<typename AnalysisT>
AnalysisT &	getAnalysis ()
	Query an analysis for the current ir unit.
template<typename AnalysisT, typename OpT>
AnalysisT &	getAnalysis ()
	Query an analysis for the current ir unit of a specific derived operation type.
template<typename AnalysisT>
std::optional< std::reference_wrapper< AnalysisT > >	getCachedAnalysis ()
	Query a cached instance of an analysis for the current ir unit if one exists.
void	markAllAnalysesPreserved ()
	Mark all analyses as preserved.
template<typename... AnalysesT>
void	markAnalysesPreserved ()
	Mark the provided analyses as preserved.
void	markAnalysesPreserved (TypeID id)
template<typename AnalysisT>
std::optional< std::reference_wrapper< AnalysisT > >	getCachedParentAnalysis (Operation *parent)
	Returns the analysis for the given parent operation if it exists.
template<typename AnalysisT>
std::optional< std::reference_wrapper< AnalysisT > >	getCachedParentAnalysis ()
	Returns the analysis for the parent operation if it exists.
template<typename AnalysisT>
std::optional< std::reference_wrapper< AnalysisT > >	getCachedChildAnalysis (Operation *child)
	Returns the analysis for the given child operation if it exists.
template<typename AnalysisT>
AnalysisT &	getChildAnalysis (Operation *child)
	Returns the analysis for the given child operation, or creates it if it doesn't exist.
template<typename AnalysisT, typename OpTy>
AnalysisT &	getChildAnalysis (OpTy child)
	Returns the analysis for the given child operation of specific derived operation type, or creates it if it doesn't exist.
AnalysisManager	getAnalysisManager ()
	Returns the current analysis manager.
void	copyOptionValuesFrom (const Pass *other)
	Copy the option values from 'other', which is another instance of this pass.
Static Protected Member Functions inherited from mlir::OperationPass< gpu::GPUModuleOp >
static bool	classof (const Pass *pass)
	Support isa/dyn_cast functionality.

Detailed Description

template<typename DerivedT>
class mlir::impl::ConvertGpuOpsToROCDLOpsBase< DerivedT >

Definition at line 2486 of file LowerGpuOpsToROCDLOps.cpp.

Member Typedef Documentation

◆ Base

template<typename DerivedT>

using mlir::impl::ConvertGpuOpsToROCDLOpsBase< DerivedT >::Base = ConvertGpuOpsToROCDLOpsBase

Definition at line 2488 of file LowerGpuOpsToROCDLOps.cpp.

Constructor & Destructor Documentation

◆ ConvertGpuOpsToROCDLOpsBase() [1/4]

template<typename DerivedT>

mlir::impl::ConvertGpuOpsToROCDLOpsBase< DerivedT >::ConvertGpuOpsToROCDLOpsBase ( )

inline

Definition at line 2490 of file LowerGpuOpsToROCDLOps.cpp.

◆ ConvertGpuOpsToROCDLOpsBase() [2/4]

template<typename DerivedT>

mlir::impl::ConvertGpuOpsToROCDLOpsBase< DerivedT >::ConvertGpuOpsToROCDLOpsBase ( const ConvertGpuOpsToROCDLOpsBase< DerivedT > & other )

inline

Definition at line 2491 of file LowerGpuOpsToROCDLOps.cpp.

◆ ConvertGpuOpsToROCDLOpsBase() [3/4]

template<typename DerivedT>

mlir::impl::ConvertGpuOpsToROCDLOpsBase< DerivedT >::ConvertGpuOpsToROCDLOpsBase ( ConvertGpuOpsToROCDLOpsBase< DerivedT > && )

delete

◆ ~ConvertGpuOpsToROCDLOpsBase()

template<typename DerivedT>

mlir::impl::ConvertGpuOpsToROCDLOpsBase< DerivedT >::~ConvertGpuOpsToROCDLOpsBase ( )

default

◆ ConvertGpuOpsToROCDLOpsBase() [4/4]

template<typename DerivedT>

mlir::impl::ConvertGpuOpsToROCDLOpsBase< DerivedT >::ConvertGpuOpsToROCDLOpsBase ( ConvertGpuOpsToROCDLOpsOptions options )

inline

Explicitly declare the TypeID for this class.

We declare an explicit private instantiation because Pass classes should only be visible by the current library.

Definition at line 2534 of file LowerGpuOpsToROCDLOps.cpp.

Member Function Documentation

◆ classof()

template<typename DerivedT>

bool mlir::impl::ConvertGpuOpsToROCDLOpsBase< DerivedT >::classof ( const ::mlir::Pass * pass )

inlinestatic

Support isa/dyn_cast functionality for the derived pass class.

Definition at line 2512 of file LowerGpuOpsToROCDLOps.cpp.

◆ clonePass()

template<typename DerivedT>

std::unique_ptr<::mlir::Pass > mlir::impl::ConvertGpuOpsToROCDLOpsBase< DerivedT >::clonePass ( ) const

inlineoverridevirtual

A clone method to create a copy of this pass.

Implements mlir::Pass.

Definition at line 2517 of file LowerGpuOpsToROCDLOps.cpp.

◆ getArgument()

template<typename DerivedT>

::llvm::StringRef mlir::impl::ConvertGpuOpsToROCDLOpsBase< DerivedT >::getArgument ( ) const

inlineoverridevirtual

Return the command line argument used when registering this pass.

Return an empty string if one does not exist.

Reimplemented from mlir::Pass.

Definition at line 2501 of file LowerGpuOpsToROCDLOps.cpp.

◆ getArgumentName()

template<typename DerivedT>

constexpr ::llvm::StringLiteral mlir::impl::ConvertGpuOpsToROCDLOpsBase< DerivedT >::getArgumentName ( )

inlinestatic

Returns the command-line argument attached to this pass.

Definition at line 2498 of file LowerGpuOpsToROCDLOps.cpp.

◆ getDependentDialects()

template<typename DerivedT>

void mlir::impl::ConvertGpuOpsToROCDLOpsBase< DerivedT >::getDependentDialects ( ::mlir::DialectRegistry & registry ) const

inlineoverride

Return the dialect that must be loaded in the context before this pass.

Definition at line 2522 of file LowerGpuOpsToROCDLOps.cpp.

◆ getDescription()

template<typename DerivedT>

::llvm::StringRef mlir::impl::ConvertGpuOpsToROCDLOpsBase< DerivedT >::getDescription ( ) const

inlineoverridevirtual

Return the command line description used when registering this pass.

Return an empty string if one does not exist.

Reimplemented from mlir::Pass.

Definition at line 2503 of file LowerGpuOpsToROCDLOps.cpp.

◆ getName()

template<typename DerivedT>

::llvm::StringRef mlir::impl::ConvertGpuOpsToROCDLOpsBase< DerivedT >::getName ( ) const

inlineoverridevirtual

Returns the derived pass name.

Implements mlir::Pass.

Definition at line 2509 of file LowerGpuOpsToROCDLOps.cpp.

◆ getPassName()

template<typename DerivedT>

constexpr ::llvm::StringLiteral mlir::impl::ConvertGpuOpsToROCDLOpsBase< DerivedT >::getPassName ( )

inlinestatic

Returns the derived pass name.

Definition at line 2506 of file LowerGpuOpsToROCDLOps.cpp.

◆ operator=() [1/2]

template<typename DerivedT>

ConvertGpuOpsToROCDLOpsBase & mlir::impl::ConvertGpuOpsToROCDLOpsBase< DerivedT >::operator= ( const ConvertGpuOpsToROCDLOpsBase< DerivedT > & )

delete

◆ operator=() [2/2]

template<typename DerivedT>

ConvertGpuOpsToROCDLOpsBase & mlir::impl::ConvertGpuOpsToROCDLOpsBase< DerivedT >::operator= ( ConvertGpuOpsToROCDLOpsBase< DerivedT > && )

delete

◆ createConvertGpuOpsToROCDLOps [1/2]

template<typename DerivedT>

std::unique_ptr<::mlir::Pass > createConvertGpuOpsToROCDLOps ( )

friend

Definition at line 2558 of file LowerGpuOpsToROCDLOps.cpp.

◆ createConvertGpuOpsToROCDLOps [2/2]

template<typename DerivedT>

std::unique_ptr<::mlir::Pass > createConvertGpuOpsToROCDLOps ( ConvertGpuOpsToROCDLOpsOptions options )

friend

Definition at line 2562 of file LowerGpuOpsToROCDLOps.cpp.

Member Data Documentation

◆ allowedDialects

template<typename DerivedT>

::mlir::Pass::ListOption<std::string> mlir::impl::ConvertGpuOpsToROCDLOpsBase< DerivedT >::allowedDialects {*this, "allowed-dialects", ::llvm::cl::desc(R"PO(Run conversion patterns of only the specified dialects)PO")}

protected

Definition at line 2555 of file LowerGpuOpsToROCDLOps.cpp.

◆ arch

template<typename DerivedT>

::mlir::Pass::Option<std::string> mlir::impl::ConvertGpuOpsToROCDLOpsBase< DerivedT >::arch {*this, "arch", ::llvm::cl::desc(R"PO(Target architecture, as in Clang, with optional target-ID modifiers. New-style triples such as amdgpu9.42-amd-amdhsa are preferred, and can be extended to a full target ID like amdgpu9.42-amd-amdhsa--gfx942:xnack+:sramecc-. Bare chip names like gfx1250 or gfx942:xnack- are also supported. Defaults to an invalid target so that one must be given explicitly)PO"), ::llvm::cl::init("invalid")}

protected

Definition at line 2544 of file LowerGpuOpsToROCDLOps.cpp.

◆ chipset

template<typename DerivedT>

::mlir::Pass::Option<std::string> mlir::impl::ConvertGpuOpsToROCDLOpsBase< DerivedT >::chipset {*this, "chipset", ::llvm::cl::desc(R"PO(Deprecated alias for 'arch'.)PO"), ::llvm::cl::init("")}

protected

Definition at line 2545 of file LowerGpuOpsToROCDLOps.cpp.

◆ indexBitwidth

template<typename DerivedT>

::mlir::Pass::Option<unsigned> mlir::impl::ConvertGpuOpsToROCDLOpsBase< DerivedT >::indexBitwidth {*this, "index-bitwidth", ::llvm::cl::desc(R"PO(Bitwidth of the index type, 0 to use size of machine word)PO"), ::llvm::cl::init(0)}

protected

Definition at line 2547 of file LowerGpuOpsToROCDLOps.cpp.

◆ runtime

template<typename DerivedT>

::mlir::Pass::Option<::mlir::gpu::amd::Runtime> mlir::impl::ConvertGpuOpsToROCDLOpsBase< DerivedT >::runtime

protected

Initial value:

{*this, "runtime", ::llvm::cl::desc(R"PO(Runtime code will be run on (default is Unknown, can also use HIP or OpenCL))PO"), ::llvm::cl::init(::mlir::gpu::amd::Runtime::Unknown), ::llvm::cl::values(
               clEnumValN(::mlir::gpu::amd::Runtime::Unknown, "unknown",
                          "Unknown (default)"),
               clEnumValN(::mlir::gpu::amd::Runtime::HIP, "HIP", "HIP"),
               clEnumValN(::mlir::gpu::amd::Runtime::OpenCL, "OpenCL",
                          "OpenCL"))}

Definition at line 2549 of file LowerGpuOpsToROCDLOps.cpp.

◆ useBarePtrCallConv

template<typename DerivedT>

::mlir::Pass::Option<bool> mlir::impl::ConvertGpuOpsToROCDLOpsBase< DerivedT >::useBarePtrCallConv {*this, "use-bare-ptr-memref-call-conv", ::llvm::cl::desc(R"PO(Replace memref arguments in GPU functions with bare pointers.All memrefs must have static shape)PO"), ::llvm::cl::init(false)}

protected

Definition at line 2548 of file LowerGpuOpsToROCDLOps.cpp.

◆ waveSize

template<typename DerivedT>

::mlir::Pass::Option<unsigned> mlir::impl::ConvertGpuOpsToROCDLOpsBase< DerivedT >::waveSize {*this, "wavesize", ::llvm::cl::desc(R"PO(Wavefront size (32 or 64) for targets that run at either, or 0 to use the architecture's default)PO"), ::llvm::cl::init(0)}

protected

Definition at line 2546 of file LowerGpuOpsToROCDLOps.cpp.

The documentation for this class was generated from the following file:

lib/Conversion/GPUToROCDL/LowerGpuOpsToROCDLOps.cpp

Public Types

Public Member Functions

Static Public Member Functions

Protected Attributes

Friends

Additional Inherited Members

Detailed Description

Member Typedef Documentation

◆ Base

Constructor & Destructor Documentation

◆ ConvertGpuOpsToROCDLOpsBase() [1/4]

◆ ConvertGpuOpsToROCDLOpsBase() [2/4]

◆ ConvertGpuOpsToROCDLOpsBase() [3/4]

◆ ~ConvertGpuOpsToROCDLOpsBase()

◆ ConvertGpuOpsToROCDLOpsBase() [4/4]

Member Function Documentation

◆ classof()

◆ clonePass()

◆ getArgument()

◆ getArgumentName()

◆ getDependentDialects()

◆ getDescription()

◆ getName()

◆ getPassName()

◆ operator=() [1/2]

◆ operator=() [2/2]

Friends And Related Symbol Documentation

◆ createConvertGpuOpsToROCDLOps [1/2]

◆ createConvertGpuOpsToROCDLOps [2/2]

Member Data Documentation

◆ allowedDialects

◆ arch

◆ chipset

◆ indexBitwidth

◆ runtime

◆ useBarePtrCallConv

◆ waveSize