Передача данных с устройства на хост
Загружайте результаты обратно на CPU.
«Передача данных с устройства на хост» — бесплатный урок 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 — локальная установка не требуется.
Все уроки этого курса
- Передача данных с хоста на устройство
- Передача данных с устройства на хост
- Перечисление направления копирования
- Узкое место передачи через PCIe