[flang-commits] [flang] [flang][cuda] Add cuf.register_kernel operation (PR #112268)

Mon Oct 14 21:05:57 PDT 2024

llvm-ci wrote:

LLVM Buildbot has detected a new failure on builder `flang-aarch64-libcxx` running on `linaro-flang-aarch64-libcxx` while building `flang` at step 5 "build-unified-tree".

Full details are available at: https://lab.llvm.org/buildbot/#/builders/89/builds/8418

<details>
<summary>Here is the relevant piece of the build log for the reference</summary>

```
Step 5 (build-unified-tree) failure: build (failure)
...
83.240 [167/12/7052] Creating library symlink lib/libFortranSemantics.so
83.383 [162/16/7053] Linking CXX executable tools/flang/unittests/Evaluate/integer.test
83.384 [162/15/7054] Linking CXX executable tools/flang/unittests/Evaluate/logical.test
83.391 [162/14/7055] Linking CXX executable tools/flang/unittests/Evaluate/real.test
83.530 [162/13/7056] Linking CXX executable tools/flang/unittests/Evaluate/folding.test
83.585 [162/12/7057] Linking CXX executable tools/flang/unittests/Evaluate/expression.test
85.714 [162/11/7058] Building CXX object tools/flang/lib/Optimizer/Dialect/CUF/CMakeFiles/CUFDialect.dir/CUFDialect.cpp.o
87.478 [162/10/7059] Building CXX object tools/flang/lib/Optimizer/Transforms/CMakeFiles/FIRTransforms.dir/CufImplicitDeviceGlobal.cpp.o
88.562 [162/9/7060] Building CXX object tools/flang/lib/Optimizer/Dialect/CUF/CMakeFiles/CUFDialect.dir/CUFOps.cpp.o
88.719 [161/9/7061] Linking CXX shared library lib/libCUFDialect.so.20.0git
FAILED: lib/libCUFDialect.so.20.0git 
: && /usr/local/bin/c++ -fPIC -stdlib=libc++ -fPIC -fno-semantic-interposition -fvisibility-inlines-hidden -Werror=date-time -Werror=unguarded-availability-new -Wall -Wextra -Wno-unused-parameter -Wwrite-strings -Wcast-qual -Wmissing-field-initializers -pedantic -Wno-long-long -Wc++98-compat-extra-semi -Wimplicit-fallthrough -Wcovered-switch-default -Wno-noexcept-type -Wnon-virtual-dtor -Wdelete-non-virtual-dtor -Wsuggest-override -Wstring-conversion -Wmisleading-indentation -Wctad-maybe-unsupported -fdiagnostics-color -ffunction-sections -fdata-sections -Werror -Wno-deprecated-copy -Wno-string-conversion -Wno-ctad-maybe-unsupported -Wno-unused-command-line-argument -Wstring-conversion           -Wcovered-switch-default -Wno-nested-anon-types -O3 -DNDEBUG  -stdlib=libc++ -Wl,-z,defs -Wl,-z,nodelete   -Wl,-rpath-link,/home/tcwg-buildbot/worker/flang-aarch64-libcxx/build/./lib  -Wl,--gc-sections -shared -Wl,-soname,libCUFDialect.so.20.0git -o lib/libCUFDialect.so.20.0git tools/flang/lib/Optimizer/Dialect/CUF/CMakeFiles/CUFDialect.dir/CUFDialect.cpp.o tools/flang/lib/Optimizer/Dialect/CUF/CMakeFiles/CUFDialect.dir/CUFOps.cpp.o  -Wl,-rpath,"\$ORIGIN/../lib:/home/tcwg-buildbot/worker/flang-aarch64-libcxx/build/lib:"  lib/libFIRDialect.so.20.0git  lib/libFIRDialectSupport.so.20.0git  lib/libCUFAttrs.so.20.0git  lib/libLLVMAsmPrinter.so.20.0git  lib/libMLIRTargetLLVMIRExport.so.20.0git  lib/libMLIRDLTIDialect.so.20.0git  lib/libMLIRLLVMIRTransforms.so.20.0git  lib/libMLIRFuncDialect.so.20.0git  lib/libMLIRTransforms.so.20.0git  lib/libMLIRRuntimeVerifiableOpInterface.so.20.0git  lib/libMLIRNVVMDialect.so.20.0git  lib/libMLIRTranslateLib.so.20.0git  lib/libMLIRParser.so.20.0git  lib/libMLIRBytecodeReader.so.20.0git  lib/libMLIRAsmParser.so.20.0git  lib/libMLIRTransformUtils.so.20.0git  lib/libMLIRSubsetOpInterface.so.20.0git  lib/libMLIRValueBoundsOpInterface.so.20.0git  lib/libMLIRDestinationStyleOpInterface.so.20.0git  lib/libMLIRRewrite.so.20.0git  lib/libMLIRRewritePDL.so.20.0git  lib/libMLIRPDLToPDLInterp.so.20.0git  lib/libMLIRPass.so.20.0git  lib/libMLIRAnalysis.so.20.0git  lib/libMLIRLoopLikeInterface.so.20.0git  lib/libMLIRInferIntRangeInterface.so.20.0git  lib/libMLIRPresburger.so.20.0git  lib/libMLIRViewLikeInterface.so.20.0git  lib/libMLIRPDLInterpDialect.so.20.0git  lib/libMLIRPDLDialect.so.20.0git  lib/libLLVMFrontendOpenMP.so.20.0git  lib/libLLVMTransformUtils.so.20.0git  lib/libMLIRLLVMDialect.so.20.0git  lib/libMLIRDataLayoutInterfaces.so.20.0git  lib/libMLIRCallInterfaces.so.20.0git  lib/libMLIRControlFlowInterfaces.so.20.0git  lib/libMLIRFunctionInterfaces.so.20.0git  lib/libMLIRInferTypeOpInterface.so.20.0git  lib/libMLIRMemorySlotInterfaces.so.20.0git  lib/libMLIRSideEffectInterfaces.so.20.0git  lib/libMLIRIR.so.20.0git  lib/libMLIRSupport.so.20.0git  lib/libLLVMBitWriter.so.20.0git  lib/libLLVMAsmParser.so.20.0git  lib/libLLVMBitReader.so.20.0git  lib/libLLVMCore.so.20.0git  lib/libLLVMRemarks.so.20.0git  lib/libLLVMBinaryFormat.so.20.0git  lib/libLLVMTargetParser.so.20.0git  lib/libLLVMSupport.so.20.0git  -Wl,-rpath-link,/home/tcwg-buildbot/worker/flang-aarch64-libcxx/build/lib && :
/usr/bin/ld: tools/flang/lib/Optimizer/Dialect/CUF/CMakeFiles/CUFDialect.dir/CUFOps.cpp.o: in function `llvm::DefaultDoCastIfPossible<mlir::gpu::GPUModuleOp, mlir::Operation*, llvm::CastInfo<mlir::gpu::GPUModuleOp, mlir::Operation*, void> >::doCastIfPossible(mlir::Operation*)':
CUFOps.cpp:(.text._ZN4llvm23DefaultDoCastIfPossibleIN4mlir3gpu11GPUModuleOpEPNS1_9OperationENS_8CastInfoIS3_S5_vEEE16doCastIfPossibleES5_[_ZN4llvm23DefaultDoCastIfPossibleIN4mlir3gpu11GPUModuleOpEPNS1_9OperationENS_8CastInfoIS3_S5_vEEE16doCastIfPossibleES5_]+0x24): undefined reference to `mlir::detail::TypeIDResolver<mlir::gpu::GPUModuleOp, void>::id'
/usr/bin/ld: CUFOps.cpp:(.text._ZN4llvm23DefaultDoCastIfPossibleIN4mlir3gpu11GPUModuleOpEPNS1_9OperationENS_8CastInfoIS3_S5_vEEE16doCastIfPossibleES5_[_ZN4llvm23DefaultDoCastIfPossibleIN4mlir3gpu11GPUModuleOpEPNS1_9OperationENS_8CastInfoIS3_S5_vEEE16doCastIfPossibleES5_]+0x28): undefined reference to `mlir::detail::TypeIDResolver<mlir::gpu::GPUModuleOp, void>::id'
/usr/bin/ld: tools/flang/lib/Optimizer/Dialect/CUF/CMakeFiles/CUFDialect.dir/CUFOps.cpp.o: in function `llvm::DefaultDoCastIfPossible<mlir::gpu::GPUFuncOp, mlir::Operation*, llvm::CastInfo<mlir::gpu::GPUFuncOp, mlir::Operation*, void> >::doCastIfPossible(mlir::Operation*)':
CUFOps.cpp:(.text._ZN4llvm23DefaultDoCastIfPossibleIN4mlir3gpu9GPUFuncOpEPNS1_9OperationENS_8CastInfoIS3_S5_vEEE16doCastIfPossibleES5_[_ZN4llvm23DefaultDoCastIfPossibleIN4mlir3gpu9GPUFuncOpEPNS1_9OperationENS_8CastInfoIS3_S5_vEEE16doCastIfPossibleES5_]+0x24): undefined reference to `mlir::detail::TypeIDResolver<mlir::gpu::GPUFuncOp, void>::id'
/usr/bin/ld: CUFOps.cpp:(.text._ZN4llvm23DefaultDoCastIfPossibleIN4mlir3gpu9GPUFuncOpEPNS1_9OperationENS_8CastInfoIS3_S5_vEEE16doCastIfPossibleES5_[_ZN4llvm23DefaultDoCastIfPossibleIN4mlir3gpu9GPUFuncOpEPNS1_9OperationENS_8CastInfoIS3_S5_vEEE16doCastIfPossibleES5_]+0x28): undefined reference to `mlir::detail::TypeIDResolver<mlir::gpu::GPUFuncOp, void>::id'
clang++: error: linker command failed with exit code 1 (use -v to see invocation)
93.279 [161/8/7062] Building CXX object tools/flang/lib/Optimizer/Transforms/CMakeFiles/FIRTransforms.dir/CUFAddConstructor.cpp.o
95.667 [161/7/7063] Building CXX object tools/flang/lib/Optimizer/Transforms/CMakeFiles/FIRTransforms.dir/CufOpConversion.cpp.o
98.962 [161/6/7064] Building CXX object tools/flang/lib/Optimizer/Builder/CMakeFiles/FIRBuilder.dir/FIRBuilder.cpp.o
159.523 [161/5/7065] Building CXX object tools/flang/tools/fir-opt/CMakeFiles/fir-opt.dir/fir-opt.cpp.o
190.893 [161/4/7066] Building CXX object tools/flang/lib/Lower/CMakeFiles/FortranLower.dir/Allocatable.cpp.o
206.072 [161/3/7067] Building CXX object tools/flang/lib/Lower/CMakeFiles/FortranLower.dir/ConvertVariable.cpp.o
238.392 [161/2/7068] Building CXX object tools/flang/lib/Lower/CMakeFiles/FortranLower.dir/ConvertCall.cpp.o
354.255 [161/1/7069] Building CXX object tools/flang/lib/Lower/CMakeFiles/FortranLower.dir/Bridge.cpp.o
ninja: build stopped: subcommand failed.

```

</details>

https://github.com/llvm/llvm-project/pull/112268