setup.py 15.8 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
import warnings
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
bnellnm's avatar
bnellnm committed
16
from torch.utils.cpp_extension import CUDA_HOME
17

18
19
20
21
22
23
24
25
26

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


27
ROOT_DIR = os.path.dirname(__file__)
28
logger = logging.getLogger(__name__)
29

30
31
32

def embed_commit_hash():
    try:
youkaichao's avatar
youkaichao committed
33
34
35
36
37
38
39
        if "BUILDKITE_COMMIT" in os.environ:
            # ci build
            commit_id = os.environ["BUILDKITE_COMMIT"]
        else:
            commit_id = subprocess.check_output(["git", "rev-parse", "HEAD"],
                                                encoding="utf-8").strip()

40
41
42
43
44
45
46
47
48
49
50
51
52
53
54
55
56
57
        commit_contents = f'__commit__ = "{commit_id}"\n'

        version_file = os.path.join(ROOT_DIR, "vllm", "commit_id.py")
        with open(version_file, "w", encoding="utf-8") as f:
            f.write(commit_contents)

    except subprocess.CalledProcessError as e:
        warnings.warn(f"Failed to get commit hash:\n{e}",
                      RuntimeWarning,
                      stacklevel=2)
    except Exception as e:
        warnings.warn(f"Failed to embed commit hash:\n{e}",
                      RuntimeWarning,
                      stacklevel=2)


embed_commit_hash()

58
59
60
61
62
# 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
63

64
65
66
67
# vLLM only supports Linux platform
assert sys.platform.startswith(
    "linux"), "vLLM only supports Linux platform (including WSL)."

68
69
MAIN_CUDA_VERSION = "12.1"

bnellnm's avatar
bnellnm committed
70
71
72
73
74
75
76
77
78
79
80
81
82
83
84
85
86
87
88
89
90
91

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:
92
        super().__init__(name, sources=[], py_limited_api=True, **kwa)
bnellnm's avatar
bnellnm committed
93
94
95
96
97
        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.
98
    did_config: Dict[str, bool] = {}
bnellnm's avatar
bnellnm committed
99
100
101
102
103

    #
    # Determine number of compilation jobs and optionally nvcc compile threads.
    #
    def compute_num_jobs(self):
104
105
        # `num_jobs` is either the value of the MAX_JOBS environment variable
        # (if defined) or the number of CPUs available.
106
        num_jobs = envs.MAX_JOBS
107
108
        if num_jobs is not None:
            num_jobs = int(num_jobs)
109
            logger.info("Using MAX_JOBS=%d as the number of jobs.", num_jobs)
110
111
112
113
114
115
116
        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
117

118
        nvcc_threads = None
119
120
121
122
123
        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.
124
            nvcc_threads = envs.NVCC_THREADS
125
126
            if nvcc_threads is not None:
                nvcc_threads = int(nvcc_threads)
127
128
129
                logger.info(
                    "Using NVCC_THREADS=%d as the number of nvcc threads.",
                    nvcc_threads)
130
131
132
            else:
                nvcc_threads = 1
            num_jobs = max(1, num_jobs // nvcc_threads)
bnellnm's avatar
bnellnm committed
133
134
135
136
137
138
139
140
141
142
143
144
145
146
147
148
149

        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"
150
        cfg = envs.CMAKE_BUILD_TYPE or default_cfg
bnellnm's avatar
bnellnm committed
151
152
153
154
155
156
157
158
159
160

        # 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),
161
            '-DVLLM_TARGET_DEVICE={}'.format(VLLM_TARGET_DEVICE),
bnellnm's avatar
bnellnm committed
162
163
        ]

164
        verbose = envs.VERBOSE
bnellnm's avatar
bnellnm committed
165
166
167
168
169
170
171
        if verbose:
            cmake_args += ['-DCMAKE_VERBOSE_MAKEFILE=ON']

        if is_sccache_available():
            cmake_args += [
                '-DCMAKE_CXX_COMPILER_LAUNCHER=sccache',
                '-DCMAKE_CUDA_COMPILER_LAUNCHER=sccache',
172
                '-DCMAKE_C_COMPILER_LAUNCHER=sccache',
bnellnm's avatar
bnellnm committed
173
174
175
176
177
178
179
180
181
182
183
184
185
186
187
188
189
190
191
192
193
194
195
196
197
198
199
200
201
202
203
204
205
206
207
208
209
210
211
212
213
214
215
216
217
218
            ]
        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)

219
        targets = []
bnellnm's avatar
bnellnm committed
220
221
222
        # Build all the extensions
        for ext in self.extensions:
            self.configure(ext)
