2

我正在用cuFFT试验批次。但我不认为我得到了正确的输出。

int NX = 16;    // size of the array
int BATCH = 16; // # of batch

我在 GPU 上分配两个数组:

float *src;
cufftComplex *dst;
cudaMalloc((void**)&src, sizeof(float)*NX*BATCH);
cudaMalloc((void**)&dst, sizeof(cufftComplex)*NX*BATCH);

我正在使用这样的简单内核初始化源数组:

__global__ void initFloatArray(float *data, const int size) {
  const int i = (blockIdx.x * blockDim.x) + threadIdx.x;
  if (i < size) {
    data[i] = i % NX;
  }
}

所以基本上,每个数组都有从 0 到 15 的值。我得到了 16 次。

我这样制定我的计划:

cufftPlanMany(&plan, 1, &NX, nullptr, 1, NX, nullptr, 1, NX, CUFFT_R2C, BATCH);

然后我正在执行我的计划:

cufftExecR2C(plan, src, dst);

最后,我将dst的内容传回主机。但是当我打印出这些值时,我得到了这个:

 BATCH 0:
  <120, 0>.length = 120
  <-8, 40.2187>.length = 41.0066
  <-8, 19.3137>.length = 20.905
  <-8, 11.9728>.length = 14.3996
  <-8, 8>.length = 11.3137
  <-8, 5.34543>.length = 9.62152
  <-8, 3.31371>.length = 8.65914
  <-8, 1.5913>.length = 8.15673
  <-8, 0>.length = 8
  <120, 0>.length = 120
  <-8, 40.2187>.length = 41.0066
  <-8, 19.3137>.length = 20.905
  <-8, 11.9728>.length = 14.3996
  <-8, 8>.length = 11.3137
  <-8, 5.34543>.length = 9.62152
  <-8, 3.31371>.length = 8.65914
 BATCH 1:
  <-8, 1.5913>.length = 8.15673
  <-8, 0>.length = 8
  <120, 0>.length = 120
  <-8, 40.2187>.length = 41.0066
  <-8, 19.3137>.length = 20.905
  <-8, 11.9728>.length = 14.3996
  ...

我期待一个重复的输出,但它每 9 个数字重复一次,而不是应该的每 16 个重复。

难道我做错了什么?或者有什么我不明白的。

4

1 回答 1

3

实值信号的 DFT 表现出 Hermitian 对称性(参见wikipedia 上的实输入 DFT)。因此,点 DFT 的完整N复数输出值N可以仅由第一个N/2+1输出值构成(即其他输出是冗余的)。

相应地,与许多实值输入的 FFT 实现一样,cuFFT 不会返回频谱的冗余上部(如cuFFT 库用户指南的第 2.4 节所示)。在您使用 16 点 FFT 的情况下,您将因此获得16/2 + 1 = 9非冗余输出。然后每个 FFT 的这 9 个值在您的最终缓冲区中背靠背地打包dst(因此每 9 个复数开始一个新的 FFT 结果)。

于 2016-01-23T00:56:13.383 回答