• コマンドプロンプトで、 aoc -list-boards コマンドを呼び出します。
  インテル^® FPGA SDK for OpenCL™オフライン・コンパイラーは、以下のような出力を生成します。

  Board list: <board_name_1> <board_name_2>
  ...

  この <board_name_N> は、特定のFPGAボードをターゲットにするためにaocコマンドで使用するボード名です。

• 複数のカスタム・プラットフォームがインストールされている場合に、特定のカスタム・プラットフォームで利用可能なFPGAボードの一覧を表示するには、-board-package=<custom_platform_path> オプションをaocコマンドに含めます。コマンドプロンプトで、次のようにコマンドを呼び出します。

  aoc -board-package=<custom_platform_path> -list-boards

  インテル^® FPGA SDK for OpenCL™オフライン・コンパイラーは、カスタム・プラットフォームで利用可能なボードの一覧を表示します。
• システムで利用可能なカスタム・プラットフォームを一覧表示するには、-list-board-packagesオプションをaocコマンドに含めます。コマンドプロンプトで、 aoc -list-board-packages コマンドを呼び出します。
  インテル^® FPGA SDK for OpenCL™オフライン・コンパイラーは、次のような出力を生成します。

  Installed board packages:
  <board_package_1>
  <board_package_2>
  ...
  Board packages shipped with Intel(R) FPGA SDK for OpenCL(TM):
  <board_package_3>
  <board_package_4>
  ...

  この <board_package_N> は、ご自身のシステムにインストールされているカスタム・プラットフォームのボードパッケージ、または、 インテル^® FPGA SDK for OpenCL™ に同梱されているボードパッケージです。

1. ボードメーカーが案内している手順に従い、FPGAボードをシステムに接続します。
2. ボードメーカーのWebサイトから、ご自身のFPGAボード用のカスタム・プラットフォームをダウンロードします。 インテル^® FPGA SDK for OpenCLリファレンス・プラットフォームのダウンロードついては、 インテル^® FPGA SDK for OpenCLプラットフォームのページを参照ください。
   ヒント: インテル^® FPGA SDK for OpenCL™ とともに提供されているBSP (a10_ref、 s10_ref、a10socなど) をインストールする場合は、カスタム・プラットフォームのインストールは不要です。BSPファイルは、 INTELFPGAOCLSDKROOT/hld/boardsにあります。手順4 に進んでください。
3. システムフォルダー以外の任意のフォルダーにカスタム・プラットフォームをインストールします。

   複数のカスタム・プラットフォームでのaocl diagnoseなど、SDKユーティリティーを使用し、同じシステムに複数のカスタム・プラットフォームを同時にインストールできます。カスタム・プラットフォームのサブディレクトリーは、board_env.xmlファイルを含みます。

   複数のカスタム・プラットフォームがあるシステムでは、カスタム・プラットフォームのメモリーマップド・デバイス (MMD) ライブラリー・ディレクトリーに直接リンクするのではなく、ホストプログラムがFPGAクライアント・ドライバー (FCD) を使用しボードを検出するようにしてください。FCDがカスタム・プラットフォームに対し正しく設定されている限り、FCDはインストールされているボードすべてをランタイムに検出します。

4. QUARTUS_ROOTDIR_OVERRIDEユーザー環境変数が、 インテル^® Quartus^® Prime開発ソフトウェア・プロ・エディションのソフトウェアのインストール・ディレクトリーを指定するように設定します。
5. カスタム・プラットフォーム・ライブラリーへのパス (ボード・サポート・パッケージのMMDライブリーへのパスであれば、<path_to_customplatform>/windows64/binなど) を、PATH (Windows) もしくはLD_LIBRARY_PATH (Linux) 環境変数設定に追加します。
   インテル^® FPGA SDK for OpenCL™ スタート・ガイドは、init_openclスクリプトに関するより詳細な情報を提供しています。ユーザー環境変数の設定およびinit_openclスクリプトの実行に関しては、 インテル^® FPGA SDK for OpenCL™ ユーザー環境変数の設定 の章を参照ください。
6. コマンドプロンプトで、 aocl install <path_to_customplatform> を呼び出します。
   aocl install <path_to_customplatform> を呼び出すと、FCDとボードドライバーがインストールされ、ホスト・アプリケーションとハードウェアのカーネルプログラムの通信が可能になります。

   要確認:

   • ボードのインストールには管理者権限が必要です。Windowsコマンドプロンプトを管理者として実行するには、Start > All Programs > Accessoriesをクリックします。AccessoriesのCommand Promptを右クリックし、右クリックメニューにあるRun as Administratorをクリックします。

     Windows 8.1またはWindows 10のシステムでは、署名付きドライバーの検証を無効にしなければならない場合があります。詳細については以下の内容を参照してください。

     • Windows 8: https://www.intel.com/content/altera-www/global/en_us/index/support/support-resources/knowledge-base/solutions/fb321729.html
     • Windows 10: https://www.intel.com/content/altera-www/global/en_us/index/support/support-resources/knowledge-base/embedded/2017/Why-does-aocl-diagnose-fail-while-using-Windows-10.html
   • システムにドライバーがすでにインストールされており、管理者権限なしでFCDをインストールする必要がある場合、以下のようにaocl installコマンドを-fcd-onlyフラグとともに呼び出し、FCDインストールのプロンプトに従ってください。

     aocl install <path_to_customplatform> -fcd-only

7. ご自身のマシンにインストールされたFPGA デバイスのリストを照会するには、 aocl diagnose コマンドを呼び出します。
   ソフトウェアは、<device_name> を含む出力を生成します。<device_name> は、acl0からacl127のacl番号です。

   重要: aocl diagnoseユーティリティーを実装した後に発生する可能性があるエラーに関しては、Intel Arria 10 GX FPGA Development Kit Reference Platform Porting Guideの、Possible Errors After Running the diagnose Utilityの章を参照ください。ご自身のアクセラレーター・ボードの <device_name> の照会に関しては、FPGAボードのデバイス名の照会の章を参照ください。
8. FPGAボードが正常にインストールされていることを確認するには、 aocl diagnose <device_name> コマンドを呼び出し、ボードメーカーが推奨する診断テストを実行します。

1. ボードメーカーから提供されている手順に従い、マシンからボードを外します。
2. aocl uninstall <path_to_customplatform> ユーティリティー・コマンドを呼び出し、現在のホスト・コンピューター・ドライバーを削除します (PCIe^®ドライバーなど)。 インテル^® FPGA SDK for OpenCL™ は、FPGAボードと通信するためにそれらのドライバーを使用します。
   要確認:

   • カスタム・プラットフォームのアンインストールには、root権限が必要です。ドライバーを維持しながらインストールされているFCDを削除するには、以下のように aocl uninstall コマンドを-fcd-onlyフラグとともに呼び出し、FCDのアンインストールのプロンプトに従ってください。

     aocl uninstall <path_to_customplatform> -fcd-only

   • Linuxシステムにおいて、FCDをデフォルト・ディレクトリーである/ opt / Intel / OpenCL / Boards /以外の特定のディレクトリーにインストールした場合、アンインストールを実行する前に、環境変数ACL_BOARD_VENDOR_PATHが、その特定のFCDのインストール・ディレクトリーを指すよう設定されていることを確認してください。
