{"id":1493,"date":"2021-11-25T03:06:32","date_gmt":"2021-11-24T18:06:32","guid":{"rendered":"https:\/\/www.xlsoft.com\/jp\/blog\/intel\/?p=1493"},"modified":"2022-02-25T10:30:41","modified_gmt":"2022-02-25T01:30:41","slug":"migrate_to_c_from_opencl","status":"publish","type":"post","link":"https:\/\/www.xlsoft.com\/jp\/blog\/intel\/2021\/11\/25\/migrate_to_c_from_opencl\/","title":{"rendered":"GPU-Quicksort \uff5eOpenCL* \u304b\u3089\u30c7\u30fc\u30bf\u4e26\u5217 C++ \u3078\u306e\u79fb\u884c\uff5e"},"content":{"rendered":"

\u30c7\u30fc\u30bf\u4e26\u5217 C++ (DPC++) \u306f\u3001 Khronos SYCL* \u6a19\u6e96\u30d9\u30fc\u30b9\u306e\u30d8\u30c6\u30ed\u30b8\u30cb\u30a2\u30b9\u3067\u79fb\u690d\u6027\u306e\u9ad8\u3044\u30d7\u30ed\u30b0\u30e9\u30df\u30f3\u30b0<\/span>\u8a00\u8a9e\u3067\u3059\u3002 \u3053\u306e\u30b7\u30f3\u30b0\u30eb\u30bd\u30fc\u30b9\u30fb\u30d7\u30ed\u30b0\u30e9\u30df\u30f3\u30b0\u8a00\u8a9e\u306f\u3001 CPU\u3001 \u7d71\u5408 \/ \u30c7\u30a3\u30b9\u30af\u30ea\u30fc\u30c8 GPU\u3001 FPGA\u3001 \u305d\u306e\u4ed6\u306e<\/span>\u30a2\u30af\u30bb\u30e9\u30ec\u30fc\u30bf\u30fc\u306a\u3069\u3001 \u3055\u307e\u3056\u307e\u306a\u30d7\u30e9\u30c3\u30c8\u30d5\u30a9\u30fc\u30e0\u3092\u30bf\u30fc\u30b2\u30c3\u30c8\u306b\u3059\u308b\u3053\u3068\u304c\u3067\u304d\u307e\u3059\u3002 \u3053\u3053\u3067\u306f\u3001 DPC++ \u3067<\/span>\u4f55\u304c\u3067\u304d\u308b\u306e\u304b\u7406\u89e3\u3059\u308b\u305f\u3081\u3001 \u91cd\u8981\u306a OpenCL* \u30a2\u30d7\u30ea\u30b1\u30fc\u30b7\u30e7\u30f3\u3067\u3042\u308b GPU-Quicksort \u3092 DPC++ \u306b\u79fb\u884c<\/span>\u3057\u307e\u3059\u3002 \u76ee\u6a19\u306f\u3001 OpenCL* \u30a2\u30d7\u30ea\u30b1\u30fc\u30b7\u30e7\u30f3\u306e\u6027\u80fd\u3092\u8d85\u3048\u308b\u3053\u3068\u3067\u3059\u3002 OpenCL* C \u3067\u6c4e\u7528\u30a2\u30eb\u30b4\u30ea\u30ba\u30e0\u3092\u8a18<\/span>\u8ff0\u3059\u308b\u3053\u3068\u306f\u975e\u5e38\u306b\u56f0\u96e3\u3067\u3042\u308a\u3001 \u7570\u306a\u308b\u30c7\u30fc\u30bf\u578b\u3092\u6271\u3046\u30bd\u30fc\u30c8\u306e\u3088\u3046\u306a\u30a2\u30eb\u30b4\u30ea\u30ba\u30e0\u306e\u5b9f\u88c5\u3067\u306f\u3001 \u3053\u308c\u304c\u6df1\u523b<\/span>\u306a\u554f\u984c\u3068\u306a\u308a\u307e\u3059\u3002 OpenCL* \u3067\u8a18\u8ff0\u3055\u308c\u305f\u30aa\u30ea\u30b8\u30ca\u30eb\u306e GPU-Quicksort \u306f\u3001 \u7b26\u53f7\u306a\u3057\u6574\u6570\u3092\u30bd\u30fc\u30c8\u3057\u307e\u3059\u3002<\/span><\/p>\n

\u3053\u3053\u3067\u306f\u3001 DPC++ \u3067\u30c6\u30f3\u30d7\u30ec\u30fc\u30c8\u3092\u4f7f\u7528\u3057\u3066\u3001 \u8907\u6570\u306e\u30c7\u30fc\u30bf\u578b\u306b\u5bfe\u5fdc\u3057\u305f GPU-Quicksort \u3092\u5b9f\u88c5\u3059\u308b\u65b9\u6cd5<\/span>\u3092\u793a\u3057\u307e\u3059\u3002 \u305d\u3057\u3066\u3001 DPC++ \u304c\u79fb\u690d\u6027\u306b\u512a\u308c\u3066\u3044\u308b\u3053\u3068\u3092\u793a\u3059\u305f\u3081\u3001 GPU-Quicksort \u3092 Windows* \u3068 RHEL<\/span>\u306b\u79fb\u690d\u3057\u307e\u3059\u3002<\/span><\/p>\n

GPU-Quicksort \u3068\u306f<\/span><\/h2>\n

GPU-Quicksort \u306f\u3001 \u9ad8\u5ea6\u306b\u4e26\u5217\u5316\u3055\u308c\u305f\u30de\u30eb\u30c1\u30b3\u30a2 \u30fb \u30b0\u30e9\u30d5\u30a3\u30c3\u30af\u30b9\u30fb\u30d7\u30ed\u30bb\u30c3\u30b5\u30fc\u5411\u3051\u306b\u8a2d\u8a08\u3055\u308c\u305f\u3001 \u30cf\u30a4\u30d1\u30d5\u30a9\u30fc\u30de\u30f3\u30b9\u306a\u30bd\u30fc\u30c8\u30fb\u30a2\u30eb\u30b4\u30ea\u30ba\u30e0\u3067\u3059\u3002 2009 \u5e74\u306b\u3001\u5f53\u6642\u30b9\u30a6\u30a7\u30fc\u30c7\u30f3\u306e\u30c1\u30e3\u30eb\u30de\u30fc\u30b9\u5de5\u79d1\u5927\u5b66\u306e\u5b66\u751f\u3067\u3042\u3063\u305f Daniel Cederman \u6c0f\u3068 Phillippas Tsigas \u6559\u6388\u306b\u3088\u3063\u3066\u958b\u767a\u3055\u308c\u307e\u3057\u305f\u3002 \u5143\u3005 CUDA* \u3067\u5b9f\u88c5\u3055\u308c\u3066\u3044\u307e\u3057\u305f\u304c\u3001 2014 \u5e74\u306b\u7b46\u8005\u304c\u30a4\u30f3\u30c6\u30eb\u00ae<\/sup> \u30a4\u30f3\u30c6\u30b0\u30ec\u30fc\u30c6\u30c3\u30c9 \u30fb\u30d7\u30ed\u30bb\u30c3\u30b5\u30fc \u30fb \u30b0\u30e9\u30d5\u30a3\u30c3\u30af\u30b9\u4e0a\u3067\u30cf\u30a4\u30d1\u30d5\u30a9\u30fc\u30de\u30f3\u30b9\u3092\u5b9f\u8a3c\u3057\u3001 \u5165\u308c\u5b50\u306e\u4e26\u5217\u51e6\u7406\u3068\u30ef\u30fc\u30af\u30b0\u30eb\u30fc\u30d7 \u30fb\u30b9\u30ad\u30e3\u30f3\u95a2\u6570\u3092\u4f7f\u7528\u3059\u308b\u305f\u3081 OpenCL* 1.2 \u3068 OpenCL*2.0 \u3067\u5b9f\u88c5\u3057\u76f4\u3057\u3001 \u30a4\u30f3\u30c6\u30eb\u306e OpenCL* \u30c9\u30e9\u30a4\u30d0\u30fc\u3067\u5b8c\u5168\u306b\u5b9f\u88c5\u3055\u308c\u307e\u3057\u305f\u3002 \u3053\u3053\u3067\u306f\u3001 GPU-Quicksort \u306eOpenCL* 1.2 \u5b9f\u88c5\u3092 DPC++ \u306b\u79fb\u884c\u3057\u3066\u3001 \u7b26\u53f7\u306a\u3057\u6574\u6570\u3060\u3051\u3067\u306a\u304f\u3001 \u5358\u7cbe\u5ea6\u3084\u500d\u7cbe\u5ea6\u306e\u6d6e\u52d5\u5c0f\u6570\u70b9\u3082\u30bd\u30fc\u30c8\u3067\u304d\u308b\u3088\u3046\u306b\u5b9f\u88c5\u3092\u6c4e\u7528\u5316\u3057\u307e\u3059\u3002<\/span><\/p>\n

OpenCL* \u3068\u306f<\/span><\/h2>\n

OpenCL* 1.2 \u5b9f\u88c5\u3092\u30d9\u30fc\u30b9\u306b\u4f5c\u696d\u3092\u958b\u59cb\u3057\u307e\u3059\u3002 \u30a4\u30f3\u30c6\u30eb\u306f\u3001 \u30d8\u30c6\u30ed\u30b8\u30cb\u30a2\u30b9\u4e26\u5217\u30b7\u30b9\u30c6\u30e0\u3092\u30d7\u30ed\u30b0\u30e9\u30df\u30f3\u30b0\u3059\u308b\u305f\u3081\u306e Khronos \u6a19\u6e96\u898f\u683c\u3067\u3042\u308b OpenCL* \u3092\u3001 \u3055\u307e\u3056\u307e\u306a\u30aa\u30da\u30ec\u30fc\u30c6\u30a3\u30f3\u30b0 \u30fb \u30b7\u30b9\u30c6\u30e0\u3068\u30d7\u30e9\u30c3\u30c8\u30d5\u30a9\u30fc\u30e0\u3067\u5b8c\u5168\u306b\u30b5\u30dd\u30fc\u30c8\u3057\u3066\u3044\u307e\u3059\u3002 OpenCL* \u306f\u4ee5\u4e0b\u3067\u69cb\u6210\u3055\u308c\u307e\u3059\u3002<\/span><\/p>\n

    \n
  • \u30e9\u30f3\u30bf\u30a4\u30e0<\/span><\/li>\n
  • \u30db\u30b9\u30c8 API <\/span><\/li>\n
  • \u30c7\u30d0\u30a4\u30b9 C \u30d9\u30fc\u30b9\u306e\u30d7\u30ed\u30b0\u30e9\u30df\u30f3\u30b0\u8a00\u8a9e\u3067\u3042\u308b OpenCL* C<\/span><\/li>\n<\/ul>\n

    \u3053\u308c\u306f OpenCL* \u306e\u5229\u70b9\u3067\u3082\u3042\u308a\u3001 \u5236\u9650\u3067\u3082\u3042\u308a\u307e\u3059\u3002 \u5229\u70b9\u306f\u3001 \u30cf\u30a4\u30d1\u30d5\u30a9\u30fc\u30de\u30f3\u30b9\u3067\u79fb\u690d\u6027\u306e\u9ad8\u3044\u30d8\u30c6\u30ed\u30b8<\/span>\u30cb\u30a2\u30b9\u4e26\u5217\u30a2\u30d7\u30ea\u30b1\u30fc\u30b7\u30e7\u30f3\u3092\u8a18\u8ff0\u3067\u304d\u308b\u3053\u3068\u3067\u3059\u3002 \u4e3b\u306a\u5236\u9650\u306f\u3001 \u30db\u30b9\u30c8\u5074\u3068\u30c7\u30d0\u30a4\u30b9\u5074\u3067\u5225\u3005\u306e\u30b3\u30fc\u30c9\u3092\u8a18\u8ff0<\/span>\u3057\u3066\u30c7\u30d0\u30c3\u30b0\u3059\u308b\u5fc5\u8981\u304c\u3042\u308b\u3053\u3068\u3001 \u304a\u3088\u3073\u30d7\u30ed\u30b0\u30e9\u30de\u30fc\u306b\u99b4\u67d3\u307f\u306e\u3042\u308b\u30c6\u30f3\u30d7\u30ec\u30fc\u30c8\u3084\u305d\u306e\u4ed6\u306e C++ \u6a5f\u80fd\u3092\u5229<\/span>\u7528\u3067\u304d\u306a\u3044\u305f\u3081\u3001 \u6c4e\u7528\u30e9\u30a4\u30d6\u30e9\u30ea\u30fc\u306e\u8a18\u8ff0\u304c\u56f0\u96e3\u306a\u3053\u3068\u3067\u3059\u3002<\/span><\/p>\n

    \u30c7\u30fc\u30bf\u4e26\u5217 C++ \u3068\u306f<\/span><\/h2>\n

    \u30c7\u30fc\u30bf\u4e26\u5217 C++ (DPC++) \u306f\u3001 Khronos SYCL* \u3092\u62e1\u5f35\u3057\u305f\u30a4\u30f3\u30c6\u30eb\u306e\u5b9f\u88c5\u3067\u3059\u3002 SYCL* \u6a19\u6e96\u306f\u3001 \u4e0a\u8a18\u306eOpenCL* \u306e\u5236\u9650\u306b\u5bfe\u5fdc\u3059\u308b\u3088\u3046\u306b\u8a2d\u8a08\u3055\u308c\u3066\u3044\u307e\u3059\u3002 DPC++ \u306f\u6b21\u306e\u6a5f\u80fd\u3092\u63d0\u4f9b\u3057\u307e\u3059\u3002<\/span><\/p>\n

      \n
    • \u30b7\u30f3\u30b0\u30eb\u30bd\u30fc\u30b9\u306e\u30d7\u30ed\u30b0\u30e9\u30df\u30f3\u30b0 \u30fb \u30e2\u30c7\u30eb\u3002 \u30db\u30b9\u30c8\u3068\u30c7\u30d0\u30a4\u30b9\u3092\u540c\u3058\u30b3\u30fc\u30c9\u30d9\u30fc\u30b9\u3067\u30d7\u30ed\u30b0\u30e9\u30df\u30f3\u30b0\u3067\u304d\u307e\u3059\u3002<\/span><\/li>\n
    • C++ \u30c6\u30f3\u30d7\u30ec\u30fc\u30c8\u3068\u30c6\u30f3\u30d7\u30ec\u30fc\u30c8 \u30fb\u30e1\u30bf\u30d7\u30ed\u30b0\u30e9\u30df\u30f3\u30b0\u3002 \u79fb\u690d\u6027\u3092\u640d\u306a\u3046\u3053\u3068\u306a\u304f\u3001 \u30d1\u30d5\u30a9\u30fc\u30de\u30f3\u30b9\u3078\u306e\u5f71\u97ff\u3092<\/span>\u6700\u5c0f\u9650\u306b\u6291\u3048\u3066\u3001 \u30c7\u30d0\u30a4\u30b9\u4e0a\u3067\u3053\u308c\u3089\u3092\u6d3b\u7528\u3067\u304d\u307e\u3059\u3002<\/span><\/li>\n<\/ul>\n

      DPC++ \u3067\u306f\u3001 \u30d7\u30ed\u30b0\u30e9\u30de\u30fc\u306f CPU\u3001 GPU\u3001 \u304a\u3088\u3073 FPGA \u3092\u30bf\u30fc\u30b2\u30c3\u30c8\u306b\u3057\u3066\u3001 \u30a2\u30af\u30bb\u30e9\u30ec\u30fc\u30bf\u30fc\u56fa\u6709\u306e\u30c1\u30e5\u30fc<\/span>\u30cb\u30f3\u30b0\u3092\u884c\u3046\u3053\u3068\u304c\u3067\u304d\u3001 OpenCL* \u3088\u308a\u3082\u78ba\u5b9f\u306b\u6539\u5584\u3055\u308c\u3066\u3044\u307e\u3059\u3002 \u307e\u305f\u3001 \u30a4\u30f3\u30c6\u30eb\u00ae<\/sup> VTune™ \u30d7\u30ed\u30d5\u30a1\u30a4<\/span>\u30e9\u30fc\u3084\u30a4\u30f3\u30c6\u30eb\u00ae<\/sup> Advisor \u306a\u3069\u306e\u30a4\u30f3\u30c6\u30eb\u00ae<\/sup> \u30bd\u30d5\u30c8\u30a6\u30a7\u30a2 \u30fb \u30c4\u30fc\u30eb\u3068\u3001 GDB \u3067\u30b5\u30dd\u30fc\u30c8\u3055\u308c\u3066\u3044\u307e\u3059\u3002 \u3053\u3053\u3067\u306f\u3001<\/span>DPC++ \u306e\u7279\u306b\u30c6\u30f3\u30d7\u30ec\u30fc\u30c8\u6a5f\u80fd\u3092\u6d3b\u7528\u3057\u307e\u3059\u3002<\/span><\/p>\n

      \u958b\u59cb\u70b9 : 2014 \u5e74\u306e Windows* \u30a2\u30d7\u30ea\u30b1\u30fc\u30b7\u30e7\u30f3<\/span><\/h2>\n

      \u300cOpenCL* 2.0 \u306e GPU-Quicksort: \u5165\u308c\u5b50\u306e\u4e26\u5217\u51e6\u7406\u3068\u30ef\u30fc\u30af\u30b0\u30eb\u30fc\u30d7 \u30fb \u30b9\u30ad\u30e3\u30f3\u95a2\u6570\u300d\u306b\u3042\u308b\u3001OpenCL* 1.2 \u3067\u5b9f\u88c5\u3055\u308c\u305f GPU-Quicksort \u3092\u958b\u59cb\u70b9\u3068\u3057\u3066\u4f7f\u7528\u3057\u307e\u3059\u3002\u3053\u306e\u30a2\u30d7\u30ea\u30b1\u30fc\u30b7\u30e7\u30f3\u306f\u3001Windows*\u5411\u3051\u306b\u8a18\u8ff0\u3055\u308c\u3066\u3044\u308b\u305f\u3081\u3001 \u4f5c\u696d\u3092\u59cb\u3081\u308b\u524d\u306b\u3001\u6642\u9593\u3092\u6e2c\u5b9a\u3059\u308b\u30af\u30ed\u30b9\u30d7\u30e9\u30c3\u30c8\u30d5\u30a9\u30fc\u30e0 \u30fb\u30b3\u30fc\u30c9\u3092\u8ffd\u52a0\u3057\u3001\u30a2\u30e9\u30a4\u30e1\u30f3\u30c8\u3055\u308c\u305f\u30e1\u30e2\u30ea\u30fc\u306e\u5272\u308a\u5f53\u3066 \/ \u89e3\u653e\u3092 Windows* \u306e _alligned_malloc\/_aligned_free\u00a0<\/em>\u304b\u3089\u00a0aligned_alloc\/free\u00a0<\/em>\u306b\u5909\u66f4\u3057\u3066\u3001Ubuntu 18.04 \u306b\u79fb\u884c\u3057\u307e\u3057\u305f\u3002<\/span><\/p>\n

      GPU-Quicksort \u30a2\u30fc\u30ad\u30c6\u30af\u30c1\u30e3\u30fc\u306b\u3064\u3044\u3066\u7c21\u5358\u306b\u898b\u3066\u307f\u307e\u3057\u3087\u3046\u3002 2 \u3064\u306e\u30ab\u30fc\u30cd\u30eb\u3067\u69cb\u6210\u3055\u308c\u307e\u3059\u3002<\/span><\/p>\n

      1. gqsort_kernel<\/em><\/span>
      \n2. lqsort_kernel<\/em><\/span><\/p>\n

      OpenCL* 1.2 \u3067\u8a18\u8ff0\u3055\u308c\u305f\u3053\u308c\u3089\u306e\u30ab\u30fc\u30cd\u30eb\u306f\u3001 \u30c7\u30a3\u30b9\u30d1\u30c3\u30c1\u30e3\u30fc \u30fb \u30b3\u30fc\u30c9\u306b\u3088\u3063\u3066\u7d50\u5408\u3055\u308c\u3001 \u5165\u529b\u304c\u00a0<\/span>lqsort_kernel<\/em> \u3067\u30bd\u30fc\u30c8\u3067\u304d\u308b\u5c0f\u3055\u306a\u30c1\u30e3\u30f3\u30af\u306b\u5206\u5272\u3055\u308c\u308b\u307e\u3067\u7e70\u308a\u8fd4\u3057 gqsort_kernel<\/em> \u3092\u547c\u3073\u51fa\u3057<\/span>
      \n\u307e\u3059\u3002 \u30e6\u30fc\u30b6\u30fc\u306f\u30a2\u30d7\u30ea\u30b1\u30fc\u30b7\u30e7\u30f3\u3067\u4ee5\u4e0b\u3092\u6307\u5b9a\u3067\u304d\u307e\u3059\u3002<\/span><\/p>\n

        \n
      • \u6e2c\u5b9a\u306e\u305f\u3081\u30bd\u30fc\u30c8\u3092\u5b9f\u884c\u3059\u308b\u56de\u6570\u3002<\/span><\/li>\n
      • \u30ab\u30fc\u30cd\u30eb\u3092\u5b9f\u884c\u3059\u308b\u30d9\u30f3\u30c0\u30fc\u3068\u30c7\u30d0\u30a4\u30b9\u3002<\/span><\/li>\n
      • \u30ab\u30fc\u30cd\u30eb\u3092\u5b9f\u884c\u3059\u308b\u30d9\u30f3\u30c0\u30fc\u3068\u30c7\u30d0\u30a4\u30b9\u3002<\/span><\/li>\n
      • \u5165\u529b\u306e\u30b5\u30a4\u30ba\u3002<\/span><\/li>\n
      • \u00a0\u30c7\u30d0\u30a4\u30b9\u306e\u8a73\u7d30\u3092\u8868\u793a\u3059\u308b\u304b\u3069\u3046\u304b\u3002<\/span><\/li>\n<\/ul>\n

        \u3053\u306e\u30a2\u30d7\u30ea\u30b1\u30fc\u30b7\u30e7\u30f3\u306f\u3001\u5178\u578b\u7684\u306a OpenCL* \u30a2\u30fc\u30ad\u30c6\u30af\u30c1\u30e3\u30fc\u306b\u5f93\u3063\u3066\u3001OpenCL* \u30d7\u30e9\u30c3\u30c8\u30d5\u30a9\u30fc\u30e0\u3068\u30c7\u30d0<\/span>\u30a4\u30b9\u3092\u521d\u671f\u5316\u3057\u3001\u30b3\u30fc\u30c9\u3092\u30d3\u30eb\u30c9\u3059\u308b\u30e6\u30fc\u30c6\u30a3\u30ea\u30c6\u30a3\u30fc\u3092\u30b5\u30dd\u30fc\u30c8\u3057\u307e\u3059\u3002 OpenCL* \u30ab\u30fc\u30cd\u30eb\u3068\u30b5\u30dd\u30fc\u30c8\u95a2\u6570\u306f\u3001<\/span>\u30e6\u30fc\u30b6\u30fc\u5f15\u6570\u3092\u53d7\u3051\u53d6\u308b\u30e1\u30a4\u30f3 \u30fb\u30a2\u30d7\u30ea\u30b1\u30fc\u30b7\u30e7\u30f3\u3068\u306f\u5225\u306e\u30d5\u30a1\u30a4\u30eb\u306b\u3042\u308a\u3001 \u30d7\u30e9\u30c3\u30c8\u30d5\u30a9\u30fc\u30e0\u3068\u30c7\u30d0\u30a4\u30b9\u3092\u521d\u671f<\/span>\u5316\u3057\u3001\u30ab\u30fc\u30cd\u30eb\u3092\u30d3\u30eb\u30c9\u3057\u3001 \u30e1\u30e2\u30ea\u30fc\u3092\u9069\u5207\u306b\u5272\u308a\u5f53\u3066\u3001 \u30d0\u30c3\u30d5\u30a1\u30fc\u3092\u4f5c\u6210\u3057\u3066\u30ab\u30fc\u30cd\u30eb\u5f15\u6570\u306b\u30d0\u30a4\u30f3\u30c9\u3057\u3001\u30c7\u30a3<\/span>\u30b9\u30d1\u30c3\u30c1\u30e3\u30fc\u95a2\u6570\u3092\u8d77\u52d5\u3057\u307e\u3059\u3002<\/span><\/p>\n

        \u30c7\u30fc\u30bf\u4e26\u5217 C++\/OpenCL* \u306e\u76f8\u4e92\u904b\u7528\u6027 : \u30d7\u30e9\u30c3\u30c8\u30d5\u30a9\u30fc\u30e0\u306e\u521d\u671f\u5316<\/span><\/h2>\n

        \u6700\u521d\u306b\u3001 \u30a4\u30f3\u30c6\u30eb\u00ae<\/sup> oneAPI \u30d9\u30fc\u30b9\u30fb \u30c4\u30fc\u30eb\u30ad\u30c3\u30c8\u3092\u30a4\u30f3\u30b9\u30c8\u30fc\u30eb\u3057\u307e\u3059\u3002 \u3053\u308c\u306b\u306f\u3001 \u30a4\u30f3\u30c6\u30eb\u00ae<\/sup> oneAPI\u00a0<\/span>DPC++ \u30b3\u30f3\u30d1\u30a4\u30e9\u30fc\u304c\u542b\u307e\u308c\u307e\u3059\u3002 CL\/sycl.hpp<\/em> \u30d8\u30c3\u30c0\u30fc\u3092\u30a4\u30f3\u30af\u30eb\u30fc\u30c9\u3057\u3066\u3001 DPC++ \u306e\u5197\u9577\u6027\u3092<\/span>\u907f\u3051\u308b\u305f\u3081\u540d\u524d\u7a7a\u9593 cl::sycl \u3092\u4f7f\u7528\u3057\u3066 DPC++ \u3078\u306e\u79fb\u884c\u3092\u958b\u59cb\u3057\u307e\u3059\u3002<\/span><\/p>\n

        \"\"<\/p>\n

        \u30d7\u30e9\u30c3\u30c8\u30d5\u30a9\u30fc\u30e0\u3001\u30c7\u30d0\u30a4\u30b9\u3001\u30b3\u30f3\u30c6\u30ad\u30b9\u30c8\u3001\u304a\u3088\u3073\u30ad\u30e5\u30fc\u306f\u3001OpenCL* \u3067\u306f\u306a\u304f\u3001\u7c21\u6f54\u306a DPC++ \u3067\u521d\u671f\u5316\u3057\u307e\u3059\u3002<\/span><\/p>\n

        \"\"<\/p>\n

        \u30a2\u30d7\u30ea\u30b1\u30fc\u30b7\u30e7\u30f3\u306e\u6b8b\u308a\u306e\u90e8\u5206\u306f OpenCL* \u30d9\u30fc\u30b9\u3067\u3042\u308b\u305f\u3081\u3001 OpenCL* \u30b3\u30f3\u30c6\u30ad\u30b9\u30c8\u3001 \u30c7\u30d0\u30a4\u30b9\u3001 \u304a\u3088\u3073\u30ad\u30e5\u30fc<\/span>\u3092\u53d6\u5f97\u3059\u308b\u5fc5\u8981\u304c\u3042\u308a\u307e\u3059\u3002<\/span><\/p>\n

        \"\"<\/p>\n

        \u3053\u308c\u304c\u6700\u521d\u306e\u53cd\u5fa9\u3067\u3059\u3002 \u30a4\u30f3\u30c6\u30eb\u00ae<\/sup> DPC++ \u30b3\u30f3\u30d1\u30a4\u30e9\u30fc\u3067\u8a2d\u5b9a\u3057\u3066\u30b3\u30f3\u30d1\u30a4\u30eb\u3057\u3001 \u5b9f\u884c\u3057\u307e\u3059\u3002<\/span><\/p>\n

        \u30c7\u30fc\u30bf\u4e26\u5217 C++: \u30a4\u30f3\u30c6\u30eb\u306e GPU \u306e\u9078\u629e<\/span><\/h2>\n

        \u6700\u521d\u306e\u53cd\u5fa9\u306e\u6b20\u70b9\u306f\u3001 \u5e38\u306b\u30c7\u30d5\u30a9\u30eb\u30c8\u306e\u30c7\u30d0\u30a4\u30b9\u3092\u9078\u629e\u3059\u308b\u3053\u3068\u3067\u3059\u3002 \u9078\u629e\u3055\u308c\u308b\u30c7\u30d0\u30a4\u30b9\u306f\u3001 \u30a4\u30f3\u30c6\u30eb\u306e GPU \u3067\u3042\u308b\u3068\u306f\u9650\u308a\u307e\u305b\u3093\u3002 \u30a4\u30f3\u30c6\u30eb\u306e GPU \u3092\u6307\u5b9a\u3059\u308b\u306b\u306f\u3001 \u30ab\u30b9\u30bf\u30e0 \u30fb \u30c7\u30d0\u30a4\u30b9 \u30fb \u30bb\u30ec\u30af\u30bf\u30fc\u3092\u8a18\u8ff0\u3059\u308b\u5fc5\u8981\u304c\u3042\u308a\u307e\u3059\u3002<\/span><\/p>\n

        \"\"<\/p>\n

        \u30e6\u30fc\u30b6\u30fc\u304c\u8981\u6c42\u3057\u305f\u5834\u5408\u3001 intel_gpu_selector \u3092\u4f7f\u7528\u3057\u3066\u30a4\u30f3\u30c6\u30eb\u306e GPU \u3092\u9078\u629e\u3057\u307e\u3059\u3002<\/span><\/p>\n

        \"\"<\/p>\n

        \u30c7\u30fc\u30bf\u4e26\u5217 C++: \u30ab\u30fc\u30cd\u30eb\u5f15\u6570\u306e\u8a2d\u5b9a\u3068\u30ab\u30fc\u30cd\u30eb\u306e\u8d77\u52d5<\/span><\/h2>\n

        \u7b2c 3 \u53cd\u5fa9\u3067\u306f\u3001 DPC++ \u3092\u4f7f\u7528\u3057\u3066\u30ab\u30fc\u30cd\u30eb\u5f15\u6570\u3092\u8a2d\u5b9a\u3057\u3001 \u30ab\u30fc\u30cd\u30eb\u3092\u8d77\u52d5\u3057\u307e\u3059\u3002 \u30d7\u30ed\u30b0\u30e9\u30e0\u306e\u30d3\u30eb\u30c9\u3068\u30ab\u30fc<\/span>\u30cd\u30eb\u306e\u53d6\u5f97\u306f\u3001 OpenCL* \u3067\u884c\u3044\u307e\u3059\u3002 cl::sycl::kernel<\/em> \u30aa\u30d6\u30b8\u30a7\u30af\u30c8\u3092\u4f7f\u7528\u3057\u3066\u30aa\u30ea\u30b8\u30ca\u30eb\u306e OpenCL*\u00a0<\/span>\u30ab\u30fc\u30cd\u30eb\u3092\u30e9\u30c3\u30d7\u3057\u307e\u3059\u3002 \u6b21\u306b\u4f8b\u3092\u793a\u3057\u307e\u3059\u3002<\/span><\/p>\n

        \"\"<\/p>\n

        clSetKernelArg<\/em> \u30e1 \u30bd \u30c3\u30c9 \u3092 DPC++ \u306e set_arg<\/em> \u30e1 \u30bd \u30c3\u30c9 \u306b\u3001clEnqueueNDRange<\/em> \u547c\u3073\u51fa\u3057\u3092<\/span>
        \nparallel_for \u547c\u3073\u51fa\u3057\u306b\u305d\u308c\u305e\u308c\u7f6e\u304d\u63db\u3048\u307e\u3059\u3002 \u4ee5\u4e0b\u306e\u4f8b\u306f\u3001gqsort_kernel<\/em> \u3067\u3059\u304c\u3001 lqsort_<\/em><\/span>
        \nkernel<\/em> \u306e\u5909\u66f4\u3082\u975e\u5e38\u306b\u4f3c\u3066\u3044\u307e\u3059\u3002<\/span><\/p>\n

        \"\"<\/p>\n

        \u4ee5\u4e0b\u306e\u3088\u3046\u306b\u3001 1 \u56de\u306e set_args<\/em> \u547c\u3073\u51fa\u3057\u3067\u3059\u3079\u3066\u306e\u30ab\u30fc\u30cd\u30eb\u5f15\u6570\u3092\u8a2d\u5b9a\u3059\u308b\u3053\u3068\u3082\u3067\u304d\u307e\u3059\u3002<\/span><\/p>\n

        \"\"<\/p>\n

        parallel_for<\/em> \u3082\u6b21\u306e\u3088\u3046\u306b\u7c21\u6f54\u306b\u6307\u5b9a\u3059\u308b\u3053\u3068\u304c\u3067\u304d\u307e\u3059\u3002<\/span><\/p>\n

        \"\"<\/p>\n

        \u30c7\u30fc\u30bf\u4e26\u5217 C++: \u30d0\u30c3\u30d5\u30a1\u30fc\u306e\u4f5c\u6210\u3068\u30a2\u30af\u30bb\u30b9\u30e2\u30fc\u30c9\u306e\u8a2d\u5b9a<\/span><\/h2>\n

        OpenCL* \u30d0\u30c3\u30d5\u30a1\u30fc\u3092 DPC++ \u30d0\u30c3\u30d5\u30a1\u30fc\u306b\u5909\u63db\u3057\u307e\u3059 (\u6700\u521d\u306e 2 \u3064\u306f\u3001 \u30a2\u30e9\u30a4\u30e1\u30f3\u30c8\u3055\u308c\u305f\u5272\u308a\u5f53\u3066\u3067\u95a2\u6570\u306b\u53c2\u7167\u6e21\u3057\u3055\u308c\u308b\u30e1\u30e2\u30ea\u30fc\u3092\u30e9\u30c3\u30d7\u3057\u3066\u304a\u308a\u3001 \u6b8b\u308a\u306e 3 \u3064\u306f STL \u30d9\u30af\u30c8\u30eb\u304b\u3089\u4f5c\u6210\u3055\u308c\u307e\u3059)\u3002 \u53c2\u7167\u6e21\u3057\u306e\u30d0\u30c3\u30d5\u30a1\u30fc\u306f\u3001 get_access<\/em> \u30e1\u30f3\u30d0\u30fc\u95a2\u6570\u306e\u524d\u306b template<\/em> \u30ad\u30fc\u30ef\u30fc\u30c9\u3092\u4f7f\u7528\u3057\u307e\u3059\u3002 \u5fc5\u8981\u306a\u30a2\u30af\u30bb\u30b9(\u8aad\u307f\u53d6\u308a\u3001 \u66f8\u304d\u8fbc\u307f\u3001 \u3042\u308b\u3044\u306f\u4e21\u65b9) \u306b\u5fdc\u3058\u3066\u3001 \u30d0\u30c3\u30d5\u30a1\u30fc\u306e\u30a2\u30af\u30bb\u30b9\u30e2\u30fc\u30c9\u306f\u7570\u306a\u308a\u307e\u3059\u3002 \u30ab\u30fc\u30cd\u30eb\u5f15\u6570\u3068\u3057\u3066\u30d0\u30c3\u30d5\u30a1\u30fc\u3092\u76f4\u63a5\u6e21\u3059\u306e\u3067\u306f\u306a\u304f\u3001 \u30d0\u30c3\u30d5\u30a1\u30fc\u3078\u306e\u30a2\u30af\u30bb\u30b5\u30fc\u3092\u6e21\u3057\u307e\u3059\u3002<\/span><\/p>\n

        \"\"<\/p>\n

        \u30c7\u30fc\u30bf\u4e26\u5217 C++: \u30d7\u30e9\u30c3\u30c8\u30d5\u30a9\u30fc\u30e0\u3068\u30c7\u30d0\u30a4\u30b9\u306e\u30d7\u30ed\u30d1\u30c6\u30a3\u30fc\u306e\u7167\u4f1a<\/span><\/h2>\n

        OpenCL* \u3067\u306f\u3001clGetPlatformInfo<\/em> \u30e1\u30bd\u30c3\u30c9\u3068 clGetDeviceInfo<\/em> \u30e1\u30bd\u30c3\u30c9\u3092\u4f7f\u7528\u3057\u3066\u30d7\u30e9\u30c3\u30c8\u30d5\u30a9\u30fc<\/span>
        \n\u30e0\u3068\u30c7\u30d0\u30a4\u30b9\u306e\u30d7\u30ed\u30d1\u30c6\u30a3\u30fc\u3092\u7167\u4f1a\u3057\u307e\u3059\u3002 \u3053\u308c\u3089\u306e\u60c5\u5831\u306e\u7167\u4f1a\u306b\u306f\u3001 get_info<><\/em> \u30e1\u30bd\u30c3\u30c9\u3092\u4f7f\u7528\u3057\u307e\u3059\u3002\u6b21\u306b\u4f8b\u3092\u793a\u3057\u307e\u3059\u3002<\/span><\/p>\n

        \"\"<\/p>\n

        \u307e\u305f\u306f\u3001 \u6b21\u306e\u3088\u3046\u306a\u3088\u308a\u8907\u96d1\u306a\u69cb\u9020\u306e\u30d7\u30ed\u30d1\u30c6\u30a3\u30fc\u3092\u7167\u4f1a\u3059\u308b\u3053\u3068\u3082\u3067\u304d\u307e\u3059\u3002<\/span><\/p>\n

        \"\"<\/p>\n

        OpenCL* \u30ab\u30fc\u30cd\u30eb\u304b\u3089\u30c7\u30fc\u30bf\u4e26\u5217 C++ \u3078\u306e\u79fb\u884c – \u30d1\u30fc\u30c8 1: gqsort_kernel<\/span><\/h2>\n

        \u3053\u3053\u307e\u3067\u306f\u3001 DPC++ \u3067\u30d7\u30e9\u30c3\u30c8\u30d5\u30a9\u30fc\u30e0\u3068\u30c7\u30d0\u30a4\u30b9\u3092\u521d\u671f\u5316\u3057\u3001 \u30d0\u30c3\u30d5\u30a1\u30fc\u3068\u30a2\u30af\u30bb\u30b5\u30fc\u3092\u4f5c\u6210\u3057\u3066\u30ab\u30fc\u30cd\u30eb\u306b\u30d0\u30a4\u30f3\u30c9\u3057\u3001 \u30c7\u30d0\u30a4\u30b9\u3067\u30ab\u30fc\u30cd\u30eb\u3092\u8d77\u52d5\u3057\u307e\u3057\u305f\u3002 \u3057\u304b\u3057\u3001 \u30ab\u30fc\u30cd\u30eb\u306e\u4f5c\u6210\u306f OpenCL* \u3067\u884c\u3046\u5fc5\u8981\u304c\u3042\u308a\u307e\u3059\u3002<\/span>OpenCL* C \u3068 clBuildProgram\/clCreateKernel<\/em> API \u3092\u4f7f\u7528\u3057\u3066\u3001 \u30d7\u30ed\u30b0\u30e9\u30e0\u3092\u30d3\u30eb\u30c9\u3057\u30ab\u30fc\u30cd\u30eb\u3092\u4f5c<\/span>\u6210\u3057\u307e\u3059\u3002 OpenCL* C \u30ab\u30fc\u30cd\u30eb\u306f\u3001 \u5b9f\u884c\u6642\u306b\u30d3\u30eb\u30c9\u306e\u524d\u306b\u30d7\u30ed\u30b0\u30e9\u30e0\u306b\u30ed\u30fc\u30c9\u3055\u308c\u308b\u5225\u306e\u30d5\u30a1\u30a4\u30eb\u306b\u683c\u7d0d\u3055\u308c\u307e\u3059\u3002 \u3053\u308c\u3092\u5909\u66f4\u3057\u307e\u3059\u3002 2 \u3064\u306e\u30ab\u30fc\u30cd\u30eb\u306e\u3046\u3061\u3001 \u7c21\u5358\u306a gqsort_kernel<\/em> \u304b\u3089\u4f5c\u696d\u3057\u307e\u3059\u3002<\/span><\/p>\n

        DPC++ \u3067\u306f\u3001 \u30e9\u30e0\u30c0\u307e\u305f\u306f\u30d5\u30a1\u30f3\u30af\u30bf\u30fc\u3092\u4f7f\u7528\u3057\u3066\u30ab\u30fc\u30cd\u30eb\u3092\u4f5c\u6210\u3057\u307e\u3059\u3002 \u901a\u5e38\u3001 \u5c0f\u3055\u306a\u30ab\u30fc\u30cd\u30eb\u306f\u30e9\u30e0\u30c0\u3092\u4f7f\u7528\u3057\u3066\u4f5c\u6210\u3057\u307e\u3059\u3002 \u30b5\u30dd\u30fc\u30c8\u95a2\u6570\u3092\u4f7f\u7528\u3059\u308b\u8907\u96d1\u306a\u30ab\u30fc\u30cd\u30eb\u3067\u306f\u3001 \u30d5\u30a1\u30f3\u30af\u30bf\u30fc \u30fb \u30af\u30e9\u30b9\u3092\u4f5c\u6210\u3057\u305f\u307b\u3046\u304c\u826f\u3044\u3067\u3057\u3087\u3046\u3002 gqsort_kernel_class<\/em> \u30d5\u30a1\u30f3\u30af\u30bf\u30fc\u3092\u4f5c\u6210\u3057\u3066\u3001 \u5f8c\u3067\u8907\u6570\u306e\u30c7\u30fc\u30bf\u578b\u3092\u30bd\u30fc\u30c8\u3067\u304d\u308b\u3088\u3046\u306b\u30c6\u30f3\u30d7\u30ec\u30fc\u30c8\u5316\u3057\u307e\u3059\u3002<\/span><\/p>\n

        \"\"<\/p>\n

        \u5178\u578b\u7684\u306a\u30d5\u30a1\u30f3\u30af\u30bf\u30fc \u30fb \u30af\u30e9\u30b9\u306b\u306f\u3001 \u30d1\u30e9\u30e1\u30fc\u30bf\u30fc\u3068\u3057\u3066\u53cd\u5fa9 ID (\u3053\u306e\u4f8b\u3067\u306f nd_item<1> id<\/em>) \u3092\u53d7\u3051\u53d6 \u308b void operator()<\/em> \u304c\u3042\u308a\u307e\u3059\u3002 \u30ab\u30fc\u30cd\u30eb\u672c\u4f53\u306f void operator()<\/em> \u306b\u3042\u308a\u307e\u3059\u3002 \u30d5\u30a1\u30f3\u30af\u30bf\u30fc\u306b\u306f\u3001 OpenCL* \u30ab\u30fc\u30cd\u30eb\u306e\u30b0\u30ed\u30fc\u30d0\u30eb\u304a\u3088\u3073\u30ed\u30fc\u30ab\u30eb \u30fb\u30e1\u30e2\u30ea\u30fc \u30fb \u30dd\u30a4\u30f3\u30bf\u30fc\u3068\u540c\u7b49\u306e\u3001 \u30b0\u30ed\u30fc\u30d0\u30eb\u304a\u3088\u3073\u30ed\u30fc\u30ab\u30eb \u30a2\u30af\u30bb\u30b5\u30fc\u3092\u53d7\u3051\u53d6\u308b\u30b3\u30f3\u30b9\u30c8\u30e9\u30af\u30bf\u30fc\u304c\u3042\u308a\u307e\u3059\u3002 \u5178\u578b\u7684\u306a DPC++ \u30d5\u30a1\u30f3\u30af\u30bf\u30fc\u306b\u306f\u3001 \u30b0\u30ed\u30fc\u30d0\u30eb\u304a\u3088\u3073 \u30ed\u30fc\u30ab\u30eb\u30a2\u30af\u30bb\u30b5\u30fc\u306e\u578b\u3092\u5b9a\u7fa9\u3059\u308b using<\/em> \u53e5\u3092\u6301\u3064\u30d7\u30ea\u30a2\u30f3\u30d6\u30eb\u304c\u3042\u308a\u307e\u3059\u3002gqsort_kernel<\/em> \u306e\u4f8b\u3067\u306f\u3001 \u6b21\u306e\u3088\u3046\u306b\u306a\u308a\u307e\u3059\u3002<\/span><\/p>\n

        \"\"<\/p>\n

        \u30d5\u30a1\u30f3\u30af\u30bf\u30fc\u306e private<\/em> \u30bb\u30af\u30b7\u30e7\u30f3\u306b\u306f\u3001 void operator()<\/em> \u306e\u672c\u4f53\u3067\u4f7f\u7528\u3055\u308c\u308b\u3059\u3079\u3066\u306e\u30b0\u30ed\u30fc\u30d0\u30eb\u304a\u3088<\/span>
        \n\u3073\u30ed\u30fc\u30ab\u30eb\u30a2\u30af\u30bb\u30b5\u30fc\u304c\u542b\u307e\u308c\u307e\u3059\u3002 \u3053\u306e\u4f8b\u3067\u306f\u3001 \u6b21\u306e\u3088\u3046\u306b\u306a\u308a\u307e\u3059\u3002 \u6700\u521d\u306e 5 \u3064\u306f\u3001 \u30b0\u30ed\u30fc\u30d0\u30eb\u30d0\u30c3\u30d5\u30a1\u30fc\u3078\u306e\u30a2\u30af\u30bb\u30b5\u30fc\u3067\u3001 \u6b8b\u308a\u306f\u30ed\u30fc\u30ab\u30eb\u30d0\u30c3\u30d5\u30a1\u30fc\u3078\u306e\u30a2\u30af\u30bb\u30b5\u30fc\u3067\u3059\u3002<\/span><\/p>\n

        \"\"<\/p>\n

        gqsort_kernel<\/em> \u306f\u3001 \u30b5\u30dd\u30fc\u30c8\u69cb\u9020\u4f53\u3068 2 \u3064\u306e\u30b5\u30dd\u30fc\u30c8\u95a2\u6570 plus_prescan<\/em> \u3068 median<\/em> \u3092\u4f7f\u7528\u3059\u308b\u8907\u96d1<\/span>
        \n\u306a\u30ab\u30fc\u30cd\u30eb\u3067\u3059\u3002 \u3053\u308c\u3089\u306e\u30b5\u30dd\u30fc\u30c8\u95a2\u6570\u306f\u3001\u7279\u6b8a\u306a OpenCL* \u95a2\u6570\u3092\u4f7f\u7528\u3057\u3001\u30ed\u30fc\u30ab\u30eb\u30e1\u30e2\u30ea\u30fc\u914d\u5217\u304a\u3088\u3073\u5909\u6570\u3001\u30ed\u30fc\u30ab\u30eb\u304a\u3088\u3073\u30b0\u30ed\u30fc\u30d0\u30eb\u30d0\u30ea\u30a2\u3001 \u30a2\u30c8\u30df\u30c3\u30af\u64cd\u4f5c\u3092\u5e45\u5e83\u304f\u4f7f\u7528\u3057\u307e\u3059\u3002 \u3053\u308c\u3089\u306e\u8981\u7d20\u3092\u3059\u3079\u3066 DPC++ \u306b\u5909\u63db\u3059\u308b\u5fc5\u8981\u304c\u3042\u308a\u307e\u3059\u3002<\/span><\/p>\n

        \u95a2\u6570\u304b\u3089\u958b\u59cb\u3057\u307e\u3057\u3087\u3046\u3002 \u69cb\u9020\u4f53\u306f\u30c6\u30f3\u30d7\u30ec\u30fc\u30c8\u5316\u3055\u308c\u3066\u3044\u308b\u305f\u3081\u7701\u7565\u3057\u307e\u3059\u3002 \u30b9\u30ad\u30e3\u30f3\u5408\u8a08\u3092\u8a08\u7b97\u3059\u308b plus_prescan<\/em> \u95a2\u6570\u306f\u6bd4\u8f03\u7684\u5358\u7d14\u306a\u305f\u3081\u3001 \u30bd\u30fc\u30c8\u3092\u6c4e\u7528\u7684\u306b\u3059\u308b\u6e96\u5099\u3068\u3057\u3066\u30c6\u30f3\u30d7\u30ec\u30fc\u30c8\u95a2\u6570\u306b\u3059\u308b\u3060\u3051\u3067 DPC++ \u306b\u79fb\u884c\u3067\u304d\u307e\u3059\u3002<\/span><\/p>\n

        \"\"<\/p>\n

        median<\/em> \u95a2 \u6570 \u306f\u3001 \u30c6 \u30f3 \u30d7 \u30ec \u30fc\u30c8 \u95a2 \u6570 \u306b \u3059 \u308b \u3060 \u3051 \u3067 \u306a\u304f\u3001 OpenCL* C \u306e select<\/em> \u95a2 \u6570 \u3092 DPC++ \u306e\u00a0<\/span>cl::sycl::select<\/em> \u95a2\u6570\u306b\u7f6e\u304d\u63db\u3048\u3066\u3001 \u540c\u69d8\u306e\u30db\u30b9\u30c8\u95a2\u6570\u3068\u533a\u5225\u3059\u308b\u305f\u3081\u540d\u524d\u3092 median_select<\/em> \u306b<\/span>
        \n\u5909\u66f4\u3057\u307e\u3059\u3002<\/span><\/p>\n

        \"\"<\/p>\n

        OpenCL* C \u3067\u306f\u3001 \u30ed\u30fc\u30ab\u30eb\u30e1\u30e2\u30ea\u30fc\u5909\u6570\u3068\u914d\u5217\u3092\u30ab\u30fc\u30cd\u30eb\u306e\u672c\u4f53\u5185\u3067\u4f5c\u6210\u3057\u3066\u3001 \u30ab\u30fc\u30cd\u30eb\u5f15\u6570\u3068\u3057\u3066\u6e21\u3059\u3053\u3068\u304c\u53ef\u80fd\u3067\u3059\u3002 \u3057\u304b\u3057\u3001 DPC++ \u3067\u306f\u3001 \u30d5\u30a1\u30f3\u30af\u30bf\u30fc\u3092\u4f7f\u7528\u3059\u308b\u5834\u5408\u3001 \u30d5\u30a1\u30f3\u30af\u30bf\u30fc\u3092\u69cb\u7bc9\u3059\u308b\u969b\u306b\u30ed\u30fc\u30ab\u30eb \u30fb \u30d0\u30c3\u30d5\u30a1\u30fc \u30fb\u30a2\u30af\u30bb\u30b5\u30fc\u3092\u6e21\u3057\u307e\u3059\u3002 \u3053\u306e\u4f8b\u3067\u306f\u3001 \u3059\u3079\u3066\u306e\u30ed\u30fc\u30ab\u30eb\u30e1\u30e2\u30ea\u30fc\u5909\u6570\u3068\u914d\u5217\u306f\u7b26\u53f7\u306a\u3057\u6574\u6570\u3092\u683c\u7d0d\u3059\u308b\u305f\u3081\u3001 \u7279\u6b8a\u306a local_read_write_accessor<\/em> \u578b\u3092\u4f5c\u6210\u3057\u307e\u3059\u3002<\/span><\/p>\n

        \"\"<\/p>\n

        \u3059\u3079\u3066\u306e\u30ed\u30fc\u30ab\u30eb\u30e1\u30e2\u30ea\u30fc\u5909\u6570\u3092\u5ba3\u8a00\u3057\u307e\u3059\u3002<\/span><\/p>\n

        \"\"<\/p>\n

        \u305d\u3057\u3066\u3001 \u305d\u308c\u3089\u3092\u30d1\u30e9\u30e1\u30fc\u30bf\u30fc\u3068\u3057\u3066\u3001 \u30b0\u30ed\u30fc\u30d0\u30eb\u30fb\u30d0\u30c3\u30d5\u30a1\u30fc\u30fb\u30a2\u30af\u30bb\u30b5\u30fc\u3068\u3068\u3082\u306b\u30d5\u30a1\u30f3\u30af\u30bf\u30fc\u30fb\u30b3\u30f3\u30b9\u30c8\u30e9\u30af\u30bf\u30fc\u306b\u6e21\u3057\u307e\u3059\u3002 \u6b21\u306b\u3001 \u751f\u6210\u3055\u308c\u305f\u30aa\u30d6\u30b8\u30a7\u30af\u30c8\u3092 parallel_for<\/em> \u306b\u6e21\u3057\u307e\u3059\u3002<\/span><\/p>\n

        \"\"<\/p>\n

        \u3053\u306e\u70b9\u306b\u304a\u3044\u3066\u3001 DPC++ \u306f OpenCL* C \u3088\u308a\u3082\u8907\u96d1\u3067\u3059\u3002 get_group_id<\/em> \u95a2\u6570\u3068 get_local_id<\/em> \u95a2\u6570\u306f<\/span>
        \n\u6b21\u306e\u3088\u3046\u306b\u306a\u308a\u307e\u3059\u3002<\/span><\/p>\n

        \"\"<\/p>\n

        \u30ed\u30fc\u30ab\u30eb\u30d0\u30ea\u30a2\u306f\u3001<\/span><\/p>\n

        \"\"<\/p>\n

        \u304b\u3089\u4ee5\u4e0b\u306b\u5909\u66f4\u3055\u308c\u307e\u3059\u3002<\/span><\/p>\n

        \"\"<\/p>\n

        \u30b0\u30ed\u30fc\u30d0\u30eb\u304a\u3088\u3073\u30ed\u30fc\u30ab\u30eb\u30d0\u30ea\u30a2\u306f\u3001<\/span><\/p>\n

        \"\"<\/p>\n

        \u304b\u3089\u4ee5\u4e0b\u306b\u5909\u66f4\u3055\u308c\u307e\u3059\u3002<\/span><\/p>\n

        \"\"<\/p>\n

        DPC++ \u306e\u30a2\u30c8\u30df\u30c3\u30af\u64cd\u4f5c\u306f\u3001 OpenCL* C \u306e\u3088\u3046\u306b\u6d17\u7df4\u3055\u308c\u3066\u3044\u307e\u305b\u3093\u3002<\/span>
        \nOpenCL* C \u3067\u306f\u7c21\u6f54\u306a\u4ee5\u4e0b\u306e\u30b3\u30fc\u30c9\u304c<\/span><\/p>\n

        \"\"<\/p>\n

        DPC++ \u3067\u306f\u6b21\u306e\u3088\u3046\u306b\u306a\u308a\u307e\u3059\u3002<\/span><\/p>\n

        \"\"<\/p>\n

        DPC++ \u306e\u30a2\u30c8\u30df\u30c3\u30af\u64cd\u4f5c\u306f\u3001 \u30b0\u30ed\u30fc\u30d0\u30eb\u307e\u305f\u306f\u30ed\u30fc\u30ab\u30eb \u30fb\u30e1\u30e2\u30ea\u30fc \u30fb \u30dd\u30a4\u30f3\u30bf\u30fc\u3092\u76f4\u63a5\u64cd\u4f5c\u3067\u304d\u306a\u3044\u305f\u3081\u3001cl::sycl::atomic<><\/em> \u5909\u6570\u3092\u30a2\u30c8\u30df\u30c3\u30af\u64cd\u4f5c\u3092\u884c\u3046\u305f\u3081\u306b\u4f5c\u6210\u3057\u3066\u3044\u307e\u3059\u3002<\/span><\/p>\n

        \u3053\u3053\u307e\u3067\u3067\u3001 \u30b5\u30dd\u30fc\u30c8\u69cb\u9020\u4f53\u3068\u30b5\u30dd\u30fc\u30c8\u95a2\u6570\u3092\u5909\u63db\u3057\u3066\u30c6\u30f3\u30d7\u30ec\u30fc\u30c8\u5316\u3057\u3001 \u7279\u6b8a\u306a OpenCL* C \u95a2\u6570\u3092 DPC++ \u306b\u5909\u63db\u3057\u307e\u3057\u305f\u3002 \u307e\u305f\u3001 \u30ed\u30fc\u30ab\u30eb\u30a2\u30af\u30bb\u30b5\u30fc\u3092\u6301\u3064\u30c6\u30f3\u30d7\u30ec\u30fc\u30c8\u95a2\u6570\u3092\u4f5c\u6210\u3057\u3001 \u30d0\u30ea\u30a2\u3068\u30a2\u30c8\u30df\u30c3\u30af\u64cd\u4f5c\u3092\u5909\u63db\u3057\u307e\u3057\u305f\u3002<\/span><\/p>\n

        OpenCL* \u30ab\u30fc\u30cd\u30eb\u304b\u3089\u30c7\u30fc\u30bf\u4e26\u5217 C++ \u3078\u306e\u79fb\u884c – \u30d1\u30fc\u30c8 2: lqsort_kernel<\/em><\/span><\/h2>\n

        lqsort_kernel<\/em> \u306e\u5909\u63db\u3082 gqsort_kernel<\/em> \u306e\u5909\u63db\u3068\u4f3c\u3066\u3044\u307e\u3059\u3002lqsort_kernel_class<\/em> \u30d5\u30a1\u30f3\u30af<\/span>\u30bf\u30fc\u3092\u4f5c\u6210\u3057\u3066\u3001 \u30ed\u30fc\u30ab\u30eb\u30e1\u30e2\u30ea\u30fc\u914d\u5217\u3068\u5909\u6570\u3001 \u304a\u3088\u3073\u30d0\u30ea\u30a2\u3092\u5909\u63db\u3057\u307e\u3059 (\u30a2\u30c8\u30df\u30c3\u30af\u64cd\u4f5c\u306f\u3042\u308a\u307e\u305b\u3093)\u3002lqsort_kernel<\/em> \u3082\u30b5\u30dd\u30fc\u30c8\u95a2\u6570\u3068\u30b5\u30dd\u30fc\u30c8\u69cb \u9020\u4f53\u3092 \u4f7f\u7528\u3057\u307e\u3059\u3002 gqsort_kernel<\/em> \u3067\u4f7f\u7528\u3055\u308c\u308b<\/span>plus_prescan<\/em> \u3068 median_select<\/em> \u306b\u52a0\u3048\u3066\u3001 lqsort_kernel<\/em> \u306b\u306f\u3088\u308a\u8907\u96d1\u306a bitonic_sort<\/em> \u3068sort_threshold<\/em> \u304c\u3042\u308a\u307e\u3059\u3002 \u5909\u63db\u5f8c\u3001 \u3053\u308c\u3089\u306e\u95a2\u6570\u306f lqsort_kernel_class<\/em> \u306e\u30e1\u30f3\u30d0\u30fc\u95a2\u6570\u306b\u306a\u308a\u307e\u3059\u3002 DPC++ \u3067\u306f\u53cd\u5fa9\u30aa\u30d6\u30b8\u30a7\u30af\u30c8\u304c\u5fc5\u8981\u306a\u30d0\u30ea\u30a2\u306e\u4f7f\u7528\u306b\u3088\u308a\u3001 \u3053\u308c\u3089\u306e\u95a2\u6570\u306e\u30b7\u30b0\u30cd\u30c1\u30e3\u30fc\u306f\u5909\u308f\u308a\u307e\u3059\u3002 \u3053\u308c\u3089\u306e\u95a2\u6570\u306f\u3001 \u30ed\u30fc\u30ab\u30eb\u304a\u3088\u3073\u30b0\u30ed\u30fc\u30d0\u30eb \u30fb\u30e1\u30e2\u30ea\u30fc \u30fb \u30dd\u30a4\u30f3\u30bf\u30fc\u3092\u4f7f\u7528\u3059\u308b\u305f\u3081\u3001 \u7279\u5225\u306a\u51e6\u7406\u304c\u5fc5\u8981\u3067\u3059\u3002 \u305d\u306e\u305f\u3081\u3001 OpenCL* C \u30b7\u30b0\u30cd\u30c1\u30e3\u30fc\u306f\u3001<\/span><\/p>\n

        \"\"<\/p>\n

        \u304b\u3089\u4ee5\u4e0b\u306b\u5909\u308f\u308a\u307e\u3059\u3002<\/span><\/p>\n

        \"\"<\/p>\n

        \u540c\u69d8\u306b\u3001<\/span><\/p>\n

        \"\"<\/p>\n

        \u3082\u4ee5\u4e0b\u306b\u5909\u308f\u308a\u307e\u3059\u3002<\/span><\/p>\n

        \"\"<\/p>\n

        gqsort_kernel<\/em> \u3068\u540c\u69d8\u306b\u3001 \u5f8c\u3067\u8907\u6570\u306e\u30c7\u30fc\u30bf\u578b\u3092\u6271\u3048\u308b\u3088\u3046\u306b\u3001 UINT_MAX<\/em> \u30de\u30af\u30ed\u3092 std::numeric_ limits::max()<\/em> \u306b\u7f6e\u304d\u63db\u3048\u3066\u3053\u308c\u3089\u306e\u95a2\u6570\u3092\u5909\u63db\u3057\u307e\u3059\u3002 lqsort_kernel<\/em> \u3092\u5909 \u63db\u3059\u308b\u969b\u306b\u3001 \u30ed\u30fc\u30ab\u30eb\u30e1\u30e2\u30ea\u30fc\u3078 \u306e\u30dd\u30a4\u30f3\u30bf\u30fc (local uint* sn;<\/em> \u306a\u3069) \u306f local_ptr<><\/em> \u30aa\u30d6\u30b8\u30a7\u30af\u30c8 (local_ptr sn;<\/em> \u306a\u3069) \u306b\u7f6e\u304d\u63db\u3048\u3089\u308c\u307e\u3059\u3002 \u30ed\u30fc\u30ab\u30eb\u30a2\u30af\u30bb\u30b5\u30fc\u304b\u3089 \u30ed\u30fc\u30ab\u30eb\u30dd\u30a4\u30f3\u30bf\u30fc\u3092\u53d6\u5f97\u3059\u308b\u305f\u3081\u3001 \u30a2\u30af\u30bb\u30b5\u30fc\u306e get_pointer<\/em> \u30e1\u30f3\u30d0\u30fc\u95a2\u6570\u3092\u547c\u3073\u51fa\u3057\u307e\u3059\u3002<\/span><\/p>\n

        \"\"<\/p>\n

        local_ptr<><\/em> \u30aa\u30d6 \u30b8\u30a7\u30af\u30c8\u3068 global_ptr<><\/em> \u30aa \u30d6 \u30b8\u30a7 \u30af\u30c8 \u306f \u30dd\u30a4 \u30f3\u30bf\u30fc\u6f14\u7b97\u3092\u4f7f\u7528\u3059\u308b\u305f\u3081\u3001<\/span>d + d_offset<\/em> (d<\/em> \u306f\u30b0\u30ed\u30fc\u30d0\u30eb\u30dd\u30a4\u30f3\u30bf\u30fc) \u306f\u6b21\u306e\u3088\u3046\u306b\u306a\u308a\u307e\u3059\u3002<\/span><\/p>\n

        \"\"<\/p>\n

        \u30ed\u30fc\u30ab\u30eb\u30e1\u30e2\u30ea\u30fc\u5909\u6570\u306f\u3001 \u30b5\u30a4\u30ba 1 \u306e\u30a2\u30af\u30bb\u30b5\u30fc (\u3064\u307e\u308a\u3001 gtsum[0]<\/em> \u306e\u3088\u3046\u306a\u30a4\u30f3\u30c7\u30c3\u30af\u30b9 0 \u306e\u914d\u5217\u30a2\u30af\u30bb\u30b9) \u3068\u3057\u3066\u5909\u63db\u3057\u307e\u3059\u3002 lqsort_kernel<\/em> \u306e\u5909\u63db\u304c\u5b8c\u4e86\u3057\u305f\u3089\u3001 DPC++ \u3078\u5b8c\u5168\u306b\u79fb\u884c\u3067\u304d\u307e\u3059\u304c\u3001 \u3053\u306e\u6642\u70b9\u3067\u306f\u7b26\u53f7\u306a\u3057\u6574\u6570\u3057\u304b\u30bd\u30fc\u30c8\u3067\u304d\u307e\u305b\u3093\u3002 \u3057\u304b\u3057\u3001 \u30b5\u30dd\u30fc\u30c8\u69cb\u9020\u4f53\u3068\u30b5\u30dd\u30fc\u30c8\u95a2\u6570\u3001\u304a\u3088\u3073 2 \u3064\u306e\u30e1\u30a4\u30f3\u30ab\u30fc\u30cd\u30eb\u306e\u30d5\u30a1\u30f3\u30af\u30bf\u30fc\u30fb\u30af\u30e9\u30b9\u306f\u3059\u3067\u306b\u30c6\u30f3\u30d7\u30ec\u30fc\u30c8\u5316\u3055\u308c\u3066\u3044\u308b\u305f\u3081\u3001 \u8907\u6570\u306e\u30c7\u30fc\u30bf\u578b\u306b\u5bfe\u5fdc\u3059\u308b\u306e\u306f\u5bb9\u6613\u3067\u3059\u3002<\/span><\/p>\n

        \u30c7\u30fc\u30bf\u4e26\u5217 C++ \u306e\u5229\u70b9 : \u30c6\u30f3\u30d7\u30ec\u30fc\u30c8\u3068\u6ce8\u610f\u4e8b\u9805<\/span><\/h2>\n

        DPC++ \u306e\u771f\u306e\u529b\u306f\u3001 C++ \u30c6\u30f3\u30d7\u30ec\u30fc\u30c8\u3092\u4f7f\u7528\u3057\u3066\u6c4e\u7528\u30b3\u30fc\u30c9\u3092\u8a18\u8ff0\u3067\u304d\u308b\u3053\u3068\u3067\u3059\u3002 \u3053\u306e\u30bb\u30af\u30b7\u30e7\u30f3\u3067\u306f\u3001 GPU-Quicksort \u3092\u6c4e\u7528\u5316\u3057\u3066\u3001 \u7b26\u53f7\u306a\u3057\u6574\u6570\u3060\u3051\u3067\u306a\u304f\u3001 \u5358\u7cbe\u5ea6\u3084\u500d\u7cbe\u5ea6\u306e\u6d6e\u52d5\u5c0f\u6570\u70b9\u306a\u3069\u3001 \u307b\u304b\u306e\u57fa\u672c \u30c7\u30fc\u30bf\u578b\u3082\u30bd\u30fc\u30c8\u3067\u304d\u308b\u3088\u3046\u306b\u3057\u307e\u3059\u3002 \u524d\u8ff0\u306e UINT_MAX<\/em> \u304bstd::numeric_limits::max()<\/em> \u3078\u306e \u5909\u66f4\u306b\u52a0\u3048\u3066\u3001median_select<\/em> \u95a2\u6570\u3092\u5909\u66f4\u3059\u308b\u5fc5\u8981\u304c\u3042\u308a\u307e\u3059\u3002 cl::sycl::select<\/em> \u306f\u3001 \u7b2c 1 \u5f15\u6570\u3068 \u7b2c 2 \u5f15\u6570\u306e\u578b\u306e\u30b5\u30a4\u30ba\u306b\u5fdc\u3058\u3066\u3001 \u7570\u306a\u308b\u7b2c 3 \u5f15\u6570\u3092\u53d7\u3051\u53d6\u308b\u305f\u3081\u3001 select_type_selector<\/em> \u578b\u306e\u7279\u5fb4 \u30af\u30e9\u30b9\u3092\u8ffd\u52a0\u3057\u307e\u3059\u3002<\/span><\/p>\n

        \"\"<\/p>\n

        \u3053\u308c\u306b\u3088\u308a\u3001 \u30d6\u30fc\u30eb \u5024\u306e\u6bd4\u8f03\u3092 cl::sycl::select<\/em> \u3067\u5fc5\u8981\u306a\u9069\u5207\u306a\u578b\u306b\u5909\u63db\u3059\u308b\u3053\u3068\u304c\u3067\u304d\u307e\u3059\u3002<\/span>
        \nmedian_select<\/em> \u306f\u6b21\u306e\u3088\u3046\u306b\u306a\u308a\u307e\u3059\u3002<\/span><\/p>\n

        \"\"<\/p>\n

        \u8ffd\u52a0\u306e\u578b\u306b\u5bfe\u5fdc\u3059\u308b\u306b\u306f\u3001 select_type_selector<\/em> \u3092\u7de8\u96c6\u3057\u307e\u3059\u3002 \u3053\u308c\u3067\u3001 GPUQSort \u306f GPU \u3067\u5358\u7cbe<\/span>
        \n\u5ea6\u3068\u500d\u7cbe\u5ea6\u306e\u6d6e\u52d5\u5c0f\u6570\u70b9\u3082\u30bd\u30fc\u30c8\u3067\u304d\u308b\u3088\u3046\u306b\u306a\u308a\u307e\u3057\u305f\u3002<\/span><\/p>\n

        Windows* \u3068 RHEL \u3078\u306e\u79fb\u690d<\/span><\/h2>\n

        DPC++ \u306e\u79fb\u690d\u6027\u3092\u5b9f\u8a3c\u3059\u308b\u305f\u3081\u3001 Windows* \u3068 RHEL \u3078\u30b3\u30fc\u30c9\u3092\u79fb\u690d\u3057\u307e\u3059\u3002 RHEL \u3078\u306e\u79fb\u690d\u306f\u975e\u5e38\u306b\u7c21\u5358\u3067\u3059\u3002 \u30ea\u30f3\u30af\u6642\u306b\u30a4\u30f3\u30c6\u30eb\u306e imf \u6570\u5b66\u30e9\u30a4\u30d6\u30e9\u30ea\u30fc\u3092\u8ffd\u52a0\u3059\u308b\u3060\u3051\u3067\u3059\u3002 Windows* \u3078\u306e\u79fb\u690d\u306b\u306f\u3001 \u3082\u3046\u5c11\u3057\u624b\u9593\u304c\u304b\u304b\u308a\u307e\u3059\u3002 \u30b3\u30f3\u30d1\u30a4\u30eb\u6642\u306b\u6b21\u306e\u5b9a\u7fa9\u3092\u8ffd\u52a0\u3057\u307e\u3059\u3002<\/span><\/p>\n

        \"\"<\/p>\n

        \u500d\u7cbe\u5ea6\u306e cl::sycl::select<\/em> \u306f \u7b2c 3 \u5f15\u6570\u306b unsigned long long<\/em> \u578b (Linux* \u3067\u306f unsigned<\/em><\/span>
        \nlong<\/em> \u578b) \u3092\u5fc5\u8981\u3068\u3059\u308b\u3053\u3068\u304b\u3089\u3001 \u500d\u7cbe\u5ea6\u306e select_type_selector<\/em> \u3092\u6b21\u306e\u3088\u3046\u306b\u5909\u66f4\u3057\u307e\u3059\u3002<\/span><\/p>\n

        \"\"<\/p>\n

        Windows* \u3067\u306f\u3001 \u30de\u30af\u30ed\u5b9a\u7fa9\u304c std::max<\/em> \u304a\u3088\u3073 std::min<\/em> \u3068\u7af6\u5408\u3057\u306a\u3044\u3088\u3046\u306b\u3001 max<\/em> \u304a\u3088\u3073 min<\/em> \u3092\u672a\u5b9a\u7fa9\u306b\u3057\u307e\u3059\u3002 \u3053\u308c\u3067\u3001 Windows* \u304a\u3088\u3073 RHEL \u3067\u30a4\u30f3\u30c6\u30eb\u306e GPU \u3092\u4f7f\u7528\u3057\u3066\u3001 \u7b26\u53f7\u306a\u3057\u6574\u6570\u3001 \u5358\u7cbe\u5ea6\u6d6e\u52d5\u5c0f\u6570\u70b9\u3001 \u500d\u7cbe\u5ea6\u6d6e\u52d5\u5c0f\u6570\u70b9\u3092\u30bd\u30fc\u30c8\u3067\u304d\u307e\u3059\u3002<\/span><\/p>\n

        \u4eca\u3059\u3050\u5b9f\u8df5\u3057\u3066\u307f\u307e\u3057\u3087\u3046<\/span><\/h2>\n

        \u3053\u306e\u8a18\u4e8b\u3067\u306f\u3001 GPU-Quicksort \u3092\u30aa\u30ea\u30b8\u30ca\u30eb\u306e OpenCL* 1.2 \u304b\u3089 DPC++ \u3078\u79fb\u884c\u3059\u308b\u65b9\u6cd5\u3092\u30b9\u30c6\u30c3\u30d7\u3054\u3068\u306b\u8aac\u660e\u3057\u307e\u3057\u305f\u3002 \u30b9\u30c6\u30c3\u30d7\u3054\u3068\u306b\u3001 \u30a2\u30d7\u30ea\u30b1\u30fc\u30b7\u30e7\u30f3\u306e\u52d5\u4f5c\u3092\u78ba\u8a8d\u3067\u304d\u308b\u3053\u3068\u304c\u91cd\u8981\u3067\u3059\u3002 DPC++ \u3092\u30ef\u30fc\u30af\u30d5\u30ed\u30fc\u306b\u5c0e\u5165\u3059\u308b\u3053\u3068\u3092\u691c\u8a0e\u3057\u3066\u3044\u308b\u5834\u5408\u306f\u3001 \u5c0f\u898f\u6a21\u304b\u3089\u521d\u3081\u3066\u3001 \u5f90\u3005\u306b\u8ffd\u52a0\u3057\u3066\u3044\u304f\u304b\u3001 \u6642\u9593\u3092\u304b\u3051\u3066\u5b8c\u5168\u306b\u79fb\u884c\u3057\u3066\u304f\u3060\u3055\u3044\u3002 \u5bb9\u6613\u306b OpenCL* \u3068 DPC++ \u3092\u30b3\u30fc\u30c9\u30d9\u30fc\u30b9\u306b\u6df7\u5728\u3055\u305b\u3001 \u4e21\u65b9\u306e\u5229\u70b9\u3092\u5f97\u3089\u308c\u307e\u3059\u3002 \u5f93\u6765\u306e OpenCL* \u30ab\u30fc\u30cd\u30eb\u3092\u305d\u306e\u307e\u307e\u4f7f\u7528\u3057\u3064\u3064\u3001 DPC++ \u3067\u958b\u767a\u3059\u308b\u65b0\u3057\u3044\u30b3\u30fc\u30c9\u3067\u306f C++ \u30c6\u30f3\u30d7\u30ec\u30fc\u30c8\u3001 \u30af\u30e9\u30b9\u3001\u30e9\u30e0\u30c0\u3092\u6d3b\u7528\u3067\u304d\u307e\u3059\u3002 Windows* \u3084\u5404\u7a2e Linux* \u30c7\u30a3\u30b9\u30c8\u30ea\u30d3\u30e5\u30fc\u30b7\u30e7\u30f3\u3078\u306e\u30b3\u30fc\u30c9\u306e\u79fb\u690d\u3082\u5bb9\u6613\u3067\u3001 \u958b\u767a\u30d7\u30e9\u30c3\u30c8\u30d5\u30a9\u30fc\u30e0\u3092\u9078\u629e\u3067\u304d\u307e\u3059\u3002 \u3055\u3089\u306b\u3001 \u5f37\u529b\u306a\u30a4\u30f3\u30c6\u30eb\u306e\u30c4\u30fc\u30eb\u304c DPC++ \u30d7\u30ed\u30b0\u30e9\u30e0\u306e\u30c7\u30d0\u30c3\u30b0\u3001 \u30d7\u30ed\u30d5\u30a1\u30a4\u30eb\u3001 \u89e3\u6790\u3092\u652f\u63f4\u3057\u307e\u3059\u3002<\/span><\/p>\n

        \n

        \u672c\u8a18\u4e8b\u306f\u300cParallel Universe 40\u53f7\u300d\u306e\u300cGPU-Quicksort\u300d\u3088\u308a\u8ee2\u8f09\u3057\u305f\u3082\u306e\u3067\u3059\u3002\u305d\u306e\u4ed6\u300cParallel Universe\u300d\u306e\u8a18\u4e8b\u306f\u3053\u3061\u3089<\/a>\u304b\u3089\u3054\u89a7\u3044\u305f\u3060\u3051\u307e\u3059\u3002<\/span><\/p>\n

        \n","protected":false},"excerpt":{"rendered":"

        \u30c7\u30fc\u30bf\u4e26\u5217 C++ (DPC++) \u306f\u3001 Khro […]<\/a><\/p>\n<\/div>","protected":false},"author":1,"featured_media":1524,"comment_status":"closed","ping_status":"closed","sticky":false,"template":"","format":"standard","meta":{"footnotes":""},"categories":[1],"tags":[],"class_list":["post-1493","post","type-post","status-publish","format-standard","has-post-thumbnail","hentry","category-1"],"aioseo_notices":[],"_links":{"self":[{"href":"https:\/\/www.xlsoft.com\/jp\/blog\/intel\/wp-json\/wp\/v2\/posts\/1493","targetHints":{"allow":["GET"]}}],"collection":[{"href":"https:\/\/www.xlsoft.com\/jp\/blog\/intel\/wp-json\/wp\/v2\/posts"}],"about":[{"href":"https:\/\/www.xlsoft.com\/jp\/blog\/intel\/wp-json\/wp\/v2\/types\/post"}],"author":[{"embeddable":true,"href":"https:\/\/www.xlsoft.com\/jp\/blog\/intel\/wp-json\/wp\/v2\/users\/1"}],"replies":[{"embeddable":true,"href":"https:\/\/www.xlsoft.com\/jp\/blog\/intel\/wp-json\/wp\/v2\/comments?post=1493"}],"version-history":[{"count":7,"href":"https:\/\/www.xlsoft.com\/jp\/blog\/intel\/wp-json\/wp\/v2\/posts\/1493\/revisions"}],"predecessor-version":[{"id":1854,"href":"https:\/\/www.xlsoft.com\/jp\/blog\/intel\/wp-json\/wp\/v2\/posts\/1493\/revisions\/1854"}],"wp:featuredmedia":[{"embeddable":true,"href":"https:\/\/www.xlsoft.com\/jp\/blog\/intel\/wp-json\/wp\/v2\/media\/1524"}],"wp:attachment":[{"href":"https:\/\/www.xlsoft.com\/jp\/blog\/intel\/wp-json\/wp\/v2\/media?parent=1493"}],"wp:term":[{"taxonomy":"category","embeddable":true,"href":"https:\/\/www.xlsoft.com\/jp\/blog\/intel\/wp-json\/wp\/v2\/categories?post=1493"},{"taxonomy":"post_tag","embeddable":true,"href":"https:\/\/www.xlsoft.com\/jp\/blog\/intel\/wp-json\/wp\/v2\/tags?post=1493"}],"curies":[{"name":"wp","href":"https:\/\/api.w.org\/{rel}","templated":true}]}}