setup.py 13.8 KB
Newer Older
1
import io
2
import logging
3
4
import os
import re
5
import subprocess
bnellnm's avatar
bnellnm committed
6
import sys
7
from shutil import which
8
from typing import Dict, List
9

Woosuk Kwon's avatar
Woosuk Kwon committed
10
import torch
11
12
13
from packaging.version import Version, parse
from setuptools import Extension, find_packages, setup
from setuptools.command.build_ext import build_ext
bnellnm's avatar
bnellnm committed
14
from torch.utils.cpp_extension import CUDA_HOME
15
16

ROOT_DIR = os.path.dirname(__file__)
17
logger = logging.getLogger(__name__)
18
19
# Target device of vLLM, supporting [cuda (by default), rocm, neuron, cpu]
VLLM_TARGET_DEVICE = os.getenv("VLLM_TARGET_DEVICE", "cuda")
20

21
22
23
24
# vLLM only supports Linux platform
assert sys.platform.startswith(
    "linux"), "vLLM only supports Linux platform (including WSL)."

25
26
MAIN_CUDA_VERSION = "12.1"

bnellnm's avatar
bnellnm committed
27
28
29
30
31
32
33
34
35
36
37
38
39
40
41
42
43
44
45
46
47
48
49
50
51
52
53
54

def is_sccache_available() -> bool:
    return which("sccache") is not None


def is_ccache_available() -> bool:
    return which("ccache") is not None


def is_ninja_available() -> bool:
    return which("ninja") is not None


def remove_prefix(text, prefix):
    if text.startswith(prefix):
        return text[len(prefix):]
    return text


class CMakeExtension(Extension):

    def __init__(self, name: str, cmake_lists_dir: str = '.', **kwa) -> None:
        super().__init__(name, sources=[], **kwa)
        self.cmake_lists_dir = os.path.abspath(cmake_lists_dir)


class cmake_build_ext(build_ext):
    # A dict of extension directories that have been configured.
55
    did_config: Dict[str, bool] = {}
bnellnm's avatar
bnellnm committed
56
57
58
59
60

    #
    # Determine number of compilation jobs and optionally nvcc compile threads.
    #
    def compute_num_jobs(self):
61
62
        # `num_jobs` is either the value of the MAX_JOBS environment variable
        # (if defined) or the number of CPUs available.
63
64
65
        num_jobs = os.environ.get("MAX_JOBS", None)
        if num_jobs is not None:
            num_jobs = int(num_jobs)
66
            logger.info("Using MAX_JOBS=%d as the number of jobs.", num_jobs)
67
68
69
70
71
72
73
        else:
            try:
                # os.sched_getaffinity() isn't universally available, so fall
                #  back to os.cpu_count() if we get an error here.
                num_jobs = len(os.sched_getaffinity(0))
            except AttributeError:
                num_jobs = os.cpu_count()
bnellnm's avatar
bnellnm committed
74

75
        nvcc_threads = None
76
77
78
79
80
81
82
83
        if _is_cuda() and get_nvcc_cuda_version() >= Version("11.2"):
            # `nvcc_threads` is either the value of the NVCC_THREADS
            # environment variable (if defined) or 1.
            # when it is set, we reduce `num_jobs` to avoid
            # overloading the system.
            nvcc_threads = os.getenv("NVCC_THREADS", None)
            if nvcc_threads is not None:
                nvcc_threads = int(nvcc_threads)
84
85
86
                logger.info(
                    "Using NVCC_THREADS=%d as the number of nvcc threads.",
                    nvcc_threads)
