CUDA Academy · Урок

Передача данных с устройства на хост

Загружайте результаты обратно на CPU.

Урок 2 из 413 шагов

«Передача данных с устройства на хост» — бесплатный урок CUDA Academy на CoddyKit. Это урок 2 из 4. Ты можешь прочитать весь урок бесплатно ниже — а потом практиковать его прямо в браузере с встроенным редактором кода и ИИ-репетитором 24/7. Это часть пути обучения CUDA Academy, и твой прогресс синхронизируется между веб-версией и приложением CoddyKit. Курс CUDA Academy содержит 4 уроков всего.

Возвращаем результаты

Ваше ядро только что заполнило буфер устройства результатами, но CPU не может напрямую читать память GPU. Необходимо загрузить результаты обратно. 📥

Направление выгрузки

Чтобы получить данные обратно, используйте cudaMemcpyDeviceToHost. Теперь источник — память устройства, а назначение — RAM хоста.

cudaMemcpy(h_c, d_c, bytes, cudaMemcpyDeviceToHost);

Назначение по-прежнему указывается первым

Правило не меняется: сначала аргумент назначения, затем источник. При выгрузке первым указывается указатель хоста.

cudaMemcpy(h_dst, d_src, bytes, cudaMemcpyDeviceToHost);

Буфер хоста должен существовать

Для назначения должна быть подготовлена настоящая память CPU. Выделите хранилище хоста с помощью malloc или new до обратного копирования.

float* h_c = (float*)malloc(bytes);

Дождитесь завершения ядра

Блокирующий cudaMemcpy ожидает завершения предыдущей работы в стандартном потоке, поэтому ядро завершится до чтения результатов.

myKernel<<<blocks, threads>>>(d_c, n);
cudaMemcpy(h_c, d_c, bytes, cudaMemcpyDeviceToHost);

То же количество байтов

Выгружайте ровно столько байтов, сколько было загружено и обработано. Несовпадение размеров приводит к усечённым или бессмысленным результатам.

size_t bytes = n * sizeof(float);

Теперь их можно прочитать

После завершения копирования значения находятся в обычной памяти CPU. Вы можете вывести, проверить или сохранить их как любой другой массив хоста.

printf("%f\n", h_c[0]);

Полный цикл

Полная задача на GPU — это полный цикл: загрузить входные данные, запустить ядро, затем выгрузить результаты. Для каждого этапа используется cudaMemcpy.

Проверяйте, прежде чем доверять

После загрузки сравните результат GPU с быстрым эталонным вычислением на CPU. Проверка выявляет ошибки, прежде чем они начнут распространяться. ✅

Освобождайте выделенную память

Когда результаты вернулись на хост, освободите память с обеих сторон: вызовите cudaFree для буфера устройства и освободите буфер хоста, чтобы избежать утечек.

cudaFree(d_c);
free(h_c);

Загрузка тоже требует времени

Обратный путь проходит по той же медленной шине, поэтому копируйте обратно только те результаты, которые действительно нужны на хосте.

Быстрая проверка

Ваше ядро записало результаты в буфер устройства d_c. Как прочитать их на CPU?

Итоги

Вы изучили обратную передачу с помощью cudaMemcpyDeviceToHost: выделите память на хосте, укажите сначала указатель хоста, дождитесь завершения ядра, затем проверьте результат и освободите память. 🎉

Можно начать бесплатно

Изучай C++ с ИИ-репетитором — бесплатно

Пиши и запускай код прямо в браузере, получай мгновенную помощь от ИИ-репетитора 24/7 и продолжи учиться на сайте или в приложении.

Курсы
30
Уроки
120

Часто задаваемые вопросы

Урок «Передача данных с устройства на хост» бесплатный?

Да — полный текст урока «Передача данных с устройства на хост» бесплатно доступен здесь в веб-версии. Чтобы практиковать его интерактивно (встроенный редактор кода и ИИ-репетитор 24/7) и разблокировать остальной курс CUDA Academy, подпишись на CoddyKit PRO. Курс CUDA Academy содержит 4 уроков всего.

Чему я научусь в уроке «Передача данных с устройства на хост»?

Загружайте результаты обратно на CPU. Ты практикуешь CUDA Academy с помощью реального кода, который запускаешь прямо в браузере, и ИИ-репетитор 24/7 отвечает на твои вопросы во время урока.

Нужен ли мне опыт, чтобы начать CUDA Academy?

Предыдущий опыт не требуется. CUDA Academy на CoddyKit структурирован для всех уровней — от новичков до продвинутых, поэтому ты можешь начать отсюда или с самого начала и учиться в своем темпе. Это урок 2 из 4.

Сколько времени занимает урок «Передача данных с устройства на хост»?

Большинство уроков CoddyKit занимают около 5–10 минут. Каждый из них компактный и интерактивный, поэтому ты постоянно делаешь прогресс и продолжаешь с того же места в веб-версии и приложении.

Можно ли писать и запускать код в этом уроке CUDA Academy?

Да. Каждый урок CUDA Academy включает встроенный редактор кода, поэтому ты пишешь и запускаешь реальный код прямо в браузере и получаешь моментальную обратную связь от AI — локальная установка не требуется.

Все уроки этого курса

  1. Передача данных с хоста на устройство
  2. Передача данных с устройства на хост
  3. Перечисление направления копирования
  4. Узкое место передачи через PCIe
← Назад к CUDA Academy