Problema al llamar a la plantilla kernel CUDA

Question

He estado intentando crear kernels de plantillas, pero he tenido problemas para llamarlos a mi programa. Tengo una clase Matrix<T> plantilla, y algunos métodos definidos dentro de él

Matrix.h:

template <typename T> class Matrix { 
    ... 
    void sum(Matrix<T>& m1, Matrix<T>& m2, Matrix<T>& sum); 
    ... 
} 

#include "Matrix.cu" 

Matrix.cu:

#include "MatrixKernel.h" 

template<typename T> void Matrix<T>::sum(const Matrix<T>& m, Matrix<T>& sum) { 
    ... 
    sumKernel<T><<<dimGrid, dimBlock>>>(Matrix<T> m1, Matrix<T> m2, Matrix<T> sum) 
    ... 
} 

MatrixKernel.h:

template<typename T> __global__ void sumKernel(const Matrix<T> m1, const Matrix<T> m2, Matrix<T> sum) { 
... 
} 

El problema es que cuando invoco sumKernel desde el interior de la suma, el compilador me da el siguiente error:

error C2059: syntax error : '<' 

¿Alguien sabe lo que está pasando? El código compilado bien justo antes de incluir la llamada sumKernel.

Gracias.

Answer 1

Parece que tiene un #include extraño, lo que hace que el código compilado por el compilador incorrecto. Haga una distinción entre los encabezados gpu y los encabezados de la CPU usando .cu.h para encabezados cuda. Asegúrese de solo NVCC compila .cu y .cu.h archivos. Los archivos Cuda nunca deberían incluirse en archivos cpp. La llamada al kernel y kernel debe estar en los archivos .cu o .cu.h, y esos archivos no se deben incluir en ningún lado en cpps.

Debido a que su .cu está siendo incluido en una cabecera que está siendo compilado por el compilador de acogida, el compilador de acogida termina golpeando el token <<< - el cual no reconoce. Probablemente no entienda el token << por lo que consume eso, dejando un inesperado <.

Aquí es una forma alternativa de hacer las cosas que deben trabajar (no lo intentó pero es similar al código que utilizamos)

(nota, esto podría funcionar, pero también podría no ser el camino correcto para resolver el problema . Mi jefe no le gusta como solución y preferiría agregar una implementación por variación)

El problema subyacente parece ser la falta de distinción entre el host y el código del dispositivo. Dejo el detalle en mi solución: cosas como copiar resultados desde y hacia el dispositivo, implementación de suma, etc.

El problema que estoy tratando de resolver es, dado un constructo, cómo se puede moldear para usar ambos en el host y el dispositivo?

Voy a la plantilla Matrix.h tanto en el tipo como en los detalles de implementación.

template <typename T, typename Implementation<T> > class Matrix { 
    void sum(Matrix<T>& m1, Matrix<T>& m2, Matrix<T>& sum) 
    { 
     Implementation.sumImp(m1, m2, sum); 
    } 
} 

La aplicación de host, HostMatrixSum.h va a hacer las cosas los de la CPU:

#include "Matrix.h" 

template <typename T> struct HostMatrixSum 
{ 
    void sumImp(Matrix<T>& m1, Matrix<T>& m2, Matrix<T>& sum) 
    { 
     ... 
    } 
} 

Mientras GpuMatrixSum.cu.h va a cargar la matriz, hacer la suma y recuperar los resultados:

#include "Matrix.h" 

template <typename T> struct GpuMatrixSum 
{ 
    template<typename T> __global__ void sumKernel(const Matrix<T> m1, const Matrix<T> m2, Matrix<T> sum) 
    { 
     ... 
    } 

    void sumImp(Matrix<T>& m1, Matrix<T>& m2, Matrix<T>& sum) 
    { 
     ... 
     sumKernel<T> <<< dimGrid, dimBlock >>> (m1,m2); 
     ... 
    } 
} 

Entonces cuando utilizamos Matrix desde el código de host, utilizamos la plantilla en la implementación de la suma de host y nunca necesitamos ver ninguna especificación de cuda:

#include "Matrix.h" 
#include "HostMatrixSum.h" 

Matrix<int, HostMatrixSum> m1 = Matrix<int>(...); 
Matrix<int, HostMatrixSum> m2 = Matrix<int>(...); 
Matrix<int, HostMatrixSum> result; 
Matrix.sum(m1,m2,result); 

Y si estamos trabajando en la GPU podemos utilizar la aplicación GPU acelerada de la suma:

#include "Matrix.h" 
#include "GpuMatrixSum.cu.h" 

Matrix<int, GpuMatrixSum> m1 = Matrix<int>(...); 
Matrix<int, GpuMatrixSum> m2 = Matrix<int>(...); 
Matrix<int, GpuMatrixSum> result; 
Matrix.sum(m1,m2,result); 

la esperanza de que funcione para usted!

Answer 2

que tenían el mismo problema: error C2059: error de sintaxis: '<'

En primer lugar, he encontrado una buena puesta a punto/tutorial aquí (por expreso visual 2010 y CUDA 4.0): http://www.stevenmarkford.com/installing-nvidia-cuda-with-visual-studio-2010/

y para resolver el problema de error de sintaxis, esto lo resolvió: How do I start a CUDA app in Visual Studio 2010?

en concreto, el cambio de la propiedad del archivo * br tal que: Tipo se establece en "CUDA C/C++"

Finalmente funcionó para mí.