3. カスタム・プラットフォームをアンインストールします。
4. LD_LIBRARY_PATH環境変数 (Linuxの場合) またはPATH環境変数 (Windowsの場合) の設定を解除します。

• ファイル名は英数字で始めてください。
  OpenCL™アプリケーションのファイル名が英数字以外で始まっている場合、以下のコンパイルエラーが発生します。

  Error: Quartus compilation FAILED
  See quartus_sh_compile.log for the output log.

• 英数字以外の文字を使用しファイル名を区別しないでください。
  インテル^® FPGA SDK for OpenCL™オフライン・コンパイラーは、英数字以外の文字をアンダースコア ( _ ) に変換します。ファイル名の末尾のみを英数字以外の異なる文字にし、2つのファイルを区別すると (例えば、myKernel＃.clとmyKernel＆.clなど)、オフライン・コンパイラーはその2つのファイル名をどちらも、<your_kernel_filename> _.cl (前述の例の場合、myKernel_.cl) に変換します。
• Windowsシステムの場合、カーネルファイル名とそのファイルパスの合計文字数が260文字を超えないようにしてください。
  64ビットのWindows 7およびWindows 8.1には、ファイルパスの長さに260文字の制限があります。カーネルファイル名とそのファイルパスの合計文字数が260文字を超えると、オフライン・コンパイラーは次のエラーメッセージを生成します。

  The filename or extension is too long. The system cannot find the path specified.

  コンパイラーのエラーメッセージに加え、次のメッセージが <your_kernel_filename>/quartus_sh_compile.log ファイルに表示されます。

  Error: Can’t copy <file_type> files: Can’t open 
  <your_kernel_filename> for write: No such file or directory

  Windows 10では、260文字の制限を除外することができます。詳しくは、Windows 10の資料を参照してください。

• OpenCLのカーネル・ソースファイル (.cl) に、予約されているキーワードである「kernel」、「Verilog」、または「VHDL」の名前を付けないでください。
  ソースファイルにkernel.cl、Verilog.cl、またはVHDL.clの名前を付けると、オフライン・コンラパイラーは特定の内部ファイルと同じ名前の中間デザインファイルを生成するため、コンパイルエラーが発生します。

• 可能な限り展開係数を指定してください。展開係数Nを指定するには、#pragma unroll <N> ディレクティブをカーネルコードのループの前に挿入します。
  オフライン・コンパイラーは、ループ展開を最大 <N> 回試みます。
  コードの一部を下記に示します。展開係数に2の値を割り当てることにより、ループを2回展開するよう、オフライン・コンパイラーに指示しています。

  #pragma unroll 2
  for(size_t k = 0; k < 4; k++)
  {
     mac += data_in[(gid * 4) + k] * coeff[k];
  }

• ループを完全に展開する場合、カーネルコードのループの前に#pragma unrollディレクティブのみを挿入し、展開係数を省略することができます。
  オフライン・コンパイラーは、トリップカウントを認識すると完全なループ展開を試みます。展開要求が実行できない場合、オフライン・コンパイラーは警告を発行します。
• ループが展開されないようにするには、展開係数に1を指定します (＃pragma unroll 1)。

• カーネルのワークグループに向けてオフライン・コンパイラーが規定するワークアイテムの最大数を指定するには、max_work_group_size(X, Y, Z) 属性をカーネルのソースコードに挿入します。
  例:

  __attribute__((max_work_group_size(512,1,1)))
  __kernel void sum (__global const float * restrict a, __global const float * restrict b, __global float * restrict answer)
  {
   size_t gid = get_global_id(0);
   answer[gid] = a[gid] + b[gid];
  }

• カーネルのワークグループにオフライン・コンパイラーが規定するワークアイテムの必要数を指定するには、reqd_work_group_size(X, Y, Z) 属性をカーネルのソースコードに挿入します。
  例:

  __attribute__((reqd_work_group_size(64,1,1)))
  __kernel void sum (__global const float * restrict a,
                     __global const float * restrict b,
                     __global float * restrict answer)
  {
      size_t gid = get_global_id(0);
      answer[gid] = a[gid] + b[gid];
  }

• 以下の規則を使用し、カーネルのソースコードにファイルスコープ変数としてチャネルのハンドルを宣言します。channel <type> <variable_name>
  例: channel int c;
• インテル^® FPGA SDK for OpenCL™ のチャネル拡張は、データ構造で宣言された複数の変数による同時チャネルアクセスをサポートします。次の方法で、structデータ構造をチャネルに宣言します。

  typedef struct type_ {
      int a;
      int b;
  } type_t;
  
  channel type_t foo;
  

1. カスタム・プラットフォームのboard_spec.xmlファイルを参照し、ご自身のFPGAボードで使用可能な入力および出力フィーチャーを特定してください。

   例えば、board_spec.xmlファイルには次のようなI/Oフィーチャー情報が含まれています。

   <channels>
     <interface name="udp_0" port="udp0_out"  type="streamsource" width="256"
      chan_id="eth0_in"/>
     <interface name="udp_0" port="udp0_in"  type="streamsink" width="256"
      chan_id="eth0_out"/>
     <interface name="udp_0" port="udp1_out"  type="streamsource" width="256"
      chan_id="eth1_in"/>
     <interface name="udp_0" port="udp1_in"  type="streamsink" width="256"
      chan_id="eth1_out"/>
   </channels>

   interface要素のwidth属性は、そのチャネルで使用されるデータタイプの幅をビットで指定します。上の例の場合、uintとfloatのデータタイプはどちらも32ビット幅です。他のより大きいデータタイプやベクトル化されたデータタイプは、board_spec.xmlファイルで指定されている適切なビット幅と一致している必要があります。

2. 次のコード例で示されているようにioチャネル属性を実装します。ioチャネル属性の名前は、board_spec.xmlファイルで指定されているI/Oチャネル名 (chan_id) と一致していなければなりません。

   channel QUDPWord udp_in_IO __attribute__((depth(0)))
                              __attribute__((io("eth0_in"))); 
   channel QUDPWord udp_out_IO __attribute__((depth(0)))
                               __attribute__((io("eth0_out"))); 
   
   __kernel void io_in_kernel (__global ulong4 *mem_read,
                               uchar read_from,
                               int size) 
   {
     int index = 0;
     ulong4 data;
     int half_size = size >> 1;
     while (index < half_size)
     {
       if (read_from & 0x01)
       {
         data = read_channel_intel(udp_in_IO);
       } 
       else
       {
         data = mem_read[index];
       }
       write_channel_intel(udp_in, data);
       index++;
     }
   }
   
   __kernel void io_out_kernel (__global ulong2 *mem_write,
                                uchar write_to,
                                int size)
   {
     int index = 0;
     ulong4 data;
     int half_size = size >> 1;
     while (index < half_size)
     {
       ulong4 data = read_channel_intel(udp_out);
       if (write_to & 0x01)
       {
         write_channel_intel(udp_out_IO, data);
       }
       else
       {
         //only write data portion
         ulong2 udp_data;
         udp_data.s0 = data.s0;
         udp_data.s1 = data.s1;
         mem_write[index] = udp_data;
       }
       index++;
     }
   }

   重要: board_spec.xmlファイルの、XML (eXtensible Markup Language) チャネル要素で指定されている各I/Oチャネルに、固有のio("chan_id") ハンドルを宣言してください。

