Нахождение минимальной позиции элемента массива cudaMalloc с помощью thrust :: min_element - PullRequest
Новая
       15

Нахождение минимальной позиции элемента массива cudaMalloc с помощью thrust :: min_element

0 голосов
/ 13 марта 2012

Я пытаюсь найти наименьший элемент в определенном массиве CUDA 

float *p;
...    
thrust::device_ptr<float> pWrapper(p);    
thrust::device_ptr<float> pos = 
               thrust::min_element(pWrapper, pWrapper + MAXX * MAXY, thrust::minimum<float>());

p - это линейная память устройства, а pWrapper - это thrust::device_ptr.

Когда я использую device_vector, легко найти местоположение наименьшего элемента по 

min_element(someDeviceVector) - someDeviceVector.begin()

В противоположность этому, когда тип, предоставленный для вызова min_element, представляет собой device_ptr, тип возврата min_element равен float *p (согласно определенному шаблону device_vector). Из предоставленного мною фрагмента кода я не могу сказать, где находится наименьшее значение и как его извлечь из массива.

Я пытался вычесть из типа возврата min_element адреса как p, так и pWrapper, но ни один из них не работал.

Ответы [ 2 ]

2 голосов
/ 13 марта 2012

Я только что узнал, что мне просто нужно использовать оператор * в исходящем результате min_element.

0 голосов
/ 06 ноября 2014

В своем посте вы рассматриваете очень распространенный случай, когда у вас есть массив cudaMalloc ', и вы хотите найти позицию и значение его минимального элемента по thrust::min_element. Ниже я привожу полный пример этого в надежде, что это может быть полезно для других пользователей.

В основном, решение ниже разделяет ту же идею обертывания thrust::device_ptr вокруг cudaMalloc 'ed линейной памяти. Тем не менее, позиция найдена thrust::distance.

Вот полный код: 

#include <thrust/device_vector.h>
#include <thrust/extrema.h>

/********************/
/* CUDA ERROR CHECK */
/********************/
#define gpuErrchk(ans) { gpuAssert((ans), __FILE__, __LINE__); }
inline void gpuAssert(cudaError_t code, char *file, int line, bool abort=true)
{
   if (code != cudaSuccess) 
   {
      fprintf(stderr,"GPUassert: %s %s %d\n", cudaGetErrorString(code), file, line);
      if (abort) exit(code);
   }
}

/********/
/* MAIN */
/********/
int main() {

    const int N = 16;

    srand(time(NULL));

    // --- Host side memory allocation and initialization
    float *h_A = (float*)malloc(N * sizeof(float));
    for (int i=0; i<N; i++) h_A[i] = rand();

    // --- Device side memory allocation and initialization
    float *d_A; gpuErrchk(cudaMalloc((void**)&d_A, N * sizeof(float)));
    gpuErrchk(cudaMemcpy(d_A, h_A, N * sizeof(float), cudaMemcpyHostToDevice));

    thrust::device_ptr<float> dp = thrust::device_pointer_cast(d_A);
    thrust::device_ptr<float> pos = thrust::min_element(dp, dp + N);

    unsigned int pos_index = thrust::distance(dp, pos);
    float min_val;
    gpuErrchk(cudaMemcpy(&min_val, &d_A[pos_index], sizeof(float), cudaMemcpyDeviceToHost));

    for (int i=0; i<N; i++) printf("d_A[%i] = %f\n", i, h_A[i]);
    printf("\n");
    printf("Position of the minimum element = %i; Value of the minimum element = %f\n", thrust::distance(dp, pos), min_val);

    cudaDeviceReset();

    return 0;
}
...