223
            targets.append(remove_prefix(ext.name, "vllm."))
bnellnm's avatar
bnellnm committed
224

225
        num_jobs, _ = self.compute_num_jobs()
bnellnm's avatar
bnellnm committed
226

227
228
229
230
231
232
        build_args = [
            "--build",
            ".",
            f"-j={num_jobs}",
            *[f"--target={name}" for name in targets],
        ]
bnellnm's avatar
bnellnm committed
233

234
        subprocess.check_call(["cmake", *build_args], cwd=self.build_temp)
235
236


237
def _is_cuda() -> bool:
238
239
240
    has_cuda = torch.version.cuda is not None
    return (VLLM_TARGET_DEVICE == "cuda" and has_cuda
            and not (_is_neuron() or _is_tpu()))
241
242


243
def _is_hip() -> bool:
244
245
    return (VLLM_TARGET_DEVICE == "cuda"
            or VLLM_TARGET_DEVICE == "rocm") and torch.version.hip is not None
246
247


248
249
250
251
def _is_neuron() -> bool:
    torch_neuronx_installed = True
    try:
        subprocess.run(["neuron-ls"], capture_output=True, check=True)
252
    except (FileNotFoundError, PermissionError, subprocess.CalledProcessError):
253
        torch_neuronx_installed = False
254
    return torch_neuronx_installed or VLLM_TARGET_DEVICE == "neuron"
255
256


257
258
259
260
def _is_tpu() -> bool:
    return VLLM_TARGET_DEVICE == "tpu"


261
262
263
264
def _is_cpu() -> bool:
    return VLLM_TARGET_DEVICE == "cpu"


265
266
267
268
def _is_openvino() -> bool:
    return VLLM_TARGET_DEVICE == "openvino"


269
270
271
272
def _is_xpu() -> bool:
    return VLLM_TARGET_DEVICE == "xpu"


273
274
275
276
def _build_custom_ops() -> bool:
    return _is_cuda() or _is_hip() or _is_cpu()


bnellnm's avatar
bnellnm committed
277
def _install_punica() -> bool:
278
    return envs.VLLM_INSTALL_PUNICA_KERNELS
279

280
281
282
283
284
285
286
287
288
289
290
291
292
293
294
295
296
297
298
299
300

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
301

302

303
304
305
def get_neuronxcc_version():
    import sysconfig
    site_dir = sysconfig.get_paths()["purelib"]
306
307
    version_file = os.path.join(site_dir, "neuronxcc", "version",
                                "__init__.py")
308
309
310
311
312
313
314
315
316
317
318
319
320
321

    # 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
322
def get_nvcc_cuda_version() -> Version:
323
324
325
326
    """Get the CUDA version from nvcc.

    Adapted from https://github.com/NVIDIA/apex/blob/8b7a1ff183741dd8f9b87e7bafd04cfde99cea28/setup.py
    """
327
    assert CUDA_HOME is not None, "CUDA_HOME is not set"
