mirror of
https://github.com/NixOS/nixpkgs.git
synced 2026-03-08 06:24:08 +01:00
214 lines
5.6 KiB
Nix
214 lines
5.6 KiB
Nix
{
|
|
lib,
|
|
stdenv,
|
|
symlinkJoin,
|
|
buildPythonPackage,
|
|
fetchFromGitHub,
|
|
gitUpdater,
|
|
|
|
cmake,
|
|
|
|
# build-system
|
|
scikit-build-core,
|
|
setuptools,
|
|
|
|
# dependencies
|
|
torch,
|
|
scipy,
|
|
trove-classifiers,
|
|
|
|
cudaSupport ? torch.cudaSupport,
|
|
cudaPackages ? torch.cudaPackages,
|
|
rocmSupport ? torch.rocmSupport,
|
|
rocmPackages ? torch.rocmPackages,
|
|
|
|
rocmGpuTargets ? rocmPackages.clr.localGpuTargets or rocmPackages.clr.gpuTargets,
|
|
}:
|
|
|
|
let
|
|
pname = "bitsandbytes";
|
|
version = "0.49.1";
|
|
|
|
brokenConditions = lib.attrsets.filterAttrs (_: cond: cond) {
|
|
"CUDA and ROCm are mutually exclusive" = cudaSupport && rocmSupport;
|
|
"CUDA is not targeting Linux" = cudaSupport && !stdenv.hostPlatform.isLinux;
|
|
};
|
|
|
|
inherit (cudaPackages) cudaMajorMinorVersion;
|
|
rocmMajorMinorVersion = lib.versions.majorMinor rocmPackages.rocm-core.version;
|
|
|
|
cudaMajorMinorVersionString = lib.replaceStrings [ "." ] [ "" ] cudaMajorMinorVersion;
|
|
rocmMajorMinorVersionString = lib.replaceStrings [ "." ] [ "" ] rocmMajorMinorVersion;
|
|
|
|
# NOTE: torchvision doesn't use cudnn; torch does!
|
|
# For this reason it is not included.
|
|
cuda-common-redist = with cudaPackages; [
|
|
(lib.getDev cuda_cccl) # <thrust/*>
|
|
(lib.getDev libcublas) # cublas_v2.h
|
|
(lib.getLib libcublas)
|
|
(lib.getInclude libcublas) # cublasLt.h
|
|
libcurand
|
|
libcusolver # cusolverDn.h
|
|
(lib.getDev libcusparse) # cusparse.h
|
|
(lib.getLib libcusparse) # cusparse.h
|
|
(lib.getInclude libcusparse) # cusparse.h
|
|
(lib.getDev cuda_cudart) # cuda_runtime.h cuda_runtime_api.h
|
|
];
|
|
|
|
cuda-native-redist = symlinkJoin {
|
|
name = "cuda-native-redist-${cudaMajorMinorVersion}";
|
|
paths =
|
|
with cudaPackages;
|
|
[
|
|
(lib.getDev cuda_cudart) # cuda_runtime.h cuda_runtime_api.h
|
|
(lib.getLib cuda_cudart)
|
|
(lib.getStatic cuda_cudart)
|
|
cuda_nvcc
|
|
]
|
|
++ cuda-common-redist;
|
|
};
|
|
|
|
cuda-redist = symlinkJoin {
|
|
name = "cuda-redist-${cudaMajorMinorVersion}";
|
|
paths = cuda-common-redist;
|
|
};
|
|
in
|
|
buildPythonPackage {
|
|
inherit pname version;
|
|
pyproject = true;
|
|
|
|
src = fetchFromGitHub {
|
|
owner = "bitsandbytes-foundation";
|
|
repo = "bitsandbytes";
|
|
tag = version;
|
|
hash = "sha256-nNhxDJITXNIZMXuZdzpF5dl1K1kFEVQ0gbTqZnOf/sI=";
|
|
};
|
|
|
|
patches = [
|
|
./find-rocm-deps-with-cmake.patch
|
|
];
|
|
|
|
# By default, which library is loaded depends on the result of `torch.cuda.is_available()`.
|
|
# When `cudaSupport` is enabled, bypass this check and load the cuda library unconditionally.
|
|
# Indeed, in this case, only `libbitsandbytes_cuda124.so` is built. `libbitsandbytes_cpu.so` is not.
|
|
# Also, hardcode the path to the previously built library instead of relying on
|
|
# `get_cuda_bnb_library_path(cuda_specs)` which relies on `torch.cuda` too.
|
|
#
|
|
# WARNING: The cuda library is currently named `libbitsandbytes_cudaxxy` for CUDA version `xx.y`
|
|
# and `libbitsandbytes_rocmxxy` for ROCm version `xx.y`
|
|
# This upstream convention could change at some point and thus break the following patch.
|
|
postPatch = (
|
|
let
|
|
prefix = if cudaSupport then "cuda" else "rocm";
|
|
majorMinorVersionString =
|
|
if cudaSupport then cudaMajorMinorVersionString else rocmMajorMinorVersionString;
|
|
in
|
|
lib.optionalString (cudaSupport || rocmSupport) ''
|
|
substituteInPlace bitsandbytes/cextension.py \
|
|
--replace-fail "if cuda_specs:" "if True:" \
|
|
--replace-fail \
|
|
"cuda_binary_path = get_cuda_bnb_library_path(cuda_specs)" \
|
|
"cuda_binary_path = PACKAGE_DIR / 'libbitsandbytes_${prefix}${majorMinorVersionString}.so'"
|
|
''
|
|
);
|
|
|
|
nativeBuildInputs = [
|
|
cmake
|
|
]
|
|
++ lib.optionals cudaSupport [
|
|
cudaPackages.cuda_nvcc
|
|
]
|
|
++ lib.optionals rocmSupport [
|
|
rocmPackages.clr
|
|
];
|
|
|
|
build-system = [
|
|
scikit-build-core
|
|
setuptools
|
|
];
|
|
|
|
buildInputs =
|
|
lib.optional cudaSupport cuda-redist
|
|
++ lib.optionals rocmSupport (
|
|
with rocmPackages;
|
|
[
|
|
rocm-device-libs
|
|
hipblas
|
|
rocm-comgr
|
|
rocm-runtime
|
|
hiprand
|
|
rocrand
|
|
hipsparse
|
|
hipblaslt
|
|
rocblas
|
|
hipcub
|
|
rocprim
|
|
]
|
|
);
|
|
|
|
cmakeFlags = [
|
|
(lib.cmakeFeature "COMPUTE_BACKEND" (
|
|
if cudaSupport then
|
|
"cuda"
|
|
else if rocmSupport then
|
|
"hip"
|
|
else
|
|
"cpu"
|
|
))
|
|
]
|
|
++ lib.optionals rocmSupport [
|
|
# ends up using g++ to build some files it shouldn't
|
|
(lib.cmakeFeature "CMAKE_C_COMPILER" "amdclang")
|
|
(lib.cmakeFeature "CMAKE_CXX_COMPILER" "amdclang++")
|
|
|
|
(lib.cmakeFeature "CMAKE_HIP_ARCHITECTURES" (builtins.concatStringsSep ";" rocmGpuTargets))
|
|
];
|
|
|
|
env = lib.optionalAttrs cudaSupport {
|
|
CUDA_HOME = cuda-native-redist;
|
|
NVCC_PREPEND_FLAGS = toString [
|
|
"-I${cuda-native-redist}/include"
|
|
"-L${cuda-native-redist}/lib"
|
|
];
|
|
};
|
|
|
|
preBuild = ''
|
|
make -j $NIX_BUILD_CORES
|
|
cd .. # leave /build/source/build
|
|
'';
|
|
|
|
dependencies = [
|
|
scipy
|
|
torch
|
|
trove-classifiers
|
|
];
|
|
|
|
doCheck = false; # tests require CUDA and also GPU access
|
|
|
|
pythonImportsCheck = [ "bitsandbytes" ];
|
|
|
|
passthru = {
|
|
inherit
|
|
cudaSupport
|
|
cudaPackages
|
|
rocmSupport
|
|
rocmPackages
|
|
brokenConditions # To help debug when a package is broken due to CUDA support
|
|
;
|
|
|
|
updateScript = gitUpdater {
|
|
ignoredVersions = "continuous-release.*";
|
|
};
|
|
};
|
|
|
|
meta = {
|
|
description = "8-bit CUDA functions for PyTorch";
|
|
homepage = "https://github.com/bitsandbytes-foundation/bitsandbytes";
|
|
changelog = "https://github.com/bitsandbytes-foundation/bitsandbytes/releases/tag/${version}";
|
|
license = lib.licenses.mit;
|
|
maintainers = with lib.maintainers; [
|
|
bcdarwin
|
|
jk
|
|
];
|
|
};
|
|
}
|