87
88
89
            else:
                nvcc_threads = 1
            num_jobs = max(1, num_jobs // nvcc_threads)
bnellnm's avatar
bnellnm committed
90
91
92
93
94
95
96
97
98
99
100
101
102
103
104
105
106
107
108
109
110
111
112
113
114
115
116
117

        return num_jobs, nvcc_threads

    #
    # Perform cmake configuration for a single extension.
    #
    def configure(self, ext: CMakeExtension) -> None:
        # If we've already configured using the CMakeLists.txt for
        # this extension, exit early.
        if ext.cmake_lists_dir in cmake_build_ext.did_config:
            return

        cmake_build_ext.did_config[ext.cmake_lists_dir] = True

        # Select the build type.
        # Note: optimization level + debug info are set by the build type
        default_cfg = "Debug" if self.debug else "RelWithDebInfo"
        cfg = os.getenv("CMAKE_BUILD_TYPE", default_cfg)

        # where .so files will be written, should be the same for all extensions
        # that use the same CMakeLists.txt.
        outdir = os.path.abspath(
            os.path.dirname(self.get_ext_fullpath(ext.name)))

        cmake_args = [
            '-DCMAKE_BUILD_TYPE={}'.format(cfg),
            '-DCMAKE_LIBRARY_OUTPUT_DIRECTORY={}'.format(outdir),
            '-DCMAKE_ARCHIVE_OUTPUT_DIRECTORY={}'.format(self.build_temp),
118
            '-DVLLM_TARGET_DEVICE={}'.format(VLLM_TARGET_DEVICE),
bnellnm's avatar
bnellnm committed
119
120
121
122
123
124
125
126
127
128
129
130
131
132
133
134
135
136
137
138
139
140
141
142
143
144
145
146
147
148
149
150
151
152
153
154
155
156
157
158
159
160
161
162
163
164
165
166
167
168
169
170
171
172
173
174
175
176
177
178
179
180
181
182
183
184
185
186
187
188
        ]

        verbose = bool(int(os.getenv('VERBOSE', '0')))
        if verbose:
            cmake_args += ['-DCMAKE_VERBOSE_MAKEFILE=ON']

        if is_sccache_available():
            cmake_args += [
                '-DCMAKE_CXX_COMPILER_LAUNCHER=sccache',
                '-DCMAKE_CUDA_COMPILER_LAUNCHER=sccache',
            ]
        elif is_ccache_available():
            cmake_args += [
                '-DCMAKE_CXX_COMPILER_LAUNCHER=ccache',
                '-DCMAKE_CUDA_COMPILER_LAUNCHER=ccache',
            ]

        # Pass the python executable to cmake so it can find an exact
        # match.
        cmake_args += ['-DVLLM_PYTHON_EXECUTABLE={}'.format(sys.executable)]

        if _install_punica():
            cmake_args += ['-DVLLM_INSTALL_PUNICA_KERNELS=ON']

        #
        # Setup parallelism and build tool
        #
        num_jobs, nvcc_threads = self.compute_num_jobs()

        if nvcc_threads:
            cmake_args += ['-DNVCC_THREADS={}'.format(nvcc_threads)]

        if is_ninja_available():
            build_tool = ['-G', 'Ninja']
            cmake_args += [
                '-DCMAKE_JOB_POOL_COMPILE:STRING=compile',
                '-DCMAKE_JOB_POOLS:STRING=compile={}'.format(num_jobs),
            ]
        else:
            # Default build tool to whatever cmake picks.
            build_tool = []

        subprocess.check_call(
            ['cmake', ext.cmake_lists_dir, *build_tool, *cmake_args],
            cwd=self.build_temp)

    def build_extensions(self) -> None:
        # Ensure that CMake is present and working
        try:
            subprocess.check_output(['cmake', '--version'])
        except OSError as e:
            raise RuntimeError('Cannot find CMake executable') from e

        # Create build directory if it does not exist.
        if not os.path.exists(self.build_temp):
            os.makedirs(self.build_temp)

        # Build all the extensions
        for ext in self.extensions:
            self.configure(ext)

            ext_target_name = remove_prefix(ext.name, "vllm.")
            num_jobs, _ = self.compute_num_jobs()

            build_args = [
                '--build', '.', '--target', ext_target_name, '-j',
                str(num_jobs)
            ]

            subprocess.check_call(['cmake', *build_args], cwd=self.build_temp)
189
190


191
def _is_cuda() -> bool:
192
193
194
    return VLLM_TARGET_DEVICE == "cuda" \
            and torch.version.cuda is not None \
            and not _is_neuron()
195
196


197
def _is_hip() -> bool:
198
199
    return (VLLM_TARGET_DEVICE == "cuda"
            or VLLM_TARGET_DEVICE == "rocm") and torch.version.hip is not None
200
201


202
203
204
205
def _is_neuron() -> bool:
    torch_neuronx_installed = True
    try:
        subprocess.run(["neuron-ls"], capture_output=True, check=True)
206
    except (FileNotFoundError, PermissionError, subprocess.CalledProcessError):
207
        torch_neuronx_installed = False
208
209
    return torch_neuronx_installed or os.environ.get("VLLM_BUILD_WITH_NEURON",
                                                     False)
210
211


212
213
214
215
def _is_cpu() -> bool:
    return VLLM_TARGET_DEVICE == "cpu"


bnellnm's avatar
bnellnm committed
216
217
def _install_punica() -> bool:
    return bool(int(os.getenv("VLLM_INSTALL_PUNICA_KERNELS", "0")))
218

219
220
221
222
223
224
225
226
227
228
229
230
231
232
233
234
235
236
237
238
239

def get_hipcc_rocm_version():
    # Run the hipcc --version command
    result = subprocess.run(['hipcc', '--version'],
                            stdout=subprocess.PIPE,
                            stderr=subprocess.STDOUT,
                            text=True)

    # Check if the command was executed successfully
    if result.returncode != 0:
        print("Error running 'hipcc --version'")
        return None

    # Extract the version using a regular expression
    match = re.search(r'HIP version: (\S+)', result.stdout)
    if match:
        # Return the version string
        return match.group(1)
    else:
        print("Could not find HIP version in the output")
        return None
Woosuk Kwon's avatar
Woosuk Kwon committed
240

241

242
243
244
def get_neuronxcc_version():
    import sysconfig
    site_dir = sysconfig.get_paths()["purelib"]
245
246
    version_file = os.path.join(site_dir, "neuronxcc", "version",
                                "__init__.py")
247
248
249
250
251
252
253
254
255
256
257
258
259
260

    # Check if the command was executed successfully
    with open(version_file, "rt") as fp:
        content = fp.read()

    # Extract the version using a regular expression
    match = re.search(r"__version__ = '(\S+)'", content)
    if match:
        # Return the version string
        return match.group(1)
    else:
        raise RuntimeError("Could not find HIP version in the output")


bnellnm's avatar
bnellnm committed
261
def get_nvcc_cuda_version() -> Version:
262
263
264
265
    """Get the CUDA version from nvcc.

    Adapted from https://github.com/NVIDIA/apex/blob/8b7a1ff183741dd8f9b87e7bafd04cfde99cea28/setup.py
    """
266
    assert CUDA_HOME is not None, "CUDA_HOME is not set"
bnellnm's avatar
bnellnm committed
267
    nvcc_output = subprocess.check_output([CUDA_HOME + "/bin/nvcc", "-V"],
268
269
270
271
272
273
274
                                          universal_newlines=True)
    output = nvcc_output.split()
    release_idx = output.index("release") + 1
    nvcc_cuda_version = parse(output[release_idx].split(",")[0])
    return nvcc_cuda_version


275
276
277
278
def get_path(*filepath) -> str:
    return os.path.join(ROOT_DIR, *filepath)


279
def find_version(filepath: str) -> str:
280
281
282
283
284
    """Extract version information from the given filepath.

    Adapted from https://github.com/ray-project/ray/blob/0b190ee1160eeca9796bc091e07eaebf4c85b511/python/setup.py
    """
    with open(filepath) as fp:
Woosuk Kwon's avatar
Woosuk Kwon committed
285
286
        version_match = re.search(r"^__version__ = ['\"]([^'\"]*)['\"]",
                                  fp.read(), re.M)
287
288
289
290
291
        if version_match:
            return version_match.group(1)
        raise RuntimeError("Unable to find version string.")


292
293
def get_vllm_version() -> str:
    version = find_version(get_path("vllm", "__init__.py"))
294

295
    if _is_cuda():
bnellnm's avatar
bnellnm committed
296
        cuda_version = str(get_nvcc_cuda_version())
297
298
299
300
        if cuda_version != MAIN_CUDA_VERSION:
            cuda_version_str = cuda_version.replace(".", "")[:3]
            version += f"+cu{cuda_version_str}"
    elif _is_hip():
301
302
303
304
305
        # Get the HIP version
        hipcc_version = get_hipcc_rocm_version()
        if hipcc_version != MAIN_CUDA_VERSION:
            rocm_version_str = hipcc_version.replace(".", "")[:3]
            version += f"+rocm{rocm_version_str}"
306
307
    elif _is_neuron():
        # Get the Neuron version
bnellnm's avatar
bnellnm committed
308
        neuron_version = str(get_neuronxcc_version())
309
310
311
        if neuron_version != MAIN_CUDA_VERSION:
            neuron_version_str = neuron_version.replace(".", "")[:3]
            version += f"+neuron{neuron_version_str}"
312
313
    elif _is_cpu():
        version += "+cpu"
314
    else:
315
        raise RuntimeError("Unknown runtime environment")
316

317
318
319
    return version


320
def read_readme() -> str:
Stephen Krider's avatar
Stephen Krider committed
321
322
323
324
325
326
    """Read the README file if present."""
    p = get_path("README.md")
    if os.path.isfile(p):
        return io.open(get_path("README.md"), "r", encoding="utf-8").read()
    else:
        return ""
327
328


329
330
def get_requirements() -> List[str]:
    """Get Python package dependencies from requirements.txt."""
331
332
333

    def _read_requirements(filename: str) -> List[str]:
        with open(get_path(filename)) as f:
334
            requirements = f.read().strip().split("\n")
335
336
337
338
339
340
341
342
343
344
345
346
347
348
349
350
351
352
353
        resolved_requirements = []
        for line in requirements:
            if line.startswith("-r "):
                resolved_requirements += _read_requirements(line.split()[1])
            else:
                resolved_requirements.append(line)
        return resolved_requirements

    if _is_cuda():
        requirements = _read_requirements("requirements-cuda.txt")
        cuda_major = torch.version.cuda.split(".")[0]
        modified_requirements = []
        for req in requirements:
            if "vllm-nccl-cu12" in req:
                modified_requirements.append(
                    req.replace("vllm-nccl-cu12", f"vllm-nccl-cu{cuda_major}"))
            else:
                modified_requirements.append(req)
        requirements = modified_requirements
354
    elif _is_hip():
355
        requirements = _read_requirements("requirements-rocm.txt")
356
    elif _is_neuron():
357
        requirements = _read_requirements("requirements-neuron.txt")
358
    elif _is_cpu():
359
        requirements = _read_requirements("requirements-cpu.txt")
360
361
    else:
        raise ValueError(
362
            "Unsupported platform, please use CUDA, ROCm, Neuron, or CPU.")
363
364
365
    return requirements


bnellnm's avatar
bnellnm committed
366
367
368
369
370
371
372
373
374
375
376
ext_modules = []

if _is_cuda():
    ext_modules.append(CMakeExtension(name="vllm._moe_C"))

    if _install_punica():
        ext_modules.append(CMakeExtension(name="vllm._punica_C"))

if not _is_neuron():
    ext_modules.append(CMakeExtension(name="vllm._C"))

377
378
379
package_data = {
    "vllm": ["py.typed", "model_executor/layers/fused_moe/configs/*.json"]
}
Simon Mo's avatar
Simon Mo committed
380
if os.environ.get("VLLM_USE_PRECOMPILED"):
381
    ext_modules = []
Simon Mo's avatar
Simon Mo committed
382
383
    package_data["vllm"].append("*.so")

bnellnm's avatar
bnellnm committed
384
setup(
Woosuk Kwon's avatar
Woosuk Kwon committed
385
    name="vllm",
386
    version=get_vllm_version(),
Woosuk Kwon's avatar
Woosuk Kwon committed
387
    author="vLLM Team",
388
    license="Apache 2.0",
Woosuk Kwon's avatar
Woosuk Kwon committed
389
390
    description=("A high-throughput and memory-efficient inference and "
                 "serving engine for LLMs"),
391
392
    long_description=read_readme(),
    long_description_content_type="text/markdown",
393
    url="https://github.com/vllm-project/vllm",
394
    project_urls={
395
396
        "Homepage": "https://github.com/vllm-project/vllm",
        "Documentation": "https://vllm.readthedocs.io/en/latest/",
397
398
399
400
401
    },
    classifiers=[
        "Programming Language :: Python :: 3.8",
        "Programming Language :: Python :: 3.9",
        "Programming Language :: Python :: 3.10",
Woosuk Kwon's avatar
Woosuk Kwon committed
402
        "Programming Language :: Python :: 3.11",
403
404
405
        "License :: OSI Approved :: Apache Software License",
        "Topic :: Scientific/Engineering :: Artificial Intelligence",
    ],
bnellnm's avatar
bnellnm committed
406
    packages=find_packages(exclude=("benchmarks", "csrc", "docs", "examples",
407
                                    "tests*")),
408
409
    python_requires=">=3.8",
    install_requires=get_requirements(),
Woosuk Kwon's avatar
Woosuk Kwon committed
410
    ext_modules=ext_modules,
411
    extras_require={
412
        "tensorizer": ["tensorizer==2.9.0"],
413
    },
bnellnm's avatar
bnellnm committed
414
    cmdclass={"build_ext": cmake_build_ext} if not _is_neuron() else {},
Simon Mo's avatar
Simon Mo committed
415
    package_data=package_data,
Woosuk Kwon's avatar
Woosuk Kwon committed
416
)