search

vllm-project / vllm

A high-throughput and memory-efficient inference and serving engine for LLMs
https://docs.vllm.ai
Apache License 2.0
30.11k stars 4.55k forks source link

[Installation]: error: identifier "__builtin_dynamic_object_size" is undefined #10179

Open xiaoxiaosuaxuan opened 4 days ago

xiaoxiaosuaxuan commented 4 days ago

Your current environment

Collecting environment information...
PyTorch version: 2.4.0
Is debug build: False
CUDA used to build PyTorch: 12.1
ROCM used to build PyTorch: N/A

OS: Ubuntu 24.04 LTS (x86_64)
GCC version: (Ubuntu 11.4.0-9ubuntu1) 11.4.0
Clang version: Could not collect
CMake version: version 3.28.3
Libc version: glibc-2.39

Python version: 3.10.15 (main, Oct  3 2024, 07:27:34) [GCC 11.2.0] (64-bit runtime)
Python platform: Linux-6.8.0-41-generic-x86_64-with-glibc2.39
Is CUDA available: True
CUDA runtime version: 12.1.105
CUDA_MODULE_LOADING set to: LAZY
GPU models and configuration: 
GPU 0: NVIDIA RTX A6000
GPU 1: NVIDIA RTX A6000

Nvidia driver version: 550.100
cuDNN version: Could not collect
HIP runtime version: N/A
MIOpen runtime version: N/A
Is XNNPACK available: True

CPU:
Architecture:                         x86_64
CPU op-mode(s):                       32-bit, 64-bit
Address sizes:                        43 bits physical, 48 bits virtual
Byte Order:                           Little Endian
CPU(s):                               96
On-line CPU(s) list:                  0-95
Vendor ID:                            AuthenticAMD
Model name:                           AMD EPYC 7K62 48-Core Processor
CPU family:                           23
Model:                                49
Thread(s) per core:                   2
Core(s) per socket:                   48
Socket(s):                            1
Stepping:                             0
Frequency boost:                      enabled
CPU(s) scaling MHz:                   64%
CPU max MHz:                          2600.0000
CPU min MHz:                          1500.0000
BogoMIPS:                             5200.17
Flags:                                fpu vme de pse tsc msr pae mce cx8 apic sep mtrr pge mca cmov pat pse36 clflush mmx fxsr sse sse2 ht syscall nx mmxext fxsr_opt pdpe1gb rdtscp lm constant_tsc rep_good nopl nonstop_tsc cpuid extd_apicid aperfmperf rapl pni pclmulqdq monitor ssse3 fma cx16 sse4_1 sse4_2 movbe popcnt aes xsave avx f16c rdrand lahf_lm cmp_legacy svm extapic cr8_legacy abm sse4a misalignsse 3dnowprefetch osvw ibs skinit wdt tce topoext perfctr_core perfctr_nb bpext perfctr_llc mwaitx cpb cat_l3 cdp_l3 hw_pstate ssbd mba ibrs ibpb stibp vmmcall fsgsbase bmi1 avx2 smep bmi2 cqm rdt_a rdseed adx smap clflushopt clwb sha_ni xsaveopt xsavec xgetbv1 cqm_llc cqm_occup_llc cqm_mbm_total cqm_mbm_local clzero irperf xsaveerptr rdpru wbnoinvd amd_ppin arat npt lbrv svm_lock nrip_save tsc_scale vmcb_clean flushbyasid decodeassists pausefilter pfthreshold avic v_vmsave_vmload vgif v_spec_ctrl umip rdpid overflow_recov succor smca sev sev_es
Virtualization:                       AMD-V
L1d cache:                            1.5 MiB (48 instances)
L1i cache:                            1.5 MiB (48 instances)
L2 cache:                             24 MiB (48 instances)
L3 cache:                             192 MiB (12 instances)
NUMA node(s):                         1
NUMA node0 CPU(s):                    0-95
Vulnerability Gather data sampling:   Not affected
Vulnerability Itlb multihit:          Not affected
Vulnerability L1tf:                   Not affected
Vulnerability Mds:                    Not affected
Vulnerability Meltdown:               Not affected
Vulnerability Mmio stale data:        Not affected
Vulnerability Reg file data sampling: Not affected
Vulnerability Retbleed:               Mitigation; untrained return thunk; SMT enabled with STIBP protection
Vulnerability Spec rstack overflow:   Mitigation; Safe RET
Vulnerability Spec store bypass:      Mitigation; Speculative Store Bypass disabled via prctl
Vulnerability Spectre v1:             Mitigation; usercopy/swapgs barriers and __user pointer sanitization
Vulnerability Spectre v2:             Mitigation; Retpolines; IBPB conditional; STIBP always-on; RSB filling; PBRSB-eIBRS Not affected; BHI Not affected
Vulnerability Srbds:                  Not affected
Vulnerability Tsx async abort:        Not affected

