Не должно быть проблем с записью в единый буфер памяти из нескольких потоков.
Однако имейте в виду ограничения, налагаемые, когда свойство устройства concurrentManagedAccess равно , а не верно.В этом случае, когда у вас есть управляемый буфер и вы запускаете ядро, доступ к любому потоку ЦП / хосту любого типа, к этому буферу или любому другому управляемому буферу, не разрешен, , пока вы не выполните a cudaDeviceSynchronize() после вызова ядра.
В многопоточной среде это может потребовать некоторых явных усилий для обеспечения выполнения.
Я думаю, что это похоже на этот концерт , если этотакже ваша публикация.Обратите внимание, что для TX2 это свойство должно быть установлено в значение false.
Обратите внимание, что это общее правило в неконкурентном случае можно изменить путем осторожного использования streams .Однако ограничения по-прежнему применяются к буферам, прикрепленным к потокам, в которых запущено ядро (или к буферам, явно не привязанным к какому-либо потоку): когда указанное выше свойство имеет значение false, доступ к любому потоку ЦП невозможен.
Мотивация такого поведения примерно следующая.Среда выполнения CUDA не знает взаимосвязи между управляемыми буферами, независимо от того, где эти буферы были созданы.Буфер, созданный в одном потоке, может легко содержать объекты со встроенными указателями, и ничто не мешает указателям указывать на данные в другом управляемом буфере.Даже буфер, который был создан позже.Даже буфер, который был создан в другом потоке.Безопасное предположение состоит в том, что любые связи могут быть возможны, и, следовательно, без каких-либо других согласований подсистема управляемой памяти в среде выполнения CUDA должна перемещать все управляемые буферы в графический процессор при запуске ядра.Это делает все управляемые буферы, без исключения, недоступными для потоков ЦП (любой поток, где угодно).В обычном потоке программы доступ восстанавливается при следующем вызове cudaDeviceSynchronize ().Как только поток ЦП, который выдает этот вызов, завершает вызов и продолжает работу, управляемые буферы снова становятся видимыми (всем) потокам ЦП.Другой запуск ядра (где угодно) повторяет процесс и прерывает доступ.Повторим, что этот механизм действует, когда свойство concurrentManagedAccess в графическом процессоре имеет значение , а не true, и это поведение может быть несколько изменено с помощью вышеупомянутого механизма присоединения потока.