1. カスタム・プラットフォームのboard_spec.xmlファイルを確認し、FPGAボードで使用可能な入力および出力フィーチャーを特定ください。

   例えば、board_spec.xmlファイルには、I/Oフィーチャーに関する次のような情報が含まれています。

   <channels>
     <interface name="udp_0" port="udp0_out"  type="streamsource" width="256"
      chan_id="eth0_in"/>
     <interface name="udp_0" port="udp0_in"  type="streamsink" width="256"
      chan_id="eth0_out"/>
     <interface name="udp_0" port="udp1_out"  type="streamsource" width="256"
      chan_id="eth1_in"/>
     <interface name="udp_0" port="udp1_in"  type="streamsink" width="256"
      chan_id="eth1_out"/>
   </channels>

   interface要素のwidth属性は、そのパイプで使用されるデータの型の幅をビット単位で指定します。上記例の場合、uintとfloatのデータ型はどちらも32ビット幅です。その他のより大きなデータ型や、ベクトル化されたデータ型は、board_spec.xmlファイルで指定されている適切なビット幅に一致している必要があります。

2. 次のコード例で示されているようにio属性を実装します。io属性名は、board_spec.xmlファイルで指定されているI/Oチャネル名 (chan_id) に一致しなければなりません。

   __kernel void test (pipe uint pkt   __attribute__((io(“enet”))),;
                       pipe float data __attribute__((io(“pcie”))));

   重要: board_spec.xmlファイル内のチャネルのXML要素で指定されている各I/Oパイプに、固有のio("chan_id") ハンドルを宣言してください。

• デバイス固有のコード (例えばFPGA_board_1) をカーネルプログラムに含めるには、カーネルプログラムを次のように構成します。

  #if defined(AOCL_BOARD_FPGA_board_1)
      //FPGA_board_1-specific statements
  #else
      //FPGA_board_2-specific statements
  #endif

  カーネルのコンパイルを特定のボードに対して行うと、定義済みプリプロセッサー・マクロAOCL_BOARD_<board_name> が1に設定されます。<board_name> がFPGA_board_1の場合、 インテル^® FPGA SDK for OpenCL™オフライン・コンパイラーは、FPGA_board_1に固有のパラメーターとフィーチャーをコンパイルします。
• インテル^® FPGA SDK for OpenCL™オフライン・コンパイラー固有のコンパイラー・フィーチャーと最適化を導入するには、カーネルプログラムを次のように構成します。

  #if defined(INTELFPGA_CL)
      //statements
  #else
      //statements
  #endif

  このINTELFPGA_CLは、 インテル^® にて定義済みのオフライン・コンパイラー用のプリプロセッサー・マクロです。

グローバル・メモリー・バッファーを手動で分割すると、バッファー間のメモリーアクセスを制御し、メモリー帯域幅を最大化することができます。バッファーの分割は、同じメモリータイプのインターフェイス間、または異なるメモリータイプのインターフェイス間で行うことが可能です。

1. OpenCLカーネルを -no-interleaving=<global_memory_type> フラグでコンパイルし、指定されたメモリータイプのメモリーバンクを個別のアドレスでコンフィグレーションします。 -no-interleaving=<global_memory_type> フラグの使用方法に関しては、グローバルメモリーのバーストインターリーブの無効化 (-no-interleaving=<global_memory_type>) の章を参照ください。
2. ホスト・アプリケーションにOpenCLバッファーを作成し、CL_CHANNELフラグでバッファーをいずれかのバンクへ割り当てます。
   • CL_CHANNEL_1_INTELFPGAを指定し、バッファーを使用可能な最下位メモリー領域に割り当てます。
   • CL_CHANNEL_2_INTELFPGAを指定し、メモリーを2番目のバンクに割り当てます (利用可能な場合)。
   重要: それぞれのバッファーは、単一メモリーバンクにのみ割り当ててください。ランタイムに2番目のバンクが利用できない場合、メモリーは1番目のバンクに割り当てられます。グローバルメモリーが利用できない場合は、clCreateBuffer呼び出しは失敗し、エラーメッセージCL_MEM_OBJECT_ALLOCATION_FAILUREが表示されます。

異種メモリーを使用するには、.clファイルのコードを次のように変更します。

1. 次のいずれかの方法で、FPGAボードで使用可能なグローバル・メモリー・タイプの名前を確認してください。
   • ボードメーカーの資料を参照する。
   • ボードのカスタム・プラットフォームのboard_spec.xmlファイルで名前を検索する。各グローバル・メモリー・タイプの名前は、global_mem要素のname属性に割り当てられた一意の文字列です。
2. 特定のグローバル・メモリー・タイプにバッファーを割り当てるようにホストに指示するには、buffer_location("<memory_type>") 属性を挿入します。ここで <memory_type> は、ボードメーカーより提供されているグローバル・メモリー・タイプの名前です。
   例

   __kernel void foo(__global __attribute__((buffer_location("DDR"))) int *x,
                     __global __attribute__((buffer_location("QDR"))) int *y)

   buffer_location属性を指定しない場合、ホストはバッファーをデフォルトのメモリータイプに自動的に割り当てます。デフォルトのメモリータイプを確認するには、ボードメーカーから提供されている資料を参照してください。または、カスタム・プラットフォームのboard_spec.xmlファイルで、最初に定義されているメモリータイプもしくは、属性default=1が割り当てられたメモリータイプを検索します。

   インテルでは、次のようにbuffer_location属性をプリプロセッサー・マクロに定義し、再利用を容易にすることを推奨しています。

   #define QDR\
   __global __attribute__((buffer_location("QDR")))
   								
   #define DDR\
   __global __attribute__((buffer_location("DDR")))
   __kernel void foo (QDR uint * data, DDR uint * lup)
   {
   	//statements
   }							

   重要: カーネル引数をデフォルト以外のメモリーに割り当てる場合 (上記コードであればQDR uint * dataおよびDDR uint * lup)、その引数をconstantキーワードで宣言することはできません。さらに、その引数から派生するポインターでアトミック操作を実行することはできません。

clCreateProgramWithBinary関数を使用しOpenCLランタイムにカーネルをロードすると、デフォルトで、ホストはバッファーをメインメモリーに割り当てます。カーネルの呼び出し中にホストは、カーネル引数にバインドされている異種メモリーバッファーを、メインメモリーに自動的に再配置します。

