Ошибка компоновщика 2019 при соединении приложения Winusb и CUDA
У меня есть два приложения Winusb и копирование данных из процессора в графический процессор с помощью CUDA. Оба прекрасно работают как два отдельных проекта, но когда я пытаюсь объединить их в один проект, я получаю следующую ошибку компоновки.
Журнал сборки:
1>------ Build started: Project: USB Application2, Configuration: Win7 Debug Win32 ------
1> Compiling CUDA source file function.cu...
1>
1> C:\Users\bel1\documents\visual studio 2012\Projects\USB Application2\USB Application2>"C:\Program Files\NVIDIA GPU Computing Toolkit\CUDA\v5.5\bin\nvcc.exe" -gencode=arch=compute_10,code=sm_10 --use-local-env --cl-version 2010 -ccbin "C:\Program Files\Microsoft Visual Studio 11.0\VC\bin" -IWin7Debug\ -IWin7Debug\ -I"C:\Program Files\NVIDIA GPU Computing Toolkit\CUDA\v5.5\include" -I"C:\Program Files\NVIDIA GPU Computing Toolkit\CUDA\v5.5\include" -I"C:\Program Files\NVIDIA GPU Computing Toolkit\CUDA\v5.5\include" --keep-dir Win7Debug -maxrregcount=0 --machine 32 -cuda -cudart static -D_X86_=1 -Di386=1 -DSTD_CALL -DWIN32_LEAN_AND_MEAN=1 -D_WIN32_WINNT=0x0601 -DWINVER=0x0601 -DWINNT=1 -DNTDDI_VERSION=0x06010000 -DDBG=1 -D_AFXDLL -Xcompiler "/EHsc /W0 /nologo /Od /Zi /RTC1 /MT " -o Win7Debug\function.cu.obj "C:\Users\bel1\documents\visual studio 2012\Projects\USB Application2\USB Application2\function.cu"1> Compiling CUDA source file wrapper.cu...
1>
1> C:\Users\bel1\documents\visual studio 2012\Projects\USB Application2\USB Application2>"C:\Program Files\NVIDIA GPU Computing Toolkit\CUDA\v5.5\bin\nvcc.exe" -gencode=arch=compute_10,code=sm_10 --use-local-env --cl-version 2010 -ccbin "C:\Program Files\Microsoft Visual Studio 11.0\VC\bin" -IWin7Debug\ -IWin7Debug\ -I"C:\Program Files\NVIDIA GPU Computing Toolkit\CUDA\v5.5\include" -I"C:\Program Files\NVIDIA GPU Computing Toolkit\CUDA\v5.5\include" -I"C:\Program Files\NVIDIA GPU Computing Toolkit\CUDA\v5.5\include" --keep-dir Win7Debug -maxrregcount=0 --machine 32 -cuda -cudart static -D_X86_=1 -Di386=1 -DSTD_CALL -DWIN32_LEAN_AND_MEAN=1 -D_WIN32_WINNT=0x0601 -DWINVER=0x0601 -DWINNT=1 -DNTDDI_VERSION=0x06010000 -DDBG=1 -D_AFXDLL -Xcompiler "/EHsc /W0 /nologo /Od /Zi /RTC1 /MT " -o Win7Debug\wrapper.cu.obj "C:\Users\bel1\documents\visual studio 2012\Projects\USB Application2\USB Application2\wrapper.cu"1>main.obj : error LNK2019: unresolved external symbol "short * __stdcall speccud(short * const)" (?speccud@@YGPAFQAF@Z) referenced in function _main
1>C:\Users\bel1\documents\visual studio 2012\Projects\USB Application2\Win7Debug\USBApplication2.exe : fatal error LNK1120: 1 unresolved externals
========== Build: 0 succeeded, 1 failed, 0 up-to-date, 0 skipped ==========
main.cpp
#include "pch.h"short *speccud(short ispecbu[]);
LONG __cdecl _tmain(LONG Argc, LPTSTR ** Argv )
//int main(int argc, char **argv)
{
FILE *output_file1 = fopen("output_file2.txt", "w");
FILE *output_file2 = fopen("output_file3.txt", "w");
DEVICE_DATA deviceData;
HRESULT hr;
USB_DEVICE_DESCRIPTOR deviceDesc;
BOOL bResult;
BOOL noDevice;
ULONG lengthReceived;
BOOL wrResult = TRUE;
BOOL wr1Result = TRUE;
BOOL RQResult = 0;
UNREFERENCED_PARAMETER(Argc);
UNREFERENCED_PARAMETER(Argv);//////////////////////Open device ///////////////
hr = OpenDevice(&deviceData, &noDevice);
if (FAILED(hr)) {
if (noDevice) {
printf(_T("Device not connected or driver not installed\n"));
} else {
printf(_T("Failed looking for device, HRESULT 0x%x\n"), hr);
}
std::getchar();
return 0;
}
/////////////////////Get descriptor//////////////////
bResult = WinUsb_GetDescriptor(deviceData.WinusbHandle,
USB_DEVICE_DESCRIPTOR_TYPE,
0,
0,
(PBYTE) &deviceDesc,
sizeof(deviceDesc),
&lengthReceived);
if (FALSE == bResult || lengthReceived != sizeof(deviceDesc)) {
printf(_T("Error among LastError %d or lengthReceived %d\n"),
FALSE == bResult ? GetLastError() : 0,
lengthReceived);
CloseDevice(&deviceData);
return 0;
}
bool sResult = FALSE;bool syResult;
bool sResult1 = FALSE;bool syResult1;
//Initialize
UCHAR Intialize[] = {0x01};
ULONG cbISize = strlen((char*)Intialize);
ULONG InSent = 0;
wrResult = WinUsb_WritePipe(deviceData.WinusbHandle, 0x01, Intialize, 1, &InSent, 0);
//Integration time - 700ms
UCHAR Inttime[] = {0x0200100000};
ULONG cbITSize = strlen((char*)Inttime);
ULONG InttimeSent = 0;
wrResult = WinUsb_WritePipe(deviceData.WinusbHandle, 0x01, Inttime, 5, &InttimeSent, 0);
//strobe signal
UCHAR strobe1[] = {0x030001};
ULONG strobeSize1 = strlen((char*)strobe1);
ULONG strobeSent1 = 0;
wr1Result = WinUsb_WritePipe(deviceData.WinusbHandle, 0x01, strobe1, 3, &strobeSent1, 0);
//Request spectra
UCHAR Rqspectra[] = {0x09};
ULONG RqSize = strlen((char*)Rqspectra);
ULONG RqSent = 0;
RQResult = WinUsb_WritePipe(deviceData.WinusbHandle, 0x01, Rqspectra,1, &RqSent, 0);
//Pixel Values
UCHAR szBuffer[15][512];
UCHAR sz1Buffer[1];
UCHAR tBuffer[1];
ULONG tReadx;
ULONG cbReadx[16];
USHORT newbuf[15][512];
short specbu[7860];
short *fans;
for (int i=0;i<16;i++)
{
if (i<4)
{
sResult = WinUsb_ReadPipe(deviceData.WinusbHandle, 0x86, szBuffer[i], 512, &cbReadx[i], 0);
}
else if (i>=4 && i<15)
{
sResult = WinUsb_ReadPipe(deviceData.WinusbHandle, 0x82, szBuffer[i], 512, &cbReadx[i], 0);
}
else if (i = 15)
{
syResult = WinUsb_ReadPipe(deviceData.WinusbHandle, 0x82, sz1Buffer, 1, &cbReadx[i], 0);
}
}
int pon=0;
for (int k=0;k<15;k++)
{
for (int l=0;l<512;l+=2)
{
newbuf[k][l] = (szBuffer[k][(l+1)]<<8|szBuffer[k][l]);
specbu[pon]= (szBuffer[k][(l+1)]<<8|szBuffer[k][l]);
fprintf(output_file1,"%d\t\n",specbu[pon]);
pon++;
}
}
//printf("%d",sizeof(specbu));
//short ARR[5] = {1,2,3,4,5};
//fans=speccud(ARR);
fans = speccud(specbu);
for (int k=0;k<5;k++)
{printf("%d", fans[k]);
//fprintf(output_file2,"%d\t\n",fans[k]);
//tempc[k]=specbu[k];
}
std::getchar();
CloseDevice(&deviceData);
return 0;
}
Wrapper.cu
#include "cuda_runtime.h"#include <cuda.h>
#include <cstdio>
#include "device_launch_parameters.h"
__global__ void saxpy(int cn, short ca, short *cx, short *cy);
short *speccud(short ispecbu[])
{
const int cN = 7680;
short *cx, *cd_x, *cd_y;
static short *cy;
cx = (short*)malloc(cN*sizeof(short));
cy = (short*)malloc(cN*sizeof(short));
cudaMalloc(&cd_x, cN*sizeof(short));
cudaMalloc(&cd_y, cN*sizeof(short));
for (int ci = 0; ci < cN; ci++) {
cx[ci] = ispecbu[ci];
//y[i] = 2.0f;
}
cudaMemcpy(cd_x, cx, cN*sizeof(short), cudaMemcpyHostToDevice);
cudaMemcpy(cd_y, cy, cN*sizeof(short), cudaMemcpyHostToDevice);
// Perform SAXPY on 1M elements
saxpy<<<(cN+255)/256, 256>>>(cN, 1, cd_x, cd_y);
cudaMemcpy(cy, cd_y, cN*sizeof(short), cudaMemcpyDeviceToHost);
return cy;
}
Function.cu
#ifndef __Kernel_CU__
#define __Kernel_CU__
__global__ void saxpy(int cn, short ca, short *cx, short *cy)
{
int ci = blockIdx.x*blockDim.x + threadIdx.x;
cy[ci] = ca+cx[ci];
}
#endif
У меня также есть device.cpp, который имеет функции opendevice, closedevice и т. Д. (Часть Winusb и имеет слишком много строк автоматически сгенерированного кода). Это похоже на ошибку компоновщика между приложением Cuda и Winusb. когда я просто создаю два визуальных студийных проекта, один для Cuda и другой для winusb, оба работают отлично.
Решение
Компоновщик просматривает символы, необходимые для main.cpp (то есть точки входа, необходимые для main.obj), и пытается найти определения для этих точек входа в других модулях вашего проекта.
В случае main.obj был один символ (точка входа), который он не мог найти определенным в другом месте:
1>main.obj : error LNK2019: unresolved external symbol "short * __stdcall speccud(short * const)" (?speccud@@YGPAFQAF@Z) referenced in function _main
В этом случае компоновщик говорит: Я ищу функцию, определенную следующим образом:
short * __stdcall speccud(short * const)
но я не могу найти это!».
Конечно, вы не украшали свой прототип в main.cpp __stdcall, это было сделано автоматически компилятором, прежде чем он решил, какой символ нужен извне. Компилятор VS C ++ может вести себя по-разному, и в этом случае его поведение при компиляции файла main.cpp отличалось от его (декорирующего) поведения при компиляции Wrapper.cu. В результате функция speccud в Wrapper.cu экспортировалось с именем, отличным от того, которое было определено как необходимое для main.obj, поэтому компоновщик не смог сопоставить их.
Поэтому, если вы избежите этой путаницы, заставив экспортировать функцию в Wrapper.cu способом, точно совпадающим с тем, что, по словам компоновщика, он ищет в main.obj, компоновщик может найти соответствие:
Линкер сказал: Я ищу: «
short * __stdcall speccud(short * const)
так что если вы измените прототип на:
short * __stdcall speccud(short * const);
и определение функции для:
short * __stdcall speccud(short * const ispecbu)
тогда все совпадает.
(в связи C ++ фактический процесс сопоставления основан на искромсанный имя, которое это:
?speccud@@YGPAFQAF@Z
но процесс сообщения об ошибках также устраняет это для нас:
short * __stdcall speccud(short * const)
Манглинг / деманглинг следует определенной процедуре, поэтому вы можете использовать онлайн-сервис для раскрутки преобразовать искаженное имя в его деформированную версию. Искаженная версия этой функции выглядела бы иначе, если бы у функции не было __stdcall украшение.)
Другие решения