setup.py 17.2 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
294
295
296
297
298
299
300
301
302
303
304
305
306
307
308
309
310
311
312
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
313

314

315
316
317
def get_neuronxcc_version():
    import sysconfig
    site_dir = sysconfig.get_paths()["purelib"]
318
319
    version_file = os.path.join(site_dir, "neuronxcc", "version",
                                "__init__.py")
320
321
322
323
324
325
326
327
328
329
330

    # 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:
331
        raise RuntimeError("Could not find Neuron version in the output")
332
333


bnellnm's avatar
bnellnm committed
334
def get_nvcc_cuda_version() -> Version:
335
336
337
338
    """Get the CUDA version from nvcc.

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


348
349
350
351
def get_path(*filepath) -> str:
    return os.path.join(ROOT_DIR, *filepath)


352
def get_vllm_version() -> str:
353
354
355
356
    version = get_version(
        write_to="vllm/_version.py",  # TODO: move this to pyproject.toml
    )

357
    sep = "+" if "+" not in version else "."  # dev versions might contain +
358

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

392
393
394
    return version


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


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

    def _read_requirements(filename: str) -> List[str]:
        with open(get_path(filename)) as f:
409
            requirements = f.read().strip().split("\n")
410
411
412
413
        resolved_requirements = []
        for line in requirements:
            if line.startswith("-r "):
                resolved_requirements += _read_requirements(line.split()[1])
414
415
            elif line.startswith("--"):
                continue
416
417
418
419
            else:
                resolved_requirements.append(line)
        return resolved_requirements

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


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

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

458
459
460
if _is_hip():
    ext_modules.append(CMakeExtension(name="vllm._rocm_C"))

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

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

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

475
476
477
if _no_device():
    ext_modules = []

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