3. 異種メモリーバッファーが最初にメインメモリーに割り当てられるのを防ぐには、clCreateBuffer関数を呼び出す際に、CL_MEM_HETEROGENEOUS_INTELFPGAフラグを含めます。また、 clSetKernelArgを使用しcl_memバッファーをbuffer_location属性を使用した引数にまずバインドした後に、そのバッファーに対する読み取りまたは書き込みを実行してください。次に例を示します。

   mem = clCreateBuffer(context, flags|CL_MEM_HETEROGENEOUS_INTELFPGA,  memSize, NULL, &errNum);
   
   clSetKernelArg(kernel, 0, sizeof(cl_mem), &mem);
   clEnqueueWriteBuffer(queue, mem, CL_FALSE, 0, N, 0, NULL, &write_event);
   clEnqueueNDRangeKernel(queue, kernel, 1, NULL, global_work_size, NULL, 0, NULL, &kernel_event);

   例えば次のclCreateBuffer呼び出しは、デフォルト以外のメモリーバンクの、使用可能な最下位メモリー領域にメモリーを割り当てます。

   mem = clCreateBuffer(context,  (CL_MEM_HETEROGENEOUS_INTELFPGA|CL_CHANNEL_1_INTELFPGA), memSize,   NULL,   &errNum);

   clCreateBuffer呼び出しは、カーネル引数で指定した内容に基づき、メモリーを特定のグローバル・メモリー・タイプに割り当てます。メモリータイプにあるメモリー・オブジェクト (cl_mem) が、異なるメモリー・テクノロジーに対応するカーネル引数として設定されている場合、ホストはカーネルをキューする際にそのメモリー・オブジェクトを自動的に移動します。バッファーは複数のメモリー・テクノロジーに関連付けるカーネル引数として渡さないでください。

1. 構造体のコンテンツを格納するためのcl_memバッファーを割り当てます。
   重要: 異なる構造体の値を使用するカーネルごとに個別のcl_memバッファーが必要です。
2. 構造体のカーネル引数を、構造体のコンテンツへのポインターではなく、構造体のバッファーへのポインターで設定します。
3. カーネルをキューする前に構造体のバッファーのコンテンツを設定します。次のいずれかの手順を実行し、カーネルが起動する前に構造体のバッファーが設定されるようにします。
   • カーネルキューと同じコマンドキューに構造体バッファーをキューします。
   • 個別のカーネルキューと構造体のバッファーキューをイベントと同期させます。

4. アプリケーションが構造体バッファーを使用するカーネルを呼び出す必要がなくなった際には、cl_memバッファーを解放します。

1. コマンドプロンプトで aocl compile-config ユーティリティー・コマンドを呼び出します。
   ソフトウェアは、OpenCL™ APIヘッダーファイルが存在するフォルダーまたはディレクトリーへのパスを表示します。例えば、

   • Windowsシステムの場合、パスは-I%INTELFPGAOCLSDKROOT%/host/includeになります。
   • Linuxシステムの場合、パスは-I$INTELFPGAOCLSDKROOT/host/includeになります。

   このINTELFPGAOCLSDKROOTは、ソフトウェアのインストール位置を指します。

2. このパスを、Cプリプロセッサーに追加します。

1. オフライン・コンパイラーでOpenCLカーネルをコンパイルし.aocxファイルを作成します。
2. ホスト・アプリケーションにclCreateProgramWithBinary関数を含め、.aocxファイルからcl_program OpenCLプログラム・オブジェクトを作成します。
3. ホスト・アプリケーションにclBuildProgram関数を含め、指定したデバイスで実行可能なプログラムファイルを作成します。
   以下は、clCreateProgramWithBinaryを使用しFPGAデバイスをプログラムするホストコード例です。

   size_t lengths[1];
   unsigned char* binaries[1] ={NULL};
   cl_int status[1];
   cl_int error;
   cl_program program;
   const char options[] = "";
   
   FILE *fp = fopen("program.aocx","rb");
   fseek(fp,0,SEEK_END);
   lengths[0] = ftell(fp);
   binaries[0] = (unsigned char*)malloc(sizeof(unsigned char)*lengths[0]);
   rewind(fp);
   fread(binaries[0],lengths[0],1,fp);
   fclose(fp);
   
   program = clCreateProgramWithBinary(context,
                                       1,
                                       device_list,
                                       lengths,
                                       (const unsigned char **)binaries,
                                       status,
                                       &error);
   clBuildProgram(program,1,device_list,options,NULL,NULL);

   clBuildProgram関数が正常に実行されると、CL_SUCCESSが返されます。
4. clCreateKernelsInProgramまたはclCreateKernel関数を使用し、プログラム実行可能ファイルからカーネル・オブジェクトを作成します。
5. カーネルを実行するための関数を含め、スケジュールされたカーネルをFPGAで実行するようホストランタイムに指示します。
   • NDRangeカーネルを実行するためのコマンドをエンキューするには、clEnqueueNDRangeKernelを使用します。
   • 単一ワークアイテムのカーネルをエンキューするには、clEnqueueTaskを使用します。
   重要:

   インテルでは、使用されていないイベント・オブジェクトを解放することを推奨しています。SDKは、明示的な指示があるまでイベント・オブジェクトを解放せずに保持し続けます。使用していないイベント・オブジェクトを保持し続けると、不必要にメモリーが消費されます。

   イベント・オブジェクトの解放には、clReleaseEvent関数を呼び出します。

   複数のFPGAのプログラムをメモリーにロードすることができます。ホストはそれらを使用し、必要に応じてFPGAを再プログラムします。

• 共有メモリーの割り当てとアクセスには、次の例のようなホストコードを構築します。

  cl_mem src = clCreateBuffer(…, CL_MEM_ALLOC_HOST_PTR, size, …);
  int *src_ptr  = (int*)clEnqueueMapBuffer  (…, src, size, …);
  *src_ptr = input_value; //host writes to ptr directly
  clSetKernelArg (…, src);
  clEnqueueNDRangeKernel(…);
  clFinish();
  printf (“Result = %d\n”, *dst_ptr); //result is available immediately
  clEnqueueUnmapMemObject(…, src, src_ptr, …);
  clReleaseMemObject(src); // actually frees physical memory
  

  CONFIG_CMA_SIZE_MBYTESカーネル・コンフィグレーション・オプションを含め、割り当てに有効な共有メモリーの最大総量を制御することができます。実際には、割り当てられた共有メモリーの総量は、CONFIG_CMA_SIZE_MBYTESの値よりも小さくなります。
  重要:

  1. ターゲットボードに複数のDDRメモリーバンクがある場合、clCreateBuffer(..., CL_MEM_READ_WRITE, ...)関数は、メモリーを非共有DDRメモリーバンクに割り当てます。ただし、FPGAが共有メモリーである単一DDRバンクへアクセスできる場合、clCreateBuffer(..., CL_MEM_READ_WRITE, ...) は、CL_MEM_ALLOC_HOST_PTRフラグを使用するのと同様に、メモリーを共有メモリーに割り当てます。
  2. clCreateBuffer(..., CL_MEM_ALLOC_HOST_PTR, size, ...)関数で要求する共有メモリーは、Linux OpenCLカーネルドライバーに割り当てられ、Linuxカーネルの連続したメモリー割り当て (CMA) 機能に依存します。CMAを有効にしコンフィグレーションする方法に関しては、Intel FPGA SDK for OpenCL Intel Arria 10 SoC Development Kit Reference Platform Porting GuideのRecompiling the Linux Kernel for the Intel Arria 10 SoC Development Kit およびCompiling and Installing the OpenCL Linux Kernel Driverの章を参照ください。
