Kopieren Sie ein Objekt zu Gerät?

Kann ich kopieren Sie eine C++ - Objekt auf dem Gerät?

sagen, ich habe:

class CudaClass
{
public:
int* data;
CudaClass(int x) {
    data = new int[1]; data[0] = x;
}
};

__global__ void useClass(CudaClass cudaClass)
{
    printf("%d" cudaClass.data[0]);
};


int main()
{
    CudaClass c(1);
}

Nun, wie kopiere ich mit "c" device memory " und starten Sie die kernel - "useClass"?

InformationsquelleAutor SpaceMonkey | 2013-04-15
  1. 18

    Ja, Sie können ein Objekt kopieren, um das Gerät für die Verwendung auf dem Gerät. Wenn das Objekt eingebettet hat Zeiger auf dynamisch zugewiesenen Regionen, der Prozess erfordert einige zusätzliche Schritte.

    Sehen meine Antwort hier für eine Diskussion dessen, was beteiligt ist. Die Antwort hat auch noch ein paar Proben-code Antworten verknüpft.

    Auch, in Ihrer Klasse definition, wenn Sie möchten, dass bestimmte Funktionen, die verwendet werden auf dem Gerät, sollten Sie schmücken diese Funktionen angemessen (d.h. wahrscheinlich mit __device__ __host__);

    EDIT: In der Antwort auf eine Frage (jetzt gelöscht) hier ist das einfachste Beispiel-code, den ich kommen könnte, basierend auf den gelieferten code:

    #include <stdio.h>

class CudaClass
{
public:
int* data;
CudaClass(int x) {
    data = new int[1]; data[0] = x;
}
};

__global__ void useClass(CudaClass *cudaClass)
{
    printf("%d\n", cudaClass->data[0]);
};




int main()
{
    CudaClass c(1);
    //create class storage on device and copy top level class
    CudaClass *d_c;
    cudaMalloc((void **)&d_c, sizeof(CudaClass));
    cudaMemcpy(d_c, &c, sizeof(CudaClass), cudaMemcpyHostToDevice);
    //make an allocated region on device for use by pointer in class
    int *hostdata;
    cudaMalloc((void **)&hostdata, sizeof(int));
    cudaMemcpy(hostdata, c.data, sizeof(int), cudaMemcpyHostToDevice);
    //copy pointer to allocated device storage to device class
    cudaMemcpy(&(d_c->data), &hostdata, sizeof(int *), cudaMemcpyHostToDevice);
    useClass<<<1,1>>>(d_c);
    cudaDeviceSynchronize();
    return 0;
}

    Im Interesse der Kürze/übersichtlichkeit habe ich darauf verzichtet, die üblichen cuda Fehler überprüfen.

    Beantwortung der Frage, können Sie Speicherplatz zuweisen, der direkt von dem host unter Verwendung der Zeiger in der device-Klasse. Dies ist, weil cudaMalloc erwartet ein gewöhnlicher host-based-Zeiger-Speicher, wie das, was du mit:

    int *hostdata;

    cudaMalloc können mit einem Zeiger, dessen Speicherung ist bereits auf dem Gerät. Das wird nicht funktionieren:

    cudaMalloc(&(d_c->data), sizeof(int));

    da es erfordert die Dereferenzierung eines Geräts Zeiger (d_c) in host-code, der nicht erlaubt ist.

    • ok nur noch eine Frage: Was ich sehe, ist, dass Sie allozieren von Speicher auf dem Gerät, dann kopieren Sie den Zeiger-Wert, um das array in das Objekt. Warum kann ich nicht zuordnen, für myobject.array direkt anstelle der Verwendung eines "mittleren" - variable für die Daten, und kopieren Sie den Zeiger in myobject.array?
    • Diese Frage beantwortet ein edit zu meiner Antwort. Ich glaube, ich habe bereits angesprochen, wie diese Frage auch in Fragen gepostet, nachdem einer der verlinkten Antworten.
    • Danke so viel, sehr klare Antwort ! Noch eine Frage wenn ich darf: Warum kann ich das nicht CudaMalloc((void**)&Daten, 100*sizeof(int)) Im Konstruktor anstelle von data = new int[100] ? Ich dachte, dass sollte zuweisen auf dem Gerät, sondern direkt auf dem host dann auf Gerät kopieren. Cheers
    • Sie könnte das tun, ich erinnere mich nicht, sagen Sie es nicht konnte. Allerdings haben Sie dann ein host-based-Klasse mit einem Zeiger auf device-basierte storage - (nur). Solche Speicher konnte nicht initialisiert werden auf dem host, die Art, wie Ihre aktuelle Klasse definition tut: data[0]=x; Sie konnte immer noch cudaMemset vielleicht, oder etwas wesentlich komplizierter im Konstruktor. Du bist einfach der Zusammenfassung einige der code, den ich geschrieben habe in den Konstruktor, wenn Sie das tun. Live it up.
    • Ich hoffe, Sie können klären, die fahne hier cudaMemcpy(&(d_c->data), &hostdata, sizeof(int *), cudaMemcpyHostToDevice); warum nicht mit cudaMemcpyDeviceToDevice? Ich finde beide Zeiger sind auf dem Gerät
    • hostdata enthält einen Zeiger auf device memory. Aber &hostdata ist ein Zeiger auf eine Stelle in dem host-Speicher. Also Nein, der Zeiger ist nicht "auf das Gerät" und es nicht auf einen Punkt "auf dem Gerät". &hostdata Punkte auf eine Stelle in dem host-Speicher. hostdata verweist auf eine Position im Speicher des Gerätes.
    • Wie würden Sie gehen über das kopieren der class-Objekt und seine Daten zurück? Ich habe versucht, genau dies zu tun für ein paar Tage jetzt...
    • Für diese trivial einfach Klasse in diesem problem, das einzige, was notwendig wäre, um in umgekehrter cudaMemcpy operation, die Kopien der eigentlichen Daten, also, nach dem kernel, so etwas wie: cudaMemcpy(c.data, hostdata, sizeof(int), cudaMemcpyDeviceToHost);. Ein komplizierter Gegenstand würde wahrscheinlich erfordern mehrere Schritte. Da eine direkte Kopie des Objekts selbst vom Gerät zurück zum host ungültig machen würden die eingebetteten Zeiger in das Objekt, das Sie einen Weg brauchen würde, zu erhalten oder zu "reparieren" diese Zeiger, viel die gleiche Weise wie diese Antwort zeigt, "reparieren" die embedded-Zeiger in der device-Objekt.

    InformationsquelleAutor Robert Crovella
Schreibe einen Kommentar