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

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

19
20
21
22
23
24
25
26
27

def load_module_from_path(module_name, path):
    spec = importlib.util.spec_from_file_location(module_name, path)
    module = importlib.util.module_from_spec(spec)
    sys.modules[module_name] = module
    spec.loader.exec_module(module)
    return module


28
ROOT_DIR = os.path.dirname(__file__)
29
logger = logging.getLogger(__name__)
30
31
32
33
34
35

# cannot import envs directly because it depends on vllm,
#  which is not installed yet
envs = load_module_from_path('envs', os.path.join(ROOT_DIR, 'vllm', 'envs.py'))

VLLM_TARGET_DEVICE = envs.VLLM_TARGET_DEVICE
36

37
38
39
40
41
42
if not sys.platform.startswith("linux"):
    logger.warning(
        "vLLM only supports Linux platform (including WSL). "
        "Building on %s, "
        "so vLLM may not be able to run correctly", sys.platform)
    VLLM_TARGET_DEVICE = "empty"
43

44
45
MAIN_CUDA_VERSION = "12.1"

bnellnm's avatar
bnellnm committed
46
47
48
49
50
51
52
53
54
55
56
57
58
59
60
61
62
63
64
65
66
67

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:
68
        super().__init__(name, sources=[], py_limited_api=True, **kwa)
bnellnm's avatar
bnellnm committed
69
70
71
72
73
        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.
74
    did_config: Dict[str, bool] = {}
bnellnm's avatar
bnellnm committed
75
76
77
78
79

    #
    # Determine number of compilation jobs and optionally nvcc compile threads.
    #
    def compute_num_jobs(self):
80
81
        # `num_jobs` is either the value of the MAX_JOBS environment variable
        # (if defined) or the number of CPUs available.
82
        num_jobs = envs.MAX_JOBS
83
84
        if num_jobs is not None:
            num_jobs = int(num_jobs)
85
            logger.info("Using MAX_JOBS=%d as the number of jobs.", num_jobs)
86
87
88
89
90
91
92
        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
93

94
        nvcc_threads = None
95
96
97
98
99
        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.
100
            nvcc_threads = envs.NVCC_THREADS
101
102
            if nvcc_threads is not None:
                nvcc_threads = int(nvcc_threads)
103
104
105
                logger.info(
                    "Using NVCC_THREADS=%d as the number of nvcc threads.",
                    nvcc_threads)