• 共有ハード・プロセッサー・システム (HPS) DDRからFPGA DDRへの効率的なデータ転送に向け、memcpy関数を実行するカーネルを次のように含めます。

  __attribute__((num_simd_work_items(8)))
  mem_stream(__global uint * src, __global uint * dst)
  {
      size_t gid = get_global_id(0);
      dst[gid] = src[gid];
  }
  

  重要: CL_MEM_ALLOC_HOST_PTRフラグを使用し、srcポインターをHPS DDRに共有メモリーとして割り当てます。
• ホストがコンスタント・メモリーを共有HPS DDRシステムに割り当て、カーネル実行後にそれを変更すると、変更が有効にならない可能性があります。その結果、続くカーネル実行に古いデータが使用される可能性があります。カーネルの実行に古いコンスタント・メモリーが使用されないようにするため、次のいずれかを実行してください。
  1. コンスタント・メモリーの初期化後は、それを変更しない
  2. 複数の__constantデータセットが必要な場合、複数のコンスタント・メモリー・バッファーを作成する
  3. 可能であれば、アクセラレーター・ボードのFPGA DDRにコンスタント・メモリーを割り当てる

• 1つもしくは複数のカーネル・ソースファイルをコンパイルするには、コマンドプロンプトで aoc -rtl <your_kernel_filename1>.cl [<your_kernel_filename2>.cl ...]コマンドを呼び出します。
  この [ <your_kernel_filename2>.cl ...] は、カーネルのファイル名をスペースで区切ったもので、 <your_kernel_filename1>.clに加えオプションでコンパイル可能です。
  aocコマンドを-rtlフラグとともに呼び出すと、オフライン・コンパイラーはカーネルをコンパイルし、次のファイルとディレクトリーを作成します。

  • 各.clカーネル・ソースファイルの.aocoファイル。その後オフライン・コンパイラーはそれらをリンクし.aocrファイルを生成します。.aocoファイルまたは.aocrファイルの生成は、数秒から数分で行われます。
  • <your_kernel_filename> フォルダーまたはサブディレクトリー。これには、FPGAのプログラミングに必要なハードウェア・コンフィグレーション・ファイルを構築するためにSDKが使用する中間ファイルが含まれます。
• 1つ以上の.aocoオブジェクト・ファイルをコンパイルするには、 aoc -rtl <your_kernel_filename>.aoco [<your_kernel_filename2>.aoco ...]コマンドをコマンドプロンプトで呼び出します。
  この [ <your_kernel_filename2>.aoco ...] は、オブジェクト・ファイルのファイル名をスペースで区切ったもので、 <your_kernel_filename1>.aocoに加えオプションでコンパイル可能です。
  aocコマンドを-rtlフラグとともに呼び出すと、オフライン・コンパイラーは次のファイルとディレクトリーを作成します。

  • オフライン・コンパイラーはすべての.aocoファイルをリンクし、.aocrファイルを生成します。
  • <your_kernel_filename> フォルダーまたはサブディレクトリー。これには、FPGAのプログラミングに必要なハードウェア・コンフィグレーション・ファイルを構築するためにSDKが使用する中間ファイルが含まれます。

• 複数ステップでのコンパイルフローを実行する場合は、出力ファイル名を次のように指定します。
  1. 中間コンパイルの段階でオフライン・コンパイラーが作成する.aocoファイルの名前を指定するには、 aoc -rtl -o <your_object_filename>.aocr <your kernel_filename>.clコマンドを呼び出します。
  2. 最終コンパイルの段階でオフライン・コンパイラーが作成する.aocxファイルの名前を指定するには、 aoc -o <your_executable_filename>.aocx <your_object_filename>.aocrコマンドを呼び出します。
• 1ステップでのコンパイルフローを実行する場合は、 aoc -o <your_executable_filename>.aocx <your_kernel_filename>.clコマンドを呼び出し、.aocxファイル名を指定します。

• カスタム・プラットフォームで利用可能な FPGAボードの名前を取得するには、 aoc -list-boards コマンドを呼び出します。
  オフライン・コンパイラーは以下のような出力を生成します。

  Board List:
  FPGA_board_1

  このFPGA_board_1は、<board_name> です。

  特定のカスタム・プラットフォームの利用可能なFPGAボードをすべて一覧表示することも可能です。-board-package=<custom_platform_path> オプションをaocコマンドに含めてください。コマンドプロンプトで次のコマンドを呼び出します。

  aoc –board-package=<custom_platform_path> -list-boards=<board_name>

  インテル^® FPGA SDK for OpenCL™オフライン・コンパイラーは、特定のカスタム・プラットフォームで利用可能なボードの一覧を表示します。

• OpenCLカーネルをFPGA_board_1にコンパイルするには、 aoc -board=FPGA_board_1 <your_kernel_filename>.clコマンドを呼び出します。
  オフライン・コンパイラーは、プリプロセッサー・マクロAOCL_BOARD_FPGA_board_1を1に定義し、FPGA_board_1をターゲットとするカーネルコードをコンパイルします。
• 複数のカスタム・プラットフォーム (ボードパッケージ) がインストールされている場合、特定のカスタム・プラットフォームのボードバリアントでカーネルをコンパイルできます。-board-package=<custom_platform_path> オプションを -board=<board_name> とともに含めてください。コマンドプロンプトで次のコマンドを呼び出します。

  aoc -board-package=<custom_platform_path> -board=<board_name>

  インテル^® FPGA SDK for OpenCL™オフライン・コンパイラーは、<custom_platform_path> で指定されているボードでカーネルをコンパイルします。

• システムで利用可能なカスタム・プラットフォームのリストを表示するには、-list-board-packagesオプションをaocコマンドに含めます。コマンドプロンプトで aoc -list-board-packages コマンドを呼び出します。 インテル^® FPGA SDK for OpenCL™オフライン・コンパイラーは、次の例のような出力を生成します。

  Installed board packages:
  <board_package_1>
  ...
  Board packages shipped with Intel(R) FPGA SDK for OpenCL(TM):
  <board_package_2>
  ...

  この <board_package_N> は、システムにインストールされているカスタム・プラットフォームのボードパッケージ、または インテル^® FPGA SDK for OpenCL™ に同梱されているボードパッケージです。

• __attribute__((scheduler_target_fmax_mhz(__x))) ソースレベル属性を使用する
• aocコマンドの-fmax=<fmax target in Mhz> で、すべてのカーネルをグローバルにコンパイルするよう、インテル FPGA SDK for OpenCL オフライン・コンパイラーに指示する

kernel void k1(){ 
 ... 
}  
__attribute__((scheduler_target_fmax_mhz(200))) 
kernel void k2(){ 
 
...
}

