CMakeLists.txt 3.25 KB
Newer Older
Chao Liu's avatar
Chao Liu committed
1
cmake_minimum_required(VERSION 2.8.3)
Chao Liu's avatar
Chao Liu committed
2
project(modular_convolution)
Chao Liu's avatar
Chao Liu committed
3

4
5
6
7
8
list(APPEND CMAKE_MODULE_PATH "${PROJECT_SOURCE_DIR}/cmake")

include(TargetFlags)
include(AddKernels)

Chao Liu's avatar
Chao Liu committed
9
#c++
Chao Liu's avatar
Chao Liu committed
10
enable_language(CXX)
Chao Liu's avatar
Chao Liu committed
11
set(CMAKE_CXX_STANDARD 17)
Chao Liu's avatar
Chao Liu committed
12
set(CMAKE_CXX_STANDARD_REQUIRED ON)
Chao Liu's avatar
Chao Liu committed
13
set(CMAKE_CXX_EXTENSIONS OFF)
Chao Liu's avatar
Chao Liu committed
14
15
message("CMAKE_CXX_COMPILER_ID: ${CMAKE_CXX_COMPILER_ID}")

Chao Liu's avatar
Chao Liu committed
16
#OpenMP
Chao Liu's avatar
Chao Liu committed
17
18
19
20
21
22
23
24
25
26
27
if(CMAKE_CXX_COMPILER_ID MATCHES "Clang")
	# workaround issue hipcc in rocm3.5 cannot find openmp
	set(OpenMP_CXX "${CMAKE_CXX_COMPILER}")
	set(OpenMP_CXX_FLAGS "-fopenmp=libomp -Wno-unused-command-line-argument")
	set(OpenMP_CXX_LIB_NAMES "libomp" "libgomp" "libiomp5")
	set(OpenMP_libomp_LIBRARY ${OpenMP_CXX_LIB_NAMES})
	set(OpenMP_libgomp_LIBRARY ${OpenMP_CXX_LIB_NAMES})
	set(OpenMP_libiomp5_LIBRARY ${OpenMP_CXX_LIB_NAMES})
else()
	find_package(OpenMP REQUIRED)
endif()
Chao Liu's avatar
Chao Liu committed
28

Chao Liu's avatar
Chao Liu committed
29
30
31
32
message("OpenMP_CXX_LIB_NAMES: ${OpenMP_CXX_LIB_NAMES}")
message("OpenMP_gomp_LIBRARY: ${OpenMP_gomp_LIBRARY}")
message("OpenMP_pthread_LIBRARY: ${OpenMP_pthread_LIBRARY}")
message("OpenMP_CXX_FLAGS: ${OpenMP_CXX_FLAGS}")
Chao Liu's avatar
Chao Liu committed
33

Chao Liu's avatar
Chao Liu committed
34
35
36
set (CMAKE_CXX_FLAGS "${CMAKE_CXX_FLAGS} ${OpenMP_CXX_FLAGS}")
link_libraries(${OpenMP_gomp_LIBRARY})
link_libraries(${OpenMP_pthread_LIBRARY})
Chao Liu's avatar
Chao Liu committed
37

Chao Liu's avatar
Chao Liu committed
38
#GPU backend
Chao Liu's avatar
Chao Liu committed
39
if(DEVICE_BACKEND STREQUAL "AMD")
Chao Liu's avatar
Chao Liu committed
40
41
    find_package(HIP REQUIRED)
endif()
Chao Liu's avatar
Chao Liu committed
42
43

#
Chao Liu's avatar
Chao Liu committed
44
include_directories(BEFORE
Chao Liu's avatar
Chao Liu committed
45
46
47
48
49
    ${PROJECT_SOURCE_DIR}/composable_kernel/include
    ${PROJECT_SOURCE_DIR}/composable_kernel/include/utility
    ${PROJECT_SOURCE_DIR}/composable_kernel/include/tensor_description
    ${PROJECT_SOURCE_DIR}/composable_kernel/include/tensor_operation
    ${PROJECT_SOURCE_DIR}/composable_kernel/include/kernel_algorithm
Chao Liu's avatar
Chao Liu committed
50
    ${PROJECT_SOURCE_DIR}/composable_kernel/include/driver
Chao Liu's avatar
Chao Liu committed
51
    ${PROJECT_SOURCE_DIR}/external/half/include
Chao Liu's avatar
Chao Liu committed
52
53
    ${PROJECT_SOURCE_DIR}/driver/include
    ${PROJECT_BINARY_DIR}/composable_kernel/include/utility
Chao Liu's avatar
Chao Liu committed
54
)
Chao Liu's avatar
Chao Liu committed
55

Chao Liu's avatar
Chao Liu committed
56
57
58
59
60
61
if(DEVICE_BACKEND STREQUAL "AMD")
    include_directories(BEFORE
        ${PROJECT_SOURCE_DIR}/external/rocm/include
    )
endif()

Chao Liu's avatar
Chao Liu committed
62
if(DEVICE_BACKEND STREQUAL "AMD")
63
64
    configure_file("${PROJECT_SOURCE_DIR}/composable_kernel/include/utility/config.amd.hpp.in" "${PROJECT_BINARY_DIR}/composable_kernel/include/utility/config.hpp")
    configure_file("${PROJECT_SOURCE_DIR}/composable_kernel/include/utility/float_type.amd.hpp.in" "${PROJECT_BINARY_DIR}/composable_kernel/include/utility/float_type.hpp")
Chao Liu's avatar
Chao Liu committed
65
    configure_file("${PROJECT_SOURCE_DIR}/composable_kernel/include/utility/synchronization.amd.hpp.in" "${PROJECT_BINARY_DIR}/composable_kernel/include/utility/synchronization.hpp")
Chao Liu's avatar
Chao Liu committed
66
67
endif()

Chao Liu's avatar
Chao Liu committed
68
add_subdirectory(driver)
69
70
71
72
73
74
75

set(CMAKE_CXX_FLAGS "${CMAKE_CXX_FLAGS}")

message("Compiling options for drivers: ${CMAKE_CXX_FLAGS}")

if(DEVICE_BACKEND STREQUAL "AMD")
    set(CONV_V2_SOURCE driver/conv_driver_v2.cpp)
zjing14's avatar
zjing14 committed
76
    set(CONV_BWD_DATA_V2_SOURCE driver/conv_bwd_data_driver_v2.cpp)
77
78
79
80
    set(CONV_V2_OLC_SOURCE driver/conv_driver_v2_olc.cpp)
endif()

add_executable(conv_driver_v2 ${CONV_V2_SOURCE})
zjing14's avatar
zjing14 committed
81
add_executable(conv_bwd_data_driver_v2 ${CONV_BWD_DATA_V2_SOURCE})
82
83
84
85
86
add_executable(conv_driver_v2_olc ${CONV_V2_OLC_SOURCE})

target_include_directories(conv_driver_v2_olc PRIVATE driver/olCompiling/include/)

target_link_libraries(conv_driver_v2 PRIVATE modConv)
zjing14's avatar
zjing14 committed
87
target_link_libraries(conv_bwd_data_driver_v2 PRIVATE modConv)
88
89
90
target_link_libraries(conv_driver_v2_olc PRIVATE modConv)