Versions of relevant libraries:
[pip3] numpy==2.0.1
[pip3] torch==2.4.0
[pip3] torchaudio==2.4.0
[pip3] torchvision==0.19.0
[pip3] triton==3.0.0
[conda] blas                      1.0                         mkl  
[conda] cuda-cudart               12.1.105                      0    nvidia
[conda] cuda-cupti                12.1.105                      0    nvidia
[conda] cuda-libraries            12.1.0                        0    nvidia
[conda] cuda-nvrtc                12.1.105                      0    nvidia
[conda] cuda-nvtx                 12.1.105                      0    nvidia
[conda] cuda-opencl               12.6.77                       0    nvidia
[conda] cuda-runtime              12.1.0                        0    nvidia
[conda] cuda-version              12.6                          3    nvidia
[conda] ffmpeg                    4.3                  hf484d3e_0    pytorch
[conda] libcublas                 12.1.0.26                     0    nvidia
[conda] libcufft                  11.0.2.4                      0    nvidia
[conda] libcufile                 1.11.1.6                      0    nvidia
[conda] libcurand                 10.3.7.77                     0    nvidia
[conda] libcusolver               11.4.4.55                     0    nvidia
[conda] libcusparse               12.0.2.55                     0    nvidia
[conda] libjpeg-turbo             2.0.0                h9bf148f_0    pytorch
[conda] libnpp                    12.0.2.50                     0    nvidia
[conda] libnvjitlink              12.1.105                      0    nvidia
[conda] libnvjpeg                 12.1.1.14                     0    nvidia
[conda] mkl                       2023.1.0         h213fc3f_46344  
[conda] mkl-service               2.4.0           py310h5eee18b_1  
[conda] mkl_fft                   1.3.11          py310h5eee18b_0  
[conda] mkl_random                1.2.8           py310h1128e8f_0  
[conda] numpy                     2.0.1           py310h5f9d8c6_1  
[conda] numpy-base                2.0.1           py310hb5e798b_1  
[conda] pytorch                   2.4.0           py3.10_cuda12.1_cudnn9.1.0_0    pytorch
[conda] pytorch-cuda              12.1                 ha16c6d3_6    pytorch
[conda] pytorch-mutex             1.0                        cuda    pytorch
[conda] torchaudio                2.4.0               py310_cu121    pytorch
[conda] torchtriton               3.0.0                     py310    pytorch
[conda] torchvision               0.19.0              py310_cu121    pytorch
ROCM Version: Could not collect
Neuron SDK Version: N/A
vLLM Version: N/A
vLLM Build Flags:
CUDA Archs: Not Set; ROCm: Disabled; Neuron: Disabled
GPU Topology:
GPU0    GPU1    CPU Affinity    NUMA Affinity   GPU NUMA ID
GPU0     X      NV4     0-95    0               N/A
GPU1    NV4      X      0-95    0               N/A

Legend:

  X    = Self
  SYS  = Connection traversing PCIe as well as the SMP interconnect between NUMA nodes (e.g., QPI/UPI)
  NODE = Connection traversing PCIe as well as the interconnect between PCIe Host Bridges within a NUMA node
  PHB  = Connection traversing PCIe as well as a PCIe Host Bridge (typically the CPU)
  PXB  = Connection traversing multiple PCIe bridges (without traversing the PCIe Host Bridge)
  PIX  = Connection traversing at most a single PCIe bridge
  NV#  = Connection traversing a bonded set of # NVLinks```

How you are installing vllm

git clone https://github.com/vllm-project/vllm.git
cd vllm
git checkout v0.6.2
pip install -e . -v
xiaoxiaosuaxuan commented 4 days ago