• プリプロセッサー・マクロの定義をオフライン・コンパイラーに渡すには、 aoc -D <macro_name> <kernel_filename>.clコマンドを呼び出します。
• 定義済みのプリプロセッサー・マクロの既存値を上書きするには、 aoc -D <macro_name>=<value> <kernel_filename>.clコマンドを呼び出します。
  次のカーネルsumのコードを例にします。

  #ifndef UNROLL_FACTOR
    #define UNROLL_FACTOR 1
  #endif
  
  __kernel void sum (__global const int * restrict x,
                     __global int * restrict sum)
  {
    int accum = 0;
  
    #pragma unroll UNROLL_FACTOR
    for(size_t i = 0; i < 4; i++)
    {
      accum += x[i + get_global_id(0) * 4];
    }
    sum[get_global_id(0)] = accum;
  }

  UNROLL_FACTORの1を4に上書きし設定するには、 aoc -DUNROLL_FACTOR=4 sum.clコマンドを呼び出します。このコマンドを呼び出すことは、sumカーネル・ソースコードの#define UNROLL_FACTOR 1の行を#define UNROLL_FACTOR 4に置き換えることと同等です。

• プリプロセッサー・マクロを使用し、カーネルのソースコードを変更することなくオフライン・コンパイラーによるカーネルの最適化を制御するには、 aoc -o <hardware_filename>.aocx -D <macro_name>=<value> <kernel_filename>.clを呼び出します。
  以下に詳細を説明します。

  -oは、オフライン・コンパイラーが生成する.aocxファイル名を指定するために使用するオフライン・コンパイラーのオプションです。

  <hardware_filename> は、指定したプリプロセッサー・マクロの値を使用しオフライン・コンパイラーが生成する.aocxファイルの名前です。

  ヒント: コンパイル結果をどちらもファイルシステムに保存するには、aocコマンドの-oフラグを使用し、カーネルを個別のバイナリーとしてコンパイルします。
  例えば、同じカーネルを必要なワークグループ・サイズの64および128で複数回コンパイルする場合、次のようにWORK_GROUP_SIZEプリプロセッサー・マクロをカーネル属性reqd_work_group_sizeに定義できます。

  __attribute__((reqd_work_group_size(WORK_GROUP_SIZE,1,1)))
  __kernel void myKernel(...)
  for (size_t i = 0; i < 1024; i++)
  {
  	  // statements
  }

  次のコマンドを入力し、カーネルを複数回コンパイルします。

  aoc –o myKernel_64.aocx –DWORK_GROUP_SIZE=64 myKernel.cl

  aoc –o myKernel_128.aocx –DWORK_GROUP_SIZE=128 myKernel.cl

• フルコンパイルの進捗をオフライン・コンパイラーに報告させるには、 aoc -v <your_kernel_filename>.clコマンドを呼び出します。
  オフライン・コンパイラーは、次のようなコンパイル進捗レポートを生成します。

  aoc: Environment checks are completed successfully.
  You are now compiling the full flow!!
  aoc: Selected target board a10gx
  aoc: Running OpenCL parser....
  aoc: OpenCL parser completed successfully.
  aoc: Compiling....
  aoc: Linking with IP library ...
  aoc: First stage compilation completed successfully.
  aoc: Setting up project for CvP revision flow....
  aoc: Hardware generation completed successfully.
  

• ハードウェアを構築しない中間コンパイルの進捗をオフライン・コンパイラーに報告させるには、 aoc -rtl -v <your_kernel_filename>.clコマンドを呼び出します。
  オフライン・コンパイラーは、次のようなコンパイル進捗レポートを生成します。

  aoc: Environment checks are completed successfully.
  aoc: Selected target board a10gx
  aoc: Running OpenCL parser....
  aoc: OpenCL parser completed successfully.
  aoc: Compiling....
  aoc: Linking with IP library ...
  aoc: First stage compilation completed successfully.
  aoc: To compile this project, run "aoc <your_kernel_filename>.aoco"

• エミュレーションに向けたコンパイルの進捗を報告するようオフライン・コンパイラーに指示するには、 aoc -march=emulator -v <your_kernel_filename>.clコマンドを呼び出します。
  オフライン・コンパイラーは、次のようなコンパイル進捗レポートを生成します。

  aoc: Environment checks are completed successfully.
  You are now compiling the full flow!!
  aoc: Selected target board a10gx
  aoc: Running OpenCL parser....ex
  aoc: OpenCL parser completed successfully.
  aoc: Compiling for Emulation ....
  aoc: Emulator Compilation completed successfully.
  Emulator flow is successful.

• デフォルトのグローバルメモリーのバーストインターリーブを無効にするようオフライン・コンパイラーに指示するには、 aoc <your_kernel_filename>.cl -no-interleaving=default コマンドを呼び出します。
  アクセラレーター・ボードには、複数のグローバル・メモリー・タイプが含まれる場合があります。デフォルトのグローバル・メモリー・タイプを特定するには、ご利用のカスタム・プラットフォームのボードメーカーより提供されている資料を確認ください。
• 異種メモリーのシステムにおいて、特定のグローバル・メモリー・タイプのバーストインターリーブを無効にするようオフライン・コンパイラーに指示するには、次の作業を実行します。
  1. カスタム・プラットフォームのBoard_spec.xmlファイルで、利用可能なグローバル・メモリー・タイプ名を確認します (DDR、クアッド・データ・レート (QDR) など)。
  2. 例えば、DDRのメモリータイプのバーストインターリーブを無効にするには、 aoc <your_kernel_filename>.cl -no-interleaving=DDRコマンドを呼び出します。
     オフライン・コンパイラーは、DDRメモリーバンクの手動分割を有効にし、他のメモリーバンクをバーストインターリーブ方式でコンフィグレーションします。
  3. 複数のタイプのグローバル・メモリー・バッファーのバーストインターリーブを無効にするには、 -no-interleaving=<global_memory_type> オプションを各グローバル・メモリー・タイプに含めます。
     例えば、DDRとQDRのバーストインターリーブをどちらとも無効にするには、 aoc <your_kernel_filename>.cl -no-interleaving=DDR -no-interleaving=QDRコマンドを呼び出します。

aoc-incremental<your_kernel_filename>.cl

/*****Update kernels in your OpenCL design*****/

aoc-incremental-fast-compile<your_kernel_filename>.cl

1. aoc -incremental <your_kernel_filename>.clコマンドを呼び出し、インクリメンタル・モードが有効になっている状態で、初期セットアップのコンパイルをクリーンなディレクトリーに行います。
   注: セットアップをコンパイルする際は、-incrementalフラグを必ず有効にしてください。

   このセットアップのコンパイルは、以前のコンパイル結果を再利用しません。セットアップをコンパイルする際は、-fast-compileオフライン・コンパイラー・コマンド・オプションをaocコマンドに含めないでください。このオプションを含めると、今後のインクリメンタル・コンパイル時にエラーが発生する可能性が高くなります。

   ヒント: インテルでは、コンパイルの時間が問題にならない場合は必ず、セットアップのコンパイルを新しく実行し、今後のインクリメンタル・コンパイル時にコンパイルが失敗する可能性を低下させることを推奨しています。連続して多くのインクリメンタル・コンパイルを実行すると、コンパイルが失敗する可能性が高くなります。また、ハードウェアのパフォーマンスおよび、生成された.aocxファイルの効率も低下します。
2. ご自身のOpenCLデザインのカーネルを修正します。
   デザインには複数の.clファイルを含めることが可能です。
3. デザインのインクリメンタル・コンパイルを実行します。最適なコンパイル速度を得るために、-fast-compileフラグもaocコマンドに含めます。
   aoc -incremental -fast-compile <your_kernel_filename>.cl
