cuda 지원 GPU에서 병렬로 실행되도록이 조합 알고리즘을 어떻게 수정할 수 있습니까?

현재 가능한 모든 문자열 조합을 생성하는 ac 프로그램이 있습니다. 순열이 아닌 조합에 유의하십시오. 이것은 프로그램입니다 :

#include <stdio.h>
#include <string.h>
#include <stdlib.h>

//Constants
static const char set[] = "abcd";
static const int setSize = sizeof(set) - 1;

 void brute(char* temp, int index, int max){
     //Declarations
     int i;
     for(i = 0; i < setSize; i++){
         temp[index] = set[i];
         if(index == max - 1){
                printf("%s\n", temp);
         }
         else{
              brute(temp, index + 1, max);
         }
   }
}

void length(int max_len){
   //Declarations
   char* temp = (char *) malloc(max_len + 1);
   int i;

   //Execute
   for(i = 1; i <= max_len; i++){
         memset(temp, 0, max_len + 1);
         brute(temp, 0, i);
   }
   free(temp);
}


int main(void){
   //Execute
   length(2);
   getchar();
   return 0;
}

조합의 최대 길이를 수정할 수 있습니다. 현재 데모 용으로 2로 설정되어 있습니다. 현재 구성되어있는 경우 프로그램은

a, b, c, d, aa, ab, ac, ad, ba, bb, bc, bd, ca, cb, cc...

이 프로그램을 cuda로 번역했습니다.

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

#include <stdio.h>
#include <string.h>
#include <stdlib.h>

//On-Device Memory
__constant__ char set_d[] = "adcd";
__constant__ int setSize_d = 4;

__device__ void brute(char* temp, int index, int max){
  //Declarations 
  int i;
  for(i = 0; i < setSize_d; i++){
      temp[index] = set_d[i];
      if(index == max - 1){
          printf("%s\n", temp);
      }
      else{
          brute(temp, index + 1, max);
      }
  }
}


__global__ void length_d(int max_len){

      //Declarations
  char* temp = (char *) malloc(max_len + 1);
  int i;
  //Execute
  for(i = 1; i <= max_len; i++){
      memset(temp, 0, max_len+1);
      brute(temp, 0, i);
  }
  free(temp);
}


int main()
{
    //Execute
    cudaSetDevice(0);

    //Launch Kernel
    length_d<<<1, 1>>>(2);
    cudaDeviceSynchronize();

    getchar(); //Keep this console open...
    return 0;
}

원래 프로그램의 cuda 버전은 기본적으로 c 프로그램의 정확한 복사본입니다 (이 프로그램은 -arch=sm_20. 따라서 printfcuda 환경에서 다른 호스트 함수가 작동 한다는 점에 유의하십시오 ).

내 목표는 a-z, A-Z, 0-9, and other characters최대 길이의 조합을 최대 10 개까지 계산하는 것입니다 . 그렇기 때문에이 프로그램이 내 GPU에서 실행되기를 원합니다. 현재로서는 병렬 처리를 이용하지 않습니다. 이는 분명히 cuda에서 프로그램을 작성하는 전체 목적을 무너 뜨립니다. 그러나 스레드를 특정 인덱스 또는 시작 지점으로 위임하는 것 외에도 프로그램의 재귀 적 특성을 제거하는 방법을 잘 모르겠습니다.

건설적인 의견을 보내 주시면 감사하겠습니다.

또한 연속 컴파일시 가끔 경고 메시지가 나타납니다 (산발적으로 나타남) warning : Stack size for entry function '_Z8length_di' cannot be statically determined.

나는 아직 문제를 정확히 찾아 내지 못했지만, 내가 할 수 있기 전에 누군가가 원인을 알아낼 경우에 대비해 게시 할 것이라고 생각했습니다. Visual Studio 2012에서 컴파일 중입니다.

참고 : 상당히 흥미 롭습니다. cuda 프로그램이 이제는 콘솔에 대한 출력이 주기적입니다. 즉, 수십 개의 조합을 인쇄하고, 일시 중지하고, 수십 개의 조합을 인쇄하고, 일시 중지하는 등의 작업을 수행합니다. 또한보고 된 GPU 사용량에서도이 동작을 관찰합니다. 주기적으로 5 %에서 100 %로 변동합니다.