Home
last modified time | relevance | path

Searched refs:CUDA (Results 1 – 25 of 105) sorted by relevance

12345

/openbsd-src/gnu/llvm/llvm/docs/
H A DCompileCudaWithLLVM.rst2 Compiling CUDA with clang
11 This document describes how to compile CUDA code with clang, and gives some
12 details about LLVM and clang's CUDA implementations.
14 This document assumes a basic familiarity with CUDA. Information about CUDA
16 `CUDA programming guide
19 Compiling CUDA Code
25 CUDA is supported since llvm 3.9. Clang currently supports CUDA 7.0 through
26 11.5. If clang detects a newer CUDA version, it will issue a warning and will
27 attempt to use detected CUDA SDK it as if it were CUDA 11.5.
29 Before you build CUDA code, you'll need to have installed the CUDA SDK. See
[all …]
H A DNVPTXUsage.rst21 This document assumes a basic familiarity with CUDA and the PTX
22 assembly language. Information about the CUDA Driver API and the PTX assembly
23 language can be found in the `CUDA documentation
100 copy data to it by name with the CUDA Driver API.
117 generated PTX compatible with the CUDA Driver API.
119 Example: 32-bit PTX for CUDA Driver API: ``nvptx-nvidia-cuda``
121 Example: 64-bit PTX for CUDA Driver API: ``nvptx64-nvidia-cuda``
223 map in the following way to CUDA builtins:
226 CUDA Builtin PTX Special Register Intrinsic
252 instruction, equivalent to the ``__syncthreads()`` call in CUDA.
[all …]
/openbsd-src/gnu/llvm/clang/lib/Frontend/
H A DFrontendOptions.cpp22 .Case("cui", InputKind(Language::CUDA).getPreprocessed()) in getInputKindForExtension()
33 .Cases("cu", "cuh", Language::CUDA) in getInputKindForExtension()
/openbsd-src/gnu/llvm/clang/tools/nvptx-arch/
H A DCMakeLists.txt13 find_package(CUDA QUIET)
20 # If we found the CUDA library directly we just dynamically link against it.
/openbsd-src/gnu/llvm/clang/lib/Sema/
H A DSemaCUDA.cpp38 assert(getLangOpts().CUDA && "Should only be called during CUDA compilation"); in PushForceCUDAHostDevice()
43 assert(getLangOpts().CUDA && "Should only be called during CUDA compilation"); in PopForceCUDAHostDevice()
661 assert(getLangOpts().CUDA && "Should only be called during CUDA compilation"); in maybeAddCUDAHostDeviceAttrs()
727 assert(getLangOpts().CUDA && "Should only be called during CUDA compilation"); in CUDADiagIfDeviceCode()
757 assert(getLangOpts().CUDA && "Should only be called during CUDA compilation"); in CUDADiagIfHostCode()
785 assert(getLangOpts().CUDA && "Should only be called during CUDA compilation"); in CheckCUDACall()
896 assert(getLangOpts().CUDA && "Should only be called during CUDA compilation"); in CUDASetLambdaAttrs()
905 assert(getLangOpts().CUDA && "Should only be called during CUDA compilation"); in checkCUDATargetOverload()
/openbsd-src/gnu/llvm/clang/lib/Headers/cuda_wrappers/
H A Dcmath1 /*===---- cmath - CUDA wrapper for <cmath> ---------------------------------===
31 // libc++ will need long double variants of these functions, but CUDA does not
71 // which we can't handle on GPU. We need to forward those to CUDA-provided
H A Dnew1 /*===---- new - CUDA wrapper for <new> -------------------------------------===
31 // and CUDA-specific macros are not available yet.
H A Dcomplex1 /*===---- complex - CUDA wrapper for <complex> ------------------------------===
47 // functions that don't exist when compiling CUDA device code).
/openbsd-src/gnu/llvm/clang/lib/Basic/
H A DLangOptions.cpp173 Opts.CUDA = Lang == Language::CUDA || Opts.HIP; in setLangDefaults()
184 } else if (Opts.CUDA) { in setLangDefaults()
H A DLangStandards.cpp57 case Language::CUDA: in getDefaultLanguageStandard()
H A DBuiltins.cpp117 if (!LangOpts.CUDA && BuiltinInfo.Langs == CUDA_LANG) in builtinIsSupported()
/openbsd-src/gnu/llvm/clang/docs/
H A DClangOffloadPackager.rst94 | IMG_Cubin | 0x03 | The image is a CUDA object file |
96 | IMG_Fatbinary | 0x04 | The image is a CUDA fatbinary file |
98 | IMG_PTX | 0x05 | The image is a CUDA PTX file |
111 | OFK_CUDA | 0x02 | The producer was CUDA |
H A DClangLinkerWrapper.rst35 --cuda-path=<dir> Set the system CUDA path
/openbsd-src/gnu/llvm/clang/include/clang/Basic/
H A DDiagnosticDriverKinds.td54 def err_drv_cuda_bad_gpu_arch : Error<"unsupported CUDA gpu architecture: %0">;
57 "cannot find CUDA installation; provide its path via '--cuda-path', or pass "
58 "'-nocudainc' to build without CUDA includes">;
60 "cannot find libdevice for %0; provide path to different CUDA installation "
84 "GPU arch %0 is supported by CUDA versions between %1 and %2 (inclusive), "
85 "but installation at %3 is %4; use '--cuda-path' to specify a different CUDA "
89 "CUDA version%0 is newer than the latest%select{| partially}1 supported version %2">,
92 "CUDA version %0 is only partially supported">,
97 "mixed CUDA and HIP compilation is not supported">;
331 "NVPTX target requires CUDA 9.2 or above; CUDA %0 detected">;
[all …]
H A DLangStandards.def203 // CUDA
204 LANGSTANDARD(cuda, "cuda", CUDA, "NVIDIA CUDA(tm)",
H A DLangOptions.def240 LANGOPT(CUDA , 1, 0, "CUDA")
249 LANGOPT(OpenMPCUDANumSMs , 32, 0, "Number of SMs for CUDA devices.")
250 LANGOPT(OpenMPCUDABlocksPerSM , 32, 0, "Number of blocks per SM for CUDA devices.")
265 LANGOPT(CUDAIsDevice , 1, 0, "compiling for CUDA device")
266 LANGOPT(CUDAAllowVariadicFunctions, 1, 0, "allowing variadic functions in CUDA device code")
272 LANGOPT(GPUDeferDiag, 1, 0, "defer host/device related diagnostic messages for CUDA/HIP")
273 …gSideOverloads, 1, 0, "always exclude wrong side overloads in overloading resolution for CUDA/HIP")
H A DLangStandard.h40 CUDA, enumerator
H A DFeatures.def277 // CUDA/HIP Features
278 FEATURE(cuda_noinline_keyword, LangOpts.CUDA)
H A DAttr.td359 def CUDA : LangOpt<"CUDA">;
1149 // CUDA attributes are spelled __attribute__((attr)) or __declspec(__attr__),
1154 let LangOpts = [CUDA];
1160 let LangOpts = [CUDA];
1166 let LangOpts = [CUDA];
1172 let LangOpts = [CUDA];
1178 let LangOpts = [CUDA];
1188 let LangOpts = [CUDA];
1200 let LangOpts = [CUDA];
1208 let LangOpts = [CUDA];
[all …]
/openbsd-src/gnu/llvm/llvm/lib/Target/NVPTX/
H A DNVPTXSubtarget.cpp58 if (TM.getDrvInterface() == NVPTX::CUDA) in hasImageHandles()
H A DNVPTX.h73 CUDA enumerator
H A DNVPTXLowerArgs.cpp424 if (TM && TM->getDrvInterface() == NVPTX::CUDA) { in runOnKernelFunction()
448 else if (TM && TM->getDrvInterface() == NVPTX::CUDA) in runOnKernelFunction()
H A DNVPTXAsmPrinter.h252 NVPTX::CUDA) {} in NVPTXAsmPrinter()
/openbsd-src/gnu/llvm/clang/lib/AST/
H A DMicrosoftCXXABI.cpp124 if (Context.getLangOpts().CUDA && Context.getAuxTargetInfo()) { in MicrosoftCXXABI()
194 if (Context.getLangOpts().CUDA && Context.getAuxTargetInfo()) { in createMangleNumberingContext()
/openbsd-src/gnu/llvm/clang/lib/Headers/openmp_wrappers/
H A Dcmath39 // Overloads not provided by the CUDA wrappers but by the CUDA system headers.

12345