Comment appeler une fonction hôte dans un noyau CUDA?

Comme l'erreur suivante l'indique, l'appel d'une fonction d'hôte ('rand') n'est pas autorisé dans le noyau, et je me demande si il y a une solution, si j'ai besoin de le faire.

error: calling a host function("rand") from a __device__/__global__ function("xS_v1_cuda") is not allowed

source d'informationauteur Hailiang Zhang

  1. 26

    Malheureusement vous ne pouvez pas appeler des fonctions dans l'appareil qui ne sont pas spécifiés avec __device__ modificateur. Si vous avez besoin de nombres aléatoires dans le code de l'appareil de regarder cuda générateur aléatoire curand http://developer.nvidia.com/curand

    Si vous avez votre propre fonction d'hôte que vous voulez l'appeler à partir d'un noyau d'utiliser à la fois le __host__ et __device__ modificateurs:

    __host__ __device__ int add( int a, int b )
{
    return a + b;
}

    Lorsque ce fichier est compilé par le compilateur NVCC pilote, deux versions de l'fonctions sont rassemblés: un appelable par le code d'hôte et un autre appelable par le code de l'appareil. Et c'est pourquoi cette fonction peut être appelée maintenant à la fois par l'hôte et le code de l'appareil.

  2. 7

    La réponse courte est qu'il y a pas de solution à ce problème.

    Tout ce qui est normalement exécuté sur un PROCESSEUR doivent être adaptés à un environnement CUDA, sans aucune garantie qu'il est encore possible de le faire. Hôte fonctions sont juste un autre nom dans CUDA pour les fonctions C. Qui est, les fonctions en cours d'exécution sur un PROCESSEUR-mémoire d'architecture de Von Neumann comme tous les C/C++ a été jusqu'à ce point dans les Pc. Les gpu de vous donner d'énormes quantités de puissance de calcul, mais le coût est qu'il n'est pas près d'aussi flexible ou compatible. Plus important encore, les fonctions de s'exécuter sans la possibilité d'accéder à la mémoire principale et la mémoire qu'ils peuvent l'accès est limité.

    Si ce que vous essayez d'obtenir un générateur de nombre aléatoire vous avez de la chance considérant que Nvidia est allé à la peine, en particulier de la mise en œuvre d'une très efficace Mersenne Twister qui peut prendre en charge jusqu'à 256 threads par SMP. Elle est exigible à l'intérieur d'une fonction du dispositif, décrit dans un précédent post de la mine ici. Si quelqu'un trouve un meilleur lien qui décrit cette fonctionnalité, veuillez retirer la mine et de remplacer le texte approprié ici avec le lien.

    Une chose que je suis sans cesse surpris par est de savoir comment de nombreux programmeurs ne semblent pas conscients de la façon dont standardisés de haute qualité de la pseudo-aléatoire nombre de générateurs. "Le déploiement de votre propre" n'est vraiment pas une bonne idée compte tenu de la quantité d'un art de nombres pseudo-aléatoires. La vérification d'un générateur fournissant suffisamment imprévisible numéros prend beaucoup de travail et de talent universitaire...

  3. 5

    Alors que pas applicable aux " rand ()", mais quelques hôte des fonctions comme "printf" sont disponibles lors de la compilation avec calcul de compatibilité >= 2.0

    e.g:

    nvcc.exe -gencode=arch=compute_10,code=\sm_10,compute_10\...
error : calling a host function("printf") from a __device__/__global__ function("myKernel") is not allowed

    Compile et fonctionne avec sm_20,compute_20

  4. -1

    Je suis en désaccord avec certains des autres réponses dans le sens suivant:

    OP ne décrit pas un problème: il n'est pas malheureux que vous ne pouvez pas appeler __host__ fonctions de code de l'appareil - il est tout à fait impossible pour qu'il soit de toute autre manière, et ce n'est pas une mauvaise chose.

    À expliquer: Pensez à l'hôte (CPU) code comme un lecteur de CD qui vous a mis dans un lecteur de CD; et sur le code de l'appareil comme un, disons, de la carte SD qui vous a mis dans une miniature lecteur de musique. OP la question est "comment puis-je met un disque dans ma figurine de joueur de musique"? Vous ne pouvez pas, et il n'a pas de sens de vouloir. Il pourrait être la même musique essentiellement (code avec les mêmes fonctionnalités; bien que généralement, l'hôte de code et de code de l'appareil ne fonctionnent pas tout à fait la même tâche de calcul) - mais les médias ne sont pas interchangeables.