CMakeLists.txt 34 KB

123456789101112131415161718192021222324252627282930313233343536373839404142434445464748495051525354555657585960616263646566676869707172737475767778798081828384858687888990919293949596979899100101102103104105106107108109110111112113114115116117118119120121122123124125126127128129130131132133134135136137138139140141142143144145146147148149150151152153154155156157158159160161162163164165166167168169170171172173174175176177178179180181182183184185186187188189190191192193194195196197198199200201202203204205206207208209210211212213214215216217218219220221222223224225226227228229230231232233234235236237238239240241242243244245246247248249250251252253254255256257258259260261262263264265266267268269270271272273274275276277278279280281282283284285286287288289290291292293294295296297298299300301302303304305306307308309310311312313314315316317318319320321322323324325326327328329330331332333334335336337338339340341342343344345346347348349350351352353354355356357358359360361362363364365366367368369370371372373374375376377378379380381382383384385386387388389390391392393394395396397398399400401402403404405406407408409410411412413414415416417418419420421422423424425426427428429430431432433434435436437438439440441442443444445446447448449450451452453454455456457458459460461462463464465466467468469470471472473474475476477478479480481482483484485486487488489490491492493494495496497498499500501502503504505506507508509510511512513514515516517518519520521522523524525526527528529530531532533534535536537538539540541542543544545546547548549550551552553554555556557558559560561562563564565566567568569570571572573574575576577578579580581582583584585586587588589590591592593594595596597598599600601602603604605606607608609610611612613614615616617618619620621622623624625626627628629630631632633634635636637638639640641642643644645646647648649650651652653654655656657658659660661662663664665666667668669670671672673674675676677678679680681682683684685686687688689690691692693694695696697698699700701702703704705706707708709710711712713714715716717718719720721722723724725726727728729730731732733734735736737738739740741742743744745746747748749750751752753754755756757758759760761762763764765766767768769770771772773774775776777778779780781782783784785786787788789790791792793794795796797798799800801802803804805806807808809810811812813814815816817818819820821822823824825826827828829830831832833834835836837838839840841842843844845846847848849850851852853854855856857858859860861862863864865866867868869870871872873874875876877878879880881882883884885886887888889890891892893894895896897898899900901902903904905906907908909910911912913914915916917918919920921922923924925926927928929930
  1. cmake_minimum_required(VERSION 3.14) # for add_link_options and implicit target directories.
  2. project("llama.cpp" C CXX)
  3. set(CMAKE_EXPORT_COMPILE_COMMANDS ON)
  4. if (NOT XCODE AND NOT MSVC AND NOT CMAKE_BUILD_TYPE)
  5. set(CMAKE_BUILD_TYPE Release CACHE STRING "Build type" FORCE)
  6. set_property(CACHE CMAKE_BUILD_TYPE PROPERTY STRINGS "Debug" "Release" "MinSizeRel" "RelWithDebInfo")
  7. endif()
  8. set(CMAKE_RUNTIME_OUTPUT_DIRECTORY ${CMAKE_BINARY_DIR}/bin)
  9. if (CMAKE_SOURCE_DIR STREQUAL CMAKE_CURRENT_SOURCE_DIR)
  10. set(LLAMA_STANDALONE ON)
  11. # configure project version
  12. # TODO
  13. else()
  14. set(LLAMA_STANDALONE OFF)
  15. endif()
  16. if (EMSCRIPTEN)
  17. set(BUILD_SHARED_LIBS_DEFAULT OFF)
  18. option(LLAMA_WASM_SINGLE_FILE "llama: embed WASM inside the generated llama.js" ON)
  19. else()
  20. if (MINGW)
  21. set(BUILD_SHARED_LIBS_DEFAULT OFF)
  22. else()
  23. set(BUILD_SHARED_LIBS_DEFAULT ON)
  24. endif()
  25. endif()
  26. #
  27. # Option list
  28. #
  29. if (APPLE)
  30. set(LLAMA_METAL_DEFAULT ON)
  31. else()
  32. set(LLAMA_METAL_DEFAULT OFF)
  33. endif()
  34. # general
  35. option(BUILD_SHARED_LIBS "build shared libraries" OFF)
  36. option(LLAMA_STATIC "llama: static link libraries" OFF)
  37. option(LLAMA_NATIVE "llama: enable -march=native flag" ON)
  38. option(LLAMA_LTO "llama: enable link time optimization" OFF)
  39. option(LLAMA_CCACHE "llama: use ccache if available" ON)
  40. # debug
  41. option(LLAMA_ALL_WARNINGS "llama: enable all compiler warnings" ON)
  42. option(LLAMA_ALL_WARNINGS_3RD_PARTY "llama: enable all compiler warnings in 3rd party libs" OFF)
  43. option(LLAMA_GPROF "llama: enable gprof" OFF)
  44. # sanitizers
  45. option(LLAMA_SANITIZE_THREAD "llama: enable thread sanitizer" OFF)
  46. option(LLAMA_SANITIZE_ADDRESS "llama: enable address sanitizer" OFF)
  47. option(LLAMA_SANITIZE_UNDEFINED "llama: enable undefined sanitizer" OFF)
  48. # instruction set specific
  49. if (LLAMA_NATIVE)
  50. set(INS_ENB OFF)
  51. else()
  52. set(INS_ENB ON)
  53. endif()
  54. option(LLAMA_AVX "llama: enable AVX" ${INS_ENB})
  55. option(LLAMA_AVX2 "llama: enable AVX2" ${INS_ENB})
  56. option(LLAMA_AVX512 "llama: enable AVX512" OFF)
  57. option(LLAMA_AVX512_VBMI "llama: enable AVX512-VBMI" OFF)
  58. option(LLAMA_AVX512_VNNI "llama: enable AVX512-VNNI" OFF)
  59. option(LLAMA_FMA "llama: enable FMA" ${INS_ENB})
  60. # in MSVC F16C is implied with AVX2/AVX512
  61. if (NOT MSVC)
  62. option(LLAMA_F16C "llama: enable F16C" ${INS_ENB})
  63. endif()
  64. if (WIN32)
  65. option(LLAMA_WIN_VER "llama: Windows Version" 0x602)
  66. endif()
  67. # 3rd party libs
  68. option(LLAMA_ACCELERATE "llama: enable Accelerate framework" ON)
  69. option(LLAMA_BLAS "llama: use BLAS" OFF)
  70. set(LLAMA_BLAS_VENDOR "Generic" CACHE STRING "llama: BLAS library vendor")
  71. option(LLAMA_CUBLAS "llama: use CUDA" OFF)
  72. #option(LLAMA_CUDA_CUBLAS "llama: use cuBLAS for prompt processing" OFF)
  73. option(LLAMA_CUDA_FORCE_DMMV "llama: use dmmv instead of mmvq CUDA kernels" OFF)
  74. option(LLAMA_CUDA_FORCE_MMQ "llama: use mmq kernels instead of cuBLAS" OFF)
  75. set(LLAMA_CUDA_DMMV_X "32" CACHE STRING "llama: x stride for dmmv CUDA kernels")
  76. set(LLAMA_CUDA_MMV_Y "1" CACHE STRING "llama: y block size for mmv CUDA kernels")
  77. option(LLAMA_CUDA_F16 "llama: use 16 bit floats for some calculations" OFF)
  78. set(LLAMA_CUDA_KQUANTS_ITER "2" CACHE STRING "llama: iters./thread per block for Q2_K/Q6_K")
  79. set(LLAMA_CUDA_PEER_MAX_BATCH_SIZE "128" CACHE STRING
  80. "llama: max. batch size for using peer access")
  81. option(LLAMA_HIPBLAS "llama: use hipBLAS" OFF)
  82. option(LLAMA_HIP_UMA "llama: use HIP unified memory architecture" OFF)
  83. option(LLAMA_CLBLAST "llama: use CLBlast" OFF)
  84. option(LLAMA_METAL "llama: use Metal" ${LLAMA_METAL_DEFAULT})
  85. option(LLAMA_METAL_NDEBUG "llama: disable Metal debugging" OFF)
  86. option(LLAMA_METAL_SHADER_DEBUG "llama: compile Metal with -fno-fast-math" OFF)
  87. option(LLAMA_MPI "llama: use MPI" OFF)
  88. option(LLAMA_QKK_64 "llama: use super-block size of 64 for k-quants" OFF)
  89. option(LLAMA_BUILD_TESTS "llama: build tests" ${LLAMA_STANDALONE})
  90. option(LLAMA_BUILD_EXAMPLES "llama: build examples" ${LLAMA_STANDALONE})
  91. option(LLAMA_BUILD_SERVER "llama: build server example" ON)
  92. # add perf arguments
  93. option(LLAMA_PERF "llama: enable perf" OFF)
  94. if (LLAMA_PERF)
  95. add_definitions(-DGGML_PERF)
  96. endif()
  97. # Required for relocatable CMake package
  98. include(${CMAKE_CURRENT_SOURCE_DIR}/scripts/build-info.cmake)
  99. #
  100. # Compile flags
  101. #
  102. set(CMAKE_CXX_STANDARD 11)
  103. set(CMAKE_CXX_STANDARD_REQUIRED true)
  104. set(CMAKE_C_STANDARD 11)
  105. set(CMAKE_C_STANDARD_REQUIRED true)
  106. set(THREADS_PREFER_PTHREAD_FLAG ON)
  107. find_package(Threads REQUIRED)
  108. include(CheckCXXCompilerFlag)
  109. # enable libstdc++ assertions for debug builds
  110. if (CMAKE_SYSTEM_NAME MATCHES "Linux")
  111. add_compile_definitions($<$<CONFIG:Debug>:_GLIBCXX_ASSERTIONS>)
  112. endif()
  113. if (NOT MSVC)
  114. if (LLAMA_SANITIZE_THREAD)
  115. add_compile_options(-fsanitize=thread)
  116. link_libraries(-fsanitize=thread)
  117. endif()
  118. if (LLAMA_SANITIZE_ADDRESS)
  119. add_compile_options(-fsanitize=address -fno-omit-frame-pointer)
  120. link_libraries(-fsanitize=address)
  121. endif()
  122. if (LLAMA_SANITIZE_UNDEFINED)
  123. add_compile_options(-fsanitize=undefined)
  124. link_libraries(-fsanitize=undefined)
  125. endif()
  126. endif()
  127. if (APPLE AND LLAMA_ACCELERATE)
  128. find_library(ACCELERATE_FRAMEWORK Accelerate)
  129. if (ACCELERATE_FRAMEWORK)
  130. message(STATUS "Accelerate framework found")
  131. add_compile_definitions(GGML_USE_ACCELERATE)
  132. add_compile_definitions(ACCELERATE_NEW_LAPACK)
  133. add_compile_definitions(ACCELERATE_LAPACK_ILP64)
  134. set(LLAMA_EXTRA_LIBS ${LLAMA_EXTRA_LIBS} ${ACCELERATE_FRAMEWORK})
  135. else()
  136. message(WARNING "Accelerate framework not found")
  137. endif()
  138. endif()
  139. if (LLAMA_METAL)
  140. find_library(FOUNDATION_LIBRARY Foundation REQUIRED)
  141. find_library(METAL_FRAMEWORK Metal REQUIRED)
  142. find_library(METALKIT_FRAMEWORK MetalKit REQUIRED)
  143. message(STATUS "Metal framework found")
  144. set(GGML_HEADERS_METAL ggml-metal.h)
  145. set(GGML_SOURCES_METAL ggml-metal.m)
  146. add_compile_definitions(GGML_USE_METAL)
  147. if (LLAMA_METAL_NDEBUG)
  148. add_compile_definitions(GGML_METAL_NDEBUG)
  149. endif()
  150. # get full path to the file
  151. #add_compile_definitions(GGML_METAL_DIR_KERNELS="${CMAKE_CURRENT_SOURCE_DIR}/")
  152. # copy ggml-metal.metal to bin directory
  153. configure_file(ggml-metal.metal ${CMAKE_RUNTIME_OUTPUT_DIRECTORY}/ggml-metal.metal COPYONLY)
  154. if (LLAMA_METAL_SHADER_DEBUG)
  155. # custom command to do the following:
  156. # xcrun -sdk macosx metal -fno-fast-math -c ggml-metal.metal -o ggml-metal.air
  157. # xcrun -sdk macosx metallib ggml-metal.air -o default.metallib
  158. #
  159. # note: this is the only way I found to disable fast-math in Metal. it's ugly, but at least it works
  160. # disabling fast math is needed in order to pass tests/test-backend-ops
  161. # note: adding -fno-inline fixes the tests when using MTL_SHADER_VALIDATION=1
  162. # note: unfortunately, we have to call it default.metallib instead of ggml.metallib
  163. # ref: https://github.com/ggerganov/whisper.cpp/issues/1720
  164. set(XC_FLAGS -fno-fast-math -fno-inline -g)
  165. if (LLAMA_QKK_64)
  166. set(XC_FLAGS ${XC_FLAGS} -DQK_K=64)
  167. endif()
  168. add_custom_command(
  169. OUTPUT ${CMAKE_RUNTIME_OUTPUT_DIRECTORY}/default.metallib
  170. COMMAND xcrun -sdk macosx metal ${XC_FLAGS} -c ${CMAKE_RUNTIME_OUTPUT_DIRECTORY}/ggml-metal.metal -o ${CMAKE_RUNTIME_OUTPUT_DIRECTORY}/ggml-metal.air
  171. COMMAND xcrun -sdk macosx metallib ${CMAKE_RUNTIME_OUTPUT_DIRECTORY}/ggml-metal.air -o ${CMAKE_RUNTIME_OUTPUT_DIRECTORY}/default.metallib
  172. DEPENDS ggml-metal.metal
  173. COMMENT "Compiling Metal kernels"
  174. )
  175. add_custom_target(
  176. ggml-metal ALL
  177. DEPENDS ${CMAKE_RUNTIME_OUTPUT_DIRECTORY}/default.metallib
  178. )
  179. endif()
  180. set(LLAMA_EXTRA_LIBS ${LLAMA_EXTRA_LIBS}
  181. ${FOUNDATION_LIBRARY}
  182. ${METAL_FRAMEWORK}
  183. ${METALKIT_FRAMEWORK}
  184. )
  185. endif()
  186. if (LLAMA_BLAS)
  187. if (LLAMA_STATIC)
  188. set(BLA_STATIC ON)
  189. endif()
  190. if ($(CMAKE_VERSION) VERSION_GREATER_EQUAL 3.22)
  191. set(BLA_SIZEOF_INTEGER 8)
  192. endif()
  193. set(BLA_VENDOR ${LLAMA_BLAS_VENDOR})
  194. find_package(BLAS)
  195. if (BLAS_FOUND)
  196. message(STATUS "BLAS found, Libraries: ${BLAS_LIBRARIES}")
  197. if ("${BLAS_INCLUDE_DIRS}" STREQUAL "")
  198. # BLAS_INCLUDE_DIRS is missing in FindBLAS.cmake.
  199. # see https://gitlab.kitware.com/cmake/cmake/-/issues/20268
  200. find_package(PkgConfig REQUIRED)
  201. if (${LLAMA_BLAS_VENDOR} MATCHES "Generic")
  202. pkg_check_modules(DepBLAS REQUIRED blas)
  203. elseif (${LLAMA_BLAS_VENDOR} MATCHES "OpenBLAS")
  204. # As of openblas v0.3.22, the 64-bit is named openblas64.pc
  205. pkg_check_modules(DepBLAS openblas64)
  206. if (NOT DepBLAS_FOUND)
  207. pkg_check_modules(DepBLAS REQUIRED openblas)
  208. endif()
  209. elseif (${LLAMA_BLAS_VENDOR} MATCHES "FLAME")
  210. pkg_check_modules(DepBLAS REQUIRED blis)
  211. elseif (${LLAMA_BLAS_VENDOR} MATCHES "ATLAS")
  212. pkg_check_modules(DepBLAS REQUIRED blas-atlas)
  213. elseif (${LLAMA_BLAS_VENDOR} MATCHES "FlexiBLAS")
  214. pkg_check_modules(DepBLAS REQUIRED flexiblas_api)
  215. elseif (${LLAMA_BLAS_VENDOR} MATCHES "Intel")
  216. # all Intel* libraries share the same include path
  217. pkg_check_modules(DepBLAS REQUIRED mkl-sdl)
  218. elseif (${LLAMA_BLAS_VENDOR} MATCHES "NVHPC")
  219. # this doesn't provide pkg-config
  220. # suggest to assign BLAS_INCLUDE_DIRS on your own
  221. if ("${NVHPC_VERSION}" STREQUAL "")
  222. message(WARNING "Better to set NVHPC_VERSION")
  223. else()
  224. set(DepBLAS_FOUND ON)
  225. set(DepBLAS_INCLUDE_DIRS "/opt/nvidia/hpc_sdk/${CMAKE_SYSTEM_NAME}_${CMAKE_SYSTEM_PROCESSOR}/${NVHPC_VERSION}/math_libs/include")
  226. endif()
  227. endif()
  228. if (DepBLAS_FOUND)
  229. set(BLAS_INCLUDE_DIRS ${DepBLAS_INCLUDE_DIRS})
  230. else()
  231. message(WARNING "BLAS_INCLUDE_DIRS neither been provided nor been automatically"
  232. " detected by pkgconfig, trying to find cblas.h from possible paths...")
  233. find_path(BLAS_INCLUDE_DIRS
  234. NAMES cblas.h
  235. HINTS
  236. /usr/include
  237. /usr/local/include
  238. /usr/include/openblas
  239. /opt/homebrew/opt/openblas/include
  240. /usr/local/opt/openblas/include
  241. /usr/include/x86_64-linux-gnu/openblas/include
  242. )
  243. endif()
  244. endif()
  245. message(STATUS "BLAS found, Includes: ${BLAS_INCLUDE_DIRS}")
  246. add_compile_options(${BLAS_LINKER_FLAGS})
  247. add_compile_definitions(GGML_USE_OPENBLAS)
  248. if (${BLAS_INCLUDE_DIRS} MATCHES "mkl" AND (${LLAMA_BLAS_VENDOR} MATCHES "Generic" OR ${LLAMA_BLAS_VENDOR} MATCHES "Intel"))
  249. add_compile_definitions(GGML_BLAS_USE_MKL)
  250. endif()
  251. set(LLAMA_EXTRA_LIBS ${LLAMA_EXTRA_LIBS} ${BLAS_LIBRARIES})
  252. set(LLAMA_EXTRA_INCLUDES ${LLAMA_EXTRA_INCLUDES} ${BLAS_INCLUDE_DIRS})
  253. else()
  254. message(WARNING "BLAS not found, please refer to "
  255. "https://cmake.org/cmake/help/latest/module/FindBLAS.html#blas-lapack-vendors"
  256. " to set correct LLAMA_BLAS_VENDOR")
  257. endif()
  258. endif()
  259. if (LLAMA_QKK_64)
  260. add_compile_definitions(GGML_QKK_64)
  261. endif()
  262. if (LLAMA_CUBLAS)
  263. cmake_minimum_required(VERSION 3.17)
  264. find_package(CUDAToolkit)
  265. if (CUDAToolkit_FOUND)
  266. message(STATUS "cuBLAS found")
  267. enable_language(CUDA)
  268. set(GGML_HEADERS_CUDA ggml-cuda.h)
  269. set(GGML_SOURCES_CUDA ggml-cuda.cu)
  270. add_compile_definitions(GGML_USE_CUBLAS)
  271. # if (LLAMA_CUDA_CUBLAS)
  272. # add_compile_definitions(GGML_CUDA_CUBLAS)
  273. # endif()
  274. if (LLAMA_CUDA_FORCE_DMMV)
  275. add_compile_definitions(GGML_CUDA_FORCE_DMMV)
  276. endif()
  277. if (LLAMA_CUDA_FORCE_MMQ)
  278. add_compile_definitions(GGML_CUDA_FORCE_MMQ)
  279. endif()
  280. add_compile_definitions(GGML_CUDA_DMMV_X=${LLAMA_CUDA_DMMV_X})
  281. add_compile_definitions(GGML_CUDA_MMV_Y=${LLAMA_CUDA_MMV_Y})
  282. if (DEFINED LLAMA_CUDA_DMMV_Y)
  283. add_compile_definitions(GGML_CUDA_MMV_Y=${LLAMA_CUDA_DMMV_Y}) # for backwards compatibility
  284. endif()
  285. if (LLAMA_CUDA_F16 OR LLAMA_CUDA_DMMV_F16)
  286. add_compile_definitions(GGML_CUDA_F16)
  287. endif()
  288. add_compile_definitions(K_QUANTS_PER_ITERATION=${LLAMA_CUDA_KQUANTS_ITER})
  289. add_compile_definitions(GGML_CUDA_PEER_MAX_BATCH_SIZE=${LLAMA_CUDA_PEER_MAX_BATCH_SIZE})
  290. if (LLAMA_STATIC)
  291. if (WIN32)
  292. # As of 12.3.1 CUDA Tookit for Windows does not offer a static cublas library
  293. set(LLAMA_EXTRA_LIBS ${LLAMA_EXTRA_LIBS} CUDA::cudart_static CUDA::cublas CUDA::cublasLt)
  294. else ()
  295. set(LLAMA_EXTRA_LIBS ${LLAMA_EXTRA_LIBS} CUDA::cudart_static CUDA::cublas_static CUDA::cublasLt_static)
  296. endif()
  297. else()
  298. set(LLAMA_EXTRA_LIBS ${LLAMA_EXTRA_LIBS} CUDA::cudart CUDA::cublas CUDA::cublasLt)
  299. endif()
  300. set(LLAMA_EXTRA_LIBS ${LLAMA_EXTRA_LIBS} CUDA::cuda_driver)
  301. if (NOT DEFINED CMAKE_CUDA_ARCHITECTURES)
  302. # 52 == lowest CUDA 12 standard
  303. # 60 == f16 CUDA intrinsics
  304. # 61 == integer CUDA intrinsics
  305. # 70 == compute capability at which unrolling a loop in mul_mat_q kernels is faster
  306. if (LLAMA_CUDA_F16 OR LLAMA_CUDA_DMMV_F16)
  307. set(CMAKE_CUDA_ARCHITECTURES "60;61;70") # needed for f16 CUDA intrinsics
  308. else()
  309. set(CMAKE_CUDA_ARCHITECTURES "52;61;70") # lowest CUDA 12 standard + lowest for integer intrinsics
  310. #set(CMAKE_CUDA_ARCHITECTURES "") # use this to compile much faster, but only F16 models work
  311. endif()
  312. endif()
  313. message(STATUS "Using CUDA architectures: ${CMAKE_CUDA_ARCHITECTURES}")
  314. else()
  315. message(WARNING "cuBLAS not found")
  316. endif()
  317. endif()
  318. if (LLAMA_MPI)
  319. cmake_minimum_required(VERSION 3.10)
  320. find_package(MPI)
  321. if (MPI_C_FOUND)
  322. message(STATUS "MPI found")
  323. set(GGML_HEADERS_MPI ggml-mpi.h)
  324. set(GGML_SOURCES_MPI ggml-mpi.c ggml-mpi.h)
  325. add_compile_definitions(GGML_USE_MPI)
  326. add_compile_definitions(${MPI_C_COMPILE_DEFINITIONS})
  327. if (NOT MSVC)
  328. add_compile_options(-Wno-cast-qual)
  329. endif()
  330. set(LLAMA_EXTRA_LIBS ${LLAMA_EXTRA_LIBS} ${MPI_C_LIBRARIES})
  331. set(LLAMA_EXTRA_INCLUDES ${LLAMA_EXTRA_INCLUDES} ${MPI_C_INCLUDE_DIRS})
  332. # Even if you're only using the C header, C++ programs may bring in MPI
  333. # C++ functions, so more linkage is needed
  334. if (MPI_CXX_FOUND)
  335. set(LLAMA_EXTRA_LIBS ${LLAMA_EXTRA_LIBS} ${MPI_CXX_LIBRARIES})
  336. endif()
  337. else()
  338. message(WARNING "MPI not found")
  339. endif()
  340. endif()
  341. if (LLAMA_CLBLAST)
  342. find_package(CLBlast)
  343. if (CLBlast_FOUND)
  344. message(STATUS "CLBlast found")
  345. set(GGML_HEADERS_OPENCL ggml-opencl.h)
  346. set(GGML_SOURCES_OPENCL ggml-opencl.cpp)
  347. add_compile_definitions(GGML_USE_CLBLAST)
  348. set(LLAMA_EXTRA_LIBS ${LLAMA_EXTRA_LIBS} clblast)
  349. else()
  350. message(WARNING "CLBlast not found")
  351. endif()
  352. endif()
  353. if (LLAMA_HIPBLAS)
  354. list(APPEND CMAKE_PREFIX_PATH /opt/rocm)
  355. if (NOT ${CMAKE_C_COMPILER_ID} MATCHES "Clang")
  356. message(WARNING "Only LLVM is supported for HIP, hint: CC=/opt/rocm/llvm/bin/clang")
  357. endif()
  358. if (NOT ${CMAKE_CXX_COMPILER_ID} MATCHES "Clang")
  359. message(WARNING "Only LLVM is supported for HIP, hint: CXX=/opt/rocm/llvm/bin/clang++")
  360. endif()
  361. find_package(hip)
  362. find_package(hipblas)
  363. find_package(rocblas)
  364. if (${hipblas_FOUND} AND ${hip_FOUND})
  365. message(STATUS "HIP and hipBLAS found")
  366. add_compile_definitions(GGML_USE_HIPBLAS GGML_USE_CUBLAS)
  367. if (LLAMA_HIP_UMA)
  368. add_compile_definitions(GGML_HIP_UMA)
  369. endif()
  370. add_library(ggml-rocm OBJECT ggml-cuda.cu ggml-cuda.h)
  371. if (BUILD_SHARED_LIBS)
  372. set_target_properties(ggml-rocm PROPERTIES POSITION_INDEPENDENT_CODE ON)
  373. endif()
  374. if (LLAMA_CUDA_FORCE_DMMV)
  375. target_compile_definitions(ggml-rocm PRIVATE GGML_CUDA_FORCE_DMMV)
  376. endif()
  377. if (LLAMA_CUDA_FORCE_MMQ)
  378. target_compile_definitions(ggml-rocm PRIVATE GGML_CUDA_FORCE_MMQ)
  379. endif()
  380. target_compile_definitions(ggml-rocm PRIVATE GGML_CUDA_DMMV_X=${LLAMA_CUDA_DMMV_X})
  381. target_compile_definitions(ggml-rocm PRIVATE GGML_CUDA_MMV_Y=${LLAMA_CUDA_MMV_Y})
  382. target_compile_definitions(ggml-rocm PRIVATE K_QUANTS_PER_ITERATION=${LLAMA_CUDA_KQUANTS_ITER})
  383. set_source_files_properties(ggml-cuda.cu PROPERTIES LANGUAGE CXX)
  384. target_link_libraries(ggml-rocm PRIVATE hip::device PUBLIC hip::host roc::rocblas roc::hipblas)
  385. if (LLAMA_STATIC)
  386. message(FATAL_ERROR "Static linking not supported for HIP/ROCm")
  387. endif()
  388. set(LLAMA_EXTRA_LIBS ${LLAMA_EXTRA_LIBS} ggml-rocm)
  389. else()
  390. message(WARNING "hipBLAS or HIP not found. Try setting CMAKE_PREFIX_PATH=/opt/rocm")
  391. endif()
  392. endif()
  393. function(get_flags CCID CCVER)
  394. set(C_FLAGS "")
  395. set(CXX_FLAGS "")
  396. if (CCID MATCHES "Clang")
  397. set(C_FLAGS -Wunreachable-code-break -Wunreachable-code-return)
  398. set(CXX_FLAGS -Wunreachable-code-break -Wunreachable-code-return -Wmissing-prototypes -Wextra-semi)
  399. if (
  400. (CCID STREQUAL "Clang" AND CCVER VERSION_GREATER_EQUAL 3.8.0) OR
  401. (CCID STREQUAL "AppleClang" AND CCVER VERSION_GREATER_EQUAL 7.3.0)
  402. )
  403. set(C_FLAGS ${C_FLAGS} -Wdouble-promotion)
  404. endif()
  405. elseif (CCID STREQUAL "GNU")
  406. set(C_FLAGS -Wdouble-promotion)
  407. set(CXX_FLAGS -Wno-array-bounds)
  408. if (CCVER VERSION_GREATER_EQUAL 7.1.0)
  409. set(CXX_FLAGS ${CXX_FLAGS} -Wno-format-truncation)
  410. endif()
  411. if (CCVER VERSION_GREATER_EQUAL 8.1.0)
  412. set(CXX_FLAGS ${CXX_FLAGS} -Wextra-semi)
  413. endif()
  414. elseif (CCID MATCHES "Intel")
  415. # enable max optimization level when using Intel compiler
  416. set(C_FLAGS -ipo -O3 -static -fp-model=fast -flto -fno-stack-protector)
  417. set(CXX_FLAGS -ipo -O3 -static -fp-model=fast -flto -fno-stack-protector)
  418. add_link_options(-fuse-ld=lld -static-intel)
  419. endif()
  420. set(GF_C_FLAGS ${C_FLAGS} PARENT_SCOPE)
  421. set(GF_CXX_FLAGS ${CXX_FLAGS} PARENT_SCOPE)
  422. endfunction()
  423. if (LLAMA_ALL_WARNINGS)
  424. if (NOT MSVC)
  425. set(WARNING_FLAGS -Wall -Wextra -Wpedantic -Wcast-qual -Wno-unused-function)
  426. set(C_FLAGS -Wshadow -Wstrict-prototypes -Wpointer-arith -Wmissing-prototypes
  427. -Werror=implicit-int -Werror=implicit-function-declaration)
  428. set(CXX_FLAGS -Wmissing-declarations -Wmissing-noreturn)
  429. set(C_FLAGS ${WARNING_FLAGS} ${C_FLAGS})
  430. set(CXX_FLAGS ${WARNING_FLAGS} ${CXX_FLAGS})
  431. get_flags(${CMAKE_CXX_COMPILER_ID} ${CMAKE_CXX_COMPILER_VERSION})
  432. add_compile_options("$<$<COMPILE_LANGUAGE:C>:${C_FLAGS};${GF_C_FLAGS}>"
  433. "$<$<COMPILE_LANGUAGE:CXX>:${CXX_FLAGS};${GF_CXX_FLAGS}>")
  434. else()
  435. # todo : msvc
  436. set(C_FLAGS "")
  437. set(CXX_FLAGS "")
  438. endif()
  439. endif()
  440. if (LLAMA_CUBLAS)
  441. set(CUDA_FLAGS ${CXX_FLAGS} -use_fast_math)
  442. if (NOT MSVC)
  443. set(CUDA_FLAGS ${CUDA_FLAGS} -Wno-pedantic)
  444. endif()
  445. if (LLAMA_ALL_WARNINGS AND NOT MSVC)
  446. set(NVCC_CMD ${CMAKE_CUDA_COMPILER} .c)
  447. if (NOT CMAKE_CUDA_HOST_COMPILER STREQUAL "")
  448. set(NVCC_CMD ${NVCC_CMD} -ccbin ${CMAKE_CUDA_HOST_COMPILER})
  449. endif()
  450. execute_process(
  451. COMMAND ${NVCC_CMD} -Xcompiler --version
  452. OUTPUT_VARIABLE CUDA_CCFULLVER
  453. ERROR_QUIET
  454. )
  455. if (NOT CUDA_CCFULLVER MATCHES clang)
  456. set(CUDA_CCID "GNU")
  457. execute_process(
  458. COMMAND ${NVCC_CMD} -Xcompiler "-dumpfullversion -dumpversion"
  459. OUTPUT_VARIABLE CUDA_CCVER
  460. ERROR_QUIET
  461. )
  462. else()
  463. if (CUDA_CCFULLVER MATCHES Apple)
  464. set(CUDA_CCID "AppleClang")
  465. else()
  466. set(CUDA_CCID "Clang")
  467. endif()
  468. string(REGEX REPLACE "^.* version ([0-9.]*).*$" "\\1" CUDA_CCVER ${CUDA_CCFULLVER})
  469. endif()
  470. message("-- CUDA host compiler is ${CUDA_CCID} ${CUDA_CCVER}")
  471. get_flags(${CUDA_CCID} ${CUDA_CCVER})
  472. list(JOIN GF_CXX_FLAGS " " CUDA_CXX_FLAGS) # pass host compiler flags as a single argument
  473. if (NOT CUDA_CXX_FLAGS STREQUAL "")
  474. set(CUDA_FLAGS ${CUDA_FLAGS} -Xcompiler ${CUDA_CXX_FLAGS})
  475. endif()
  476. endif()
  477. add_compile_options("$<$<COMPILE_LANGUAGE:CUDA>:${CUDA_FLAGS}>")
  478. endif()
  479. if (WIN32)
  480. add_compile_definitions(_CRT_SECURE_NO_WARNINGS)
  481. if (BUILD_SHARED_LIBS)
  482. set(CMAKE_WINDOWS_EXPORT_ALL_SYMBOLS ON)
  483. endif()
  484. endif()
  485. if (LLAMA_LTO)
  486. include(CheckIPOSupported)
  487. check_ipo_supported(RESULT result OUTPUT output)
  488. if (result)
  489. set(CMAKE_INTERPROCEDURAL_OPTIMIZATION TRUE)
  490. else()
  491. message(WARNING "IPO is not supported: ${output}")
  492. endif()
  493. endif()
  494. if (LLAMA_CCACHE)
  495. find_program(LLAMA_CCACHE_FOUND ccache)
  496. if (LLAMA_CCACHE_FOUND)
  497. set_property(GLOBAL PROPERTY RULE_LAUNCH_COMPILE ccache)
  498. set(ENV{CCACHE_SLOPPINESS} time_macros)
  499. message(STATUS "Using ccache")
  500. else()
  501. message(STATUS "Warning: ccache not found - consider installing it or use LLAMA_CCACHE=OFF")
  502. endif ()
  503. endif()
  504. # this version of Apple ld64 is buggy
  505. execute_process(
  506. COMMAND ${CMAKE_C_COMPILER} ${CMAKE_EXE_LINKER_FLAGS} -Wl,-v
  507. ERROR_VARIABLE output
  508. OUTPUT_QUIET
  509. )
  510. if (output MATCHES "dyld-1015\.7")
  511. add_compile_definitions(HAVE_BUGGY_APPLE_LINKER)
  512. endif()
  513. # Architecture specific
  514. # TODO: probably these flags need to be tweaked on some architectures
  515. # feel free to update the Makefile for your architecture and send a pull request or issue
  516. message(STATUS "CMAKE_SYSTEM_PROCESSOR: ${CMAKE_SYSTEM_PROCESSOR}")
  517. if (MSVC)
  518. string(TOLOWER "${CMAKE_GENERATOR_PLATFORM}" CMAKE_GENERATOR_PLATFORM_LWR)
  519. message(STATUS "CMAKE_GENERATOR_PLATFORM: ${CMAKE_GENERATOR_PLATFORM}")
  520. else ()
  521. set(CMAKE_GENERATOR_PLATFORM_LWR "")
  522. endif ()
  523. if (NOT MSVC)
  524. if (LLAMA_STATIC)
  525. add_link_options(-static)
  526. if (MINGW)
  527. add_link_options(-static-libgcc -static-libstdc++)
  528. endif()
  529. endif()
  530. if (LLAMA_GPROF)
  531. add_compile_options(-pg)
  532. endif()
  533. endif()
  534. function(add_compile_option_cpp ARG)
  535. # Adds a compile option to C/C++ only, but not for Cuda.
  536. # Use, e.g., for CPU-architecture flags.
  537. add_compile_options($<$<COMPILE_LANGUAGE:CXX>:${ARG}>)
  538. add_compile_options($<$<COMPILE_LANGUAGE:C>:${ARG}>)
  539. endfunction()
  540. if ((${CMAKE_SYSTEM_PROCESSOR} MATCHES "arm") OR (${CMAKE_SYSTEM_PROCESSOR} MATCHES "aarch64") OR ("${CMAKE_GENERATOR_PLATFORM_LWR}" MATCHES "arm64"))
  541. message(STATUS "ARM detected")
  542. if (MSVC)
  543. add_compile_definitions(__ARM_NEON)
  544. add_compile_definitions(__ARM_FEATURE_FMA)
  545. add_compile_definitions(__ARM_FEATURE_DOTPROD)
  546. # add_compile_definitions(__ARM_FEATURE_FP16_VECTOR_ARITHMETIC) # MSVC doesn't support vdupq_n_f16, vld1q_f16, vst1q_f16
  547. add_compile_definitions(__aarch64__) # MSVC defines _M_ARM64 instead
  548. else()
  549. check_cxx_compiler_flag(-mfp16-format=ieee COMPILER_SUPPORTS_FP16_FORMAT_I3E)
  550. if (NOT "${COMPILER_SUPPORTS_FP16_FORMAT_I3E}" STREQUAL "")
  551. add_compile_options(-mfp16-format=ieee)
  552. endif()
  553. if (${CMAKE_SYSTEM_PROCESSOR} MATCHES "armv6")
  554. # Raspberry Pi 1, Zero
  555. add_compile_options(-mfpu=neon-fp-armv8 -mno-unaligned-access)
  556. endif()
  557. if (${CMAKE_SYSTEM_PROCESSOR} MATCHES "armv7")
  558. # Raspberry Pi 2
  559. add_compile_options(-mfpu=neon-fp-armv8 -mno-unaligned-access -funsafe-math-optimizations)
  560. endif()
  561. if (${CMAKE_SYSTEM_PROCESSOR} MATCHES "armv8")
  562. # Raspberry Pi 3, 4, Zero 2 (32-bit)
  563. add_compile_options(-mno-unaligned-access)
  564. endif()
  565. endif()
  566. elseif (${CMAKE_SYSTEM_PROCESSOR} MATCHES "^(x86_64|i686|AMD64)$" OR "${CMAKE_GENERATOR_PLATFORM_LWR}" MATCHES "^(x86_64|i686|amd64|x64)$" )
  567. message(STATUS "x86 detected")
  568. if (MSVC)
  569. # instruction set detection for MSVC only
  570. if (LLAMA_NATIVE)
  571. include(cmake/FindSIMD.cmake)
  572. endif ()
  573. if (LLAMA_AVX512)
  574. add_compile_option_cpp(/arch:AVX512)
  575. # MSVC has no compile-time flags enabling specific
  576. # AVX512 extensions, neither it defines the
  577. # macros corresponding to the extensions.
  578. # Do it manually.
  579. if (LLAMA_AVX512_VBMI)
  580. add_compile_definitions($<$<COMPILE_LANGUAGE:C>:__AVX512VBMI__>)
  581. add_compile_definitions($<$<COMPILE_LANGUAGE:CXX>:__AVX512VBMI__>)
  582. endif()
  583. if (LLAMA_AVX512_VNNI)
  584. add_compile_definitions($<$<COMPILE_LANGUAGE:C>:__AVX512VNNI__>)
  585. add_compile_definitions($<$<COMPILE_LANGUAGE:CXX>:__AVX512VNNI__>)
  586. endif()
  587. elseif (LLAMA_AVX2)
  588. add_compile_option_cpp(/arch:AVX2)
  589. elseif (LLAMA_AVX)
  590. add_compile_option_cpp(/arch:AVX)
  591. endif()
  592. else()
  593. if (LLAMA_NATIVE)
  594. add_compile_option_cpp(-march=native)
  595. endif()
  596. if (LLAMA_F16C)
  597. add_compile_option_cpp(-mf16c)
  598. endif()
  599. if (LLAMA_FMA)
  600. add_compile_option_cpp(-mfma)
  601. endif()
  602. if (LLAMA_AVX)
  603. add_compile_option_cpp(-mavx)
  604. endif()
  605. if (LLAMA_AVX2)
  606. add_compile_option_cpp(-mavx2)
  607. endif()
  608. if (LLAMA_AVX512)
  609. add_compile_option_cpp(-mavx512f)
  610. add_compile_option_cpp(-mavx512bw)
  611. endif()
  612. if (LLAMA_AVX512_VBMI)
  613. add_compile_option_cpp(-mavx512vbmi)
  614. endif()
  615. if (LLAMA_AVX512_VNNI)
  616. add_compile_option_cpp(-mavx512vnni)
  617. endif()
  618. endif()
  619. elseif (${CMAKE_SYSTEM_PROCESSOR} MATCHES "ppc64")
  620. message(STATUS "PowerPC detected")
  621. if (${CMAKE_SYSTEM_PROCESSOR} MATCHES "ppc64le")
  622. add_compile_options(-mcpu=powerpc64le)
  623. else()
  624. add_compile_options(-mcpu=native -mtune=native)
  625. #TODO: Add targets for Power8/Power9 (Altivec/VSX) and Power10(MMA) and query for big endian systems (ppc64/le/be)
  626. endif()
  627. else()
  628. message(STATUS "Unknown architecture")
  629. endif()
  630. if (MINGW)
  631. # Target Windows 8 for PrefetchVirtualMemory
  632. add_compile_definitions(_WIN32_WINNT=${LLAMA_WIN_VER})
  633. endif()
  634. #
  635. # POSIX conformance
  636. #
  637. # clock_gettime came in POSIX.1b (1993)
  638. # CLOCK_MONOTONIC came in POSIX.1-2001 / SUSv3 as optional
  639. # posix_memalign came in POSIX.1-2001 / SUSv3
  640. # M_PI is an XSI extension since POSIX.1-2001 / SUSv3, came in XPG1 (1985)
  641. add_compile_definitions(_XOPEN_SOURCE=600)
  642. # Somehow in OpenBSD whenever POSIX conformance is specified
  643. # some string functions rely on locale_t availability,
  644. # which was introduced in POSIX.1-2008, forcing us to go higher
  645. if (CMAKE_SYSTEM_NAME MATCHES "OpenBSD")
  646. remove_definitions(-D_XOPEN_SOURCE=600)
  647. add_compile_definitions(_XOPEN_SOURCE=700)
  648. endif()
  649. # Data types, macros and functions related to controlling CPU affinity and
  650. # some memory allocation are available on Linux through GNU extensions in libc
  651. if (CMAKE_SYSTEM_NAME MATCHES "Linux")
  652. add_compile_definitions(_GNU_SOURCE)
  653. endif()
  654. # RLIMIT_MEMLOCK came in BSD, is not specified in POSIX.1,
  655. # and on macOS its availability depends on enabling Darwin extensions
  656. # similarly on DragonFly, enabling BSD extensions is necessary
  657. if (
  658. CMAKE_SYSTEM_NAME MATCHES "Darwin" OR
  659. CMAKE_SYSTEM_NAME MATCHES "iOS" OR
  660. CMAKE_SYSTEM_NAME MATCHES "tvOS" OR
  661. CMAKE_SYSTEM_NAME MATCHES "DragonFly"
  662. )
  663. add_compile_definitions(_DARWIN_C_SOURCE)
  664. endif()
  665. # alloca is a non-standard interface that is not visible on BSDs when
  666. # POSIX conformance is specified, but not all of them provide a clean way
  667. # to enable it in such cases
  668. if (CMAKE_SYSTEM_NAME MATCHES "FreeBSD")
  669. add_compile_definitions(__BSD_VISIBLE)
  670. endif()
  671. if (CMAKE_SYSTEM_NAME MATCHES "NetBSD")
  672. add_compile_definitions(_NETBSD_SOURCE)
  673. endif()
  674. if (CMAKE_SYSTEM_NAME MATCHES "OpenBSD")
  675. add_compile_definitions(_BSD_SOURCE)
  676. endif()
  677. #
  678. # libraries
  679. #
  680. # ggml
  681. if (GGML_USE_CPU_HBM)
  682. add_definitions(-DGGML_USE_CPU_HBM)
  683. find_library(memkind memkind REQUIRED)
  684. endif()
  685. add_library(ggml OBJECT
  686. ggml.c
  687. ggml.h
  688. ggml-alloc.c
  689. ggml-alloc.h
  690. ggml-backend.c
  691. ggml-backend.h
  692. ggml-quants.c
  693. ggml-quants.h
  694. ${GGML_SOURCES_CUDA} ${GGML_HEADERS_CUDA}
  695. ${GGML_SOURCES_OPENCL} ${GGML_HEADERS_OPENCL}
  696. ${GGML_SOURCES_METAL} ${GGML_HEADERS_METAL}
  697. ${GGML_SOURCES_MPI} ${GGML_HEADERS_MPI}
  698. ${GGML_SOURCES_EXTRA} ${GGML_HEADERS_EXTRA}
  699. )
  700. target_include_directories(ggml PUBLIC . ${LLAMA_EXTRA_INCLUDES})
  701. target_compile_features(ggml PUBLIC c_std_11) # don't bump
  702. target_link_libraries(ggml PUBLIC Threads::Threads ${LLAMA_EXTRA_LIBS})
  703. if (GGML_USE_CPU_HBM)
  704. target_link_libraries(ggml PUBLIC memkind)
  705. endif()
  706. add_library(ggml_static STATIC $<TARGET_OBJECTS:ggml>)
  707. if (BUILD_SHARED_LIBS)
  708. set_target_properties(ggml PROPERTIES POSITION_INDEPENDENT_CODE ON)
  709. add_library(ggml_shared SHARED $<TARGET_OBJECTS:ggml>)
  710. target_link_libraries(ggml_shared PUBLIC Threads::Threads ${LLAMA_EXTRA_LIBS})
  711. install(TARGETS ggml_shared LIBRARY)
  712. endif()
  713. # llama
  714. add_library(llama
  715. llama.cpp
  716. llama.h
  717. )
  718. target_include_directories(llama PUBLIC .)
  719. target_compile_features(llama PUBLIC cxx_std_11) # don't bump
  720. target_link_libraries(llama PRIVATE
  721. ggml
  722. ${LLAMA_EXTRA_LIBS}
  723. )
  724. if (BUILD_SHARED_LIBS)
  725. set_target_properties(llama PROPERTIES POSITION_INDEPENDENT_CODE ON)
  726. target_compile_definitions(llama PRIVATE LLAMA_SHARED LLAMA_BUILD)
  727. if (LLAMA_METAL)
  728. set_target_properties(llama PROPERTIES RESOURCE "${CMAKE_CURRENT_SOURCE_DIR}/ggml-metal.metal")
  729. endif()
  730. endif()
  731. #
  732. # install
  733. #
  734. include(GNUInstallDirs)
  735. include(CMakePackageConfigHelpers)
  736. set(LLAMA_INCLUDE_INSTALL_DIR ${CMAKE_INSTALL_INCLUDEDIR}
  737. CACHE PATH "Location of header files")
  738. set(LLAMA_LIB_INSTALL_DIR ${CMAKE_INSTALL_LIBDIR}
  739. CACHE PATH "Location of library files")
  740. set(LLAMA_BIN_INSTALL_DIR ${CMAKE_INSTALL_BINDIR}
  741. CACHE PATH "Location of binary files")
  742. set(LLAMA_BUILD_NUMBER ${BUILD_NUMBER})
  743. set(LLAMA_BUILD_COMMIT ${BUILD_COMMIT})
  744. set(LLAMA_INSTALL_VERSION 0.0.${BUILD_NUMBER})
  745. get_directory_property(LLAMA_TRANSIENT_DEFINES COMPILE_DEFINITIONS)
  746. configure_package_config_file(
  747. ${CMAKE_CURRENT_SOURCE_DIR}/scripts/LlamaConfig.cmake.in
  748. ${CMAKE_CURRENT_BINARY_DIR}/LlamaConfig.cmake
  749. INSTALL_DESTINATION ${CMAKE_INSTALL_LIBDIR}/cmake/Llama
  750. PATH_VARS LLAMA_INCLUDE_INSTALL_DIR
  751. LLAMA_LIB_INSTALL_DIR
  752. LLAMA_BIN_INSTALL_DIR )
  753. write_basic_package_version_file(
  754. ${CMAKE_CURRENT_BINARY_DIR}/LlamaConfigVersion.cmake
  755. VERSION ${LLAMA_INSTALL_VERSION}
  756. COMPATIBILITY SameMajorVersion)
  757. install(FILES ${CMAKE_CURRENT_BINARY_DIR}/LlamaConfig.cmake
  758. ${CMAKE_CURRENT_BINARY_DIR}/LlamaConfigVersion.cmake
  759. DESTINATION ${CMAKE_INSTALL_LIBDIR}/cmake/Llama)
  760. set(GGML_PUBLIC_HEADERS "ggml.h" "ggml-alloc.h" "ggml-backend.h"
  761. "${GGML_HEADERS_CUDA}" "${GGML_HEADERS_OPENCL}"
  762. "${GGML_HEADERS_METAL}" "${GGML_HEADERS_MPI}" "${GGML_HEADERS_EXTRA}")
  763. set_target_properties(ggml PROPERTIES PUBLIC_HEADER "${GGML_PUBLIC_HEADERS}")
  764. install(TARGETS ggml PUBLIC_HEADER)
  765. set_target_properties(llama PROPERTIES PUBLIC_HEADER ${CMAKE_CURRENT_SOURCE_DIR}/llama.h)
  766. install(TARGETS llama LIBRARY PUBLIC_HEADER)
  767. install(
  768. FILES convert.py
  769. PERMISSIONS
  770. OWNER_READ
  771. OWNER_WRITE
  772. OWNER_EXECUTE
  773. GROUP_READ
  774. GROUP_EXECUTE
  775. WORLD_READ
  776. WORLD_EXECUTE
  777. DESTINATION ${CMAKE_INSTALL_BINDIR})
  778. install(
  779. FILES convert-lora-to-ggml.py
  780. PERMISSIONS
  781. OWNER_READ
  782. OWNER_WRITE
  783. OWNER_EXECUTE
  784. GROUP_READ
  785. GROUP_EXECUTE
  786. WORLD_READ
  787. WORLD_EXECUTE
  788. DESTINATION ${CMAKE_INSTALL_BINDIR})
  789. if (LLAMA_METAL)
  790. install(
  791. FILES ggml-metal.metal
  792. PERMISSIONS
  793. OWNER_READ
  794. OWNER_WRITE
  795. GROUP_READ
  796. WORLD_READ
  797. DESTINATION ${CMAKE_INSTALL_BINDIR})
  798. endif()
  799. #
  800. # programs, examples and tests
  801. #
  802. add_subdirectory(common)
  803. if (LLAMA_BUILD_TESTS AND NOT CMAKE_JS_VERSION)
  804. include(CTest)
  805. add_subdirectory(tests)
  806. endif ()
  807. if (LLAMA_BUILD_EXAMPLES)
  808. add_subdirectory(examples)
  809. add_subdirectory(pocs)
  810. endif()