bnellnm's avatar
bnellnm committed
328
    nvcc_output = subprocess.check_output([CUDA_HOME + "/bin/nvcc", "-V"],
329
330
331
332
333
334
335
                                          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


336
337
338
339
def get_path(*filepath) -> str:
    return os.path.join(ROOT_DIR, *filepath)


340
def find_version(filepath: str) -> str:
341
342
343
344
345
    """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
346
347
        version_match = re.search(r"^__version__ = ['\"]([^'\"]*)['\"]",
                                  fp.read(), re.M)
348
349
350
351
352
        if version_match:
            return version_match.group(1)
        raise RuntimeError("Unable to find version string.")


353
def get_vllm_version() -> str:
354
    version = find_version(get_path("vllm", "version.py"))
355

356
    if _is_cuda():
bnellnm's avatar
bnellnm committed
357
        cuda_version = str(get_nvcc_cuda_version())
358
359
360
361
        if cuda_version != MAIN_CUDA_VERSION:
            cuda_version_str = cuda_version.replace(".", "")[:3]
            version += f"+cu{cuda_version_str}"
    elif _is_hip():
362
363
364
365
366
        # 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}"
367
368
    elif _is_neuron():
        # Get the Neuron version
bnellnm's avatar
bnellnm committed
369
        neuron_version = str(get_neuronxcc_version())
370
371
372
        if neuron_version != MAIN_CUDA_VERSION:
            neuron_version_str = neuron_version.replace(".", "")[:3]
            version += f"+neuron{neuron_version_str}"
373
374
    elif _is_openvino():
        version += "+openvino"
375
376
    elif _is_tpu():
        version += "+tpu"
377
378
    elif _is_cpu():
        version += "+cpu"
379
380
    elif _is_xpu():
        version += "+xpu"
381
    else:
382
        raise RuntimeError("Unknown runtime environment")
383

384
385
386
    return version


387
def read_readme() -> str:
Stephen Krider's avatar
Stephen Krider committed
388
389
390
391
392
393
    """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 ""
394
395


396
397
def get_requirements() -> List[str]:
    """Get Python package dependencies from requirements.txt."""
398
399
400

    def _read_requirements(filename: str) -> List[str]:
        with open(get_path(filename)) as f:
401
            requirements = f.read().strip().split("\n")
402
403
404
405
406
407
408
409
410
411
        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")
412
        cuda_major, cuda_minor = torch.version.cuda.split(".")
413
414
        modified_requirements = []
        for req in requirements:
415
416
            if ("vllm-flash-attn" in req
                    and not (cuda_major == "12" and cuda_minor == "1")):
417
418
419
420
                # vllm-flash-attn is built only for CUDA 12.1.
                # Skip for other versions.
                continue
            modified_requirements.append(req)
421
        requirements = modified_requirements
422
    elif _is_hip():
423
        requirements = _read_requirements("requirements-rocm.txt")
424
    elif _is_neuron():
425
        requirements = _read_requirements("requirements-neuron.txt")
426
427
    elif _is_openvino():
        requirements = _read_requirements("requirements-openvino.txt")
428
429
    elif _is_tpu():
        requirements = _read_requirements("requirements-tpu.txt")
430
    elif _is_cpu():
431
        requirements = _read_requirements("requirements-cpu.txt")
432
433
    elif _is_xpu():
        requirements = _read_requirements("requirements-xpu.txt")
434
435
    else:
        raise ValueError(
436
437
            "Unsupported platform, please use CUDA, ROCm, Neuron, "
            "OpenVINO, or CPU.")
438
439
440
    return requirements


bnellnm's avatar
bnellnm committed
441
442
ext_modules = []

443
if _is_cuda() or _is_hip():
bnellnm's avatar
bnellnm committed
444
445
    ext_modules.append(CMakeExtension(name="vllm._moe_C"))

446
if _build_custom_ops():
bnellnm's avatar
bnellnm committed
447
448
    ext_modules.append(CMakeExtension(name="vllm._C"))

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

452
453
454
package_data = {
    "vllm": ["py.typed", "model_executor/layers/fused_moe/configs/*.json"]
}
455
if envs.VLLM_USE_PRECOMPILED:
456
    ext_modules = []
Simon Mo's avatar
Simon Mo committed
457
458
    package_data["vllm"].append("*.so")

bnellnm's avatar
bnellnm committed
459
setup(
Woosuk Kwon's avatar
Woosuk Kwon committed
460
    name="vllm",
461
    version=get_vllm_version(),
Woosuk Kwon's avatar
Woosuk Kwon committed
462
    author="vLLM Team",
463
    license="Apache 2.0",
Woosuk Kwon's avatar
Woosuk Kwon committed
464
465
    description=("A high-throughput and memory-efficient inference and "
                 "serving engine for LLMs"),
466
467
    long_description=read_readme(),
    long_description_content_type="text/markdown",
468
    url="https://github.com/vllm-project/vllm",
469
    project_urls={
470
471
        "Homepage": "https://github.com/vllm-project/vllm",
        "Documentation": "https://vllm.readthedocs.io/en/latest/",
472
473
474
475
476
    },
    classifiers=[
        "Programming Language :: Python :: 3.8",
        "Programming Language :: Python :: 3.9",
        "Programming Language :: Python :: 3.10",
Woosuk Kwon's avatar
Woosuk Kwon committed
477
        "Programming Language :: Python :: 3.11",
478
479
480
        "License :: OSI Approved :: Apache Software License",
        "Topic :: Scientific/Engineering :: Artificial Intelligence",
    ],
bnellnm's avatar
bnellnm committed
481
    packages=find_packages(exclude=("benchmarks", "csrc", "docs", "examples",
482
                                    "tests*")),
483
484
    python_requires=">=3.8",
    install_requires=get_requirements(),
Woosuk Kwon's avatar
Woosuk Kwon committed
485
    ext_modules=ext_modules,
486
    extras_require={
487
        "tensorizer": ["tensorizer>=2.9.0"],
488
    },
489
    cmdclass={"build_ext": cmake_build_ext} if _build_custom_ops() else {},
Simon Mo's avatar
Simon Mo committed
490
    package_data=package_data,
Woosuk Kwon's avatar
Woosuk Kwon committed
491
)