Error:

 running build_py
  running build_ext
  -- The CXX compiler identification is GNU 11.4.0
  -- Detecting CXX compiler ABI info
  -- Detecting CXX compiler ABI info - done
  -- Check for working CXX compiler: /usr/bin/c++ - skipped
  -- Detecting CXX compile features
  -- Detecting CXX compile features - done
  -- Build type: RelWithDebInfo
  -- Target device: cuda
  -- Found Python: /home/hang/miniconda3/envs/vllm-v062/bin/python (found version "3.10.15") found components: Interpreter Development.Module Development.SABIModule
  -- Found python matching: /home/hang/miniconda3/envs/vllm-v062/bin/python.
  -- Found CUDA: /usr/local/cuda-12.1 (found version "12.1")
  -- The CUDA compiler identification is NVIDIA 12.0.140
  -- Detecting CUDA compiler ABI info
  -- Detecting CUDA compiler ABI info - done
  -- Check for working CUDA compiler: /usr/bin/nvcc - skipped
  -- Detecting CUDA compile features
  -- Detecting CUDA compile features - done
  -- Found CUDAToolkit: /usr/include (found version "12.0.140")
  -- Performing Test CMAKE_HAVE_LIBC_PTHREAD
  -- Performing Test CMAKE_HAVE_LIBC_PTHREAD - Success
  -- Found Threads: TRUE
  -- Caffe2: CUDA detected: 12.1
  -- Caffe2: CUDA nvcc is: /usr/local/cuda-12.1/bin/nvcc
  -- Caffe2: CUDA toolkit directory: /usr/local/cuda-12.1
  -- Caffe2: Header version is: 12.1
  -- /usr/local/cuda-12.1/lib64/libnvrtc.so shorthash is b51b459d
  -- USE_CUDNN is set to 0. Compiling without cuDNN support
  -- USE_CUSPARSELT is set to 0. Compiling without cuSPARSELt support
  -- Autodetected CUDA architecture(s):  8.6 8.6
  -- Added CUDA NVCC flags for: -gencode;arch=compute_86,code=sm_86
  CMake Warning at /tmp/pip-build-env-qxkzns9r/overlay/lib/python3.10/site-packages/torch/share/cmake/Torch/TorchConfig.cmake:22 (message):
    static library kineto_LIBRARY-NOTFOUND not found.
  Call Stack (most recent call first):
    /tmp/pip-build-env-qxkzns9r/overlay/lib/python3.10/site-packages/torch/share/cmake/Torch/TorchConfig.cmake:120 (append_torchlib_if_found)
    CMakeLists.txt:84 (find_package)

  -- Found Torch: /tmp/pip-build-env-qxkzns9r/overlay/lib/python3.10/site-packages/torch/lib/libtorch.so
  -- Enabling core extension.
  -- CUDA supported arches: 7.0;7.5;8.0;8.6;8.9;9.0
  -- CUDA target arches: 86-real
  -- CMake Version: 3.30.5
  -- CUTLASS 3.5.1
  -- CUDART: /usr/local/cuda-12.1/lib64/libcudart.so
  -- CUDA Driver: /usr/local/cuda-12.1/lib64/stubs/libcuda.so
  -- NVRTC: /usr/local/cuda-12.1/lib64/libnvrtc.so
  -- Default Install Location: install
  -- Found Python3: /home/hang/miniconda3/envs/vllm-v062/bin/python3.10 (found suitable version "3.10.15", minimum required is "3.5") found components: Interpreter
  -- Make cute::tuple be the new standard-layout tuple type
  -- CUDA Compilation Architectures: 70;72;75;80;86;87;89;90;90a
  -- Enable caching of reference results in conv unit tests
  -- Enable rigorous conv problem sizes in conv unit tests
  -- Using NVCC flags: --expt-relaxed-constexpr;-DCUTE_USE_PACKED_TUPLE=1;-DCUTLASS_TEST_LEVEL=0;-DCUTLASS_TEST_ENABLE_CACHED_RESULTS=1;-DCUTLASS_CONV_UNIT_TEST_RIGOROUS_SIZE_ENABLED=1;-DCUTLASS_DEBUG_TRACE_LEVEL=0;-Xcompiler=-Wconversion;-Xcompiler=-fno-strict-aliasing;-lineinfo
  -- Configuring cublas ...
  -- cuBLAS Disabled.
  -- Configuring cuBLAS ... done.
  -- Machete generation completed successfully.
  -- Machete generated sources: /home/hang/workdir/os-hw/vllm/csrc/quantization/machete/generated/machete_mm_bf16u4.cu;/home/hang/workdir/os-hw/vllm/csrc/quantization/machete/generated/machete_mm_bf16u4_impl_part0.cu;/home/hang/workdir/os-hw/vllm/csrc/quantization/machete/generated/machete_mm_bf16u4_impl_part1.cu;/home/hang/workdir/os-hw/vllm/csrc/quantization/machete/generated/machete_mm_bf16u4b8.cu;/home/hang/workdir/os-hw/vllm/csrc/quantization/machete/generated/machete_mm_bf16u4b8_impl_part0.cu;/home/hang/workdir/os-hw/vllm/csrc/quantization/machete/generated/machete_mm_bf16u4b8_impl_part1.cu;/home/hang/workdir/os-hw/vllm/csrc/quantization/machete/generated/machete_mm_bf16u8.cu;/home/hang/workdir/os-hw/vllm/csrc/quantization/machete/generated/machete_mm_bf16u8_impl_part0.cu;/home/hang/workdir/os-hw/vllm/csrc/quantization/machete/generated/machete_mm_bf16u8_impl_part1.cu;/home/hang/workdir/os-hw/vllm/csrc/quantization/machete/generated/machete_mm_bf16u8b128.cu;/home/hang/workdir/os-hw/vllm/csrc/quantization/machete/generated/machete_mm_bf16u8b128_impl_part0.cu;/home/hang/workdir/os-hw/vllm/csrc/quantization/machete/generated/machete_mm_bf16u8b128_impl_part1.cu;/home/hang/workdir/os-hw/vllm/csrc/quantization/machete/generated/machete_mm_f16u4.cu;/home/hang/workdir/os-hw/vllm/csrc/quantization/machete/generated/machete_mm_f16u4_impl_part0.cu;/home/hang/workdir/os-hw/vllm/csrc/quantization/machete/generated/machete_mm_f16u4_impl_part1.cu;/home/hang/workdir/os-hw/vllm/csrc/quantization/machete/generated/machete_mm_f16u4b8.cu;/home/hang/workdir/os-hw/vllm/csrc/quantization/machete/generated/machete_mm_f16u4b8_impl_part0.cu;/home/hang/workdir/os-hw/vllm/csrc/quantization/machete/generated/machete_mm_f16u4b8_impl_part1.cu;/home/hang/workdir/os-hw/vllm/csrc/quantization/machete/generated/machete_mm_f16u8.cu;/home/hang/workdir/os-hw/vllm/csrc/quantization/machete/generated/machete_mm_f16u8_impl_part0.cu;/home/hang/workdir/os-hw/vllm/csrc/quantization/machete/generated/machete_mm_f16u8_impl_part1.cu;/home/hang/workdir/os-hw/vllm/csrc/quantization/machete/generated/machete_mm_f16u8b128.cu;/home/hang/workdir/os-hw/vllm/csrc/quantization/machete/generated/machete_mm_f16u8b128_impl_part0.cu;/home/hang/workdir/os-hw/vllm/csrc/quantization/machete/generated/machete_mm_f16u8b128_impl_part1.cu;/home/hang/workdir/os-hw/vllm/csrc/quantization/machete/generated/machete_prepack_bf16u4.cu;/home/hang/workdir/os-hw/vllm/csrc/quantization/machete/generated/machete_prepack_bf16u4b8.cu;/home/hang/workdir/os-hw/vllm/csrc/quantization/machete/generated/machete_prepack_bf16u8.cu;/home/hang/workdir/os-hw/vllm/csrc/quantization/machete/generated/machete_prepack_bf16u8b128.cu;/home/hang/workdir/os-hw/vllm/csrc/quantization/machete/generated/machete_prepack_f16u4.cu;/home/hang/workdir/os-hw/vllm/csrc/quantization/machete/generated/machete_prepack_f16u4b8.cu;/home/hang/workdir/os-hw/vllm/csrc/quantization/machete/generated/machete_prepack_f16u8.cu;/home/hang/workdir/os-hw/vllm/csrc/quantization/machete/generated/machete_prepack_f16u8b128.cu
  -- Enabling C extension.
  -- Enabling moe extension.
  -- Build type: RelWithDebInfo
  -- Target device: cuda
  -- Building vllm-flash-attn inside vLLM. Skipping flag detection and relying on parent build.
  -- vllm-flash-attn is available at /tmp/tmp_b9gxugc.build-temp/_deps/vllm-flash-attn-src
  -- Configuring done (29.1s)
  CMake Warning at /tmp/pip-build-env-qxkzns9r/overlay/lib/python3.10/site-packages/cmake/data/share/cmake-3.30/Modules/FindPython/Support.cmake:4239 (add_library):
    Cannot generate a safe runtime search path for target _core_C because files
    in some directories may conflict with libraries in implicit directories:

      runtime library [libnvToolsExt.so.1] in /usr/lib/x86_64-linux-gnu may be hidden by files in:
        /usr/local/cuda-12.1/lib64

    Some of these libraries may not be found correctly.
  Call Stack (most recent call first):
    /tmp/pip-build-env-qxkzns9r/overlay/lib/python3.10/site-packages/cmake/data/share/cmake-3.30/Modules/FindPython.cmake:692 (__Python_add_library)
    cmake/utils.cmake:327 (Python_add_library)
    CMakeLists.txt:95 (define_gpu_extension_target)

  -- Generating done (0.1s)
  -- Build files have been written to: /tmp/tmp_b9gxugc.build-temp
  [1/137] Building CUDA object CMakeFiles/_C.dir/csrc/cuda_utils_kernels.cu.o
  FAILED: CMakeFiles/_C.dir/csrc/cuda_utils_kernels.cu.o
  /usr/bin/nvcc -forward-unknown-to-host-compiler -DCUTLASS_ENABLE_DIRECT_CUDA_DRIVER_CALL=1 -DPy_LIMITED_API=3 -DTORCH_EXTENSION_NAME=_C -DUSE_C10D_GLOO -DUSE_C10D_NCCL -DUSE_DISTRIBUTED -DUSE_RPC -DUSE_TENSORPIPE -D_C_EXPORTS -I/home/hang/workdir/os-hw/vllm/csrc -I/tmp/tmp_b9gxugc.build-temp/_deps/cutlass-src/include -isystem /home/hang/miniconda3/envs/vllm-v062/include/python3.10 -isystem /tmp/pip-build-env-qxkzns9r/overlay/lib/python3.10/site-packages/torch/include -isystem /tmp/pip-build-env-qxkzns9r/overlay/lib/python3.10/site-packages/torch/include/torch/csrc/api/include -DONNX_NAMESPACE=onnx_c2 -Xcudafe --diag_suppress=cc_clobber_ignored,--diag_suppress=field_without_dll_interface,--diag_suppress=base_class_has_different_dll_interface,--diag_suppress=dll_interface_conflict_none_assumed,--diag_suppress=dll_interface_conflict_dllexport_assumed,--diag_suppress=bad_friend_decl --expt-relaxed-constexpr --expt-extended-lambda -O2 -g -DNDEBUG -std=c++17 "--generate-code=arch=compute_86,code=[sm_86]" -Xcompiler=-fPIC --expt-relaxed-constexpr -DENABLE_FP8 --threads=1 -D_GLIBCXX_USE_CXX11_ABI=0 -MD -MT CMakeFiles/_C.dir/csrc/cuda_utils_kernels.cu.o -MF CMakeFiles/_C.dir/csrc/cuda_utils_kernels.cu.o.d -x cu -c /home/hang/workdir/os-hw/vllm/csrc/cuda_utils_kernels.cu -o CMakeFiles/_C.dir/csrc/cuda_utils_kernels.cu.o
  /usr/include/x86_64-linux-gnu/bits/stdlib.h(39): error: identifier "__builtin_dynamic_object_size" is undefined
      size_t sz = __builtin_dynamic_object_size (__resolved, 1);
                  ^

  /usr/include/x86_64-linux-gnu/bits/stdlib.h(67): error: identifier "__builtin_dynamic_object_size" is undefined
      return (((__builtin_constant_p (__builtin_dynamic_object_size (__buf, 1)) && (__builtin_dynamic_object_size (__buf, 1)) == (long unsigned int) -1) || (((__typeof (__buflen)) 0 < (__typeof (__buflen)) -1 || (__builtin_constant_p (__buflen) && (__buflen) > 0)) && __builtin_constant_p ((((long unsigned int) (__buflen)) <= ((__builtin_dynamic_object_size (__buf, 1))) / ((sizeof (char))))) && (((long unsigned int) (__buflen)) <= ((__builtin_dynamic_object_size (__buf, 1))) / ((sizeof (char)))))) ? __ptsname_r_alias (__fd, __buf, __buflen) : ((((__typeof (__buflen)) 0 < (__typeof (__buflen)) -1 || (__builtin_constant_p (__buflen) && (__buflen) > 0)) && __builtin_constant_p ((((long unsigned int) (__buflen)) <= (__builtin_dynamic_object_size (__buf, 1)) / (sizeof (char)))) && !(((long unsigned int) (__buflen)) <= (__builtin_dynamic_object_size (__buf, 1)) / (sizeof (char)))) ? __ptsname_r_chk_warn (__fd, __buf, __buflen, __builtin_dynamic_object_size (__buf, 1)) : __ptsname_r_chk (__fd, __buf, __buflen, __builtin_dynamic_object_size (__buf, 1))))
                                      ^

  /usr/include/x86_64-linux-gnu/bits/stdlib.h(88): error: identifier "__builtin_dynamic_object_size" is undefined
      if (__builtin_dynamic_object_size (__s, 1) != (size_t) -1
          ^

  /usr/include/x86_64-linux-gnu/bits/stdlib.h(123): error: identifier "__builtin_dynamic_object_size" is undefined
        return (((__builtin_constant_p (__builtin_dynamic_object_size (__dst, 1)) && (__builtin_dynamic_object_size (__dst, 1)) == (long unsigned int) -1) || (((__typeof (__len)) 0 < (__typeof (__len)) -1 || (__builtin_constant_p (__len) && (__len) > 0)) && __builtin_constant_p ((((long unsigned int) (__len)) <= ((__builtin_dynamic_object_size (__dst, 1))) / ((sizeof (wchar_t))))) && (((long unsigned int) (__len)) <= ((__builtin_dynamic_object_size (__dst, 1))) / ((sizeof (wchar_t)))))) ? __mbstowcs_alias (__dst, __src, __len) : ((((__typeof (__len)) 0 < (__typeof (__len)) -1 || (__builtin_constant_p (__len) && (__len) > 0)) && __builtin_constant_p ((((long unsigned int) (__len)) <= (__builtin_dynamic_object_size (__dst, 1)) / (sizeof (wchar_t)))) && !(((long unsigned int) (__len)) <= (__builtin_dynamic_object_size (__dst, 1)) / (sizeof (wchar_t)))) ? __mbstowcs_chk_warn (__dst, __src, __len, (__builtin_dynamic_object_size (__dst, 1)) / (sizeof (wchar_t))) : __mbstowcs_chk (__dst, __src, __len, (__builtin_dynamic_object_size (__dst, 1)) / (sizeof (wchar_t)))))
                                        ^

  /usr/include/x86_64-linux-gnu/bits/stdlib.h(146): error: identifier "__builtin_dynamic_object_size" is undefined
      return (((__builtin_constant_p (__builtin_dynamic_object_size (__dst, 1)) && (__builtin_dynamic_object_size (__dst, 1)) == (long unsigned int) -1) || (((__typeof (__len)) 0 < (__typeof (__len)) -1 || (__builtin_constant_p (__len) && (__len) > 0)) && __builtin_constant_p ((((long unsigned int) (__len)) <= ((__builtin_dynamic_object_size (__dst, 1))) / ((sizeof (char))))) && (((long unsigned int) (__len)) <= ((__builtin_dynamic_object_size (__dst, 1))) / ((sizeof (char)))))) ? __wcstombs_alias (__dst, __src, __len) : ((((__typeof (__len)) 0 < (__typeof (__len)) -1 || (__builtin_constant_p (__len) && (__len) > 0)) && __builtin_constant_p ((((long unsigned int) (__len)) <= (__builtin_dynamic_object_size (__dst, 1)) / (sizeof (char)))) && !(((long unsigned int) (__len)) <= (__builtin_dynamic_object_size (__dst, 1)) / (sizeof (char)))) ? __wcstombs_chk_warn (__dst, __src, __len, __builtin_dynamic_object_size (__dst, 1)) : __wcstombs_chk (__dst, __src, __len, __builtin_dynamic_object_size (__dst, 1))))
                                      ^

  /usr/include/x86_64-linux-gnu/bits/strings_fortified.h(26): error: identifier "__builtin_dynamic_object_size" is undefined
          __builtin_dynamic_object_size (__dest, 0));
          ^

  /usr/include/x86_64-linux-gnu/bits/strings_fortified.h(33): error: identifier "__builtin_dynamic_object_size" is undefined
         __builtin_dynamic_object_size (__dest, 0));
         ^

  /usr/include/x86_64-linux-gnu/bits/string_fortified.h(30): error: identifier "__builtin_dynamic_object_size" is undefined
         __builtin_dynamic_object_size (__dest, 0));
         ^

  /usr/include/x86_64-linux-gnu/bits/string_fortified.h(37): error: identifier "__builtin_dynamic_object_size" is undefined
          __builtin_dynamic_object_size (__dest, 0));
          ^

  /usr/include/x86_64-linux-gnu/bits/string_fortified.h(46): error: identifier "__builtin_dynamic_object_size" is undefined
          __builtin_dynamic_object_size (__dest, 0));
          ^

  /usr/include/x86_64-linux-gnu/bits/string_fortified.h(60): error: identifier "__builtin_dynamic_object_size" is undefined
         __builtin_dynamic_object_size (__dest, 0));
         ^

  /usr/include/x86_64-linux-gnu/bits/string_fortified.h(72): error: identifier "__builtin_dynamic_object_size" is undefined
      __explicit_bzero_chk (__dest, __len, __builtin_dynamic_object_size (__dest, 0));
                                           ^

  /usr/include/x86_64-linux-gnu/bits/string_fortified.h(79): error: identifier "__builtin_dynamic_object_size" is undefined
      return __builtin___strcpy_chk (__dest, __src, __builtin_dynamic_object_size (__dest, 1));
                                                    ^

  /usr/include/x86_64-linux-gnu/bits/string_fortified.h(86): error: identifier "__builtin_dynamic_object_size" is undefined
      return __builtin___stpcpy_chk (__dest, __src, __builtin_dynamic_object_size (__dest, 1));
                                                    ^

  /usr/include/x86_64-linux-gnu/bits/string_fortified.h(96): error: identifier "__builtin_dynamic_object_size" is undefined
          __builtin_dynamic_object_size (__dest, 1));
          ^

  /usr/include/x86_64-linux-gnu/bits/string_fortified.h(105): error: identifier "__builtin_dynamic_object_size" is undefined
          __builtin_dynamic_object_size (__dest, 1));
          ^

  /usr/include/x86_64-linux-gnu/bits/string_fortified.h(130): error: identifier "__builtin_dynamic_object_size" is undefined
      return __builtin___strcat_chk (__dest, __src, __builtin_dynamic_object_size (__dest, 1));
                                                    ^

  /usr/include/x86_64-linux-gnu/bits/string_fortified.h(139): error: identifier "__builtin_dynamic_object_size" is undefined
          __builtin_dynamic_object_size (__dest, 1));
          ^

  /usr/include/x86_64-linux-gnu/bits/string_fortified.h(153): error: identifier "__builtin_dynamic_object_size" is undefined
      if (__builtin_dynamic_object_size (__dest, 1) != (size_t) -1
          ^

  /usr/include/x86_64-linux-gnu/bits/string_fortified.h(170): error: identifier "__builtin_dynamic_object_size" is undefined
      if (__builtin_dynamic_object_size (__dest, 1) != (size_t) -1
          ^

  20 errors detected in the compilation of "/home/hang/workdir/os-hw/vllm/csrc/cuda_utils_kernels.cu".

... 
... 
... 

      /usr/include/x86_64-linux-gnu/bits/stdio2.h(198): error: identifier "__builtin_dynamic_object_size" is undefined
          size_t sz = __builtin_dynamic_object_size (__s, 1);
                      ^

      /usr/include/x86_64-linux-gnu/bits/stdio2.h(210): error: identifier "__builtin_dynamic_object_size" is undefined
          size_t sz = __builtin_dynamic_object_size (__ptr, 0);
                      ^

      /usr/include/x86_64-linux-gnu/bits/stdio2.h(223): error: identifier "__builtin_dynamic_object_size" is undefined
          size_t sz = __builtin_dynamic_object_size (__s, 1);
                      ^

      /usr/include/x86_64-linux-gnu/bits/stdio2.h(238): error: identifier "__builtin_dynamic_object_size" is undefined
          size_t sz = __builtin_dynamic_object_size (__ptr, 0);
                      ^

      49 errors detected in the compilation of "/home/hang/workdir/os-hw/vllm/csrc/moe/marlin_kernels/marlin_moe_kernel_ku4b8.cu".
      [95/137] Building CXX object CMakeFiles/_moe_C.dir/csrc/moe/torch_bindings.cpp.o
      [96/137] Building CXX object CMakeFiles/_C.dir/csrc/torch_bindings.cpp.o
      ninja: build stopped: subcommand failed.
      Traceback (most recent call last):
        File "/tmp/pip-build-env-8i21mc29/overlay/lib/python3.10/site-packages/setuptools/command/editable_wheel.py", line 137, in run
          self._create_wheel_file(bdist_wheel)
        File "/tmp/pip-build-env-8i21mc29/overlay/lib/python3.10/site-packages/setuptools/command/editable_wheel.py", line 338, in _create_wheel_file
          files, mapping = self._run_build_commands(dist_name, unpacked, lib, tmp)
        File "/tmp/pip-build-env-8i21mc29/overlay/lib/python3.10/site-packages/setuptools/command/editable_wheel.py", line 261, in _run_build_commands
          self._run_build_subcommands()
        File "/tmp/pip-build-env-8i21mc29/overlay/lib/python3.10/site-packages/setuptools/command/editable_wheel.py", line 288, in _run_build_subcommands
          self.run_command(name)
        File "/tmp/pip-build-env-8i21mc29/overlay/lib/python3.10/site-packages/setuptools/_distutils/cmd.py", line 316, in run_command
          self.distribution.run_command(command)
        File "/tmp/pip-build-env-8i21mc29/overlay/lib/python3.10/site-packages/setuptools/dist.py", line 999, in run_command
          super().run_command(command)
        File "/tmp/pip-build-env-8i21mc29/overlay/lib/python3.10/site-packages/setuptools/_distutils/dist.py", line 973, in run_command
          cmd_obj.run()
        File "<string>", line 235, in run
        File "/tmp/pip-build-env-8i21mc29/overlay/lib/python3.10/site-packages/setuptools/command/build_ext.py", line 98, in run
          _build_ext.run(self)
        File "/tmp/pip-build-env-8i21mc29/overlay/lib/python3.10/site-packages/setuptools/_distutils/command/build_ext.py", line 359, in run
          self.build_extensions()
        File "<string>", line 209, in build_extensions
        File "/home/hang/miniconda3/envs/vllm-v062/lib/python3.10/subprocess.py", line 369, in check_call
          raise CalledProcessError(retcode, cmd)
      subprocess.CalledProcessError: Command '['cmake', '--build', '.', '-j=96', '--target=_core_C', '--target=_moe_C', '--target=vllm_flash_attn_c', '--target=_C']' returned non-zero exit status 1.
      /tmp/pip-build-env-8i21mc29/overlay/lib/python3.10/site-packages/setuptools/_distutils/dist.py:973: _DebuggingTips: Problem in editable installation.
      !!

              ********************************************************************************
              An error happened while installing `vllm` in editable mode.

              The following steps are recommended to help debug this problem:

              - Try to install the project normally, without using the editable mode.
                Does the error still persist?
                (If it does, try fixing the problem before attempting the editable mode).
              - If you are using binary extensions, make sure you have all OS-level
                dependencies installed (e.g. compilers, toolchains, binary libraries, ...).
              - Try the latest version of setuptools (maybe the error was already fixed).
              - If you (or your project dependencies) are using any setuptools extension
                or customization, make sure they support the editable mode.

              After following the steps above, if the problem still persists and
              you think this is related to how setuptools handles editable installations,
              please submit a reproducible example
              (see https://stackoverflow.com/help/minimal-reproducible-example) to:

                  https://github.com/pypa/setuptools/issues

              See https://setuptools.pypa.io/en/latest/userguide/development_mode.html for details.
              ********************************************************************************

      !!
        cmd_obj.run()
      Traceback (most recent call last):
        File "/home/hang/miniconda3/envs/vllm-v062/lib/python3.10/site-packages/pip/_vendor/pyproject_hooks/_in_process/_in_process.py", line 353, in <module>
          main()
        File "/home/hang/miniconda3/envs/vllm-v062/lib/python3.10/site-packages/pip/_vendor/pyproject_hooks/_in_process/_in_process.py", line 335, in main
          json_out['return_val'] = hook(**hook_input['kwargs'])
        File "/home/hang/miniconda3/envs/vllm-v062/lib/python3.10/site-packages/pip/_vendor/pyproject_hooks/_in_process/_in_process.py", line 273, in build_editable
          return hook(wheel_directory, config_settings, metadata_directory)
        File "/tmp/pip-build-env-8i21mc29/overlay/lib/python3.10/site-packages/setuptools/build_meta.py", line 475, in build_editable
          return self._build_with_temp_dir(
        File "/tmp/pip-build-env-8i21mc29/overlay/lib/python3.10/site-packages/setuptools/build_meta.py", line 406, in _build_with_temp_dir
          self.run_setup()
        File "/tmp/pip-build-env-8i21mc29/overlay/lib/python3.10/site-packages/setuptools/build_meta.py", line 319, in run_setup
          exec(code, locals())
        File "<string>", line 483, in <module>
        File "/tmp/pip-build-env-8i21mc29/overlay/lib/python3.10/site-packages/setuptools/__init__.py", line 117, in setup
          return distutils.core.setup(**attrs)
        File "/tmp/pip-build-env-8i21mc29/overlay/lib/python3.10/site-packages/setuptools/_distutils/core.py", line 183, in setup
          return run_commands(dist)
        File "/tmp/pip-build-env-8i21mc29/overlay/lib/python3.10/site-packages/setuptools/_distutils/core.py", line 199, in run_commands
          dist.run_commands()
        File "/tmp/pip-build-env-8i21mc29/overlay/lib/python3.10/site-packages/setuptools/_distutils/dist.py", line 954, in run_commands
          self.run_command(cmd)
        File "/tmp/pip-build-env-8i21mc29/overlay/lib/python3.10/site-packages/setuptools/dist.py", line 999, in run_command
          super().run_command(command)
        File "/tmp/pip-build-env-8i21mc29/overlay/lib/python3.10/site-packages/setuptools/_distutils/dist.py", line 973, in run_command
          cmd_obj.run()
        File "/tmp/pip-build-env-8i21mc29/overlay/lib/python3.10/site-packages/setuptools/command/editable_wheel.py", line 137, in run
          self._create_wheel_file(bdist_wheel)
        File "/tmp/pip-build-env-8i21mc29/overlay/lib/python3.10/site-packages/setuptools/command/editable_wheel.py", line 338, in _create_wheel_file
          files, mapping = self._run_build_commands(dist_name, unpacked, lib, tmp)
        File "/tmp/pip-build-env-8i21mc29/overlay/lib/python3.10/site-packages/setuptools/command/editable_wheel.py", line 261, in _run_build_commands
          self._run_build_subcommands()
        File "/tmp/pip-build-env-8i21mc29/overlay/lib/python3.10/site-packages/setuptools/command/editable_wheel.py", line 288, in _run_build_subcommands
          self.run_command(name)
        File "/tmp/pip-build-env-8i21mc29/overlay/lib/python3.10/site-packages/setuptools/_distutils/cmd.py", line 316, in run_command
          self.distribution.run_command(command)
        File "/tmp/pip-build-env-8i21mc29/overlay/lib/python3.10/site-packages/setuptools/dist.py", line 999, in run_command
          super().run_command(command)
        File "/tmp/pip-build-env-8i21mc29/overlay/lib/python3.10/site-packages/setuptools/_distutils/dist.py", line 973, in run_command
          cmd_obj.run()
        File "<string>", line 235, in run
        File "/tmp/pip-build-env-8i21mc29/overlay/lib/python3.10/site-packages/setuptools/command/build_ext.py", line 98, in run
          _build_ext.run(self)
        File "/tmp/pip-build-env-8i21mc29/overlay/lib/python3.10/site-packages/setuptools/_distutils/command/build_ext.py", line 359, in run
          self.build_extensions()
        File "<string>", line 209, in build_extensions
        File "/home/hang/miniconda3/envs/vllm-v062/lib/python3.10/subprocess.py", line 369, in check_call
          raise CalledProcessError(retcode, cmd)
      subprocess.CalledProcessError: Command '['cmake', '--build', '.', '-j=96', '--target=_core_C', '--target=_moe_C', '--target=vllm_flash_attn_c', '--target=_C']' returned non-zero exit status 1.
      [end of output]

  note: This error originates from a subprocess, and is likely not a problem with pip.
  ERROR: Failed building editable for vllm
Failed to build vllm
ERROR: ERROR: Failed to build installable wheels for some pyproject.toml based projects (vllm)