diff --git a/.gitignore b/.gitignore index 9bead862d8..6e3022484f 100644 --- a/.gitignore +++ b/.gitignore @@ -12,45 +12,45 @@ __pycache__/ .benchmarks/ *.cpp !*_impl.cpp -!cuda_bindings/cuda/bindings/_lib/param_packer.cpp -!cuda_bindings/cuda/bindings/_bindings/loader.cpp +!cuda_bindings/src/cuda/bindings/_lib/param_packer.cpp +!cuda_bindings/src/cuda/bindings/_bindings/loader.cpp cache_driver cache_runtime cache_nvrtc -cuda_bindings/cuda/bindings/_lib/utils.pxi +cuda_bindings/src/cuda/bindings/_lib/utils.pxi # CUDA Python specific (auto-generated) -cuda_bindings/cuda/bindings/_bindings/cydriver.pxd -cuda_bindings/cuda/bindings/_bindings/cydriver.pyx -cuda_bindings/cuda/bindings/_bindings/cyruntime.pxd -cuda_bindings/cuda/bindings/_bindings/cyruntime.pyx -cuda_bindings/cuda/bindings/_bindings/cyruntime_ptds.pxd -cuda_bindings/cuda/bindings/_bindings/cyruntime_ptds.pyx -cuda_bindings/cuda/bindings/_bindings/cynvrtc.pxd -cuda_bindings/cuda/bindings/_bindings/cynvrtc.pyx -cuda_bindings/cuda/bindings/_internal/_nvml.pyx -cuda_bindings/cuda/bindings/_internal/cufile.pyx -cuda_bindings/cuda/bindings/_internal/nvfatbin.pyx -cuda_bindings/cuda/bindings/_internal/nvjitlink.pyx -cuda_bindings/cuda/bindings/_internal/nvml.pyx -cuda_bindings/cuda/bindings/_internal/nvvm.pyx -cuda_bindings/cuda/bindings/_lib/utils.pxd -cuda_bindings/cuda/bindings/_lib/utils.pyx -cuda_bindings/cuda/bindings/cydriver.pxd -cuda_bindings/cuda/bindings/cydriver.pyx -cuda_bindings/cuda/bindings/cyruntime.pxd -cuda_bindings/cuda/bindings/cyruntime.pyx -cuda_bindings/cuda/bindings/cyruntime_functions.pxi -cuda_bindings/cuda/bindings/cyruntime_types.pxi -cuda_bindings/cuda/bindings/cynvrtc.pxd -cuda_bindings/cuda/bindings/cynvrtc.pyx -cuda_bindings/cuda/bindings/driver.pxd -cuda_bindings/cuda/bindings/driver.pyx -cuda_bindings/cuda/bindings/runtime.pxd -cuda_bindings/cuda/bindings/runtime.pyx -cuda_bindings/cuda/bindings/nvrtc.pxd -cuda_bindings/cuda/bindings/nvrtc.pyx -cuda_bindings/cuda/bindings/utils/_get_handle.pyx +cuda_bindings/src/cuda/bindings/_bindings/cydriver.pxd +cuda_bindings/src/cuda/bindings/_bindings/cydriver.pyx +cuda_bindings/src/cuda/bindings/_bindings/cyruntime.pxd +cuda_bindings/src/cuda/bindings/_bindings/cyruntime.pyx +cuda_bindings/src/cuda/bindings/_bindings/cyruntime_ptds.pxd +cuda_bindings/src/cuda/bindings/_bindings/cyruntime_ptds.pyx +cuda_bindings/src/cuda/bindings/_bindings/cynvrtc.pxd +cuda_bindings/src/cuda/bindings/_bindings/cynvrtc.pyx +cuda_bindings/src/cuda/bindings/_internal/_nvml.pyx +cuda_bindings/src/cuda/bindings/_internal/cufile.pyx +cuda_bindings/src/cuda/bindings/_internal/nvfatbin.pyx +cuda_bindings/src/cuda/bindings/_internal/nvjitlink.pyx +cuda_bindings/src/cuda/bindings/_internal/nvml.pyx +cuda_bindings/src/cuda/bindings/_internal/nvvm.pyx +cuda_bindings/src/cuda/bindings/_lib/utils.pxd +cuda_bindings/src/cuda/bindings/_lib/utils.pyx +cuda_bindings/src/cuda/bindings/cydriver.pxd +cuda_bindings/src/cuda/bindings/cydriver.pyx +cuda_bindings/src/cuda/bindings/cyruntime.pxd +cuda_bindings/src/cuda/bindings/cyruntime.pyx +cuda_bindings/src/cuda/bindings/cyruntime_functions.pxi +cuda_bindings/src/cuda/bindings/cyruntime_types.pxi +cuda_bindings/src/cuda/bindings/cynvrtc.pxd +cuda_bindings/src/cuda/bindings/cynvrtc.pyx +cuda_bindings/src/cuda/bindings/driver.pxd +cuda_bindings/src/cuda/bindings/driver.pyx +cuda_bindings/src/cuda/bindings/runtime.pxd +cuda_bindings/src/cuda/bindings/runtime.pyx +cuda_bindings/src/cuda/bindings/nvrtc.pxd +cuda_bindings/src/cuda/bindings/nvrtc.pyx +cuda_bindings/src/cuda/bindings/utils/_get_handle.pyx # Version files from setuptools_scm _version.py diff --git a/cuda_bindings/MANIFEST.in b/cuda_bindings/MANIFEST.in index 39073c42fd..cf965dfd0a 100644 --- a/cuda_bindings/MANIFEST.in +++ b/cuda_bindings/MANIFEST.in @@ -1,8 +1,8 @@ -# SPDX-FileCopyrightText: Copyright (c) 2024-2025 NVIDIA CORPORATION & AFFILIATES. All rights reserved. +# SPDX-FileCopyrightText: Copyright (c) 2024-2026 NVIDIA CORPORATION & AFFILIATES. All rights reserved. # SPDX-License-Identifier: LicenseRef-NVIDIA-SOFTWARE-LICENSE -recursive-include cuda/ *.pyx *.pxd *.pxi *.pyx.in *.pxd.in *.pxi.in *.h +recursive-include src/cuda/ *.pyx *.pxd *.pxi *.pyx.in *.pxd.in *.pxi.in *.h # at least with setuptools 75.0.0 this folder was added erroneously # to the payload, causing file copying to the build environment failed -exclude cuda/bindings cuda?bindings -exclude cuda/bindings/_bindings cuda?bindings?_bindings +exclude src/cuda/bindings src?cuda?bindings +exclude src/cuda/bindings/_bindings src?cuda?bindings?_bindings diff --git a/cuda_bindings/build_hooks.py b/cuda_bindings/build_hooks.py index b08b0d24d8..d055a5d795 100644 --- a/cuda_bindings/build_hooks.py +++ b/cuda_bindings/build_hooks.py @@ -33,40 +33,10 @@ _extensions = None -# Please keep in sync with the copy in cuda_core/build_hooks.py. -def _import_get_cuda_path_or_home(): - """Import get_cuda_path_or_home, working around PEP 517 namespace shadowing. - - See https://github.com/NVIDIA/cuda-python/issues/1824 for why this helper is needed. - """ - try: - import cuda.pathfinder - except ModuleNotFoundError as exc: - if exc.name not in ("cuda", "cuda.pathfinder"): - raise - try: - import cuda - except ModuleNotFoundError: - cuda = None - - for p in sys.path: - sp_cuda = os.path.join(p, "cuda") - if os.path.isdir(os.path.join(sp_cuda, "pathfinder")): - cuda.__path__ = list(cuda.__path__) + [sp_cuda] - break - else: - raise ModuleNotFoundError( - "cuda-pathfinder is not installed in the build environment. " - "Ensure 'cuda-pathfinder>=1.5' is in build-system.requires." - ) - import cuda.pathfinder - - return cuda.pathfinder.get_cuda_path_or_home - - @functools.cache def _get_cuda_path() -> str: - get_cuda_path_or_home = _import_get_cuda_path_or_home() + from cuda.pathfinder import get_cuda_path_or_home + cuda_path = get_cuda_path_or_home() if not cuda_path: raise RuntimeError("Environment variable CUDA_PATH or CUDA_HOME is not set") @@ -266,7 +236,7 @@ def _generate_output(infile, template_vars): def _rename_architecture_specific_files(): - path = os.path.join("cuda", "bindings", "_internal") + path = os.path.join("src", "cuda", "bindings", "_internal") if sys.platform == "linux": src_files = glob.glob(os.path.join(path, "*_linux.pyx")) elif sys.platform == "win32": @@ -290,7 +260,10 @@ def _prep_extensions(sources, libraries, include_dirs, library_dirs, extra_compi libraries = libraries if libraries else [] exts = [] for pyx in files: - mod_name = pyx.replace(".pyx", "").replace(os.sep, ".").replace("/", ".") + mod_path = pyx.replace(".pyx", "").replace(os.sep, "/") + if mod_path.startswith("src/"): + mod_path = mod_path[len("src/") :] + mod_name = mod_path.replace("/", ".") exts.append( Extension( mod_name, @@ -346,12 +319,12 @@ def _build_cuda_bindings(strip=False): # Generate code from .in templates path_list = [ - os.path.join("cuda"), - os.path.join("cuda", "bindings"), - os.path.join("cuda", "bindings", "_bindings"), - os.path.join("cuda", "bindings", "_internal"), - os.path.join("cuda", "bindings", "_lib"), - os.path.join("cuda", "bindings", "utils"), + os.path.join("src", "cuda"), + os.path.join("src", "cuda", "bindings"), + os.path.join("src", "cuda", "bindings", "_bindings"), + os.path.join("src", "cuda", "bindings", "_internal"), + os.path.join("src", "cuda", "bindings", "_lib"), + os.path.join("src", "cuda", "bindings", "utils"), ] input_files = [] for path in path_list: @@ -375,6 +348,7 @@ def _build_cuda_bindings(strip=False): # Prepare compile/link arguments include_dirs = [ os.path.dirname(sysconfig.get_path("include")), + "src", ] + include_path_list library_dirs = [sysconfig.get_path("platlib"), os.path.join(os.sys.prefix, "lib")] cudalib_subdirs = [r"lib\x64"] if sys.platform == "win32" else ["lib64", "lib"] @@ -415,21 +389,21 @@ def _cleanup_dst_files(): # Build extension list extensions = [] static_runtime_libraries = ["cudart_static", "rt"] if sys.platform == "linux" else ["cudart_static"] - cuda_bindings_files = glob.glob("cuda/bindings/*.pyx") + cuda_bindings_files = glob.glob("src/cuda/bindings/*.pyx") if sys.platform == "win32": cuda_bindings_files = [f for f in cuda_bindings_files if "cufile" not in f] sources_list = [ # private - (["cuda/bindings/_bindings/cydriver.pyx", "cuda/bindings/_bindings/loader.cpp"], None), - (["cuda/bindings/_bindings/cynvrtc.pyx"], None), - (["cuda/bindings/_bindings/cyruntime.pyx"], static_runtime_libraries), - (["cuda/bindings/_bindings/cyruntime_ptds.pyx"], static_runtime_libraries), + (["src/cuda/bindings/_bindings/cydriver.pyx", "src/cuda/bindings/_bindings/loader.cpp"], None), + (["src/cuda/bindings/_bindings/cynvrtc.pyx"], None), + (["src/cuda/bindings/_bindings/cyruntime.pyx"], static_runtime_libraries), + (["src/cuda/bindings/_bindings/cyruntime_ptds.pyx"], static_runtime_libraries), # utils - (["cuda/bindings/utils/*.pyx"], None), + (["src/cuda/bindings/utils/*.pyx"], None), # public *(([f], None) for f in cuda_bindings_files), # internal files used by generated bindings - (["cuda/bindings/_internal/utils.pyx"], None), + (["src/cuda/bindings/_internal/utils.pyx"], None), *(([f], None) for f in dst_files if f.endswith(".pyx")), ] @@ -446,6 +420,7 @@ def _cleanup_dst_files(): _extensions = cythonize( extensions, nthreads=nthreads, + include_path=["src"], build_dir="." if compile_for_coverage else "build/cython", compiler_directives=cython_directives, **extra_cythonize_kwargs, diff --git a/cuda_bindings/pyproject.toml b/cuda_bindings/pyproject.toml index 3aa9c62556..4eff7bab1f 100644 --- a/cuda_bindings/pyproject.toml +++ b/cuda_bindings/pyproject.toml @@ -58,6 +58,7 @@ Repository = "https://github.com/NVIDIA/cuda-python" Documentation = "https://nvidia.github.io/cuda-python/" [tool.setuptools.packages.find] +where = ["src"] include = ["cuda*"] [tool.setuptools] @@ -92,7 +93,7 @@ xfail_strict = true [tool.setuptools_scm] root = ".." -version_file = "cuda/bindings/_version.py" +version_file = "src/cuda/bindings/_version.py" # Preserve a/b pre-release suffixes, but intentionally strip rc suffixes. tag_regex = "^(?Pv\\d+\\.\\d+\\.\\d+(?:[ab]\\d+)?)" git_describe_command = ["git", "describe", "--dirty", "--tags", "--long", "--match", "v*[0-9]*"] diff --git a/cuda_bindings/setup.py b/cuda_bindings/setup.py index 2f6069c738..76d037ee58 100644 --- a/cuda_bindings/setup.py +++ b/cuda_bindings/setup.py @@ -59,6 +59,7 @@ def finalize_options(self): setup( ext_modules=build_hooks._extensions, + package_dir={"": "src"}, cmdclass={ "build_ext": build_ext, "build_py": build_py, diff --git a/cuda_bindings/cuda/bindings/__init__.pxd b/cuda_bindings/src/cuda/bindings/__init__.pxd similarity index 100% rename from cuda_bindings/cuda/bindings/__init__.pxd rename to cuda_bindings/src/cuda/bindings/__init__.pxd diff --git a/cuda_bindings/cuda/bindings/__init__.py b/cuda_bindings/src/cuda/bindings/__init__.py similarity index 73% rename from cuda_bindings/cuda/bindings/__init__.py rename to cuda_bindings/src/cuda/bindings/__init__.py index 38d71fcfde..103ebbb2de 100644 --- a/cuda_bindings/cuda/bindings/__init__.py +++ b/cuda_bindings/src/cuda/bindings/__init__.py @@ -1,4 +1,4 @@ -# SPDX-FileCopyrightText: Copyright (c) 2021-2025 NVIDIA CORPORATION & AFFILIATES. All rights reserved. +# SPDX-FileCopyrightText: Copyright (c) 2021-2026 NVIDIA CORPORATION & AFFILIATES. All rights reserved. # SPDX-License-Identifier: LicenseRef-NVIDIA-SOFTWARE-LICENSE from cuda.bindings import utils diff --git a/cuda_bindings/cuda/bindings/_bindings/__init__.py b/cuda_bindings/src/cuda/bindings/_bindings/__init__.py similarity index 100% rename from cuda_bindings/cuda/bindings/_bindings/__init__.py rename to cuda_bindings/src/cuda/bindings/_bindings/__init__.py diff --git a/cuda_bindings/cuda/bindings/_bindings/cydriver.pxd.in b/cuda_bindings/src/cuda/bindings/_bindings/cydriver.pxd.in similarity index 99% rename from cuda_bindings/cuda/bindings/_bindings/cydriver.pxd.in rename to cuda_bindings/src/cuda/bindings/_bindings/cydriver.pxd.in index 0b19de67d0..aaacdaa95a 100644 --- a/cuda_bindings/cuda/bindings/_bindings/cydriver.pxd.in +++ b/cuda_bindings/src/cuda/bindings/_bindings/cydriver.pxd.in @@ -2458,4 +2458,3 @@ cdef CUresult _cuGraphicsVDPAURegisterVideoSurface(CUgraphicsResource* pCudaReso cdef CUresult _cuGraphicsVDPAURegisterOutputSurface(CUgraphicsResource* pCudaResource, VdpOutputSurface vdpSurface, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil {{endif}} - diff --git a/cuda_bindings/cuda/bindings/_bindings/cydriver.pyx.in b/cuda_bindings/src/cuda/bindings/_bindings/cydriver.pyx.in similarity index 100% rename from cuda_bindings/cuda/bindings/_bindings/cydriver.pyx.in rename to cuda_bindings/src/cuda/bindings/_bindings/cydriver.pyx.in diff --git a/cuda_bindings/cuda/bindings/_bindings/cynvrtc.pxd.in b/cuda_bindings/src/cuda/bindings/_bindings/cynvrtc.pxd.in similarity index 99% rename from cuda_bindings/cuda/bindings/_bindings/cynvrtc.pxd.in rename to cuda_bindings/src/cuda/bindings/_bindings/cynvrtc.pxd.in index 5a53b926d1..1eca8180fe 100644 --- a/cuda_bindings/cuda/bindings/_bindings/cynvrtc.pxd.in +++ b/cuda_bindings/src/cuda/bindings/_bindings/cynvrtc.pxd.in @@ -133,4 +133,3 @@ cdef nvrtcResult _nvrtcGetTileIRSize(nvrtcProgram prog, size_t* TileIRSizeRet) e cdef nvrtcResult _nvrtcGetTileIR(nvrtcProgram prog, char* TileIR) except ?NVRTC_ERROR_INVALID_INPUT nogil {{endif}} - diff --git a/cuda_bindings/cuda/bindings/_bindings/cynvrtc.pyx.in b/cuda_bindings/src/cuda/bindings/_bindings/cynvrtc.pyx.in similarity index 100% rename from cuda_bindings/cuda/bindings/_bindings/cynvrtc.pyx.in rename to cuda_bindings/src/cuda/bindings/_bindings/cynvrtc.pyx.in diff --git a/cuda_bindings/cuda/bindings/_bindings/cyruntime.pxd.in b/cuda_bindings/src/cuda/bindings/_bindings/cyruntime.pxd.in similarity index 100% rename from cuda_bindings/cuda/bindings/_bindings/cyruntime.pxd.in rename to cuda_bindings/src/cuda/bindings/_bindings/cyruntime.pxd.in diff --git a/cuda_bindings/cuda/bindings/_bindings/cyruntime.pyx.in b/cuda_bindings/src/cuda/bindings/_bindings/cyruntime.pyx.in similarity index 100% rename from cuda_bindings/cuda/bindings/_bindings/cyruntime.pyx.in rename to cuda_bindings/src/cuda/bindings/_bindings/cyruntime.pyx.in diff --git a/cuda_bindings/cuda/bindings/_bindings/cyruntime_ptds.pxd.in b/cuda_bindings/src/cuda/bindings/_bindings/cyruntime_ptds.pxd.in similarity index 100% rename from cuda_bindings/cuda/bindings/_bindings/cyruntime_ptds.pxd.in rename to cuda_bindings/src/cuda/bindings/_bindings/cyruntime_ptds.pxd.in diff --git a/cuda_bindings/cuda/bindings/_bindings/cyruntime_ptds.pyx.in b/cuda_bindings/src/cuda/bindings/_bindings/cyruntime_ptds.pyx.in similarity index 100% rename from cuda_bindings/cuda/bindings/_bindings/cyruntime_ptds.pyx.in rename to cuda_bindings/src/cuda/bindings/_bindings/cyruntime_ptds.pyx.in diff --git a/cuda_bindings/cuda/bindings/_bindings/loader.cpp b/cuda_bindings/src/cuda/bindings/_bindings/loader.cpp similarity index 99% rename from cuda_bindings/cuda/bindings/_bindings/loader.cpp rename to cuda_bindings/src/cuda/bindings/_bindings/loader.cpp index a692eddc93..fa009af6be 100644 --- a/cuda_bindings/cuda/bindings/_bindings/loader.cpp +++ b/cuda_bindings/src/cuda/bindings/_bindings/loader.cpp @@ -1,4 +1,4 @@ -// SPDX-FileCopyrightText: Copyright (c) 2021-2024 NVIDIA CORPORATION & AFFILIATES. All rights reserved. +// SPDX-FileCopyrightText: Copyright (c) 2021-2026 NVIDIA CORPORATION & AFFILIATES. All rights reserved. // SPDX-License-Identifier: LicenseRef-NVIDIA-SOFTWARE-LICENSE #include diff --git a/cuda_bindings/cuda/bindings/_bindings/loader.h b/cuda_bindings/src/cuda/bindings/_bindings/loader.h similarity index 88% rename from cuda_bindings/cuda/bindings/_bindings/loader.h rename to cuda_bindings/src/cuda/bindings/_bindings/loader.h index 2411037b03..dd6d3d0334 100644 --- a/cuda_bindings/cuda/bindings/_bindings/loader.h +++ b/cuda_bindings/src/cuda/bindings/_bindings/loader.h @@ -1,4 +1,4 @@ -// SPDX-FileCopyrightText: Copyright (c) 2021-2024 NVIDIA CORPORATION & AFFILIATES. All rights reserved. +// SPDX-FileCopyrightText: Copyright (c) 2021-2026 NVIDIA CORPORATION & AFFILIATES. All rights reserved. // SPDX-License-Identifier: LicenseRef-NVIDIA-SOFTWARE-LICENSE // // Please refer to the NVIDIA end user license agreement (EULA) associated diff --git a/cuda_bindings/cuda/bindings/_bindings/loader.pxd b/cuda_bindings/src/cuda/bindings/_bindings/loader.pxd similarity index 74% rename from cuda_bindings/cuda/bindings/_bindings/loader.pxd rename to cuda_bindings/src/cuda/bindings/_bindings/loader.pxd index 805b849cc6..3e0d58f367 100644 --- a/cuda_bindings/cuda/bindings/_bindings/loader.pxd +++ b/cuda_bindings/src/cuda/bindings/_bindings/loader.pxd @@ -1,4 +1,4 @@ -# SPDX-FileCopyrightText: Copyright (c) 2021-2024 NVIDIA CORPORATION & AFFILIATES. All rights reserved. +# SPDX-FileCopyrightText: Copyright (c) 2021-2026 NVIDIA CORPORATION & AFFILIATES. All rights reserved. # SPDX-License-Identifier: LicenseRef-NVIDIA-SOFTWARE-LICENSE cdef extern from "loader.h": diff --git a/cuda_bindings/cuda/bindings/_example_helpers/__init__.py b/cuda_bindings/src/cuda/bindings/_example_helpers/__init__.py similarity index 100% rename from cuda_bindings/cuda/bindings/_example_helpers/__init__.py rename to cuda_bindings/src/cuda/bindings/_example_helpers/__init__.py diff --git a/cuda_bindings/cuda/bindings/_example_helpers/common.py b/cuda_bindings/src/cuda/bindings/_example_helpers/common.py similarity index 100% rename from cuda_bindings/cuda/bindings/_example_helpers/common.py rename to cuda_bindings/src/cuda/bindings/_example_helpers/common.py diff --git a/cuda_bindings/cuda/bindings/_example_helpers/helper_cuda.py b/cuda_bindings/src/cuda/bindings/_example_helpers/helper_cuda.py similarity index 100% rename from cuda_bindings/cuda/bindings/_example_helpers/helper_cuda.py rename to cuda_bindings/src/cuda/bindings/_example_helpers/helper_cuda.py diff --git a/cuda_bindings/cuda/bindings/_example_helpers/helper_string.py b/cuda_bindings/src/cuda/bindings/_example_helpers/helper_string.py similarity index 100% rename from cuda_bindings/cuda/bindings/_example_helpers/helper_string.py rename to cuda_bindings/src/cuda/bindings/_example_helpers/helper_string.py diff --git a/cuda_bindings/cuda/bindings/_internal/__init__.py b/cuda_bindings/src/cuda/bindings/_internal/__init__.py similarity index 100% rename from cuda_bindings/cuda/bindings/_internal/__init__.py rename to cuda_bindings/src/cuda/bindings/_internal/__init__.py diff --git a/cuda_bindings/cuda/bindings/_internal/_fast_enum.py b/cuda_bindings/src/cuda/bindings/_internal/_fast_enum.py similarity index 100% rename from cuda_bindings/cuda/bindings/_internal/_fast_enum.py rename to cuda_bindings/src/cuda/bindings/_internal/_fast_enum.py diff --git a/cuda_bindings/cuda/bindings/_internal/cufile.pxd b/cuda_bindings/src/cuda/bindings/_internal/cufile.pxd similarity index 100% rename from cuda_bindings/cuda/bindings/_internal/cufile.pxd rename to cuda_bindings/src/cuda/bindings/_internal/cufile.pxd diff --git a/cuda_bindings/cuda/bindings/_internal/cufile_linux.pyx b/cuda_bindings/src/cuda/bindings/_internal/cufile_linux.pyx similarity index 100% rename from cuda_bindings/cuda/bindings/_internal/cufile_linux.pyx rename to cuda_bindings/src/cuda/bindings/_internal/cufile_linux.pyx diff --git a/cuda_bindings/cuda/bindings/_internal/nvfatbin.pxd b/cuda_bindings/src/cuda/bindings/_internal/nvfatbin.pxd similarity index 100% rename from cuda_bindings/cuda/bindings/_internal/nvfatbin.pxd rename to cuda_bindings/src/cuda/bindings/_internal/nvfatbin.pxd diff --git a/cuda_bindings/cuda/bindings/_internal/nvfatbin_linux.pyx b/cuda_bindings/src/cuda/bindings/_internal/nvfatbin_linux.pyx similarity index 100% rename from cuda_bindings/cuda/bindings/_internal/nvfatbin_linux.pyx rename to cuda_bindings/src/cuda/bindings/_internal/nvfatbin_linux.pyx diff --git a/cuda_bindings/cuda/bindings/_internal/nvfatbin_windows.pyx b/cuda_bindings/src/cuda/bindings/_internal/nvfatbin_windows.pyx similarity index 100% rename from cuda_bindings/cuda/bindings/_internal/nvfatbin_windows.pyx rename to cuda_bindings/src/cuda/bindings/_internal/nvfatbin_windows.pyx diff --git a/cuda_bindings/cuda/bindings/_internal/nvjitlink.pxd b/cuda_bindings/src/cuda/bindings/_internal/nvjitlink.pxd similarity index 100% rename from cuda_bindings/cuda/bindings/_internal/nvjitlink.pxd rename to cuda_bindings/src/cuda/bindings/_internal/nvjitlink.pxd diff --git a/cuda_bindings/cuda/bindings/_internal/nvjitlink_linux.pyx b/cuda_bindings/src/cuda/bindings/_internal/nvjitlink_linux.pyx similarity index 100% rename from cuda_bindings/cuda/bindings/_internal/nvjitlink_linux.pyx rename to cuda_bindings/src/cuda/bindings/_internal/nvjitlink_linux.pyx diff --git a/cuda_bindings/cuda/bindings/_internal/nvjitlink_windows.pyx b/cuda_bindings/src/cuda/bindings/_internal/nvjitlink_windows.pyx similarity index 100% rename from cuda_bindings/cuda/bindings/_internal/nvjitlink_windows.pyx rename to cuda_bindings/src/cuda/bindings/_internal/nvjitlink_windows.pyx diff --git a/cuda_bindings/cuda/bindings/_internal/nvml.pxd b/cuda_bindings/src/cuda/bindings/_internal/nvml.pxd similarity index 100% rename from cuda_bindings/cuda/bindings/_internal/nvml.pxd rename to cuda_bindings/src/cuda/bindings/_internal/nvml.pxd diff --git a/cuda_bindings/cuda/bindings/_internal/nvml_linux.pyx b/cuda_bindings/src/cuda/bindings/_internal/nvml_linux.pyx similarity index 100% rename from cuda_bindings/cuda/bindings/_internal/nvml_linux.pyx rename to cuda_bindings/src/cuda/bindings/_internal/nvml_linux.pyx diff --git a/cuda_bindings/cuda/bindings/_internal/nvml_windows.pyx b/cuda_bindings/src/cuda/bindings/_internal/nvml_windows.pyx similarity index 100% rename from cuda_bindings/cuda/bindings/_internal/nvml_windows.pyx rename to cuda_bindings/src/cuda/bindings/_internal/nvml_windows.pyx diff --git a/cuda_bindings/cuda/bindings/_internal/nvvm.pxd b/cuda_bindings/src/cuda/bindings/_internal/nvvm.pxd similarity index 100% rename from cuda_bindings/cuda/bindings/_internal/nvvm.pxd rename to cuda_bindings/src/cuda/bindings/_internal/nvvm.pxd diff --git a/cuda_bindings/cuda/bindings/_internal/nvvm_linux.pyx b/cuda_bindings/src/cuda/bindings/_internal/nvvm_linux.pyx similarity index 100% rename from cuda_bindings/cuda/bindings/_internal/nvvm_linux.pyx rename to cuda_bindings/src/cuda/bindings/_internal/nvvm_linux.pyx diff --git a/cuda_bindings/cuda/bindings/_internal/nvvm_windows.pyx b/cuda_bindings/src/cuda/bindings/_internal/nvvm_windows.pyx similarity index 100% rename from cuda_bindings/cuda/bindings/_internal/nvvm_windows.pyx rename to cuda_bindings/src/cuda/bindings/_internal/nvvm_windows.pyx diff --git a/cuda_bindings/cuda/bindings/_internal/utils.pxd b/cuda_bindings/src/cuda/bindings/_internal/utils.pxd similarity index 98% rename from cuda_bindings/cuda/bindings/_internal/utils.pxd rename to cuda_bindings/src/cuda/bindings/_internal/utils.pxd index 50484727b7..46a785b33a 100644 --- a/cuda_bindings/cuda/bindings/_internal/utils.pxd +++ b/cuda_bindings/src/cuda/bindings/_internal/utils.pxd @@ -1,4 +1,4 @@ -# SPDX-FileCopyrightText: Copyright (c) 2024-2025 NVIDIA CORPORATION & AFFILIATES. All rights reserved. +# SPDX-FileCopyrightText: Copyright (c) 2024-2026 NVIDIA CORPORATION & AFFILIATES. All rights reserved. # # SPDX-License-Identifier: LicenseRef-NVIDIA-SOFTWARE-LICENSE diff --git a/cuda_bindings/cuda/bindings/_internal/utils.pyx b/cuda_bindings/src/cuda/bindings/_internal/utils.pyx similarity index 100% rename from cuda_bindings/cuda/bindings/_internal/utils.pyx rename to cuda_bindings/src/cuda/bindings/_internal/utils.pyx diff --git a/cuda_bindings/cuda/bindings/_lib/__init__.py b/cuda_bindings/src/cuda/bindings/_lib/__init__.py similarity index 100% rename from cuda_bindings/cuda/bindings/_lib/__init__.py rename to cuda_bindings/src/cuda/bindings/_lib/__init__.py diff --git a/cuda_bindings/cuda/bindings/_lib/cyruntime/cyruntime.pxd b/cuda_bindings/src/cuda/bindings/_lib/cyruntime/cyruntime.pxd similarity index 98% rename from cuda_bindings/cuda/bindings/_lib/cyruntime/cyruntime.pxd rename to cuda_bindings/src/cuda/bindings/_lib/cyruntime/cyruntime.pxd index 48f87f29ca..8818189a6f 100644 --- a/cuda_bindings/cuda/bindings/_lib/cyruntime/cyruntime.pxd +++ b/cuda_bindings/src/cuda/bindings/_lib/cyruntime/cyruntime.pxd @@ -1,4 +1,4 @@ -# SPDX-FileCopyrightText: Copyright (c) 2021-2025 NVIDIA CORPORATION & AFFILIATES. All rights reserved. +# SPDX-FileCopyrightText: Copyright (c) 2021-2026 NVIDIA CORPORATION & AFFILIATES. All rights reserved. # SPDX-License-Identifier: LicenseRef-NVIDIA-SOFTWARE-LICENSE cimport cuda.bindings.cyruntime as cyruntime diff --git a/cuda_bindings/cuda/bindings/_lib/cyruntime/cyruntime.pxi b/cuda_bindings/src/cuda/bindings/_lib/cyruntime/cyruntime.pxi similarity index 99% rename from cuda_bindings/cuda/bindings/_lib/cyruntime/cyruntime.pxi rename to cuda_bindings/src/cuda/bindings/_lib/cyruntime/cyruntime.pxi index c18bd1ca2e..05cc23db6f 100644 --- a/cuda_bindings/cuda/bindings/_lib/cyruntime/cyruntime.pxi +++ b/cuda_bindings/src/cuda/bindings/_lib/cyruntime/cyruntime.pxi @@ -1,4 +1,4 @@ -# SPDX-FileCopyrightText: Copyright (c) 2021-2025 NVIDIA CORPORATION & AFFILIATES. All rights reserved. +# SPDX-FileCopyrightText: Copyright (c) 2021-2026 NVIDIA CORPORATION & AFFILIATES. All rights reserved. # SPDX-License-Identifier: LicenseRef-NVIDIA-SOFTWARE-LICENSE # These graphics API are the reimplemented version of what's supported by CUDA Runtime. diff --git a/cuda_bindings/cuda/bindings/_lib/dlfcn.pxd b/cuda_bindings/src/cuda/bindings/_lib/dlfcn.pxd similarity index 84% rename from cuda_bindings/cuda/bindings/_lib/dlfcn.pxd rename to cuda_bindings/src/cuda/bindings/_lib/dlfcn.pxd index 2ae9581439..11b16b0a00 100644 --- a/cuda_bindings/cuda/bindings/_lib/dlfcn.pxd +++ b/cuda_bindings/src/cuda/bindings/_lib/dlfcn.pxd @@ -1,4 +1,4 @@ -# SPDX-FileCopyrightText: Copyright (c) 2021-2024 NVIDIA CORPORATION & AFFILIATES. All rights reserved. +# SPDX-FileCopyrightText: Copyright (c) 2021-2026 NVIDIA CORPORATION & AFFILIATES. All rights reserved. # SPDX-License-Identifier: LicenseRef-NVIDIA-SOFTWARE-LICENSE cdef extern from "" nogil: diff --git a/cuda_bindings/cuda/bindings/_lib/param_packer.h b/cuda_bindings/src/cuda/bindings/_lib/param_packer.h similarity index 98% rename from cuda_bindings/cuda/bindings/_lib/param_packer.h rename to cuda_bindings/src/cuda/bindings/_lib/param_packer.h index 96c56b4fe4..d6f413d587 100644 --- a/cuda_bindings/cuda/bindings/_lib/param_packer.h +++ b/cuda_bindings/src/cuda/bindings/_lib/param_packer.h @@ -1,4 +1,4 @@ -// SPDX-FileCopyrightText: Copyright (c) 2021-2024 NVIDIA CORPORATION & AFFILIATES. All rights reserved. +// SPDX-FileCopyrightText: Copyright (c) 2021-2026 NVIDIA CORPORATION & AFFILIATES. All rights reserved. // SPDX-License-Identifier: LicenseRef-NVIDIA-SOFTWARE-LICENSE // Please refer to the NVIDIA end user license agreement (EULA) associated diff --git a/cuda_bindings/cuda/bindings/_lib/param_packer.pxd b/cuda_bindings/src/cuda/bindings/_lib/param_packer.pxd similarity index 82% rename from cuda_bindings/cuda/bindings/_lib/param_packer.pxd rename to cuda_bindings/src/cuda/bindings/_lib/param_packer.pxd index ad7fd95668..2e70b454d8 100644 --- a/cuda_bindings/cuda/bindings/_lib/param_packer.pxd +++ b/cuda_bindings/src/cuda/bindings/_lib/param_packer.pxd @@ -1,4 +1,4 @@ -# SPDX-FileCopyrightText: Copyright (c) 2021-2024 NVIDIA CORPORATION & AFFILIATES. All rights reserved. +# SPDX-FileCopyrightText: Copyright (c) 2021-2026 NVIDIA CORPORATION & AFFILIATES. All rights reserved. # SPDX-License-Identifier: LicenseRef-NVIDIA-SOFTWARE-LICENSE # Include "param_packer.h" so its contents get compiled into every diff --git a/cuda_bindings/cuda/bindings/_lib/utils.pxd.in b/cuda_bindings/src/cuda/bindings/_lib/utils.pxd.in similarity index 99% rename from cuda_bindings/cuda/bindings/_lib/utils.pxd.in rename to cuda_bindings/src/cuda/bindings/_lib/utils.pxd.in index 353a07a09c..69bc885504 100644 --- a/cuda_bindings/cuda/bindings/_lib/utils.pxd.in +++ b/cuda_bindings/src/cuda/bindings/_lib/utils.pxd.in @@ -19,7 +19,7 @@ cdef struct _HelperInputVoidPtrStruct: Py_buffer _pybuffer cdef class _HelperInputVoidPtr: - cdef _HelperInputVoidPtrStruct _helper + cdef _HelperInputVoidPtrStruct _helper cdef void* _cptr cdef void * _helper_input_void_ptr(ptr, _HelperInputVoidPtrStruct *buffer) diff --git a/cuda_bindings/cuda/bindings/_lib/utils.pxi.in b/cuda_bindings/src/cuda/bindings/_lib/utils.pxi.in similarity index 99% rename from cuda_bindings/cuda/bindings/_lib/utils.pxi.in rename to cuda_bindings/src/cuda/bindings/_lib/utils.pxi.in index c88ec49721..1d63ca307b 100644 --- a/cuda_bindings/cuda/bindings/_lib/utils.pxi.in +++ b/cuda_bindings/src/cuda/bindings/_lib/utils.pxi.in @@ -135,13 +135,13 @@ cdef class _HelperInputVoidPtr: @property def cptr(self): - return self._cptr + return self._cptr cdef void * _helper_input_void_ptr(ptr, _HelperInputVoidPtrStruct *helper): helper[0]._pybuffer.buf = NULL try: - return ptr + return ptr except: if ptr is None: return NULL @@ -633,7 +633,7 @@ cdef class _HelperCUcoredumpSettings: {{if 'CU_COREDUMP_ENABLE_USER_TRIGGER' in found_values}}cydriver.CUcoredumpSettings_enum.CU_COREDUMP_ENABLE_USER_TRIGGER,{{endif}}): if self._is_getter == False: self._bool = init_value - + self._cptr = &self._bool self._size = 1 else: diff --git a/cuda_bindings/cuda/bindings/_lib/windll.pxd b/cuda_bindings/src/cuda/bindings/_lib/windll.pxd similarity index 95% rename from cuda_bindings/cuda/bindings/_lib/windll.pxd rename to cuda_bindings/src/cuda/bindings/_lib/windll.pxd index 7b190f3595..2e226e3103 100644 --- a/cuda_bindings/cuda/bindings/_lib/windll.pxd +++ b/cuda_bindings/src/cuda/bindings/_lib/windll.pxd @@ -1,4 +1,4 @@ -# SPDX-FileCopyrightText: Copyright (c) 2021-2024 NVIDIA CORPORATION & AFFILIATES. All rights reserved. +# SPDX-FileCopyrightText: Copyright (c) 2021-2026 NVIDIA CORPORATION & AFFILIATES. All rights reserved. # SPDX-License-Identifier: LicenseRef-NVIDIA-SOFTWARE-LICENSE from libc.stddef cimport wchar_t diff --git a/cuda_bindings/cuda/bindings/_test_helpers/__init__.py b/cuda_bindings/src/cuda/bindings/_test_helpers/__init__.py similarity index 100% rename from cuda_bindings/cuda/bindings/_test_helpers/__init__.py rename to cuda_bindings/src/cuda/bindings/_test_helpers/__init__.py diff --git a/cuda_bindings/cuda/bindings/_test_helpers/arch_check.py b/cuda_bindings/src/cuda/bindings/_test_helpers/arch_check.py similarity index 100% rename from cuda_bindings/cuda/bindings/_test_helpers/arch_check.py rename to cuda_bindings/src/cuda/bindings/_test_helpers/arch_check.py diff --git a/cuda_bindings/cuda/bindings/_test_helpers/pep723.py b/cuda_bindings/src/cuda/bindings/_test_helpers/pep723.py similarity index 100% rename from cuda_bindings/cuda/bindings/_test_helpers/pep723.py rename to cuda_bindings/src/cuda/bindings/_test_helpers/pep723.py diff --git a/cuda_bindings/cuda/bindings/cufile.pxd b/cuda_bindings/src/cuda/bindings/cufile.pxd similarity index 100% rename from cuda_bindings/cuda/bindings/cufile.pxd rename to cuda_bindings/src/cuda/bindings/cufile.pxd diff --git a/cuda_bindings/cuda/bindings/cufile.pyx b/cuda_bindings/src/cuda/bindings/cufile.pyx similarity index 100% rename from cuda_bindings/cuda/bindings/cufile.pyx rename to cuda_bindings/src/cuda/bindings/cufile.pyx diff --git a/cuda_bindings/cuda/bindings/cycufile.pxd b/cuda_bindings/src/cuda/bindings/cycufile.pxd similarity index 100% rename from cuda_bindings/cuda/bindings/cycufile.pxd rename to cuda_bindings/src/cuda/bindings/cycufile.pxd diff --git a/cuda_bindings/cuda/bindings/cycufile.pyx b/cuda_bindings/src/cuda/bindings/cycufile.pyx similarity index 100% rename from cuda_bindings/cuda/bindings/cycufile.pyx rename to cuda_bindings/src/cuda/bindings/cycufile.pyx diff --git a/cuda_bindings/cuda/bindings/cydriver.pxd.in b/cuda_bindings/src/cuda/bindings/cydriver.pxd.in similarity index 99% rename from cuda_bindings/cuda/bindings/cydriver.pxd.in rename to cuda_bindings/src/cuda/bindings/cydriver.pxd.in index 6ed16b51ba..c811fcbe51 100644 --- a/cuda_bindings/cuda/bindings/cydriver.pxd.in +++ b/cuda_bindings/src/cuda/bindings/cydriver.pxd.in @@ -5409,4 +5409,4 @@ cdef enum: CU_DEVICE_INVALID = -2 cdef enum: MAX_PLANES = 3 -cdef enum: CUDA_EGL_INFINITE_TIMEOUT = 4294967295 \ No newline at end of file +cdef enum: CUDA_EGL_INFINITE_TIMEOUT = 4294967295 diff --git a/cuda_bindings/cuda/bindings/cydriver.pyx.in b/cuda_bindings/src/cuda/bindings/cydriver.pyx.in similarity index 100% rename from cuda_bindings/cuda/bindings/cydriver.pyx.in rename to cuda_bindings/src/cuda/bindings/cydriver.pyx.in diff --git a/cuda_bindings/cuda/bindings/cynvfatbin.pxd b/cuda_bindings/src/cuda/bindings/cynvfatbin.pxd similarity index 100% rename from cuda_bindings/cuda/bindings/cynvfatbin.pxd rename to cuda_bindings/src/cuda/bindings/cynvfatbin.pxd diff --git a/cuda_bindings/cuda/bindings/cynvfatbin.pyx b/cuda_bindings/src/cuda/bindings/cynvfatbin.pyx similarity index 100% rename from cuda_bindings/cuda/bindings/cynvfatbin.pyx rename to cuda_bindings/src/cuda/bindings/cynvfatbin.pyx diff --git a/cuda_bindings/cuda/bindings/cynvjitlink.pxd b/cuda_bindings/src/cuda/bindings/cynvjitlink.pxd similarity index 100% rename from cuda_bindings/cuda/bindings/cynvjitlink.pxd rename to cuda_bindings/src/cuda/bindings/cynvjitlink.pxd diff --git a/cuda_bindings/cuda/bindings/cynvjitlink.pyx b/cuda_bindings/src/cuda/bindings/cynvjitlink.pyx similarity index 100% rename from cuda_bindings/cuda/bindings/cynvjitlink.pyx rename to cuda_bindings/src/cuda/bindings/cynvjitlink.pyx diff --git a/cuda_bindings/cuda/bindings/cynvml.pxd b/cuda_bindings/src/cuda/bindings/cynvml.pxd similarity index 100% rename from cuda_bindings/cuda/bindings/cynvml.pxd rename to cuda_bindings/src/cuda/bindings/cynvml.pxd diff --git a/cuda_bindings/cuda/bindings/cynvml.pyx b/cuda_bindings/src/cuda/bindings/cynvml.pyx similarity index 100% rename from cuda_bindings/cuda/bindings/cynvml.pyx rename to cuda_bindings/src/cuda/bindings/cynvml.pyx diff --git a/cuda_bindings/cuda/bindings/cynvrtc.pxd.in b/cuda_bindings/src/cuda/bindings/cynvrtc.pxd.in similarity index 99% rename from cuda_bindings/cuda/bindings/cynvrtc.pxd.in rename to cuda_bindings/src/cuda/bindings/cynvrtc.pxd.in index 209b361c05..1fcf26f332 100644 --- a/cuda_bindings/cuda/bindings/cynvrtc.pxd.in +++ b/cuda_bindings/src/cuda/bindings/cynvrtc.pxd.in @@ -160,4 +160,3 @@ cdef nvrtcResult nvrtcGetTileIRSize(nvrtcProgram prog, size_t* TileIRSizeRet) ex cdef nvrtcResult nvrtcGetTileIR(nvrtcProgram prog, char* TileIR) except ?NVRTC_ERROR_INVALID_INPUT nogil {{endif}} - diff --git a/cuda_bindings/cuda/bindings/cynvrtc.pyx.in b/cuda_bindings/src/cuda/bindings/cynvrtc.pyx.in similarity index 100% rename from cuda_bindings/cuda/bindings/cynvrtc.pyx.in rename to cuda_bindings/src/cuda/bindings/cynvrtc.pyx.in diff --git a/cuda_bindings/cuda/bindings/cynvvm.pxd b/cuda_bindings/src/cuda/bindings/cynvvm.pxd similarity index 100% rename from cuda_bindings/cuda/bindings/cynvvm.pxd rename to cuda_bindings/src/cuda/bindings/cynvvm.pxd diff --git a/cuda_bindings/cuda/bindings/cynvvm.pyx b/cuda_bindings/src/cuda/bindings/cynvvm.pyx similarity index 100% rename from cuda_bindings/cuda/bindings/cynvvm.pyx rename to cuda_bindings/src/cuda/bindings/cynvvm.pyx diff --git a/cuda_bindings/cuda/bindings/cyruntime.pxd.in b/cuda_bindings/src/cuda/bindings/cyruntime.pxd.in similarity index 99% rename from cuda_bindings/cuda/bindings/cyruntime.pxd.in rename to cuda_bindings/src/cuda/bindings/cyruntime.pxd.in index 85108b68a9..9cc7288c2f 100644 --- a/cuda_bindings/cuda/bindings/cyruntime.pxd.in +++ b/cuda_bindings/src/cuda/bindings/cyruntime.pxd.in @@ -2086,4 +2086,4 @@ cdef enum: CUDART_VERSION = 13020 cdef enum: __CUDART_API_VERSION = 13020 -cdef enum: CUDA_EGL_MAX_PLANES = 3 \ No newline at end of file +cdef enum: CUDA_EGL_MAX_PLANES = 3 diff --git a/cuda_bindings/cuda/bindings/cyruntime.pyx.in b/cuda_bindings/src/cuda/bindings/cyruntime.pyx.in similarity index 100% rename from cuda_bindings/cuda/bindings/cyruntime.pyx.in rename to cuda_bindings/src/cuda/bindings/cyruntime.pyx.in diff --git a/cuda_bindings/cuda/bindings/cyruntime_functions.pxi.in b/cuda_bindings/src/cuda/bindings/cyruntime_functions.pxi.in similarity index 99% rename from cuda_bindings/cuda/bindings/cyruntime_functions.pxi.in rename to cuda_bindings/src/cuda/bindings/cyruntime_functions.pxi.in index 8cbdb881a7..61ba2e1367 100644 --- a/cuda_bindings/cuda/bindings/cyruntime_functions.pxi.in +++ b/cuda_bindings/src/cuda/bindings/cyruntime_functions.pxi.in @@ -1610,4 +1610,3 @@ cdef extern from "cuda_profiler_api.h": cudaError_t cudaProfilerStop() nogil {{endif}} - diff --git a/cuda_bindings/cuda/bindings/cyruntime_types.pxi.in b/cuda_bindings/src/cuda/bindings/cyruntime_types.pxi.in similarity index 100% rename from cuda_bindings/cuda/bindings/cyruntime_types.pxi.in rename to cuda_bindings/src/cuda/bindings/cyruntime_types.pxi.in diff --git a/cuda_bindings/cuda/bindings/driver.pxd.in b/cuda_bindings/src/cuda/bindings/driver.pxd.in similarity index 100% rename from cuda_bindings/cuda/bindings/driver.pxd.in rename to cuda_bindings/src/cuda/bindings/driver.pxd.in diff --git a/cuda_bindings/cuda/bindings/driver.pyx.in b/cuda_bindings/src/cuda/bindings/driver.pyx.in similarity index 99% rename from cuda_bindings/cuda/bindings/driver.pyx.in rename to cuda_bindings/src/cuda/bindings/driver.pyx.in index 2c02494148..3df5c09cf9 100644 --- a/cuda_bindings/cuda/bindings/driver.pyx.in +++ b/cuda_bindings/src/cuda/bindings/driver.pyx.in @@ -33984,7 +33984,7 @@ def cuMemcpy3DBatchAsync(size_t numOps, opList : Optional[tuple[CUDA_MEMCPY3D_BA @cython.embedsignature(True) def cuMemcpyWithAttributesAsync(dst, src, size_t size, attr : Optional[CUmemcpyAttributes], hStream): - """ + """ Performs asynchronous memory copy operation with the specified attributes. @@ -34054,7 +34054,7 @@ def cuMemcpyWithAttributesAsync(dst, src, size_t size, attr : Optional[CUmemcpyA @cython.embedsignature(True) def cuMemcpy3DWithAttributesAsync(op : Optional[CUDA_MEMCPY3D_BATCH_OP], unsigned long long flags, hStream): - """ + """ Performs 3D memory copy with attributes asynchronously @@ -54750,7 +54750,7 @@ def cuCoredumpDeregisterCompleteCallback(callback): @cython.embedsignature(True) def cuGetExportTable(pExportTableId : Optional[CUuuid]): - """ + """ Parameters ---------- @@ -58400,4 +58400,3 @@ cdef int _add_native_handle_getters() except?-1: {{endif}} return 0 _add_native_handle_getters() - diff --git a/cuda_bindings/cuda/bindings/nvfatbin.pxd b/cuda_bindings/src/cuda/bindings/nvfatbin.pxd similarity index 100% rename from cuda_bindings/cuda/bindings/nvfatbin.pxd rename to cuda_bindings/src/cuda/bindings/nvfatbin.pxd diff --git a/cuda_bindings/cuda/bindings/nvfatbin.pyx b/cuda_bindings/src/cuda/bindings/nvfatbin.pyx similarity index 100% rename from cuda_bindings/cuda/bindings/nvfatbin.pyx rename to cuda_bindings/src/cuda/bindings/nvfatbin.pyx diff --git a/cuda_bindings/cuda/bindings/nvjitlink.pxd b/cuda_bindings/src/cuda/bindings/nvjitlink.pxd similarity index 100% rename from cuda_bindings/cuda/bindings/nvjitlink.pxd rename to cuda_bindings/src/cuda/bindings/nvjitlink.pxd diff --git a/cuda_bindings/cuda/bindings/nvjitlink.pyx b/cuda_bindings/src/cuda/bindings/nvjitlink.pyx similarity index 100% rename from cuda_bindings/cuda/bindings/nvjitlink.pyx rename to cuda_bindings/src/cuda/bindings/nvjitlink.pyx diff --git a/cuda_bindings/cuda/bindings/nvml.pxd b/cuda_bindings/src/cuda/bindings/nvml.pxd similarity index 100% rename from cuda_bindings/cuda/bindings/nvml.pxd rename to cuda_bindings/src/cuda/bindings/nvml.pxd diff --git a/cuda_bindings/cuda/bindings/nvml.pyx b/cuda_bindings/src/cuda/bindings/nvml.pyx similarity index 100% rename from cuda_bindings/cuda/bindings/nvml.pyx rename to cuda_bindings/src/cuda/bindings/nvml.pyx diff --git a/cuda_bindings/cuda/bindings/nvrtc.pxd.in b/cuda_bindings/src/cuda/bindings/nvrtc.pxd.in similarity index 100% rename from cuda_bindings/cuda/bindings/nvrtc.pxd.in rename to cuda_bindings/src/cuda/bindings/nvrtc.pxd.in diff --git a/cuda_bindings/cuda/bindings/nvrtc.pyx.in b/cuda_bindings/src/cuda/bindings/nvrtc.pyx.in similarity index 99% rename from cuda_bindings/cuda/bindings/nvrtc.pyx.in rename to cuda_bindings/src/cuda/bindings/nvrtc.pyx.in index 2f50afa726..77a77b7973 100644 --- a/cuda_bindings/cuda/bindings/nvrtc.pyx.in +++ b/cuda_bindings/src/cuda/bindings/nvrtc.pyx.in @@ -1050,7 +1050,7 @@ def nvrtcSetFlowCallback(prog, callback, payload): @cython.embedsignature(True) def nvrtcGetTileIRSize(prog): - """ + """ Parameters ---------- @@ -1084,7 +1084,7 @@ def nvrtcGetTileIRSize(prog): @cython.embedsignature(True) def nvrtcGetTileIR(prog, char* TileIR): - """ + """ Parameters ---------- diff --git a/cuda_bindings/cuda/bindings/nvvm.pxd b/cuda_bindings/src/cuda/bindings/nvvm.pxd similarity index 100% rename from cuda_bindings/cuda/bindings/nvvm.pxd rename to cuda_bindings/src/cuda/bindings/nvvm.pxd diff --git a/cuda_bindings/cuda/bindings/nvvm.pyx b/cuda_bindings/src/cuda/bindings/nvvm.pyx similarity index 100% rename from cuda_bindings/cuda/bindings/nvvm.pyx rename to cuda_bindings/src/cuda/bindings/nvvm.pyx diff --git a/cuda_bindings/cuda/bindings/runtime.pxd.in b/cuda_bindings/src/cuda/bindings/runtime.pxd.in similarity index 100% rename from cuda_bindings/cuda/bindings/runtime.pxd.in rename to cuda_bindings/src/cuda/bindings/runtime.pxd.in diff --git a/cuda_bindings/cuda/bindings/runtime.pyx.in b/cuda_bindings/src/cuda/bindings/runtime.pyx.in similarity index 99% rename from cuda_bindings/cuda/bindings/runtime.pyx.in rename to cuda_bindings/src/cuda/bindings/runtime.pyx.in index 279a8c1759..dae61548bf 100644 --- a/cuda_bindings/cuda/bindings/runtime.pyx.in +++ b/cuda_bindings/src/cuda/bindings/runtime.pyx.in @@ -21715,7 +21715,7 @@ def cudaIpcOpenMemHandle(handle not None : cudaIpcMemHandle_t, unsigned int flag Notes ----- - No guarantees are made about the address returned in `*devPtr`. + No guarantees are made about the address returned in `*devPtr`. In particular, multiple processes may not receive the same address for the same `handle`. """ cdef void_ptr devPtr = 0 @@ -28783,7 +28783,7 @@ def cudaMemcpy3DBatchAsync(size_t numOps, opList : Optional[tuple[cudaMemcpy3DBa @cython.embedsignature(True) def cudaMemcpyWithAttributesAsync(dst, src, size_t size, attr : Optional[cudaMemcpyAttributes], stream): - """ + """ Performs asynchronous memory copy operation with the specified attributes. @@ -28843,7 +28843,7 @@ def cudaMemcpyWithAttributesAsync(dst, src, size_t size, attr : Optional[cudaMem @cython.embedsignature(True) def cudaMemcpy3DWithAttributesAsync(op : Optional[cudaMemcpy3DBatchOp], unsigned long long flags, stream): - """ + """ Performs 3D asynchronous memory copy with the specified attributes. @@ -41862,4 +41862,3 @@ cdef int _add_native_handle_getters() except?-1: {{endif}} return 0 _add_native_handle_getters() - diff --git a/cuda_bindings/cuda/bindings/utils/__init__.py b/cuda_bindings/src/cuda/bindings/utils/__init__.py similarity index 89% rename from cuda_bindings/cuda/bindings/utils/__init__.py rename to cuda_bindings/src/cuda/bindings/utils/__init__.py index e4fcb15e8f..4e62915460 100644 --- a/cuda_bindings/cuda/bindings/utils/__init__.py +++ b/cuda_bindings/src/cuda/bindings/utils/__init__.py @@ -1,4 +1,4 @@ -# SPDX-FileCopyrightText: Copyright (c) 2025 NVIDIA CORPORATION & AFFILIATES. All rights reserved. +# SPDX-FileCopyrightText: Copyright (c) 2025-2026 NVIDIA CORPORATION & AFFILIATES. All rights reserved. # SPDX-License-Identifier: LicenseRef-NVIDIA-SOFTWARE-LICENSE from typing import Any, Callable diff --git a/cuda_bindings/cuda/bindings/utils/_ptx_utils.py b/cuda_bindings/src/cuda/bindings/utils/_ptx_utils.py similarity index 96% rename from cuda_bindings/cuda/bindings/utils/_ptx_utils.py rename to cuda_bindings/src/cuda/bindings/utils/_ptx_utils.py index b9df650312..9f6b3b69cc 100644 --- a/cuda_bindings/cuda/bindings/utils/_ptx_utils.py +++ b/cuda_bindings/src/cuda/bindings/utils/_ptx_utils.py @@ -1,4 +1,4 @@ -# SPDX-FileCopyrightText: Copyright (c) 2025 NVIDIA CORPORATION & AFFILIATES. All rights reserved. +# SPDX-FileCopyrightText: Copyright (c) 2025-2026 NVIDIA CORPORATION & AFFILIATES. All rights reserved. # SPDX-License-Identifier: LicenseRef-NVIDIA-SOFTWARE-LICENSE import re diff --git a/cuda_bindings/cuda/bindings/utils/_version_check.py b/cuda_bindings/src/cuda/bindings/utils/_version_check.py similarity index 95% rename from cuda_bindings/cuda/bindings/utils/_version_check.py rename to cuda_bindings/src/cuda/bindings/utils/_version_check.py index 1ebd7f3d92..25fc7884c2 100644 --- a/cuda_bindings/cuda/bindings/utils/_version_check.py +++ b/cuda_bindings/src/cuda/bindings/utils/_version_check.py @@ -1,4 +1,4 @@ -# SPDX-FileCopyrightText: Copyright (c) 2025 NVIDIA CORPORATION & AFFILIATES. All rights reserved. +# SPDX-FileCopyrightText: Copyright (c) 2025-2026 NVIDIA CORPORATION & AFFILIATES. All rights reserved. # SPDX-License-Identifier: LicenseRef-NVIDIA-SOFTWARE-LICENSE import os