4. report.htmlファイルのIncremental compileセクションで、オフライン・コンパイラーが検出した変更を確認してください。
   report.htmlファイルは、 <your_kernel_filename>/reportsディレクトリーにあります。

channel unlong4 inchannel __attribute__((io("eth0_in")));

__kernel void send (int size) {
    for (unsigned i = 0; i < size; i++) {
        ulong4 data = read_channel_intel(inchannel);
        //statements
    }
}

1. 次のいずれかの方法でカーネルコードを変更します。
   • 次のように、一致するwrite_channel_intel呼び出しを追加する

     #ifdef EMULATOR
     
     __kernel void io_in (__global char * restrict arr, int size) {
         for (unsigned i = 0; i < size; i++) {
             ulong4 data = arr[i]; //arr[i] being an alternate data source
             write_channel_intel(inchannel, data);
         }
     }
     #endif

   • I/Oチャネルアクセスを次のようにメモリーアクセスに置き換える

     __kernel void send (int size) { 
         for (unsigned i = 0; i < size; i++) {
             #ifndef EMULATOR 
     
                 ulong4 data = read_channel_intel(inchannel); 
     
             #else 
                 ulong4 data = arr[i]; //arr[i] being an alternate data source
     
             #endif 
             //statements
         }
     }

2. エミュレーション中にこの条件付きカーネルを作成および起動するよう、ホスト・アプリケーションを変更します。

• x86-64のホストシステムで実行可能なカーネルプログラムを作成するため、 aoc -march=emulator -fast-emulator <your_kernel_filename>.clコマンドを呼び出します。
• Linuxシステムに向けてインテル FPGA SDK for OpenCL オフライン・コンパイラーは、シンボリック・デバッガーのデバッグサポートを提供しています。
  オフライン・コンパイラーのデバッグサポートでは、カーネル・ソースコードの機能的なエラーの原因を特定できます。

1. ホストプログラムを変更し、エミュレーターのOpenCLプラットフォームを選択します。
   次のプラットフォーム名を選択し、ホストプログラムのエミュレーション用OpenCLプラットフォームを選択します。

   Intel(R) FPGA Emulation Platform for OpenCL(TM)

2. ホスト・アプリケーションを構築し、ホスト・アプリケーションをKhronos ICD Loader Libraryにリンクします。詳細については、ホスト・アプリケーションとKhronos ICD Loader Libraryのリンクを確認ください。
3. 必要な場合は、 <your_kernel_filename>.aocxファイルを、ホストが容易に検索できる位置へ動かします。現在の作業ディレクトリーが推奨されます。
4. エミュレーションに向けてホスト・アプリケーションを次のように実行します。
   • Windowsの場合
     1. set CL_CONFIG_CPU_EMULATE_DEVICES=<number_of_devices> コマンドを呼び出し、エミュレーションされたデバイス数を定義します。
     2. ホスト・アプリケーションを実行します。
     3. set CL_CONFIG_CPU_EMULATE_DEVICES=を呼び出し、変数の設定を解除します。
   • Linuxの場合は、 env CL_CONFIG_CPU_EMULATE_DEVICES=<number_of_devices> <host_application_filename> コマンドを呼び出します。
   このコマンドは、エミュレーターが提供する必要のある同一のエミュレーション・デバイス数を指定します。

   要確認: エミュレーション用OpenCLプラットフォーム (Intel(R) FPGA Emulation Platform for OpenCL(TM)) は、物理的なボードへのアクセスを提供しません。エミュレーションされたデバイスのみ利用可能です。

   ヒント: エミュレーター・デバイスを1つだけ使用する場合は、CL_CONFIG_CPU_EMULATE_DEVICES環境変数を設定する必要はありません。
5. ホストまたはカーネルプログラムの変更後にテストを行う場合、変更したホストまたはカーネルプログラムのみを再コンパイルし、エミュレーションを再度実行します。

1. 特定のアクセラレーター・ボードをターゲットとするデバッグの.aocxファイルを生成するため、 aoc -march=emulator -fast-emulator -g <your_kernel_filename>.clコマンドを呼び出します。
2. ホスト・アプリケーションを構築し、ホスト・アプリケーションをKhronos ICD Loader Libraryにリンクします。詳細は、ホスト・アプリケーションとKhronos ICD Loader Libraryのリンク を確認ください。
3. <your_kernel_filename>.aocxファイルが、ホストが容易に検索できる位置にあることを確認してください。現在の作業ディレクトリーが推奨されます。
4. アプリケーションの実行には、 env CL_CONFIG_CPU_EMULATE_DEVICES=<number_of_devices> gdb --args <your_host_program_name> [<host_program_arguments>] コマンドを呼び出します。この <number_of_devices> は、エミュレーターが提供する必要のある同一のエミュレーション・デバイス数です。
5. ホストまたはカーネルプログラムの変更後にテストを行う場合は、変更したホストまたはカーネルプログラムのみを再コンパイルし、デバッガーを再度実行します。

• x86-64ホストシステムで実行可能なカーネルプログラムを作成するため、 aoc -march=emulator <your_kernel_filename>.clコマンドを呼び出します。
• 特定のボードをターゲットとするエミュレーションに向けてカーネルをコンパイルするには、 aoc -march=emulator -board=<board_name> <your_kernel_filename>.clコマンドを呼び出します。
• Linuxシステムに向け、 インテル^® FPGA SDK for OpenCL™オフライン・コンパイラーは、シンボリック・デバッガーのデバッグサポートを提供しています。
  オフライン・コンパイラーのデバッグサポートにより、カーネル・ソースコードの機能的なエラーの原因を特定できるようになります。

1. ユーティリティー・コマンド aocl linkflags を実行し、ホスト・アプリケーションを構築するために必要なライブラリーを検索します。ソフトウェアは、エミュレーションおよび通常のカーネルのコンパイルフローに必要なライブラリーをどちらも表示します。
2. ホスト・アプリケーションを構築し、手順1で検索したライブラリーにリンクします。
   重要: 複数のデバイスを他のOpenCL SDKと共にエミュレーションするには、ホスト・アプリケーションをホストランタイムのライブラリーに接続する前 に、Khronos ICD Loader Libraryに接続します。ホスト・アプリケーションとICD Loader Libraryの接続は、ホスト・アプリケーションのMakefileを変更して行います。詳細は、ホスト・アプリケーションとKhronos ICD Loader Libraryのリンク を参照ください。
3. 必要な場合は、 <your_kernel_filename>.aocxファイルをホストが容易に検索できる位置に移動します。現在の作業ディレクトリーが推奨されます。
4. エミュレーションに向けてホスト・アプリケーションを実行するには
   • Windowsの場合、 set CL_CONTEXT_EMULATOR_DEVICE_INTELFPGA=<number_of_devices> コマンドを呼び出し、エミュレーションされたデバイス数を最初に定義し、その後ホスト・アプリケーションを実行します。

     ホスト・アプリケーションを実行した後、 set CL_CONTEXT_EMULATOR_DEVICE_INTELFPGA=を呼び出し変数の設定を解除します。

   • Linuxの場合、 env CL_CONTEXT_EMULATOR_DEVICE_INTELFPGA=<number_of_devices> <host_application_filename> コマンドを呼び出します。
   このコマンドは、エミュレーターが提供する必要がある同一のエミュレーション・デバイス数を指定します。

   要確認: 環境変数CL_CONTEXT_EMULATOR_DEVICE_INTELFPGAを設定すると、エミュレーションされたデバイスのみが利用可能になります。つまり、物理的なボードへのアクセスはすべて無効になります。
