장치의 포인터 배열을 복사하려고 시도 할 때 cudaMalloc 오류가 발생합니다.

Question

간단한 입자 기반의 강체 동역학 코드가 있습니다. 각 강체는 질량, 위치, 속도 등의 많은 작은 입자로 구성됩니다. 이제 포트로 이동하려고합니다. gpu 에이 CPU 코드.

구조체의 경우 포인터 배열 int** d_rigid_particle_indices을 사용하기로 선택했습니다. 각 요소는 자식 입자 인덱스의 배열을 가리 킵니다. (기수 정렬을 사용하여 모든 프레임마다 입자를 정렬하므로 인덱스가 모든 프레임을 바꿉니다. - 이중 버퍼링 방식을 사용>int** d_rigid_particle_indices[2];) 여기서

하는 데이터 구조를 호스트 장치로 데이터를 복사하는 & 함수 :

typedef struct{ 
// Particle based rigid body dynamics 
float4*  d_rb_pos;      
float4*  d_rb_vel; 
float4*  d_rb_angular_velocity; 
float4*  d_rb_linear_momentum; 
float4*  d_rb_angular_momentum; 
float4*  d_rb_force; 
float4*  d_rb_torque; 
float4*  d_rb_quaternion; 
float*  d_rb_rotation_matrix;   
float*  d_rb_inv_inertia_local;  
float*  d_rb_inv_inertia_world; 
float*  d_rb_mass; 
int**   d_rigid_particle_indices[2]; 

} d_RigidBody 단계; 이 코드 라인 :

:

void CopyRigidBodyDataHostToDevice(d_RigidBody& d_rb,std::vector<RigidBody*>& rigidbodies_h){ 
const int num_rigid_bodies = rigidbodies_h.size(); 

// allocate host mem for top level pointer array 
int** h_rigid_bodies = (int**)malloc(num_rigid_bodies*sizeof(int*)); 
for (int i = 0; i < num_rigid_bodies; ++i) 
    h_rigid_bodies[i] = NULL; 

// allocate host&device mem for child particle index array 
for (int i = 0; i < num_rigid_bodies; ++i) 
{ 
    RigidBody* rb = rigidbodies_h[i]; 
    if (rb) 
    { 
     std::vector<int>& rp_indices = rb->getRigidBodyParticleIndicesArray(); 
     const int num_particles = rp_indices.size(); 
     int* temp_rp_indices = (int*)malloc(num_particles*sizeof(int)); 
     for (int j = 0; j < num_particles; ++j) 
     { 
      temp_rp_indices[j] = rp_indices[j]; 
     }   
     int * temp_ptr; 
     CUDA_SAFE_CALL(cudaMalloc(((void**)&temp_ptr, num_particles*sizeof(int))));  // allocate device mem for child pointer 
     h_rigid_bodies[i] = temp_ptr; 
     temp_ptr = NULL; 
     for (int k = 0; k < num_particles; ++k) 
     { 
      // copy RigidParticleIndices per rigid body from host to device 
      CUDA_SAFE_CALL(cudaMemcpy(h_rigid_bodies[i], temp_rp_indices, num_particles*sizeof(int), cudaMemcpyHostToDevice)); //h_rigid_bodies[i] stores the device mem pointer 
     } 
     if (temp_rp_indices) 
      free(temp_rp_indices);    
    } 
} 

// allocate device mem for top level pointer array 
CUDA_SAFE_CALL(cudaMalloc((void**)&(d_rb.d_rigid_particle_indices[0]), num_rigid_bodies*sizeof(int*))); // pointer array 
CUDA_SAFE_CALL(cudaMalloc((void**)&(d_rb.d_rigid_particle_indices[1]), num_rigid_bodies*sizeof(int*))); // pointer array 

// now we're ready to copy top level pointer array from host to device 
CUDA_SAFE_CALL(cudaMemcpy(d_rb.d_rigid_particle_indices[0], h_rigid_bodies, num_rigid_bodies*sizeof(int*), cudaMemcpyHostToDevice)); 

// clean up 
if (h_rigid_bodies) 
{ 
    for (int i = 0; i < num_rigid_bodies; ++i) 
    { 
     if (h_rigid_bodies[i]) 
     { 
      free(h_rigid_bodies[i]); 
     } 
    } 
    free(h_rigid_bodies); 
} 

}

컴파일 후, 나는 오류 cudaMalloc "오버로드 기능없이 인스턴스를"가지고 "(부호없는 int)를 유형은 인수 목록 인수를 일치"

CUDA_SAFE_CALL(cudaMalloc(((void**)&temp_ptr, num_particles*sizeof(int))));  // allocate device mem for child pointer. 

어떤 조언이 필요합니까?

감사합니다.

Answer 1

한 쌍의 브래킷을 너무 많이 사용했습니다. 따라서 컴파일러는 cudaMalloc 호출에 전달 된 하나의 인수 만 볼 수 있습니다. 줄을

CUDA_SAFE_CALL(cudaMalloc((void**)&temp_ptr, num_particles*sizeof(int))); 

으로 변경하십시오.