106
107
108
            else:
                nvcc_threads = 1
            num_jobs = max(1, num_jobs // nvcc_threads)
bnellnm's avatar
bnellnm committed
109
110
111
112
113
114
115
116
117
118
119
120
121
122
123
124
125

        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"
126
        cfg = envs.CMAKE_BUILD_TYPE or default_cfg
bnellnm's avatar
bnellnm committed
127
128
129

        cmake_args = [
            '-DCMAKE_BUILD_TYPE={}'.format(cfg),
130
            '-DVLLM_TARGET_DEVICE={}'.format(VLLM_TARGET_DEVICE),
bnellnm's avatar
bnellnm committed
131
132
        ]

133
        verbose = envs.VERBOSE
bnellnm's avatar
bnellnm committed
134
135
136
137
138
        if verbose:
            cmake_args += ['-DCMAKE_VERBOSE_MAKEFILE=ON']

        if is_sccache_available():
            cmake_args += [
139
                '-DCMAKE_C_COMPILER_LAUNCHER=sccache',
bnellnm's avatar
bnellnm committed
140
141
                '-DCMAKE_CXX_COMPILER_LAUNCHER=sccache',
                '-DCMAKE_CUDA_COMPILER_LAUNCHER=sccache',
142
                '-DCMAKE_HIP_COMPILER_LAUNCHER=sccache',
bnellnm's avatar
bnellnm committed
143
144
145
            ]
        elif is_ccache_available():
            cmake_args += [
146
                '-DCMAKE_C_COMPILER_LAUNCHER=ccache',
bnellnm's avatar
bnellnm committed
147
148
                '-DCMAKE_CXX_COMPILER_LAUNCHER=ccache',
                '-DCMAKE_CUDA_COMPILER_LAUNCHER=ccache',
149
                '-DCMAKE_HIP_COMPILER_LAUNCHER=ccache',
bnellnm's avatar
bnellnm committed
150
151
152
153
154
155
            ]

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

156
157
158
159
        # Pass the python path to cmake so it can reuse the build dependencies
        # on subsequent calls to python.
        cmake_args += ['-DVLLM_PYTHON_PATH={}'.format(":".join(sys.path))]

bnellnm's avatar
bnellnm committed
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
189
190
191
        #
        # 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)

192
        targets = []
193
194
        target_name = lambda s: remove_prefix(remove_prefix(s, "vllm."),
                                              "vllm_flash_attn.")
bnellnm's avatar
bnellnm committed
195
196
197
        # Build all the extensions
        for ext in self.extensions:
            self.configure(ext)
198
            targets.append(target_name(ext.name))
bnellnm's avatar
bnellnm committed
199

200
        num_jobs, _ = self.compute_num_jobs()
bnellnm's avatar
bnellnm committed
201

202
203
204
205
206
207
        build_args = [
            "--build",
            ".",
            f"-j={num_jobs}",
            *[f"--target={name}" for name in targets],
        ]
bnellnm's avatar
bnellnm committed
208

209
        subprocess.check_call(["cmake", *build_args], cwd=self.build_temp)
210

211
212
213
214
215
216
217
218
219
220
221
222
223
224
225
226
227
228
229
230
231
232
        # Install the libraries
        for ext in self.extensions:
            # Install the extension into the proper location
            outdir = Path(self.get_ext_fullpath(ext.name)).parent.absolute()

            # Skip if the install directory is the same as the build directory
            if outdir == self.build_temp:
                continue

            # CMake appends the extension prefix to the install path,
            # and outdir already contains that prefix, so we need to remove it.
            prefix = outdir
            for i in range(ext.name.count('.')):
                prefix = prefix.parent

            # prefix here should actually be the same for all components
            install_args = [
                "cmake", "--install", ".", "--prefix", prefix, "--component",
                target_name(ext.name)
            ]
            subprocess.check_call(install_args, cwd=self.build_temp)

233
234
235
236
237
238
239
240
241
242
243
244
245
246
247
    def run(self):
        # First, run the standard build_ext command to compile the extensions
        super().run()

        # copy vllm/vllm_flash_attn/*.py from self.build_lib to current
        # directory so that they can be included in the editable build
        import glob
        files = glob.glob(
            os.path.join(self.build_lib, "vllm", "vllm_flash_attn", "*.py"))
        for file in files:
            dst_file = os.path.join("vllm/vllm_flash_attn",
                                    os.path.basename(file))
            print(f"Copying {file} to {dst_file}")
            self.copy_file(file, dst_file)

248

249
250
251
252
def _no_device() -> bool:
    return VLLM_TARGET_DEVICE == "empty"


253
def _is_cuda() -> bool:
254
255
256
    has_cuda = torch.version.cuda is not None
    return (VLLM_TARGET_DEVICE == "cuda" and has_cuda
            and not (_is_neuron() or _is_tpu()))
257
258


259
def _is_hip() -> bool:
260
261
    return (VLLM_TARGET_DEVICE == "cuda"
            or VLLM_TARGET_DEVICE == "rocm") and torch.version.hip is not None
262
263


264
265
266
267
def _is_neuron() -> bool:
    torch_neuronx_installed = True
    try:
        subprocess.run(["neuron-ls"], capture_output=True, check=True)
268
    except (FileNotFoundError, PermissionError, subprocess.CalledProcessError):
269
        torch_neuronx_installed = False
270
    return torch_neuronx_installed or VLLM_TARGET_DEVICE == "neuron"
271
272


273
274
275
276
def _is_tpu() -> bool:
    return VLLM_TARGET_DEVICE == "tpu"


277
278
279
280
def _is_cpu() -> bool:
    return VLLM_TARGET_DEVICE == "cpu"


281
282
283
284
def _is_openvino() -> bool:
    return VLLM_TARGET_DEVICE == "openvino"


285
286
287
288
def _is_xpu() -> bool:
    return VLLM_TARGET_DEVICE == "xpu"


289
290
291
292
def _build_custom_ops() -> bool:
    return _is_cuda() or _is_hip() or _is_cpu()


293
def _build_core_ext() -> bool:
Kunshang Ji's avatar
Kunshang Ji committed
294
    return not (_is_neuron() or _is_tpu() or _is_openvino() or _is_xpu())
295
296


297
298
299
300
301
302
303
304
305
306
307
308
309
310
311
312
313
314
315
316
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
317

318

319
320
321
def get_neuronxcc_version():
    import sysconfig
    site_dir = sysconfig.get_paths()["purelib"]
322
323
    version_file = os.path.join(site_dir, "neuronxcc", "version",
                                "__init__.py")
324
325
326
327
328
329
330
331
332
333
334
335
336
337

    # 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
338
def get_nvcc_cuda_version() -> Version:
339
340
341
342
    """Get the CUDA version from nvcc.

    Adapted from https://github.com/NVIDIA/apex/blob/8b7a1ff183741dd8f9b87e7bafd04cfde99cea28/setup.py
    """
343
    assert CUDA_HOME is not None, "CUDA_HOME is not set"
bnellnm's avatar
bnellnm committed
344
    nvcc_output = subprocess.check_output([CUDA_HOME + "/bin/nvcc", "-V"],
345
346
347
348
349
350
351
                                          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


352
353
354
355
def get_path(*filepath) -> str:
    return os.path.join(ROOT_DIR, *filepath)


356
def get_vllm_version() -> str:
357
358
    version = get_version()
    sep = "+" if "+" not in version else "."  # dev versions might contain +
359

360
    if _no_device():
361
362
        if envs.VLLM_TARGET_DEVICE == "empty":
            version += "+empty"
363
    elif _is_cuda():
bnellnm's avatar
bnellnm committed
364
        cuda_version = str(get_nvcc_cuda_version())
365
366
        if cuda_version != MAIN_CUDA_VERSION:
            cuda_version_str = cuda_version.replace(".", "")[:3]
367
368
            # skip this for source tarball, required for pypi
            if "sdist" not in sys.argv:
369
                version += f"{sep}cu{cuda_version_str}"
370
    elif _is_hip():
371
372
373
374
        # Get the HIP version
        hipcc_version = get_hipcc_rocm_version()
        if hipcc_version != MAIN_CUDA_VERSION:
            rocm_version_str = hipcc_version.replace(".", "")[:3]
375
            version += f"{sep}rocm{rocm_version_str}"
376
377
    elif _is_neuron():
        # Get the Neuron version
bnellnm's avatar
bnellnm committed
378
        neuron_version = str(get_neuronxcc_version())
379
380
        if neuron_version != MAIN_CUDA_VERSION:
            neuron_version_str = neuron_version.replace(".", "")[:3]
381
            version += f"{sep}neuron{neuron_version_str}"
382
    elif _is_openvino():
383
        version += f"{sep}openvino"
384
    elif _is_tpu():
385
        version += f"{sep}tpu"
386
    elif _is_cpu():
387
        version += f"{sep}cpu"
388
    elif _is_xpu():
389
        version += f"{sep}xpu"
390
    else:
391
        raise RuntimeError("Unknown runtime environment")
392

393
394
395
    return version


396
def read_readme() -> str:
Stephen Krider's avatar
Stephen Krider committed
397
398
399
400
401
402
    """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 ""
403
404


405
406
def get_requirements() -> List[str]:
    """Get Python package dependencies from requirements.txt."""
407
408
409

    def _read_requirements(filename: str) -> List[str]:
        with open(get_path(filename)) as f:
410
            requirements = f.read().strip().split("\n")
411
412
413
414
415
416
417
418
        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

419
420
421
    if _no_device():
        requirements = _read_requirements("requirements-cuda.txt")
    elif _is_cuda():
422
        requirements = _read_requirements("requirements-cuda.txt")
423
        cuda_major, cuda_minor = torch.version.cuda.split(".")
424
425
        modified_requirements = []
        for req in requirements:
426
427
            if ("vllm-flash-attn" in req
                    and not (cuda_major == "12" and cuda_minor == "1")):
428
429
430
431
                # vllm-flash-attn is built only for CUDA 12.1.
                # Skip for other versions.
                continue
            modified_requirements.append(req)
432
        requirements = modified_requirements
433
    elif _is_hip():
434
        requirements = _read_requirements("requirements-rocm.txt")
435
    elif _is_neuron():
436
        requirements = _read_requirements("requirements-neuron.txt")
437
438
    elif _is_openvino():
        requirements = _read_requirements("requirements-openvino.txt")
439
440
    elif _is_tpu():
        requirements = _read_requirements("requirements-tpu.txt")
441
    elif _is_cpu():
442
        requirements = _read_requirements("requirements-cpu.txt")
443
444
    elif _is_xpu():
        requirements = _read_requirements("requirements-xpu.txt")
445
446
    else:
        raise ValueError(
447
448
            "Unsupported platform, please use CUDA, ROCm, Neuron, "
            "OpenVINO, or CPU.")
449
450
451
    return requirements


bnellnm's avatar
bnellnm committed
452
453
ext_modules = []

454
455
456
if _build_core_ext():
    ext_modules.append(CMakeExtension(name="vllm._core_C"))

457
if _is_cuda() or _is_hip():
bnellnm's avatar
bnellnm committed
458
459
    ext_modules.append(CMakeExtension(name="vllm._moe_C"))

460
461
462
if _is_hip():
    ext_modules.append(CMakeExtension(name="vllm._rocm_C"))

463
464
465
466
if _is_cuda():
    ext_modules.append(
        CMakeExtension(name="vllm.vllm_flash_attn.vllm_flash_attn_c"))

467
if _build_custom_ops():
bnellnm's avatar
bnellnm committed
468
469
    ext_modules.append(CMakeExtension(name="vllm._C"))

470
471
472
package_data = {
    "vllm": ["py.typed", "model_executor/layers/fused_moe/configs/*.json"]
}
473
if envs.VLLM_USE_PRECOMPILED:
474
    ext_modules = []
Simon Mo's avatar
Simon Mo committed
475
476
    package_data["vllm"].append("*.so")

477
478
479
if _no_device():
    ext_modules = []

bnellnm's avatar
bnellnm committed
480
setup(
Woosuk Kwon's avatar
Woosuk Kwon committed
481
    name="vllm",
482
    version=get_vllm_version(),
Woosuk Kwon's avatar
Woosuk Kwon committed
483
    author="vLLM Team",
484
    license="Apache 2.0",
Woosuk Kwon's avatar
Woosuk Kwon committed
485
486
    description=("A high-throughput and memory-efficient inference and "
                 "serving engine for LLMs"),
487
488
    long_description=read_readme(),
    long_description_content_type="text/markdown",
489
    url="https://github.com/vllm-project/vllm",
490
    project_urls={
491
492
        "Homepage": "https://github.com/vllm-project/vllm",
        "Documentation": "https://vllm.readthedocs.io/en/latest/",
493
494
495
496
497
    },
    classifiers=[
        "Programming Language :: Python :: 3.8",
        "Programming Language :: Python :: 3.9",
        "Programming Language :: Python :: 3.10",
Woosuk Kwon's avatar
Woosuk Kwon committed
498
        "Programming Language :: Python :: 3.11",
499
        "Programming Language :: Python :: 3.12",
500
501
502
        "License :: OSI Approved :: Apache Software License",
        "Topic :: Scientific/Engineering :: Artificial Intelligence",
    ],
bnellnm's avatar
bnellnm committed
503
    packages=find_packages(exclude=("benchmarks", "csrc", "docs", "examples",
504
                                    "tests*")),
505
506
    python_requires=">=3.8",
    install_requires=get_requirements(),
Woosuk Kwon's avatar
Woosuk Kwon committed
507
    ext_modules=ext_modules,
508
    extras_require={
509
        "tensorizer": ["tensorizer>=2.9.0"],
510
        "video": ["opencv-python"],  # Required for video processing
511
        "audio": ["librosa", "soundfile"]  # Required for audio processing
512
    },
513
    cmdclass={"build_ext": cmake_build_ext} if len(ext_modules) > 0 else {},
Simon Mo's avatar
Simon Mo committed
514
    package_data=package_data,
Ethan Xu's avatar
Ethan Xu committed
515
516
517
518
519
    entry_points={
        "console_scripts": [
            "vllm=vllm.scripts:main",
        ],
    },
Woosuk Kwon's avatar
Woosuk Kwon committed
520
)