Çözülme oyu işlevi hakkında

Question

CUDA programlama rehberi, "_ hepsi", " _any" ve "__ballot" gibi warp oylama işlevi kavramını tanıttı.

Soruma sorum: bu 3 işlevi hangi uygulamalar kullanacak?

Answer 1

__ballotCUDA-histogram ve değerleri bir bit maskesi hızlı nesil için CUDA NPP kütüphanesinde kullanılmakta ve içsel __popc birleştirerek boolean azalma çok verimli olarak yürütülebilmesi amacıyla.

__all ve __any, __ballot girişinden önce indirgemede kullanıldı, ancak bunların başka bir kullanımını düşünemiyorum.

Answer 2

__ballot prototipi predicate sıfır ise, __ballotN iplik endeksidir N inci bit kümesi, bir değer döndürür aşağıdaki

unsigned int __ballot(int predicate); 

olduğunu.

atomicOr ve __popc ile birlikte, her bir çözgüdeki iş parçacığı sayısını gerçek bir yüklemeye sahip olarak biriktirmek için kullanılabilir.

Nitekim atomicOr prototipi

int atomicOr(int* address, int val); 

ve atomicOr, değer address tarafından işaret okur val ile arasında ikilik OR işlemi gerçekleştirir ve address geri değerini yazar ve bir şekilde eski değerini döndürür dönüş parametresi.

Diğer tarafta, __popc, 32 -bit parametresiyle ayarlanan bit sayısını döndürür.

Bu duruma göre, kullanım talimatları

volatile __shared__ u32 warp_shared_ballot[MAX_WARPS_PER_BLOCK]; 

const u32 warp_sum = threadIdx.x >> 5; 

atomicOr(&warp_shared_ballot[warp_num],__ballot(data[tid]>threshold)); 

atomicAdd(&block_shared_accumulate,__popc(warp_shared_ballot[warp_num])); 

yüklemi doğru olduğu parçacığı sayısını saymak için kullanılabilir.

fazla ayrıntı için, i D.M. Hughes ve Al tarafından In-Çekirdek Akışı Kompaksiyonu söz ediyorum __ballot API kullanır algoritmanın bir örnek olarak Shane Cook, CUDA Programlama Morgan Kaufmann

Answer 3

bakın. Önek toplamını, önceliği geçen öğelerin sayısını (çözgü başına) saymak için akış sıkıştırmasının bir parçası olarak kullanılır.

Here the paper. In-k Stream Compaction