5. ホストまたはカーネルプログラムを変更後にテストを行う場合は、変更したホストまたはカーネルプログラムのみを再コンパイルし、エミュレーションを再度実行してください。

1. レガシー・エミュレーターでのエミュレーションに向けたカーネルのコンパイル (-march=emulator) の説明に従い、カーネルをコンパイルしてください。
2. ホスト・アプリケーションを構築し、Khronos ICD Loader Libraryに接続します。詳細は、ホスト・アプリケーションとKhronos ICD Loader Libraryのリンク を参照ください。
3. <your_kernel_filename>.aocxファイルが、ホストが特定できる位置にあることを確認します。現在の作業ディレクトリーが推奨されます。
4. env CL_CONTEXT_EMULATOR_DEVICE_INTELFPGA=<number_of_devices> gdb --args <your_host_program_name> [<host_program_arguments>]コマンドを呼び出し、アプリケーションを実行します。ここで <number_of_devices> は、エミュレーターが提供する必要のある同一のエミュレーション・デバイス数です。
5. ホストまたはカーネルプログラムを変更した後にテストを行う場合は、変更したホストまたはカーネルプログラムのみを再コンパイルし、デバッガーを再度実行してください。

• <your_kernel_filename>.aocxファイルのVerilogコードをパフォーマンス・カウンターで測定するには、 aoc -profile=(all|autorun|enqueued) <your_kernel_filename>.clコマンドを呼び出します。以下に詳細を説明します。
  • all引数は、 <your_kernel_filename>.clファイルのすべてのカーネルをパフォーマンス・カウンターで測定します。これは引数が指定されていない場合のデフォルトのオプションです。
  • autorun引数は、自動実行のカーネルのみをパフォーマンス・カウンターで測定します。
  • enqueued引数は、自動実行以外のカーネルのみをパフォーマンス・カウンターで測定します。

  重要:

  • 複数の異なるカーネルをプロファイリングする際は、異なる.aocxファイルに同じカーネル名を使用しないでください。同じカーネル名が付けられている場合、それらのカーネルのプロファイル・データは正確なものになりません。
  • clGetProfileDataDeviceIntelFPGAホスト・ライブラリー呼び出しへの入力にかかわらず、 インテル^® FPGA Dynamic Profiler for OpenCL™ は、コンパイル中に示したカーネルタイプのみをプロファイルします。
  • すべてのカーネルまたはエンキューされたカーネルのOpenCLカーネル・パイプラインをパフォーマンス・カウンターで測定すると、OpenCLランタイム環境でのハードウェアのカーネル呼び出しキューの使用が無効になります。そのため、プロファイルの時間が異なる場合があります。

  注意:

  自動実行カーネルをプロファイルすると、カウンターに対するハードウェアのオーバーヘッドが発生します。大規模なデザインの場合、オーバーヘッドによってf_maxおよびデザイン周波数が低下する可能性があります。また、 インテル^® FPGA Dynamic Profiler for OpenCL™ がすべてのカーネルをプロファイルすると、デザインがチップに収まらなくなる可能性もあります。
• ローカルディスクからホスト・アプリケーションを実行し、 <your_kernel_filename>.aocxファイルをFPGAで実行します。カーネルの実行中、カーネル・パイプライン全体のパフォーマンス・カウンターはプロファイル情報を収集します。ホストは現在の作業ディレクトリーのprofile.monモニター記述ファイルにその情報を保存します。
  注意:

  ネットワーク・ディスクのアクセスが遅いため、ネットワークのディレクトリーからホスト・アプリケーションを実行すると、各カーネルの実行に遅れをもたらす可能性があります。この遅れにより、ホスト・アプリケーションの全体的な実行時間が長くなる可能性があります。さらに、ランタイムがプロファイル出力データをディスクに格納している間に、カーネルの起動に遅れが発生する可能性もあります。

1. Visual Studioソフトウェアで、Project > Propertiesを選択します。
2. Project > Properties > Code Builderのページで、Deviceを目的のFPGAデバイスに変更します。
3. C/C++ > Generalプロパティー・ページのAdditional Include Directoriesに、OpenCLコードのヘッダーファイルが配置されているディレクトリーへのフルパスを入力します。 ($(INTELFPGAOCLSDKROOT)\include).
4. Linker > Generalプロパティー・ページのAdditional Library Directoriesに、OpenCLコードのランタイム・インポート・ライブラリー・ファイルが配置されているディレクトリーへのフルパスを入力します。例えば64ビットのアプリケーションには、$(INTELFPGAOCLSDKROOT)\lib\x64を追加します。
5. Linker > Inputプロパティー・ページ、Additional DependenciesのOpenCL ICDのインポート・ライブラリー・ファイル名にOpenCL.libを入力します。

1. CodeBuilder_<version>.jarプラグインファイルを$INTELFPGAOCLSDKROOT/eclipse-plug-inから <ECLIPSE_ROOT_FOLDER>/dropinsへコピーします。
   重要: Linuxでは、$INTELFPGAOCLSDKROOT\binをLD_LIBRARY_PATH環境変数に追加する必要があります。
2. Eclipse IDEを実行します。
3. Windows > Preferencesを選択します。
4. インテル^® OpenCLダイアログに切り替えます。
5. OpenCLバイナリーのディレクトリーを$INTELFPGAOCLSDKROOT/binに設定します。

   オフライン・コンパイラーのコンフィグレーションが完了すると、Code-Builderメニューを使用し、次の基本的な操作を実行できます。

   • 新しいセッションの作成
   • 既存のセッションを開く
   • セッションの保存
   • セッションの構築
   • セッションのコンパイル
   • セッションのコンフィグレーション

   インテル^® Code Builder for OpenCL™ に関する詳細は、Developer Guide for Intel SDK for OpenCL Applicationsを参照ください。Microsoft Visual Studioに向けたインテルCode Builder for OpenCLのコンフィグレーション方法については、Intel Code Builder for OpenCL API for Microsoft Visual Studioを参照ください。Eclipseに向けたインテルCode Builder for OpenCLのコンフィグレーション方法については、Intel Code Builder for OpenCL API for Eclipseを参照ください。

1. Code-Builder > OpenCL Kernel Development > New Sessionを選択します。
2. セッション名、セッションファイルを格納するフォルダーへのパス、およびセッションのコンテンツを指定します (空のセッションまたは事前に定義されたOpenCLコードを持つセッションのどちらか)。
3. Doneをクリックします。

セッションが作成されると、新しいセッションがCode Builder Sessions Explorer ビューに表示されます。

図 16. Code Builder Session Explorer

注: Code Builder Session Explorerビューが表示されない場合は、Code-builder > OpenCL Kernel Development > Windows > Code Builder Session Explorerを選択します。