Reorganize files, Part 1 (#119)

* delete obselete files

* move files

* build

* update cmake

* update cmake

* fix build

* reorg examples

* update cmake for example and test

[ROCm/composable_kernel commit: 5d37d7bff4]

test/CMakeLists.txt

@@ -1,36 +1,41 @@
 include_directories(BEFORE
-    include
-    ${PROJECT_SOURCE_DIR}/host/host_tensor/include
-    ${PROJECT_SOURCE_DIR}/host/device/include
-    ${PROJECT_SOURCE_DIR}/device_operation/include
-    ${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/problem_transform
-    ${PROJECT_SOURCE_DIR}/external/rocm/include
-    ${PROJECT_SOURCE_DIR}/reference_operation/include
+    ${PROJECT_SOURCE_DIR}/include/ck
+    ${PROJECT_SOURCE_DIR}/include/ck/utility
+    ${PROJECT_SOURCE_DIR}/include/ck/tensor_description
+    ${PROJECT_SOURCE_DIR}/include/ck/tensor
+    ${PROJECT_SOURCE_DIR}/include/ck/problem_transform
+    ${PROJECT_SOURCE_DIR}/include/ck/tensor_operation/gpu/device
+    ${PROJECT_SOURCE_DIR}/include/ck/tensor_operation/gpu/grid
+    ${PROJECT_SOURCE_DIR}/include/ck/tensor_operation/gpu/block
+    ${PROJECT_SOURCE_DIR}/include/ck/tensor_operation/gpu/warp
+    ${PROJECT_SOURCE_DIR}/include/ck/tensor_operation/gpu/thread
+    ${PROJECT_SOURCE_DIR}/include/ck/tensor_operation/gpu/element
+    ${PROJECT_SOURCE_DIR}/library/include/ck/library/host_tensor
+    ${PROJECT_SOURCE_DIR}/library/include/ck/library/tensor_operation_instance
+    ${PROJECT_SOURCE_DIR}/library/include/ck/library/tensor_operation_instance/gpu/reduce
+    ${PROJECT_SOURCE_DIR}/library/include/ck/library/reference_tensor_operation/cpu
+    ${PROJECT_SOURCE_DIR}/library/include/ck/library/reference_tensor_operation/gpu
     ${PROJECT_SOURCE_DIR}/test/include
+    ${PROJECT_SOURCE_DIR}/external/include/half
 )
 
 add_custom_target(check COMMAND ${CMAKE_CTEST_COMMAND} --output-on-failure -C ${CMAKE_CFG_INTDIR})
 add_custom_target(tests)
 
-function(add_test_executeable TEST_NAME)
+function(add_test_executable TEST_NAME)
+    message("adding test ${TEST_NAME}")
     add_executable(${TEST_NAME} ${ARGN})
-    target_link_libraries(${TEST_NAME} PRIVATE host_tensor)
-    target_link_libraries(${TEST_NAME} PRIVATE device_gemm_instance)
-    target_link_libraries(${TEST_NAME} PRIVATE device_conv2d_fwd_instance)
-    target_link_libraries(${TEST_NAME} PRIVATE device_conv2d_bwd_data_instance)
     add_test(NAME ${TEST_NAME} COMMAND $<TARGET_FILE:${TEST_NAME}> )
     add_dependencies(tests ${TEST_NAME})
     add_dependencies(check ${TEST_NAME})
-endfunction(add_test_executeable TEST_NAME)
+endfunction(add_test_executable TEST_NAME)
 
-file(GLOB TESTS */*.cpp)
-
-foreach(TEST ${TESTS})
-    get_filename_component(BASE_NAME ${TEST} NAME_WE)
-    message("adding test ${BASE_NAME}")
-    add_test_executeable(test_${BASE_NAME} ${TEST})
-endforeach(TEST ${TESTS})
+add_subdirectory(magic_number_division)
+add_subdirectory(space_filling_curve)
+add_subdirectory(conv_util)
+add_subdirectory(reference_conv_fwd)
+add_subdirectory(gemm)
+add_subdirectory(gemm_split_k)
+add_subdirectory(conv2d_fwd)
+add_subdirectory(convnd_fwd)
+add_subdirectory(conv2d_bwd_data)

test/conv2d_bwd_data/CMakeLists.txt

@@ -0,0 +1,3 @@
+add_test_executable(test_conv2d_bwd_data conv2d_bwd_data.cpp)
+target_link_libraries(test_conv2d_bwd_data PRIVATE host_tensor)
+target_link_libraries(test_conv2d_bwd_data PRIVATE device_conv2d_bwd_data_instance)

test/conv2d_fwd/CMakeLists.txt

@@ -0,0 +1,3 @@
+add_test_executable(test_conv2d_fwd conv2d_fwd.cpp)
+target_link_libraries(test_conv2d_fwd PRIVATE host_tensor)
+target_link_libraries(test_conv2d_fwd PRIVATE device_conv2d_fwd_instance)

test/conv_util/CMakeLists.txt

@@ -0,0 +1,2 @@
+add_test_executable(test_conv_util conv_util.cpp)
+target_link_libraries(test_conv_util PRIVATE host_tensor)

test/convnd_fwd/CMakeLists.txt

@@ -0,0 +1,2 @@
+add_test_executable(test_convnd_fwd convnd_fwd.cpp)
+target_link_libraries(test_convnd_fwd PRIVATE host_tensor)

test/gemm/CMakeLists.txt

@@ -0,0 +1,11 @@
+add_test_executable(test_gemm_fp32 gemm_fp32.cpp)
+target_link_libraries(test_gemm_fp32 PRIVATE host_tensor)
+target_link_libraries(test_gemm_fp32 PRIVATE device_gemm_instance)
+
+add_test_executable(test_gemm_bf16 gemm_bf16.cpp)
+target_link_libraries(test_gemm_bf16 PRIVATE host_tensor)
+target_link_libraries(test_gemm_bf16 PRIVATE device_gemm_instance)
+
+add_test_executable(test_gemm_int8 gemm_int8.cpp)
+target_link_libraries(test_gemm_int8 PRIVATE host_tensor)
+target_link_libraries(test_gemm_int8 PRIVATE device_gemm_instance)

test/gemm_split_k/CMakeLists.txt

@@ -0,0 +1,3 @@
+add_test_executable(test_gemm_split_k gemm_split_k.cpp)
+target_link_libraries(test_gemm_split_k PRIVATE host_tensor)
+target_link_libraries(test_gemm_split_k PRIVATE device_gemm_instance)

test/magic_number_division/CMakeLists.txt

@@ -0,0 +1,2 @@
+add_test_executable(test_magic_number_division magic_number_division.cpp)
+target_link_libraries(test_magic_number_division PRIVATE host_tensor)

test/reference_conv_fwd/CMakeLists.txt

@@ -0,0 +1,2 @@
+add_test_executable(test_reference_conv_fwd reference_conv_fwd.cpp)
+target_link_libraries(test_reference_conv_fwd PRIVATE host_tensor)

test/space_filling_curve/CMakeLists.txt

@@ -0,0 +1 @@
+add_test_executable(test_space_filling_curve space_filling_curve.cpp)