c++ - 主机和设备函数 makefile 编译错误

Question

我有一个包含几个文件(.cu、.cpp、.h)的项目，我想编译并链接它。

我的文件如下:

1) Graph.cpp - 只是 c++ 代码

2) Graph.h - 上面的标题(工作正常)

3) Common.h - __host__ __device__ 函数

#ifndef COMMON_CUH
#define COMMON_CUH

#include "cuda_runtime.h"
#include "device_launch_parameters.h"

__host__ __device__ unsigned int fun1(int, int);
__host__ __device__ int fun2(int);
__host__ __device__ int fun3(int);
__host__ __device__ unsigned int fun4(int, int);

#endif

4) Common.cu - 上面的实现

#include "cuda_runtime.h"
#include "device_launch_parameters.h"

#include "Common.h"


__host__ __device__ unsigned int fun1(int a, int n) 
{
    ...
}

...other functions...

5) kernel.cu - 主文件

#include "cuda_runtime.h"
#include "device_launch_parameters.h"

#include "Graph.h"
#include "LogCreate.h"
#include "Common.h"

some __global__ functions. c++ functions, main etc.

我尝试使用的一个 makefile:

CUDA_INSTALL_PATH ?= /usr/local/cuda

# Compilers
CXX := g++
CC := gcc
LINK := g++ -fPIC
NVCC  := nvcc -ccbin /usr/bin

# Includes
INCLUDES = -I. -I$(CUDA_INSTALL_PATH)/include

# Common flags
COMMONFLAGS += $(INCLUDES)
NVCCFLAGS += $(COMMONFLAGS)
NVCCFLAGS += -arch=sm_35
# Debug mode
NVCCFLAGS += --compiler-options -Wall -G
CXXFLAGS += $(COMMONFLAGS)
CFLAGS += $(COMMONFLAGS)

LIB_CUDA := -L$(CUDA_INSTALL_PATH)/lib64 -lcudart

OBJS = Common.cuh.o Graph.cpp.o LogCreate.cpp.o kernel.cu.o
TARGET = main
LINKLINE = $(LINK) -o $(TARGET) $(OBJS) $(LIB_CUDA)

.SUFFIXES: .c .cpp .h .cu .cuh .o

%.cuh.o: %.cu %.cuh
    $(NVCC) $(NVCCFLAGS) -dc $< -o $@

%.cu.o: %.cu
    $(NVCC) $(NVCCFLAGS) -dc $< -o $@

%.cpp.o: %.cpp %.h
    $(CXX) $(CXXFLAGS) -c $< -o $@

$(TARGET): $(OBJS) Makefile
    $(LINKLINE)

clean: 
    rm -rf *.o

这给了我:

Common.cuh.o: In function `__sti____cudaRegisterAll_41_tmpxft_0000107c_00000000_6_Common_cpp1_ii__Z3Powii()':
tmpxft_0000107c_00000000-3_Common.cudafe1.cpp:(.text+0x1c1): undefined reference to `__cudaRegisterLinkedBinary_41_tmpxft_0000107c_00000000_6_Common_cpp1_ii__Z3Powii'
kernel.cu.o: In function `__sti____cudaRegisterAll_41_tmpxft_000010ad_00000000_6_kernel_cpp1_ii_filename()':
tmpxft_000010ad_00000000-3_kernel.cudafe1.cpp:(.text+0x2f33): undefined reference to `__cudaRegisterLinkedBinary_41_tmpxft_000010ad_00000000_6_kernel_cpp1_ii_filename'
collect2: error: ld returned 1 exit status
make: *** [main] Error 1

我猜是(Here's a link)可能是对我的问题的描述，但我不知道如何处理它。

另一种编写 makefile 的尝试是(不太通用):

setting like before and main part:
all:
    $(NVCC) $(NVCCFLAGS) -dc Common.cu kernel.cu
    $(NVCC) $(NVCCFLAGS) -dlink Common.o kernel.o -o link.o
    $(CXX) $(CXXFLAGS) -c Graph.cpp Graph.h -o graph.o
    $(LINK) -o main Common.o kernel.o link.o graph.o $(LIB_CUDA)

这给了我:

g++ -fPIC -o main Common.o kernel.o link.o graph.o -L/usr/local/cuda/lib64 -lcudart
graph.o: file not recognized: File format not recognized
collect2: error: ld returned 1 exit status
make: *** [all] Error 1

找了那么多网站，还是不知道怎么解决。我阅读了我之前放置的链接的一部分，但也许我错过了一些东西或者只是不明白。

请解释在 Makefile 中编译/链接时处理许多文件(带有主机和设备代码)的正确方法是什么。谢谢

Answer 1

您的第一个方法没有处理 CUDA separate compilation正确(您没有设备链接步骤)。

你的第二种方法更接近目标。

这是错误的:

$(CXX) $(CXXFLAGS) -c Graph.cpp Graph.h -o graph.o

应该是:

$(CXX) $(CXXFLAGS) -c Graph.cpp -o graph.o