{"id":267709,"date":"2015-11-08T13:22:02","date_gmt":"2015-11-08T10:22:02","guid":{"rendered":"http:\/\/savepearlharbor.com\/?p=267709"},"modified":"-0001-11-30T00:00:00","modified_gmt":"-0001-11-29T21:00:00","slug":"","status":"publish","type":"post","link":"https:\/\/savepearlharbor.com\/?p=267709","title":{"rendered":"Altera + OpenCL: \u043f\u0440\u043e\u0433\u0440\u0430\u043c\u043c\u0438\u0440\u0443\u0435\u043c \u043f\u043e\u0434 FPGA \u0431\u0435\u0437 \u0437\u043d\u0430\u043d\u0438\u044f VHDL\/Verilog"},"content":{"rendered":"<p>       <img decoding=\"async\" src=\"https:\/\/habrastorage.org\/getpro\/habr\/post_images\/4cb\/21d\/43d\/4cb21d43df4b00dac92ec93d29c15488.gif\" alt=\"image\"\/><\/p>\n<p>  \u0412\u0441\u0435\u043c \u043f\u0440\u0438\u0432\u0435\u0442!<\/p>\n<p>  <b>Altera SDK for OpenCL<\/b> \u2014 \u044d\u0442\u043e \u043d\u0430\u0431\u043e\u0440 \u0431\u0438\u0431\u043b\u0438\u043e\u0442\u0435\u043a \u0438 \u043f\u0440\u0438\u043b\u043e\u0436\u0435\u043d\u0438\u0439, \u043a\u043e\u0442\u043e\u0440\u044b\u0439 \u043f\u043e\u0437\u0432\u043e\u043b\u044f\u0435\u0442 \u043a\u043e\u043c\u043f\u0438\u043b\u0438\u0440\u043e\u0432\u0430\u0442\u044c \u043a\u043e\u0434, \u043d\u0430\u043f\u0438\u0441\u0430\u043d\u043d\u044b\u0439 \u043d\u0430 <b>OpenCL<\/b>, \u0432 \u043f\u0440\u043e\u0448\u0438\u0432\u043a\u0443 \u0434\u043b\u044f \u041f\u041b\u0418\u0421 \u0444\u0438\u0440\u043c\u044b <b>Altera<\/b>. \u042d\u0442\u043e \u0434\u0430\u0451\u0442 \u0432\u043e\u0437\u043c\u043e\u0436\u043d\u043e\u0441\u0442\u044c \u043f\u0440\u043e\u0433\u0440\u0430\u043c\u043c\u0438\u0441\u0442\u0443 \u0438\u0441\u043f\u043e\u043b\u044c\u0437\u043e\u0432\u0430\u0442\u044c FPGA \u043a\u0430\u043a \u0443\u0441\u043a\u043e\u0440\u0438\u0442\u0435\u043b\u044c \u0432\u044b\u0441\u043e\u043a\u043e\u043f\u0440\u043e\u0438\u0437\u0432\u043e\u0434\u0438\u0442\u0435\u043b\u044c\u043d\u044b\u0445 \u0432\u044b\u0447\u0438\u0441\u043b\u0435\u043d\u0438\u0439 \u0431\u0435\u0437 \u0437\u043d\u0430\u043d\u0438\u044f HDL-\u044f\u0437\u044b\u043a\u043e\u0432, \u0430 \u043f\u0438\u0441\u0430\u0442\u044c \u043d\u0430 \u0442\u043e\u043c, \u0447\u0442\u043e \u043e\u043d \u043f\u0440\u0438\u0432\u044b\u043a, \u043a\u043e\u0433\u0434\u0430 \u044d\u0442\u043e \u0434\u0435\u043b\u0430\u0435\u0442 \u043f\u043e\u0434 GPU.<\/p>\n<p>  \u042f \u043f\u043e\u0438\u0433\u0440\u0430\u043b\u0441\u044f \u0441 \u044d\u0442\u0438\u043c \u0438\u043d\u0441\u0442\u0440\u0443\u043c\u0435\u043d\u0442\u043e\u043c \u043d\u0430 \u043f\u0440\u043e\u0441\u0442\u043e\u043c \u043f\u0440\u0438\u043c\u0435\u0440\u0435 \u0438 \u0445\u043e\u0447\u0443 \u043e\u0431 \u044d\u0442\u043e\u043c \u0432\u0430\u043c \u0440\u0430\u0441\u0441\u043a\u0430\u0437\u0430\u0442\u044c.<\/p>\n<p>  \u041f\u043b\u0430\u043d:  <\/p>\n<ul>\n<li><a href=\"#fpga\">\u041f\u0430\u0440\u0443 \u0441\u043b\u043e\u0432 \u043e\u0431 FPGA<\/a><\/li>\n<li><a href=\"#where_to_run\">\u041d\u0430 \u0447\u0451\u043c \u0437\u0430\u043f\u0443\u0441\u043a\u0430\u0442\u044c?<\/a><\/li>\n<li><a href=\"#workflow\">\u041f\u0440\u043e\u0446\u0435\u0441\u0441 \u0440\u0430\u0437\u0440\u0430\u0431\u043e\u0442\u043a\u0438 (workflow)<\/a><\/li>\n<li><a href=\"#opencl_bsp\">OpenCL BSP<\/a><\/li>\n<li><a href=\"#compile\">\u041a\u043e\u043c\u043f\u0438\u043b\u0438\u0440\u0443\u0435\u043c \u043a\u0435\u0440\u043d\u0435\u043b<\/a><\/li>\n<li><a href=\"#execute_on_fpga\">\u2026 \u0438 \u0437\u0430\u043f\u0443\u0441\u043a\u0430\u0435\u043c<\/a><\/li>\n<li><a href=\"#the_end\">\u0417\u0430\u043a\u043b\u044e\u0447\u0435\u043d\u0438\u0435<\/a><\/li>\n<\/ul>\n<p>  \u0414\u043e\u0431\u0440\u043e \u043f\u043e\u0436\u0430\u043b\u043e\u0432\u0430\u0442\u044c \u043f\u043e\u0434 \u043a\u0430\u0442! <b>\u041e\u0441\u0442\u043e\u0440\u043e\u0436\u043d\u043e<\/b>, \u0431\u0443\u0434\u0443\u0442 \u043a\u0430\u0440\u0442\u0438\u043d\u043a\u0438!<br \/>  <a name=\"habracut\"><\/a><br \/>  <a name=\"fpga\"><\/a>  <\/p>\n<h2>\u041f\u0430\u0440\u0443 \u0441\u043b\u043e\u0432 \u043e\u0431 FPGA (\u041f\u041b\u0418\u0421)<\/h2>\n<p>  FPGA (Field-Programmable Gate Array) \u2014 \u044d\u0442\u043e \u043f\u0440\u043e\u0433\u0440\u0430\u043c\u043c\u0438\u0440\u0443\u0435\u043c\u0430\u044f \u043f\u043e\u043b\u044c\u0437\u043e\u0432\u0430\u0442\u0435\u043b\u0435\u043c \u0432\u0435\u043d\u0442\u0438\u043b\u044c\u043d\u0430\u044f \u043c\u0430\u0442\u0440\u0438\u0446\u0430, \u044f\u0432\u043b\u044f\u0435\u0442\u0441\u044f \u0440\u0430\u0437\u043d\u043e\u0432\u0438\u0434\u043d\u043e\u0441\u0442\u044c\u044e <abbr title=\"\u043f\u0440\u043e\u0433\u0440\u0430\u043c\u043c\u0438\u0440\u0443\u0435\u043c\u0430\u044f \u043b\u043e\u0433\u0438\u0447\u0435\u0441\u043a\u0430\u044f \u0438\u043d\u0442\u0435\u0433\u0440\u0430\u043b\u044c\u043d\u0430\u044f \u0441\u0445\u0435\u043c\u0430\">\u041f\u041b\u0418\u0421<\/abbr>. <\/p>\n<p>  \u0412 \u043e\u0441\u043d\u043e\u0432\u0435 \u0442\u0430\u043a\u0438\u0445 \u0447\u0438\u043f\u043e\u0432 \u043b\u0435\u0436\u0430\u0442 \u043d\u0435\u0431\u043e\u043b\u044c\u0448\u0438\u0435 \u0431\u043b\u043e\u043a\u0438 \u043b\u043e\u0433\u0438\u0447\u0435\u0441\u043a\u0438\u0445 \u044d\u043b\u0435\u043c\u0435\u043d\u0442\u043e\u0432. \u041d\u0430 \u0442\u0430\u043a\u0438\u0445 \u043f\u0440\u0438\u043c\u0438\u0442\u0438\u0432\u0430\u0445 \u043c\u043e\u0436\u043d\u043e \u043f\u043e\u0441\u0442\u0440\u043e\u0438\u0442\u044c \u043b\u043e\u0433\u0438\u043a\u0443 \u043b\u044e\u0431\u043e\u0433\u043e \u0447\u0438\u043f\u0430 \u2014 \u043e\u0442 8-\u0431\u0438\u0442\u043d\u043e\u0433\u043e \u043c\u0438\u043a\u0440\u043e\u043a\u043e\u043d\u0442\u0440\u043e\u043b\u043b\u0435\u0440\u0430 \u0434\u043e \u043c\u0430\u0439\u043d\u0435\u0440\u0430 \u0431\u0438\u0442\u043a\u043e\u0438\u043d\u043e\u0432. <\/p>\n<div class=\"spoiler\"><b class=\"spoiler_title\">\u041f\u043e\u0434\u0440\u043e\u0431\u043d\u0435\u0435 \u043f\u0440\u043e FPGA<\/b><\/p>\n<div class=\"spoiler_text\">\u0420\u0435\u043a\u043e\u043c\u0435\u043d\u0434\u0443\u044e \u043f\u043e\u0441\u043c\u043e\u0442\u0440\u0435\u0442\u044c \u043e\u0447\u0435\u043d\u044c \u043a\u0430\u0447\u0435\u0441\u0442\u0432\u0435\u043d\u043d\u043e\u0435 \u0432\u0438\u0434\u0435\u043e:<br \/>  <iframe loading=\"lazy\" width=\"560\" height=\"315\" src=\"https:\/\/www.youtube.com\/embed\/gUsHwi4M4xE?feature=oembed\" frameborder=\"0\" allowfullscreen><\/iframe><\/p>\n<p>  \u0422\u0430\u043a \u0436\u0435 \u0435\u0441\u0442\u044c \u043d\u0435\u043f\u043b\u043e\u0445\u0430\u044f \u043a\u043d\u0438\u0433\u0430 <a href=\"https:\/\/www.altera.com\/en_US\/pdfs\/literature\/misc\/FPGAs_For_Dummies_eBook.pdf\"><b>FPGAs for Dummies<\/b><\/a>, \u0433\u0434\u0435 \u043e\u0447\u0435\u043d\u044c \u043f\u0440\u043e\u0441\u0442\u044b\u043c \u044f\u0437\u044b\u043a\u043e\u043c \u043e\u0431\u044a\u044f\u0441\u043d\u044f\u0435\u0442\u0441\u044f \u0447\u0442\u043e \u0442\u0430\u043a\u043e\u0435 FPGA, \u0438 \u043a\u0430\u043a \u044d\u0442\u0438 \u0447\u0438\u043f\u044b \u0438\u0441\u043f\u043e\u043b\u044c\u0437\u0443\u044e\u0442\u0441\u044f.  <\/div>\n<\/div>\n<p>  \u00ab\u041a\u043b\u0430\u0441\u0441\u0438\u0447\u0435\u0441\u043a\u0430\u044f\u00bb \u0440\u0430\u0437\u0440\u0430\u0431\u043e\u0442\u043a\u0430 \u043f\u043e\u0434 FPGA \u0432\u044b\u0433\u043b\u044f\u0434\u0438\u0442 \u0442\u0430\u043a: <br \/>  <s>\u043f\u0440\u043e\u0433\u0440\u0430\u043c\u043c\u0430<\/s> \u0441\u0445\u0435\u043c\u0430 \u043e\u043f\u0438\u0441\u044b\u0432\u0430\u0435\u0442\u0441\u044f \u043d\u0430 <abbr title=\"Hardware Description Language\">HDL<\/abbr> \u044f\u0437\u044b\u043a\u0430\u0445 \u0442\u0438\u043f\u0430 VHDL\/Verilog \u0438 \u0441\u043a\u0430\u0440\u043c\u043b\u0438\u0432\u0430\u0435\u0442\u0441\u044f \u043a\u043e\u043c\u043f\u0438\u043b\u044f\u0442\u043e\u0440\u0443, \u043a\u043e\u0442\u043e\u0440\u044b\u0439 \u043f\u0435\u0440\u0435\u0432\u043e\u0434\u0438\u0442 \u043e\u043f\u0438\u0441\u0430\u043d\u0438\u0435 \u0432 \u0443\u0440\u043e\u0432\u0435\u043d\u044c \u043f\u0440\u0438\u043c\u0438\u0442\u0438\u0432\u043e\u0432, \u0430 \u0442\u0430\u043a \u0436\u0435 \u043d\u0430\u0445\u043e\u0434\u0438\u0442 \u043e\u043f\u0442\u0438\u043c\u0430\u043b\u044c\u043d\u043e\u0435 \u0440\u0430\u0441\u043f\u043e\u043b\u043e\u0436\u0435\u043d\u0438\u0435 \u044d\u0442\u0438\u0445 \u0431\u043b\u043e\u043a\u043e\u0432 \u0432 \u0447\u0438\u043f\u0435 \u0441 \u0443\u0447\u0435\u0442\u043e\u043c \u0437\u0430\u0434\u0430\u043d\u043d\u044b\u0445 \u0432\u0440\u0435\u043c\u0435\u043d\u043d\u044b\u0445 \u043e\u0433\u0440\u0430\u043d\u0438\u0447\u0435\u043d\u0438\u0439 (\u043a\u043e\u043d\u0441\u0442\u0440\u0435\u0439\u043d\u043e\u0432). \u0422\u0430\u043a\u0442\u043e\u0432\u0430\u044f \u0447\u0430\u0441\u0442\u043e\u0442\u0430 \u0441\u0445\u0435\u043c\u0430 \u2014 \u043f\u0440\u0438\u043c\u0435\u0440 \u0442\u0430\u043a\u043e\u0433\u043e \u043a\u043e\u043d\u0441\u0442\u0440\u0435\u0439\u043d\u0430.<\/p>\n<p>  \u0418\u043d\u043e\u0433\u0434\u0430 \u041f\u041b\u0418\u0421 \u0432\u043e\u0441\u043f\u0440\u0438\u043d\u0438\u043c\u0430\u0435\u0442\u0441\u044f \u043a\u0430\u043a \u0431\u043e\u043b\u0435\u0435 \u0434\u043e\u0440\u043e\u0433\u0430\u044f \u0440\u0430\u0437\u043d\u043e\u0432\u0438\u0434\u043d\u043e\u0441\u0442\u044c \u043c\u0438\u043a\u0440\u043e\u043a\u043e\u043d\u0442\u0440\u043e\u043b\u043b\u0435\u0440\u043e\u0432: \u0442\u0430\u043c \u0438 \u0442\u0430\u043c \u043c\u043e\u0436\u043d\u043e \u043c\u043e\u0440\u0433\u0430\u0442\u044c \u0441\u0432\u0435\u0442\u043e\u0434\u0438\u043e\u0434\u043e\u043c, \u043e\u0433\u0440\u0430\u043d\u0438\u0437\u043e\u0432\u044b\u0432\u0430\u0442\u044c UART, SPI, I2C. \u0420\u0430\u043d\u044c\u0448\u0435 \u043e\u0442\u0447\u0430\u0441\u0442\u0438 \u044d\u0442\u043e \u0431\u044b\u043b\u043e \u0441\u043f\u0440\u0430\u0432\u0435\u0434\u043b\u0438\u0432\u043e \u0438\u0437-\u0437\u0430 \u0442\u043e\u0433\u043e, \u0447\u0442\u043e \u041f\u041b\u0418\u0421 \u0431\u044b\u043b\u0438 \u043c\u0430\u043b\u0435\u043d\u044c\u043a\u0438\u0435 (\u043f\u043e \u0440\u0435\u0441\u0443\u0440\u0441\u0430\u043c \u0438 \u0447\u0430\u0441\u0442\u043e\u0442\u0430\u043c), \u0438 \u043e \u043a\u0430\u043a\u043e\u0439-\u0442\u043e \u0441\u0435\u0440\u044c\u0435\u0437\u043d\u043e\u0439 \u043e\u0431\u0440\u0430\u0431\u043e\u0442\u043a\u0435 \u0434\u0430\u043d\u043d\u044b\u0445 \u0438 \u043a\u043e\u043d\u043a\u0443\u0440\u0435\u043d\u0446\u0438\u0438 \u0441 \u043f\u0440\u043e\u0446\u0435\u0441\u0441\u043e\u0440\u0430\u043c \u043d\u0435\u043b\u044c\u0437\u044f \u0431\u044b\u043b\u043e \u0433\u043e\u0432\u043e\u0440\u0438\u0442\u044c. \u0421\u0435\u0439\u0447\u0430\u0441 \u0447\u0438\u043f\u044b FPGA \u0441\u0442\u0430\u043d\u043e\u0432\u0438\u0442\u0441\u044f \u0432\u0441\u0451 \u0436\u0438\u0440\u043d\u0435\u0435, \u0430 \u043f\u043e \u043f\u0440\u043e\u0438\u0437\u0432\u043e\u0434\u0438\u0442\u0435\u043b\u044c\u043d\u043e\u0441\u0442\u0438 \u0438\u0445 \u0441\u0440\u0430\u0432\u043d\u0438\u0432\u0430\u044e\u0442 \u0441 GPU. <\/p>\n<p>  FPGA \u0434\u0430\u0451\u0442 \u0432\u043e\u0437\u043c\u043e\u0436\u043d\u043e\u0441\u0442\u044c \u0443\u043f\u0440\u0430\u0432\u043b\u044f\u0442\u044c \u043e\u0431\u0440\u0430\u0431\u043e\u0442\u043a\u043e\u0439 \u043d\u0430 \u0441\u0430\u043c\u043e\u043c \u043d\u0438\u0437\u043a\u043e\u043c \u0443\u0440\u043e\u0432\u043d\u0435: \u0441\u043e\u0437\u0434\u0430\u0432\u0430\u0442\u044c \u043a\u044d\u0448\u0438 \u043d\u0443\u0436\u043d\u043e\u0433\u043e \u0440\u0430\u0437\u043c\u0435\u0440\u0430 \u0432 \u043d\u0443\u0436\u043d\u043e\u043c \u043c\u0435\u0441\u0442\u0435, \u043e\u0440\u0433\u0430\u043d\u0438\u0437\u043e\u0432\u044b\u0432\u0430\u0442\u044c \u043a\u043e\u043d\u0432\u0435\u0439\u0435\u0440\u0438\u0437\u0430\u0446\u0438\u044e, \u043e\u043f\u0438\u0441\u044b\u0432\u0430\u0442\u044c \u044f\u0432\u043d\u044b\u0439 \u043f\u0430\u0440\u0430\u043b\u043b\u0435\u043b\u0438\u0437\u043c. \u041c\u043e\u0436\u043d\u043e \u043f\u043e\u0434\u043a\u043b\u044e\u0447\u0430\u0442\u044c \u0440\u0430\u0437\u043b\u0438\u0447\u043d\u0443\u044e \u043f\u0435\u0440\u0438\u0444\u0435\u0440\u0438\u044e (\u043d\u0430\u043f\u0440\u0438\u043c\u0435\u0440, \u0432\u0438\u0434\u0435\u043e\u043a\u0430\u043c\u0435\u0440\u044b \u0438\u043b\u0438 Ethernet-\u043f\u043e\u0440\u0442\u044b) \u0438 \u043f\u0440\u043e\u0438\u0437\u0432\u043e\u0434\u0438\u0442\u044c \u0432\u044b\u0447\u0438\u0441\u043b\u0435\u043d\u0438\u044f \u0431\u0435\u0437 \u043f\u0440\u043e\u0446\u0435\u0441\u0441\u043e\u0440\u0430 \u043e\u0431\u0449\u0435\u0433\u043e \u043d\u0430\u0437\u043d\u0430\u0447\u0435\u043d\u0438\u044f.<\/p>\n<p>  \u0412\u0441\u0435 \u043f\u0440\u0435\u043b\u0435\u0441\u0442\u0438 FPGA \u043d\u0438\u0432\u0435\u043b\u0438\u0440\u0443\u044e\u0442\u0441\u044f \u0442\u0435\u043c, \u0447\u0442\u043e \u0435\u0441\u043b\u0438 \u0435\u0441\u0442\u044c \u0443\u043f\u0440\u0430\u0432\u043b\u0435\u043d\u0438\u0435 \u043d\u0438\u0437\u043a\u0438\u043c \u0443\u0440\u043e\u0432\u043d\u0435\u043c, \u0442\u043e \u044d\u0442\u043e\u0442 \u043d\u0438\u0437\u043a\u0438\u0439 \u0443\u0440\u043e\u0432\u0435\u043d\u044c \u0438 \u043d\u0430\u0434\u043e \u043f\u0440\u043e\u0433\u0440\u0430\u043c\u043c\u0438\u0440\u043e\u0432\u0430\u0442\u044c! \u041d\u0438\u0437\u043a\u0438\u0439 \u0443\u0440\u043e\u0432\u0435\u043d\u044c \u0430\u0431\u0441\u0442\u0440\u0430\u043a\u0446\u0438\u0438 \u0432\u0441\u0435\u0433\u0434\u0430 \u043f\u0440\u0438\u0432\u043e\u0434\u0438\u0442 \u043a \u0443\u0441\u043b\u043e\u0436\u043d\u0435\u043d\u0438\u044e \u0440\u0430\u0437\u0440\u0430\u0431\u043e\u0442\u043a\u0438 \u0438 \u043e\u0442\u043b\u0430\u0434\u043a\u0438, <abbr title=\"\u043f\u043e \u0441\u0440\u0430\u0432\u043d\u0435\u043d\u0438\u044e \u0441 \u0440\u0430\u0437\u0440\u0430\u0431\u043e\u0442\u043a\u043e\u0439 \u043f\u043e\u0434 CPU\">\u0443\u0432\u0435\u043b\u0438\u0447\u0435\u043d\u0438\u044e \u0441\u0440\u043e\u043a\u043e\u0432<\/abbr>. <\/p>\n<p>  \u041f\u0440\u043e\u0438\u0437\u0432\u043e\u0434\u0438\u0442\u0435\u043b\u0438 FPGA \u0432\u0435\u0441\u044c\u043c\u0430 \u0440\u0430\u0437\u0443\u043c\u043d\u043e \u0437\u0430\u0434\u0443\u043c\u0430\u043b\u0438\u0441\u044c \u043e \u0442\u043e\u043c, \u0447\u0442\u043e \u043d\u0443\u0436\u043d\u043e \u0441\u043e\u043a\u0440\u0430\u0449\u0430\u0442\u044c time-to-market: \u043f\u043e\u0437\u0432\u043e\u043b\u0438\u0442\u044c \u043f\u0440\u043e\u0433\u0440\u0430\u043c\u043c\u0438\u0441\u0442\u0430\u043c \u043e\u0447\u0435\u043d\u044c \u043b\u0435\u0433\u043a\u043e \u0438 \u0431\u044b\u0441\u0442\u0440\u043e \u043f\u0438\u0441\u0430\u0442\u044c \u043f\u043e\u0434 FPGA. \u041e\u0434\u043d\u0438\u043c \u0438\u0437 \u0441\u0442\u0430\u043d\u0434\u0430\u0440\u0442\u043d\u044b\u0445 \u0432\u0430\u0440\u0438\u0430\u043d\u0442\u043e\u0432 \u043e\u043f\u0438\u0441\u0430\u043d\u0438\u044f \u043f\u0440\u043e\u0433\u0440\u0430\u043c\u043c\u044b \u0434\u043b\u044f \u043f\u0430\u0440\u0430\u043b\u043b\u0435\u043b\u044c\u043d\u044b\u0445 \u0432\u044b\u0447\u0438\u0441\u043b\u0435\u043d\u0438\u0439 \u044f\u0432\u043b\u044f\u0435\u0442\u0441\u044f <b>OpenCL<\/b>. <b>Altera<\/b> \u0440\u0435\u0448\u0438\u043b\u0430 \u043f\u043e\u0434\u0434\u0435\u0440\u0436\u0430\u0442\u044c <b>OpenCL<\/b>: \u0431\u044b\u043b \u0440\u0430\u0437\u0440\u0430\u0431\u043e\u0442\u0430\u043d <a href=\"https:\/\/www.altera.com\/products\/design-software\/embedded-software-developers\/opencl\/overview.html\">Altera SDK for OpenCL<\/a>. <\/p>\n<p>  \u042f \u043d\u0430\u043c\u0435\u0440\u0435\u043d\u043d\u043e \u043e\u043f\u0443\u0441\u043a\u0430\u044e \u043e\u043f\u0438\u0441\u0430\u043d\u0438\u0435 <b>OpenCL<\/b>: \u0432 \u0440\u0443\u0441\u0441\u043a\u043e\u044f\u0437\u044b\u0447\u043d\u043e\u043c \u0438\u043d\u0442\u0435\u0440\u043d\u0435\u0442\u0435 \u0435\u0441\u0442\u044c \u043c\u043d\u043e\u0433\u043e \u043b\u0438\u0442\u0435\u0440\u0430\u0442\u0443\u0440\u044b \u043d\u0430 \u044d\u0442\u0443 \u0442\u0435\u043c\u0443, \u043d\u0430\u043f\u0440\u0438\u043c\u0435\u0440, <a href=\"http:\/\/habrahabr.ru\/post\/124925\/\"><b>\u0412\u0432\u0435\u0434\u0435\u043d\u0438\u0435 \u0432 OpenCL<\/b><\/a>.<\/p>\n<p>  <a name=\"where_to_run\"><\/a>  <\/p>\n<h2>\u041d\u0430 \u0447\u0451\u043c \u0437\u0430\u043f\u0443\u0441\u043a\u0430\u0442\u044c?<\/h2>\n<p>  <img decoding=\"async\" src=\"https:\/\/habrastorage.org\/getpro\/habr\/post_images\/7dc\/de5\/487\/7dcde548722fbe2169ea97b3b1972702.png\" alt=\"image\" width=\"150\"\/><\/p>\n<p>  <abbr title=\"\u0438\u0437 \u043a\u043e\u0440\u043e\u0431\u043a\u0438\">\u0417\u0430\u043f\u0443\u0441\u0442\u0438\u0442\u044c<\/abbr> OpenCL \u043c\u043e\u0436\u043d\u043e \u043d\u0435 \u043a\u0430\u0436\u0434\u043e\u0439 \u043f\u043b\u0430\u0442\u0435 \u0441 FPGA: Altera \u0441\u043e\u0437\u0434\u0430\u043b\u0430 \u0441\u043f\u0435\u0446\u0438\u0430\u043b\u044c\u043d\u0443\u044e \u043f\u0430\u0440\u0442\u043d\u0435\u0440\u0441\u043a\u0443\u044e \u043f\u0440\u043e\u0433\u0440\u0430\u043c\u043c\u0443, \u0432 \u0440\u0430\u043c\u043a\u0430\u0445 \u043a\u043e\u0442\u043e\u0440\u043e\u0439 \u0434\u0435\u0432\u043a\u0438\u0442\u044b \u043f\u043e\u043b\u0443\u0447\u0430\u044e\u0442 \u0432\u044b\u0448\u0435\u0443\u043a\u0430\u0437\u0430\u043d\u043d\u0443\u044e \u043b\u044b\u0447\u043a\u0443, \u0435\u0441\u043b\u0438 \u043f\u043b\u0430\u0442\u0430 \u0433\u043e\u0442\u043e\u0432\u0430 \u0434\u043b\u044f \u0437\u0430\u043f\u0443\u0441\u043a\u0430 OpenCL, \u043f\u0440\u043e\u0445\u043e\u0434\u0438\u0442 \u043f\u043e\u0441\u0442\u043e\u044f\u043d\u043d\u044b\u0435 \u0440\u0435\u0433\u0440\u0435\u0441\u0441\u0438\u043e\u043d\u043d\u044b\u0435 \u0442\u0435\u0441\u0442\u044b \u0438 \u043f\u0440. <\/p>\n<h3>PCIe<\/h3>\n<p>  <img decoding=\"async\" src=\"https:\/\/habrastorage.org\/getpro\/habr\/post_images\/d21\/6f7\/0b0\/d216f70b013a8ac1818d40ead6341e86.png\" alt=\"image\"\/><\/p>\n<p>  \u0427\u0438\u043f \u0441 \u041f\u041b\u0418\u0421 \u043c\u043e\u0436\u0435\u0442 \u0431\u044b\u0442\u044c \u0440\u0430\u0437\u043c\u0435\u0449\u0435\u043d \u043d\u0430 <a href=\"http:\/\/habrahabr.ru\/company\/metrotek\/blog\/267183\/\">PCIe \u043a\u0430\u0440\u0442\u043e\u0447\u043a\u0435<\/a>, \u043a\u043e\u0442\u043e\u0440\u0430\u044f \u0432\u0442\u044b\u043a\u0430\u0435\u0442\u0441\u044f \u0432 \u043c\u0430\u0442\u0435\u0440\u0438\u043d\u0441\u043a\u0443\u044e \u043f\u043b\u0430\u0442\u0443 \u0432 \u0441\u043e\u043e\u0442\u0432\u0435\u0442\u0441\u0442\u0432\u0443\u044e\u0449\u0438\u0439 \u0440\u0430\u0437\u044a\u0435\u043c (\u0445\u043e\u0442\u044c \u0432\u043c\u0435\u0441\u0442\u043e GPU). \u0427\u0435\u0440\u0435\u0437 DMA \u0438 PCIe FPGA \u043c\u043e\u0436\u0435\u0442 \u043e\u0431\u0449\u0430\u0442\u044c\u0441\u044f \u0441 DDR \u043f\u0430\u043c\u044f\u0442\u044c\u044e, \u043a\u043e\u0442\u043e\u0440\u0430\u044f \u043f\u043e\u0434\u043a\u043b\u044e\u0447\u0435\u043d\u0430 \u043a \u043f\u0440\u043e\u0446\u0435\u0441\u0441\u043e\u0440\u0443 (\u0437\u0430\u0431\u0438\u0440\u0430\u0442\u044c \u0434\u0430\u043d\u043d\u044b\u0435 \u0434\u043b\u044f \u0440\u0430\u0441\u0447\u0435\u0442\u043e\u0432). \u0422\u0430\u043a \u0436\u0435 \u043d\u0430 \u043f\u043b\u0430\u0442\u0435 \u043c\u043e\u0436\u0435\u0442 \u0431\u044b\u0442\u044c \u0440\u0430\u0437\u043c\u0435\u0449\u0435\u043d\u0430 \u0432\u043d\u0435\u0448\u043d\u044f\u044f \u043f\u0430\u043c\u044f\u0442\u044c, \u043a\u043e\u0442\u043e\u0440\u0430\u044f \u0434\u043e\u0441\u0442\u0443\u043f\u043d\u0430 \u0442\u043e\u043b\u044c\u043a\u043e \u0434\u043b\u044f FPGA (\u041e\u0421 \u043d\u0430 CPU \u0434\u043e\u0441\u0442\u0443\u043f\u0430 \u043a \u044d\u0442\u043e\u0439 \u043f\u0430\u043c\u044f\u0442\u0438 \u0438\u043c\u0435\u0442\u044c \u043d\u0435 \u0431\u0443\u0434\u0435\u0442). <\/p>\n<p>  \u0412\u043d\u0435\u0448\u043d\u044f\u044f \u043f\u0430\u043c\u044f\u0442\u044c \u043c\u043e\u0436\u0435\u0442 \u043f\u043e\u043d\u0430\u0434\u043e\u0431\u0438\u0442\u044c\u0441\u044f \u0434\u043b\u044f \u0445\u0440\u0430\u043d\u0435\u043d\u0438\u044f \u043f\u0440\u043e\u043c\u0435\u0436\u0443\u0442\u043e\u0447\u043d\u044b\u0445 \u0440\u0430\u0441\u0447\u0435\u0442\u043e\u0432: \u0434\u043e\u0441\u0442\u0443\u043f \u043a \u043d\u0435\u0439 \u0431\u0443\u0434\u0435\u0442 \u0434\u0435\u0448\u0435\u0432\u043b\u0435, \u0447\u0435\u043c \u0434\u043e\u0441\u0442\u0443\u043f \u0447\u0435\u0440\u0435\u0437 DMA \u0432 \u0445\u043e\u0441\u0442\u043e\u0432\u0443\u044e \u043f\u0430\u043c\u044f\u0442\u044c. \u041e\u043d\u0430 \u043d\u0435 \u043e\u0431\u044f\u0437\u0430\u0442\u0435\u043b\u044c\u043d\u043e \u0434\u043e\u043b\u0436\u043d\u0430 \u0431\u044b\u0442\u044c DDR: \u0434\u043b\u044f \u043d\u0435\u043a\u043e\u0442\u043e\u0440\u044b\u0445 \u0432\u044b\u0447\u0438\u0441\u043b\u0435\u043d\u0438\u0439 low-latency SRAM \u043c\u043e\u0436\u0435\u0442 \u043f\u043e\u0434\u043e\u0439\u0442\u0438 \u043b\u0443\u0447\u0448\u0435.<\/p>\n<p>  \u0414\u0430\u043d\u043d\u044b\u0435 \u0434\u043b\u044f \u043e\u0431\u0440\u0430\u0431\u043e\u0442\u043a\u0438 \u043c\u043e\u0433\u0443\u0442 \u043f\u043e\u0434\u0430\u0432\u0430\u0442\u044c\u0441\u044f \u0432 \u044f\u0434\u0440\u043e \u043d\u0435 \u0442\u043e\u043b\u044c\u043a\u043e \u0441 \u0433\u043b\u043e\u0431\u0430\u043b\u044c\u043d\u043e\u0439 \u043f\u0430\u043c\u044f\u0442\u0438, \u043d\u043e \u0435\u0449\u0435 \u0438 \u0441 I\/O \u043a\u0430\u043d\u0430\u043b\u043e\u0432, \u043d\u0430\u043f\u0440\u0438\u043c\u0435\u0440 \u0441 Ethernet-\u043f\u043e\u0440\u0442\u043e\u0432. \u0412 \u044d\u0442\u043e\u043c \u0441\u043b\u0443\u0447\u0430\u0435 \u0445\u043e\u0441\u0442 \u0442\u043e\u043b\u044c\u043a\u043e \u043d\u0430\u0441\u0442\u0440\u0430\u0438\u0432\u0430\u0435\u0442 \u043a\u0435\u0440\u043d\u0435\u043b\u044b, \u0430 \u0434\u0430\u043d\u043d\u044b\u0435 \u043e\u0431\u0440\u0430\u0431\u0430\u0442\u044b\u0432\u0430\u044e\u0442\u0441\u044f \u0441 \u043c\u0438\u043d\u0438\u043c\u0430\u043b\u044c\u043d\u043e\u0439 \u0437\u0430\u0434\u0435\u0440\u0436\u043a\u043e\u0439. (\u0415\u0441\u043b\u0438 \u0432\u044b \u0432\u0438\u0434\u0438\u0442\u0435 \u0440\u044f\u0434\u043e\u043c \u0441\u043b\u043e\u0432\u0430 Ethernet, FPGA \u0438 low-latency, \u0442\u043e \u0432 \u0431\u043e\u043b\u044c\u0448\u0438\u043d\u0441\u0442\u0432\u0435 \u0441\u043b\u0443\u0447\u0430\u0435\u0432 \u043f\u043e\u0434\u0440\u0430\u0437\u0443\u043c\u0435\u0432\u0430\u0435\u0442\u0441\u044f high-frequency trading).<\/p>\n<h3>SoC<\/h3>\n<p>  <img decoding=\"async\" src=\"https:\/\/habrastorage.org\/getpro\/habr\/post_images\/c9e\/970\/b21\/c9e970b21d238cf8042786a10dec6336.png\" alt=\"image\"\/><br \/>  \u0412\u0442\u043e\u0440\u043e\u0439 \u0432\u0430\u0440\u0438\u0430\u043d\u0442 \u0432\u043e\u0437\u043c\u043e\u0436\u0435\u043d \u043d\u0430 <abbr title=\"System On Chip\">SoC<\/abbr>&#8216;ax, \u0433\u0434\u0435 \u0432 \u043e\u0434\u043d\u043e\u043c \u043a\u0440\u0438\u0441\u0442\u0430\u043b\u0435 \u0440\u0430\u0441\u043f\u043e\u043b\u043e\u0436\u0435\u043d\u0430 \u043f\u0440\u043e\u0433\u0440\u0430\u043c\u043c\u0438\u0440\u0443\u0435\u043c\u0430\u044f \u043b\u043e\u0433\u0438\u043a\u0430 \u0438 ARM-\u043f\u0440\u043e\u0446\u0435\u0441\u0441\u043e\u0440. <\/p>\n<p>  DDR-\u043f\u0430\u043c\u044f\u0442\u044c, \u0437\u0430\u043a\u0440\u0430\u0448\u0435\u043d\u0430\u044f \u0437\u0435\u043b\u0435\u043d\u044b\u043c, \u044f\u0432\u043b\u044f\u0435\u0442\u0441\u044f \u0440\u0430\u0437\u0434\u0435\u043b\u044f\u0435\u043c\u044b\u043c \u0440\u0435\u0441\u0443\u0440\u0441\u043e\u043c: \u0441 \u043e\u0434\u043d\u043e\u0439 \u0441\u0442\u043e\u0440\u043e\u043d\u044b \u0438\u043c \u043f\u043e\u043b\u044c\u0437\u0443\u0435\u0442\u0441\u044f CPU (\u0442\u0430\u043c \u043c\u043e\u0436\u043d\u043e <a href=\"http:\/\/habrahabr.ru\/company\/metrotek\/blog\/235707\/\">\u0437\u0430\u043f\u0443\u0441\u0442\u0438\u0442\u044c linux<\/a>), \u0430 \u0441 \u0434\u0440\u0443\u0433\u043e\u0439, FPGA \u043c\u043e\u0436\u0435\u0442 \u00ab\u043d\u0430\u043f\u0440\u044f\u043c\u0443\u044e\u00bb \u0447\u0438\u0442\u0430\u0442\u044c\/\u043f\u0438\u0441\u0430\u0442\u044c \u0432 \u044d\u0442\u0443 \u043f\u0430\u043c\u044f\u0442\u044c \u0447\u0435\u0440\u0435\u0437 SDRAM-\u043a\u043e\u043d\u0442\u0440\u043e\u043b\u043b\u0435\u0440 \u0441 \u043c\u0438\u043d\u0438\u043c\u0430\u043b\u044c\u043d\u044b\u043c \u043e\u0432\u0435\u0440\u0445\u0435\u0434\u043e\u043c. \u041a\u0430\u043a \u0438 \u0441 PCIe \u043a\u0430\u0440\u0442\u043e\u0447\u043a\u043e\u0439 \u043a FPGA \u043c\u043e\u0436\u0435\u0442 \u0431\u044b\u0442\u044c \u043f\u043e\u0434\u043a\u043b\u044e\u0447\u0435\u043d\u0430 \u0432\u043d\u0435\u0448\u043d\u044f\u044f \u043f\u0430\u043c\u044f\u0442\u044c, \u043d\u043e \u043d\u0435\u043e\u0431\u0445\u043e\u0434\u0438\u043c\u043e\u0441\u0442\u044c \u0432 \u044d\u0442\u043e\u043c \u043c\u0435\u043d\u044c\u0448\u0435, \u0442.\u043a. \u0432\u0441\u0435\u0433\u0434\u0430 \u043f\u043e\u0434 \u0440\u0443\u043a\u043e\u0439 DDR. <\/p>\n<p>  \u041f\u043e\u0434\u0440\u043e\u0431\u043d\u0435\u0435 \u043e \u043f\u043b\u0430\u0442\u0444\u043e\u0440\u043c\u0430\u0445 \u043c\u043e\u0436\u043d\u043e \u043f\u0440\u043e\u0447\u0438\u0442\u0430\u0442\u044c <a href=\"https:\/\/www.altera.com\/products\/design-software\/embedded-software-developers\/opencl\/developer-zone.html#fpgaplatforms\">\u0442\u0443\u0442<\/a>.<\/p>\n<p>  \u0421\u0443\u0449\u0435\u0441\u0442\u0432\u0443\u0435\u0442 <abbr title=\"\u0432\u043f\u043e\u043b\u043d\u0435 \u043b\u0435\u0433\u0430\u043b\u044c\u043d\u0430\u044f, \u0431\u0435\u0437 \u043a\u0430\u043a\u043e\u0433\u043e-\u0442\u043e \u043f\u0430\u0442\u0447\u0438\u043d\u0433\u0430 \u0438\u043b\u0438 \u043a\u0440\u044f\u043a\u0438\u043d\u0433\u0430\">\u0432\u043e\u0437\u043c\u043e\u0436\u043d\u043e\u0441\u0442\u044c<\/abbr> \u0437\u0430\u043f\u0443\u0441\u043a\u0430 OpenCL \u043d\u0430 \u0442\u0435\u0445 \u043f\u043b\u0430\u0442\u0430\u0445, \u043a\u043e\u0442\u043e\u0440\u044b\u0435 \u043d\u0435 \u0438\u043c\u0435\u044e\u0442 \u0437\u043d\u0430\u043a\u0430 <b>Altera Preferred Board for OpenCL<\/b>. \u042f \u0440\u0430\u0441\u0441\u043a\u0430\u0437\u044b\u0432\u0430\u0442\u044c \u043e\u0431 \u044d\u0442\u043e\u043c \u043d\u0435 \u0431\u0443\u0434\u0443, \u0432 \u043a\u0430\u0447\u0435\u0441\u0442\u0432\u0435 \u043e\u0442\u043f\u0440\u0430\u0432\u043d\u043e\u0439 \u0442\u043e\u0447\u043a\u0438 \u043f\u0440\u0435\u0434\u043b\u0430\u0433\u0430\u044e \u0433\u043b\u044f\u043d\u0443\u0442\u044c \u043e\u0444\u0438\u0446\u0438\u0430\u043b\u044c\u043d\u043e\u0435 \u0440\u0443\u043a\u043e\u0432\u043e\u0434\u0441\u0442\u0432\u043e <a href=\"https:\/\/www.altera.com\/content\/dam\/altera-www\/global\/en_US\/pdfs\/literature\/hb\/opencl-sdk\/ug_aocl_custom_platform_toolkit.pdf\">Altera SDK for OpenCL: Custom Platform Toolkit User Guide<\/a>.<br \/>  <a name=\"workflow\"><\/a>  <\/p>\n<h2>\u041f\u0440\u043e\u0446\u0435\u0441\u0441 \u0440\u0430\u0437\u0440\u0430\u0431\u043e\u0442\u043a\u0438 (workflow)<\/h2>\n<p>  \u041a\u0430\u043a\u0438\u0435 \u0448\u0430\u0433\u0438 \u043d\u0430\u0434\u043e \u0432\u044b\u043f\u043e\u043b\u043d\u0438\u0442\u044c \u0434\u043b\u044f \u0437\u0430\u043f\u0443\u0441\u043a\u0430 \u044f\u0434\u0440\u0430?<\/p>\n<p>  <img decoding=\"async\" src=\"https:\/\/habrastorage.org\/files\/947\/8ee\/8c0\/9478ee8c05f646dd9bf38e50ccc1b15f.png\" width=\"600\"\/>  <\/p>\n<ul>\n<li>\u041a\u043e\u0434 \u043a\u0435\u0440\u043d\u0435\u043b\u0430 \u043e\u043f\u0438\u0441\u044b\u0432\u0430\u0435\u0442\u0441\u044f \u0432 \u0444\u0430\u0439\u043b\u0435 <b>*.cl<\/b>. <\/li>\n<li>\u0413\u043e\u0442\u043e\u0432\u0438\u0442\u0441\u044f \u0445\u043e\u0441\u0442\u043e\u0432\u043e\u0435 \u043f\u0440\u0438\u043b\u043e\u0436\u0435\u043d\u0438\u0435 \u043d\u0430 \u0421\/C++, \u043a\u043e\u0442\u043e\u0440\u043e\u0435 \u0431\u0443\u0434\u0435\u0442 \u043f\u0440\u043e\u0438\u0437\u0432\u043e\u0434\u0438\u0442\u044c \u0432\u044b\u0434\u0435\u043b\u0435\u043d\u0438\u0435 \u043d\u0435\u043e\u0431\u0445\u043e\u0434\u0438\u043c\u044b\u0445 \u043e\u0431\u044a\u0435\u043c\u043e\u0432 \u043f\u0430\u043c\u044f\u0442\u0438 \u0438 \u00ab\u0437\u0430\u0433\u0440\u0443\u0437\u043a\u0443\u00bb \u0437\u043d\u0430\u0447\u0435\u043d\u0438\u0439 \u0432 \u043a\u0435\u0440\u043d\u0435\u043b. <\/li>\n<li>\u0421 \u043f\u043e\u043c\u043e\u0449\u044c\u044e \u0443\u0442\u0438\u043b\u0438\u0442\u044b <b>aoc<\/b>, \u043a\u043e\u0442\u043e\u0440\u0430\u044f \u0432\u0445\u043e\u0434\u0438\u0442 \u0432 <b>Altera OpenCL SDK<\/b>, \u00ab\u043a\u043e\u043c\u043f\u0438\u043b\u0438\u0440\u0443\u0435\u0442\u0441\u044f\u00bb \u044f\u0434\u0440\u043e \u0432 <abbr title=\"Altera Offline Compiler Executable file\"><b>aocx<\/b><\/abbr> \u0444\u0430\u0439\u043b. \u0421 \u043f\u043e\u043c\u043e\u0449\u044c\u044e <b>gcc<\/b> \u0441\u043e\u0431\u0438\u0440\u0430\u0435\u0442\u0441\u044f \u0445\u043e\u0441\u0442\u043e\u0432\u043e\u0435 \u043f\u0440\u0438\u043b\u043e\u0436\u0435\u043d\u0438\u0435.<\/li>\n<li>\u041f\u0440\u0438 \u0437\u0430\u043f\u0443\u0441\u043a\u0435 <b>host_app<\/b> \u043f\u0440\u043e\u0438\u0437\u043e\u0439\u0434\u0435\u0442 \u0437\u0430\u0433\u0440\u0443\u0437\u043a\u0430 <abbr title=\"\u043e\u043d\u0430 \u0432 \u0441\u0435\u0431\u0435 \u0441\u043e\u0434\u0435\u0440\u0436\u0438\u0442 \u043d\u0430\u0441\u0442\u0440\u043e\u0439\u043a\u0443 \u0438 \u0441\u043e\u0435\u0434\u0438\u043d\u0435\u043d\u0438\u044f \u0432\u0441\u0435\u0445 \u043f\u0440\u0438\u043c\u0438\u0442\u0438\u0432\u043e\u0432 \u0432 \u0447\u0438\u043f\u0435\">\u043f\u0440\u043e\u0448\u0438\u0432\u043a\u0438<\/abbr> FPGA, \u0432 \u044f\u0434\u0440\u043e \u0437\u0430\u0433\u0440\u0443\u0437\u044f\u0442\u0441\u044f \u043f\u043e\u0434\u0433\u043e\u0442\u043e\u0432\u043b\u0435\u043d\u043d\u044b\u0435 \u0434\u0430\u043d\u043d\u044b\u0435 \u0438 \u043d\u0430\u0447\u043d\u0435\u0442\u0441\u044f \u0438\u0445 \u043e\u0431\u0440\u0430\u0431\u043e\u0442\u043a\u0430.<\/li>\n<li>\u0421\u0447\u0435\u0442\u0447\u0438\u043a\u0438 \u0434\u043b\u044f \u043f\u0440\u043e\u0444\u0438\u043b\u0438\u0440\u043e\u0432\u0430\u043d\u0438\u044f \u0441\u043e\u0431\u0438\u0440\u0430\u044e\u0442 \u0434\u0430\u043d\u043d\u044b\u0435, \u043a\u043e\u0442\u043e\u0440\u044b\u0435 \u043f\u043e\u043c\u0435\u0441\u0442\u044f\u0442\u0441\u044f \u0432 \u0444\u0430\u0439\u043b <b>profile.mon<\/b>. <\/li>\n<li>\u0421 \u043f\u043e\u043c\u043e\u0449\u044c\u044e \u0443\u0442\u0438\u043b\u0438\u0442\u044b <b>aocl<\/b> \u043c\u043e\u0436\u043d\u043e \u043f\u043e\u0441\u043c\u043e\u0442\u0440\u0435\u0442\u044c \u044d\u0442\u043e\u0442 \u043e\u0442\u0447\u0435\u0442 \u0438 \u0441\u0434\u0435\u043b\u0430\u0442\u044c \u0432\u044b\u0432\u043e\u0434: \u0443\u0434\u043e\u0432\u043b\u0435\u0442\u0432\u043e\u0440\u044f\u0435\u0442 \u043b\u0438 \u043f\u043e \u0432\u0440\u0435\u043c\u0435\u043d\u0438 \u0432\u044b\u043f\u043e\u043b\u043d\u0435\u043d\u0438\u044f\/\u043f\u0440\u043e\u0438\u0437\u0432\u043e\u0434\u0438\u0442\u0435\u043b\u044c\u043d\u043e\u0441\u0442\u0438 \u044d\u0442\u0430 \u0440\u0435\u0430\u043b\u0438\u0437\u0430\u0446\u0438\u044f. <\/li>\n<li>\u0415\u0441\u043b\u0438 \u0443\u0434\u043e\u0432\u043b\u0435\u0442\u0432\u043e\u0440\u044f\u0435\u0442, \u0442\u043e \u043c\u043e\u0436\u043d\u043e \u043f\u0435\u0440\u0435\u043a\u043e\u043c\u043f\u0438\u043b\u0438\u0440\u043e\u0432\u0430\u0442\u044c \u044f\u0434\u0440\u043e \u0431\u0435\u0437 <b>&#8212;profile<\/b>, \u0442.\u043a. \u043f\u0440\u043e\u0444\u0438\u043b\u0438\u0440\u0443\u044e\u0449\u0438\u0435 \u0441\u0447\u0435\u0442\u0447\u0438\u043a\u0438 \u043e\u0442\u043d\u0438\u043c\u0430\u044e\u0442 \u0440\u0435\u0441\u0443\u0440\u0441\u044b \u0432 FPGA. \u0421 \u0434\u0440\u0443\u0433\u043e\u0439 \u0441\u0442\u043e\u0440\u043e\u043d\u044b, \u0435\u0441\u043b\u0438 \u0434\u043e\u043f\u043e\u043b\u043d\u0438\u0442\u0435\u043b\u044c\u043d\u044b\u0445 \u044f\u0434\u0435\u0440 \u043d\u0435 \u043f\u043b\u0430\u043d\u0438\u0440\u0443\u0435\u0442\u0441\u044f \u0434\u043e\u0431\u0430\u0432\u043b\u044f\u0442\u044c, \u0442\u043e \u043c\u043e\u0436\u043d\u043e \u0438 \u043d\u0435 \u043f\u0435\u0440\u0435\u0441\u043e\u0431\u0438\u0440\u0430\u0442\u044c. <\/li>\n<li>\u0415\u0441\u043b\u0438 \u043d\u0435 \u0443\u0434\u043e\u0432\u043b\u0435\u0442\u0432\u043e\u0440\u044f\u0435\u0442, \u0442\u043e \u043d\u0430\u0434\u043e \u043e\u043f\u0442\u0438\u043c\u0438\u0437\u0438\u0440\u043e\u0432\u0430\u0442\u044c\/\u043f\u0438\u0441\u0430\u0442\u044c \u0440\u0443\u0447\u043a\u0430\u043c\u0438\/\u0432\u0437\u044f\u0442\u044c \u0434\u0440\u0443\u0433\u043e\u0439 \u0447\u0438\u043f \u0438\u043b\u0438 \u0441\u043c\u0438\u0440\u0438\u0442\u044c\u0441\u044f.<\/li>\n<\/ul>\n<p>  \u0417\u0430\u043c\u0435\u0447\u0443, \u0447\u0442\u043e \u043a\u043e\u043c\u043f\u0438\u043b\u044f\u0446\u0438\u044f \u0432 <b>aocx<\/b> \u0444\u0430\u0439\u043b \u043c\u043e\u0436\u0435\u0442 \u0434\u043e\u0441\u0442\u0438\u0433\u0430\u0442\u044c <b>\u043d\u0435\u0441\u043a\u043e\u043b\u044c\u043a\u0438\u0445 \u0447\u0430\u0441\u043e\u0432<\/b>!<br \/>  \u0427\u0442\u043e \u0436\u0435 \u043f\u0440\u043e\u0438\u0441\u0445\u043e\u0434\u0438\u0442, \u043a\u043e\u0433\u0434\u0430 \u0432\u044b\u0437\u044b\u0432\u0430\u0435\u0442\u0441\u044f <b>aoc kernel.cl<\/b>?<\/p>\n<h3>\u0421\u0431\u043e\u0440\u043a\u0430 aocx<\/h3>\n<p>  <img decoding=\"async\" src=\"https:\/\/habrastorage.org\/files\/156\/2c2\/9d8\/1562c29d82fd44fe86ca7efaee2c3614.png\" width=\"600\"\/>  <\/p>\n<ul>\n<li><b>kernel.cl<\/b> \u0441\u043a\u0430\u0440\u043c\u043b\u0438\u0432\u0430\u0435\u0442\u0441\u044f <b>clang<\/b>, \u043a\u043e\u0442\u043e\u0440\u044b\u0439 \u043f\u0435\u0440\u0435\u0432\u043e\u0434\u0438\u0442 \u043e\u043f\u0438\u0441\u0430\u043d\u0438\u0435 \u0432 <abbr title=\"Intermediate Representation - \u043f\u0440\u043e\u043c\u0435\u0436\u0443\u0442\u043e\u0447\u043d\u043e\u0435 \u043f\u0440\u0435\u0434\u0441\u0442\u0430\u0432\u043b\u0435\u043d\u0438\u0435 \u043a\u043e\u0434\u0430\">IR<\/abbr>, \u0430 \u0442\u0430\u043a \u0436\u0435 \u043f\u0440\u043e\u0432\u043e\u0434\u0438\u0442 \u0440\u0430\u0437\u043b\u0438\u0447\u043d\u044b\u0435 \u043e\u043f\u0442\u0438\u043c\u0438\u0437\u0430\u0446\u0438\u0438. <\/li>\n<li>\u0413\u0435\u043d\u0435\u0440\u0438\u0440\u0443\u0435\u0442\u0441\u044f <abbr title=\"Register Transfer Level\">RTL<\/abbr>-\u043d\u043e\u0435 <b>Verilog <abbr title=\"Intellectual Property - \u043e\u0431\u0449\u0435\u0435 \u043d\u0430\u0437\u0432\u0430\u043d\u0438\u0435 \u0434\u043b\u044f \u043e\u0442\u0434\u0435\u043b\u044c\u043d\u044b\u0445 \u0431\u043b\u043e\u043a\u043e\u0432\/\u043c\u043e\u0434\u0443\u043b\u0435\u0439. \u0410\u043d\u0430\u043b\u043e\u0433 \u0431\u0438\u0431\u043b\u0438\u043e\u0442\u0435\u043a\u0438 \u0432 ASIC\/FPGA \u043c\u0438\u0440\u0435\">IP<\/abbr><\/b>-\u044f\u0434\u0440\u043e. \u0421\u0433\u0435\u043d\u0435\u0440\u0435\u043d\u043d\u044b\u0435 \u0444\u0430\u0439\u043b\u044b \u0434\u043e\u0441\u0442\u0443\u043f\u043d\u044b \u0434\u043b\u044f \u0447\u0442\u0435\u043d\u0438\u044f (\u043d\u0435\u0437\u0430\u0448\u0438\u0444\u0440\u043e\u0432\u0430\u043d\u044b) \u0438 \u043c\u043e\u0433\u0443\u0442 \u0431\u044b\u0442\u044c \u043f\u0440\u043e\u0441\u0438\u043c\u0443\u043b\u0438\u0440\u043e\u0432\u0430\u0442\u044c \u0432 \u043e\u0431\u044b\u0447\u043d\u043e\u043c \u0441\u0438\u043c\u0443\u043b\u044f\u0442\u043e\u0440\u0435 (\u043d\u0430\u043f\u0440\u0438\u043c\u0435\u0440, ModelSim). \u041e\u0434\u043d\u0430\u043a\u043e, \u0442\u0430\u043c \u043d\u0435 \u0432\u0435\u0441\u044c \u043a\u043e\u0434 \u0430\u0432\u0442\u043e\u0441\u0433\u0435\u043d\u0435\u0440\u0435\u043d\u043d\u044b\u0439: \u0435\u0441\u0442\u044c \u043c\u043e\u0434\u0443\u043b\u0438, \u043a\u043e\u0442\u043e\u0440\u044b\u0435 \u044f\u0432\u043d\u043e \u043f\u0438\u0441\u0430\u043b \u0447\u0435\u043b\u043e\u0432\u0435\u043a. <\/li>\n<li>\u041f\u043e\u043b\u0443\u0447\u0435\u043d\u043d\u043e\u0435 IP \u00ab\u043f\u0440\u0438\u0441\u043e\u0435\u0434\u0438\u043d\u044f\u0435\u0442\u0441\u044f\u00bb \u043a \u0434\u0435\u0444\u043e\u043b\u0442\u043e\u043c\u0443 \u043f\u0440\u043e\u0435\u043a\u0442\u0443 \u0434\u043b\u044f \u043f\u043b\u0430\u0442\u044b \u0438 \u043f\u043e\u043b\u0443\u0447\u0430\u0435\u0442\u0441\u044f \u043e\u0431\u044b\u0447\u043d\u044b\u0439 \u043f\u0440\u043e\u0435\u043a\u0442 \u0434\u043b\u044f <abbr title=\"\u041a\u043e\u043c\u043f\u0438\u043b\u044f\u0442\u043e\u0440 \u043f\u043e\u0434 \u0447\u0438\u043f\u044b \u0444\u0438\u0440\u043c\u044b Altera\">Quartus&#8217;a<\/abbr>.<\/li>\n<li>\u041f\u0440\u043e\u0445\u043e\u0434\u0438\u0442 \u0441\u0431\u043e\u0440\u043a\u0430 \u043f\u0440\u043e\u0435\u043a\u0442\u0430 (Analysis &#038; Synthesis, Fitter, Assembler). \u0418\u043c\u0435\u043d\u043d\u043e \u044d\u0442\u043e\u0442 \u043f\u0443\u043d\u043a\u0442 \u0437\u0430\u043d\u0438\u043c\u0430\u0435\u0442 \u043d\u0430\u0438\u0431\u043e\u043b\u044c\u0448\u0435\u0435 \u0432\u0440\u0435\u043c\u044f (\u043e\u0442 \u0434\u0435\u0441\u044f\u0442\u0438 \u043c\u0438\u043d\u0443\u0442 \u0434\u043e \u043d\u0435\u0441\u043a\u043e\u043b\u044c\u043a\u0438\u0445 \u0447\u0430\u0441\u043e\u0432): \u043f\u043e\u0438\u0441\u043a \u043e\u043f\u0442\u0438\u043c\u0430\u043b\u044c\u043d\u044b\u0445 \u043c\u0435\u0441\u0442 \u0440\u0430\u0441\u043f\u043e\u043b\u043e\u0436\u0435\u043d\u0438\u044f \u043f\u0440\u0438\u043c\u0438\u0442\u0438\u0432\u043e\u0432 \u0442\u0440\u0435\u0431\u0443\u0435\u0442 \u043c\u043d\u043e\u0433\u043e \u0432\u044b\u0447\u0438\u0441\u043b\u0435\u043d\u0438\u0439. <\/li>\n<li>\u0420\u0435\u0437\u0443\u043b\u044c\u0442\u0430\u0442 \u0441\u0431\u043e\u0440\u043a\u0438, \u0438\u043d\u0444\u043e\u0440\u043c\u0430\u0446\u0438\u044f \u043e \u0431\u043e\u0440\u0434\u0435 \u0438 \u043f\u0440\u043e\u0447\u0435\u0435 \u0440\u0430\u0437\u043c\u0435\u0449\u0430\u044e\u0442 \u0432 <b>aocx<\/b>, \u043a\u043e\u0442\u043e\u0440\u044b\u0439 \u044f\u0432\u043b\u044f\u0435\u0442\u0441\u044f \u043f\u0440\u043e\u0441\u0442\u043e ELF-\u0444\u0430\u0439\u043b\u043e\u043c. <\/li>\n<\/ul>\n<p>  \u042d\u0442\u043e\u0442 <b>aocx<\/b>-\u0444\u0430\u0439\u043b \u0437\u0430\u0442\u0435\u043c \u0438 \u0438\u0441\u043f\u043e\u043b\u044c\u0437\u0443\u0435\u0442\u0441\u044f \u0434\u043b\u044f \u00ab\u0437\u0430\u0433\u0440\u0443\u0437\u043a\u0438\u00bb \u044f\u0434\u0440\u0430. <br \/>  <a name=\"opencl_bsp\"><\/a>  <\/p>\n<h2>DE1-SoC OpenCL BSP<\/h2>\n<p>  \u041d\u0430 \u0441\u043b\u043e\u0432\u0430\u0445 \u0438 \u043a\u0430\u0440\u0442\u0438\u043d\u043a\u0430\u0445 \u0432\u0441\u0451 \u0432\u044b\u0433\u043b\u044f\u0434\u0438\u0442 \u043e\u0447\u0435\u043d\u044c \u0441\u043a\u043b\u0430\u0434\u043d\u043e: \u0437\u043d\u0430\u043d\u0438\u044f Verilog&#8217;\u0430 \u043d\u0435 \u043d\u0443\u0436\u043d\u044b. <br \/>  \u0427\u0442\u043e \u0436\u0435 \u043d\u0430 \u0441\u0430\u043c\u043e\u043c \u0434\u0435\u043b\u0435?<\/p>\n<p>  \u0412 \u043c\u043e\u0438\u0445 \u0440\u0443\u043a\u0430\u0445 <a href=\"http:\/\/habrahabr.ru\/post\/247535\/\">\u0441\u043d\u043e\u0432\u0430<\/a> \u043f\u043e\u044f\u0432\u0438\u043b\u0430\u0441\u044c \u043f\u043b\u0430\u0442\u0430 <a href=\"http:\/\/de1-soc.terasic.com\/\">DE1-SoC<\/a> \u043e\u0442 Terasic\u2019a. \u0412 \u0435\u0451 \u043e\u0441\u043d\u043e\u0432\u0435 \u043b\u0435\u0436\u0438\u0442 \u043a\u0430\u043c\u0435\u043d\u044c <a href=\"https:\/\/www.altera.com\/products\/soc\/portfolio\/cyclone-v-soc\/overview.html\"><b>Cyclone V SoC<\/b><\/a> (<b>5CSEMA5F31C6<\/b>).<\/p>\n<p>  <img decoding=\"async\" src=\"http:\/\/habrastorage.org\/files\/8a1\/c1d\/b17\/8a1c1db1747c447597ac310fcb0bea72.jpg\" alt=\"image\"\/><\/p>\n<div class=\"spoiler\"><b class=\"spoiler_title\">\u0421\u043a\u0440\u044b\u0442\u044b\u0439 \u0442\u0435\u043a\u0441\u0442<\/b><\/p>\n<div class=\"spoiler_text\"><img decoding=\"async\" src=\"http:\/\/habrastorage.org\/files\/a42\/3d3\/706\/a423d37066024ff8b14642f1a68f2478.jpg\" alt=\"image\"\/>  <\/div>\n<\/div>\n<p>  \u042d\u0442\u0430 \u043f\u043b\u0430\u0442\u0430 \u0438\u043c\u0435\u0435\u0442 \u0437\u043d\u0430\u043a <b>Altera Preferred Board for OpenCL<\/b>, \u043f\u043e\u044d\u0442\u043e\u043c\u0443 \u0437\u0430\u043f\u0443\u0441\u043a OpenCL \u0434\u043e\u043b\u0436\u0435\u043d \u0431\u044b\u0442\u044c \u0438\u0437 \u043a\u043e\u0440\u043e\u0431\u043a\u0438: \u043d\u0430\u043c \u043d\u0443\u0436\u0435\u043d <b>OpenCL BSP<\/b> \u0434\u043b\u044f \u043a\u043e\u043d\u043a\u0440\u0435\u0442\u043d\u043e \u044d\u0442\u043e\u0439 \u043f\u043b\u0430\u0442\u044b. \u0415\u0433\u043e \u043c\u043e\u0436\u043d\u043e \u0432\u0437\u044f\u0442\u044c <a href=\"http:\/\/www.terasic.com.tw\/cgi-bin\/page\/archive.pl?Language=English&amp;CategoryNo=205&amp;No=836&amp;PartNo=4\">\u0442\u0443\u0442<\/a>.<\/p>\n<p>  \u0412 \u0430\u0440\u0445\u0438\u0432 \u0441 OpenCL BSP \u0432\u0445\u043e\u0434\u0438\u0442:  <\/p>\n<ul>\n<li>\u041e\u0431\u0440\u0430\u0437 \u0444\u043b\u0435\u0448\u043a\u0438 (\u0441 \u043d\u0435\u0451 \u0437\u0430\u0433\u0440\u0443\u0437\u0438\u0442\u0441\u044f linux).<\/li>\n<li>\u0414\u0435\u0444\u043e\u043b\u0442\u043d\u044b\u0439 \u043f\u0440\u043e\u0435\u043a\u0442, \u0433\u0434\u0435 \u0443\u0436\u0435 \u043d\u0430\u0441\u0442\u0440\u043e\u0435\u043d\u044b \u0432\u0441\u0435 \u043f\u0438\u043d\u044b, \u0430 \u0442\u0430\u043a \u0436\u0435 \u0438\u043d\u0442\u0435\u0440\u0444\u0435\u0439\u0441\u044b (fpga2sdram, lwhps2fpga \u0438 \u0434\u0440.).<\/li>\n<li>\u041f\u0440\u043e\u0441\u0442\u0435\u043d\u044c\u043a\u0438\u0435 \u043f\u0440\u0438\u043c\u0435\u0440\u044b. <\/li>\n<\/ul>\n<p>  \u041e\u0431\u0440\u0430\u0437 \u0437\u0430\u043f\u0438\u0441\u044b\u0432\u0430\u0435\u0442\u0441\u044f \u043d\u0430 MicroSD \u043f\u0440\u043e\u0441\u0442\u043e \u0447\u0435\u0440\u0435\u0437 <b>dd<\/b>. <br \/>  <b>\u041f\u0440\u0438\u043c\u0435\u0447\u0430\u043d\u0438\u0435<\/b>: \u0436\u0435\u043b\u0430\u0442\u0435\u043b\u044c\u043d\u043e \u0438\u0441\u043f\u043e\u043b\u044c\u0437\u043e\u0432\u0430\u0442\u044c <a href=\"https:\/\/en.wikipedia.org\/wiki\/Secure_Digital#Speed_class_rating\">\u0444\u043b\u0435\u0448\u043a\u0438 10 \u043a\u043b\u0430\u0441\u0441\u0430<\/a>. <\/p>\n<p>  \u0422\u0430\u043c \u0443\u0436\u0435 \u043b\u0435\u0436\u0438\u0442 <b>linux<\/b>:  <\/p>\n<pre><code>root@socfpga:~# uname -a Linux socfpga 3.13.0-00298-g3c7cbb9-dirty #3 SMP Fri Jul 4 15:42:32 CST 2014 armv7l GNU\/Linux  root@socfpga:~# cat \/etc\/issue      Poky 8.0 (Yocto Project 1.3 Reference Distro) 1.3 \\n \\l  root@socfpga:~# cat \/proc\/cpuinfo processor       : 0 model name      : ARMv7 Processor rev 0 (v7l) Features        : swp half thumb fastmult vfp edsp thumbee neon vfpv3 tls vfpd32 CPU implementer : 0x41 CPU architecture: 7 CPU variant     : 0x3 CPU part        : 0xc09 CPU revision    : 0  processor       : 1 model name      : ARMv7 Processor rev 0 (v7l) Features        : swp half thumb fastmult vfp edsp thumbee neon vfpv3 tls vfpd32 CPU implementer : 0x41 CPU architecture: 7 CPU variant     : 0x3 CPU part        : 0xc09 CPU revision    : 0  Hardware        : Altera SOCFPGA Revision        : 0000 Serial          : 0000000000000000 <\/code><\/pre>\n<p>  \u0422\u0430\u043c \u0436\u0435 \u043c\u043e\u0436\u043d\u043e \u043d\u0430\u0439\u0442\u0438 \u0441\u043a\u043e\u043c\u043f\u0438\u043b\u0438\u0440\u043e\u0432\u0430\u043d\u043d\u044b\u0435 \u043f\u0440\u0438\u043c\u0435\u0440\u044b \u0438 <b>OpenCL Run-Time Environment<\/b>.<\/p>\n<p>  \u0417\u0430\u0431\u043e\u0442\u043b\u0438\u0432\u0430\u044f <b>README<\/b> \u043f\u0440\u0435\u0434\u043b\u0430\u0433\u0430\u0435\u0442:  <\/p>\n<pre><code>Run &quot;source .\/init_opencl.sh&quot; to setup OpenCL Run-Time Environment, including loading driver, on this board.  Do it once right after booting the board.  OpenCL Run-Time Environment is pre-installed in opencl_arm32_rte folder. <\/code><\/pre>\n<p>  \u0421\u0430\u043c <b>init_opencl.sh<\/b> \u0432\u044b\u0433\u043b\u044f\u0434\u0438\u0442 \u043e\u0447\u0435\u043d\u044c \u0442\u0440\u0438\u0432\u0438\u0430\u043b\u044c\u043d\u043e:  <\/p>\n<pre><code>root@socfpga:~# cat init_opencl.sh export ALTERAOCLSDKROOT=\/home\/root\/opencl_arm32_rte export AOCL_BOARD_PACKAGE_ROOT=$ALTERAOCLSDKROOT\/board\/c5soc export PATH=$ALTERAOCLSDKROOT\/bin:$PATH export LD_LIBRARY_PATH=$ALTERAOCLSDKROOT\/host\/arm32\/lib:$LD_LIBRARY_PATH insmod $AOCL_BOARD_PACKAGE_ROOT\/driver\/aclsoc_drv.ko <\/code><\/pre>\n<p>  \u0412\u044b\u043f\u043e\u043b\u043d\u044f\u0435\u043c \u044d\u0442\u043e\u0442 \u0441\u043a\u0440\u0438\u043f\u0442, \u0438\u0434\u0435\u043c \u0432 \u0434\u0438\u0440\u0435\u043a\u0442\u043e\u0440\u0438\u044e <b>helloworld<\/b> \u0438 \u0437\u0430\u043f\u0443\u0441\u043a\u0430\u0435\u043c \u043e\u0434\u043d\u043e\u0438\u043c\u0435\u043d\u043d\u043e\u0435 \u043f\u0440\u0438\u043b\u043e\u0436\u0435\u043d\u0438\u0435:  <\/p>\n<pre><code>root@socfpga:~\/helloworld# .\/helloworld Querying platform for info: ========================== CL_PLATFORM_NAME                         = Altera SDK for OpenCL CL_PLATFORM_VENDOR                       = Altera Corporation CL_PLATFORM_VERSION                      = OpenCL 1.0 Altera SDK for OpenCL, Version 14.0  Querying device for info: ======================== CL_DEVICE_NAME                           = de1soc_sharedonly : Cyclone V SoC Development Kit CL_DEVICE_VENDOR                         = Altera Corporation CL_DEVICE_VENDOR_ID                      = 4466 CL_DEVICE_VERSION                        = OpenCL 1.0 Altera SDK for OpenCL, Version 14.0 CL_DRIVER_VERSION                        = 14.0 CL_DEVICE_ADDRESS_BITS                   = 64 CL_DEVICE_AVAILABLE                      = true CL_DEVICE_ENDIAN_LITTLE                  = true CL_DEVICE_GLOBAL_MEM_CACHE_SIZE          = 32768 CL_DEVICE_GLOBAL_MEM_CACHELINE_SIZE      = 0 CL_DEVICE_GLOBAL_MEM_SIZE                = 536870912 CL_DEVICE_IMAGE_SUPPORT                  = false CL_DEVICE_LOCAL_MEM_SIZE                 = 16384 CL_DEVICE_MAX_CLOCK_FREQUENCY            = 1000 CL_DEVICE_MAX_COMPUTE_UNITS              = 1 CL_DEVICE_MAX_CONSTANT_ARGS              = 8 CL_DEVICE_MAX_CONSTANT_BUFFER_SIZE       = 134217728 CL_DEVICE_MAX_WORK_ITEM_DIMENSIONS       = 3 CL_DEVICE_MAX_WORK_ITEM_DIMENSIONS       = 8192 CL_DEVICE_MIN_DATA_TYPE_ALIGN_SIZE       = 1024 CL_DEVICE_PREFERRED_VECTOR_WIDTH_CHAR    = 4 CL_DEVICE_PREFERRED_VECTOR_WIDTH_SHORT   = 2 CL_DEVICE_PREFERRED_VECTOR_WIDTH_INT     = 1 CL_DEVICE_PREFERRED_VECTOR_WIDTH_LONG    = 1 CL_DEVICE_PREFERRED_VECTOR_WIDTH_FLOAT   = 1 CL_DEVICE_PREFERRED_VECTOR_WIDTH_DOUBLE  = 0 Command queue out of order?              = false Command queue profiling enabled?         = true Using AOCX: hello_world.aocx  Kernel initialization is complete. Launching the kernel...  Thread #2: Hello from Altera's OpenCL Compiler!  Kernel execution is complete. <\/code><\/pre>\n<p>  \u041e\u043a\u0435\u0439, \u043a\u0430\u043a\u0438\u0435-\u0442\u043e \u0441\u043f\u0435\u0446\u0438\u0430\u043b\u044c\u043d\u043e \u043f\u043e\u0434\u0433\u043e\u0442\u043e\u0432\u043b\u0435\u043d\u043d\u044b\u0435 \u043f\u0440\u0438\u043c\u0435\u0440\u044b \u0438 \u0444\u0430\u0439\u043b\u044b \u043d\u0430 \u0444\u043b\u0435\u0448\u043a\u0435 \u0440\u0430\u0431\u043e\u0442\u0430\u044e\u0442 \u0438 \u0447\u0442\u043e-\u0442\u043e \u043f\u0435\u0447\u0430\u0442\u0430\u044e\u0442. <br \/>  \u0427\u0442\u043e \u043d\u0430\u0434\u043e \u0441\u0434\u0435\u043b\u0430\u0442\u044c \u0434\u043b\u044f \u0441\u0431\u043e\u0440\u043a\u0438 \u0438 \u0437\u0430\u043f\u0443\u0441\u043a\u0430 \u043f\u0440\u043e\u0441\u0442\u043e\u0433\u043e \u043f\u0440\u0438\u043c\u0435\u0440\u0430?<br \/>  <a name=\"installing_sdk\"><\/a>  <\/p>\n<h2>\u0423\u0441\u0442\u0430\u043d\u043e\u0432\u043a\u0430 SDK<\/h2>\n<p>  \u041d\u0430\u043c \u043d\u0443\u0436\u043d\u043e:  <\/p>\n<ul>\n<li><a href=\"https:\/\/dl.altera.com\/?edition=subscription\">Quartus<\/a><\/li>\n<li><a href=\"https:\/\/dl.altera.com\/opencl\/?edition=subscription\">Altera SDK for OpenCL<\/a><\/li>\n<li><a href=\"https:\/\/dl.altera.com\/soceds\/?edition=subscription\">SoC Embedded Design Suite<\/a>: \u043d\u0430\u0431\u043e\u0440 \u0442\u0443\u043b\u0437\u043e\u0432 \u0434\u043b\u044f \u0441\u0431\u043e\u0440\u043a\u0438 \u0438 \u043e\u0442\u043b\u0430\u0434\u043a\u0438 \u043f\u0440\u0438\u043b\u043e\u0436\u0435\u043d\u0438\u0439 \u043d\u0430 SoC&#8217;e. <\/li>\n<\/ul>\n<p>  \u0423\u0441\u0442\u0430\u043d\u043e\u0432\u043a\u0430 \u0432\u0441\u0435\u0445 \u044d\u0442\u0438\u0445 \u0442\u0443\u043b\u0437\u043e\u0432 \u0434\u0435\u043b\u043e \u0442\u0440\u0438\u0432\u0438\u0430\u043b\u044c\u043d\u043e\u0435, \u043d\u043e \u0435\u0441\u0442\u044c \u0442\u043e\u043d\u043a\u0438\u0435 \u043c\u043e\u043c\u0435\u043d\u0442\u044b:  <\/p>\n<ul>\n<li>\u041c\u043e\u0433\u0443\u0442 \u043f\u043e\u0442\u0440\u0435\u0431\u043e\u0432\u0430\u0442\u044c\u0441\u044f \u0440\u0443\u0442\u043e\u0432\u044b\u0435 \u043f\u0440\u0430\u0432\u0430, \u043f\u0440\u0438\u0447\u0435\u043c \u043e\u0431 \u044d\u0442\u043e\u043c \u0432\u0430\u043c \u0441\u043a\u0430\u0436\u0443\u0442 \u0442\u043e\u043b\u044c\u043a\u043e \u0432 \u043a\u043e\u043d\u0446\u0435 \u0443\u0441\u0442\u0430\u043d\u043e\u0432\u043a\u0438.<\/li>\n<li>\u041f\u043e\u0441\u043b\u0435 \u0443\u0441\u0442\u0430\u043d\u043e\u0432\u043a\u0438 \u043d\u0435\u043e\u0431\u0445\u043e\u0434\u0438\u043c\u043e \u043a\u043e\u0435-\u0447\u0435\u0433\u043e \u043f\u0440\u043e\u043f\u0438\u0441\u044b\u0432\u0430\u0442\u044c \u0432 PATH, ALTERAOCLSDKROOT, QUARTUS_ROOTDIR. \u0427\u0442\u043e \u0442\u0443\u0434\u0430 \u043f\u0440\u043e\u043f\u0438\u0441\u044b\u0432\u0430\u0442\u044c \u043c\u043e\u0436\u043d\u043e \u043f\u043e\u0434\u0447\u0435\u0440\u043f\u043d\u0443\u0442\u044c \u0438\u0437 \u0441\u043e\u043e\u0442\u0432\u0435\u0442\u0441\u0442\u0432\u0443\u044e\u0449\u0438\u0445 \u0433\u0430\u0439\u0434\u043e\u0432.<\/li>\n<\/ul>\n<p>  \u0412\u043e\u0437\u043c\u043e\u0436\u043d\u043e \u044f \u0447\u0442\u043e-\u0442\u043e \u0441\u0434\u0435\u043b\u0430\u043b \u043d\u0435 \u0442\u0430\u043a, \u043d\u043e \u0432 \u0438\u0442\u043e\u0433\u0435 \u043c\u043e\u0439 \u0441\u043a\u0440\u0438\u043f\u0442 \u0434\u043b\u044f \u043d\u0430\u0441\u0442\u0440\u043e\u0439\u043a\u0438 \u043f\u0435\u0440\u0435\u043c\u0435\u043d\u043d\u044b\u0445 \u043e\u043a\u0440\u0443\u0436\u0435\u043d\u0438\u0439 \u0441\u0442\u0430\u043b \u0432\u044b\u0433\u043b\u044f\u0434\u0435\u0442\u044c \u0432\u043e\u0442 \u0442\u0430\u043a:  <\/p>\n<pre><code>export PATH=\/home\/ish\/altera\/14.1\/quartus\/bin:$PATH export PATH=\/home\/ish\/altera\/14.1\/hld\/bin:$PATH export PATH=\/usr\/local\/DS-5\/bin:$PATH export PATH=\/usr\/local\/DS-5\/sw\/gcc\/bin:$PATH export PATH=\/home\/ish\/altera\/14.1\/hld\/linux64\/bin\/:$PATH export ALTERAOCLSDKROOT=\/home\/ish\/altera\/14.1\/hld\/ export QUARTUS_ROOTDIR=\/home\/ish\/altera\/14.1\/quartus\/ export LD_LIBRARY_PATH=\/home\/ish\/altera\/14.1\/hld\/linux64\/lib\/:$LD_LIBRARY_PATH  # \u043d\u0435\u043e\u0431\u0445\u043e\u0434\u0438\u043c\u043e\u0441\u0442\u044c \u0432 \u044d\u0442\u043e\u0439 \u0441\u0442\u0440\u043e\u0447\u043a\u0435 \u043f\u043e\u044f\u0432\u0438\u0442\u0441\u044f \u0447\u0443\u0442\u044c \u043f\u043e\u0437\u0436\u0435, \u043d\u043e \u044f \u0443\u043a\u0430\u0437\u0430\u043b \u044d\u0442\u0443 \u043f\u0435\u0440\u0435\u043c\u0435\u043d\u043d\u0443\u044e \u0432\u043c\u0435\u0441\u0442\u0435 \u0441 \u043e\u0441\u0442\u0430\u043b\u044c\u043d\u044b\u043c\u0438 export AOCL_BOARD_PACKAGE_ROOT=\/home\/ish\/altera\/14.1\/hld\/board\/de1soc <\/code><\/pre>\n<div class=\"spoiler\"><b class=\"spoiler_title\">\u0421\u043a\u0440\u044b\u0442\u044b\u0439 \u0442\u0435\u043a\u0441\u0442<\/b><\/p>\n<div class=\"spoiler_text\">\u0414\u0430, \u0443 \u043c\u0435\u043d\u044f \u0441\u0442\u043e\u0438\u0442 \u043d\u0435 \u0441\u0430\u043c\u0430\u044f \u043f\u043e\u0441\u043b\u0435\u0434\u043d\u044f\u044f Quartus&#8217;a, \u0438 \u043f\u043e\u044d\u0442\u043e\u043c\u0443, \u0432\u043e\u0437\u043c\u043e\u0436\u043d\u043e, \u0442\u043e, \u0447\u0442\u043e \u044f \u043f\u043e\u043a\u0430\u0436\u0443 \u0447\u0443\u0442\u044c \u043d\u0438\u0436\u0435 \u0431\u044b\u043b\u043e \u0443\u043b\u0443\u0447\u0448\u0435\u043d\u043e \u0432 \u043f\u044f\u0442\u043d\u0430\u0434\u0446\u0430\u0442\u043e\u0439 \u0432\u0435\u0440\u0441\u0438\u0438. <br \/>  \u0415\u0441\u043b\u0438 \u0442\u0430\u043c \u0447\u0442\u043e-\u0442\u043e \u043a\u043e\u043e\u0440\u0434\u0438\u043d\u0430\u043b\u044c\u043d\u043e \u043f\u043e\u043c\u0435\u043d\u044f\u043b\u043e\u0441\u044c \u0432 \u043f\u043b\u0430\u043d\u0435 OpenCL, \u0431\u0443\u0434\u0443 \u043f\u0440\u0438\u0437\u043d\u0430\u0442\u0435\u043b\u0435\u043d, \u0435\u0441\u043b\u0438 \u0441\u0442\u0443\u043a\u043d\u0438\u0442\u0435 \u043c\u043d\u0435 \u0432 \u043b\u0438\u0447\u043a\u0443.  <\/div>\n<\/div>\n<p>  \u041f\u043e\u0441\u043b\u0435 \u0442\u043e\u0433\u043e, \u043a\u0430\u043a \u0432\u0441\u0451 \u044d\u0442\u043e \u043f\u043e\u0441\u0442\u0430\u0432\u0438\u043b\u0438 \u0438 \u043e\u0437\u0430\u0431\u043e\u0442\u0438\u043b\u0438\u0441\u044c \u043b\u0438\u0446\u0435\u043d\u0437\u0438\u044f\u043c\u0438, \u0442\u043e \u043d\u0435\u043e\u0431\u0445\u043e\u0434\u0438\u043c\u043e \u0443\u0441\u0442\u0430\u043d\u043e\u0432\u0438\u0442\u044c \u043d\u0430\u0448\u0443 \u0431\u043e\u0440\u0434\u0443. <br \/>  \u041a\u0430\u043a \u044d\u0442\u043e \u0441\u0434\u0435\u043b\u0430\u0442\u044c \u043f\u043e\u0434\u0441\u043a\u0430\u0437\u044b\u0432\u0430\u0435\u0442 <b>README.txt<\/b>, \u043a\u043e\u0442\u043e\u0440\u044b\u0439 \u043b\u0435\u0436\u0438\u0442 \u0432 \u0430\u0440\u0445\u0438\u0432\u0435 c BSP:  <\/p>\n<pre><code>note:before the below operations,make sure you have install the opencl SDK 14.0 and SoCEDS 14.0. 1. directly unzip the de1soc_openCL_bsp.zip into %ALTERAOCLSDKROOT%\/board directory. 2. set the &quot;User variables&quot; AOCL_BOARD_PACKAGE_ROOT to %ALTERAOCLSDKROOT%\/board\/de1soc 3. open the windows command window and type &quot;aoc --list-boards&quot;, it should output &quot;de1soc_sharedonly&quot; <\/code><\/pre>\n<p>  \u0412\u044b\u043f\u043e\u043b\u043d\u044f\u0435\u043c \u0438 \u043f\u0440\u043e\u0432\u0435\u0440\u044f\u0435\u043c:  <\/p>\n<pre><code>ish@xmr:~$ aoc --list-boards Board list:   de1soc_sharedonly <\/code><\/pre>\n<p>  \u041f\u043b\u0430\u0442\u0430 \u0432 \u0441\u043f\u0438\u0441\u043a\u0435 \u043f\u043e\u044f\u0432\u0438\u043b\u0430\u0441\u044c \u2014 \u0437\u043d\u0430\u0447\u0438\u0442 \u0432\u0441\u0451 \u0441\u0434\u0435\u043b\u0430\u043b\u0438 \u0432\u0435\u0440\u043d\u043e.<br \/>  <a name=\"compile\"><\/a>  <\/p>\n<h2>\u0421\u043e\u0431\u0438\u0440\u0430\u0435\u043c \u043f\u0440\u0438\u043c\u0435\u0440<\/h2>\n<p>  \u0414\u043b\u044f \u0437\u0430\u043f\u0443\u0441\u043a\u0430 \u044f \u0432\u044b\u0431\u0440\u0430\u043b \u043e\u0447\u0435\u043d\u044c \u043f\u0440\u043e\u0441\u0442\u043e\u0439 \u043f\u0440\u0438\u043c\u0435\u0440: <br \/>  <b>Z<\/b> = <b>X<\/b> + <b>Y<\/b>,<br \/>  \u0433\u0434\u0435 <b>X<\/b> \u0438 <b>Y<\/b> \u2014 \u043c\u0430\u0441\u0441\u0438\u0432\u044b \u0438\u0437 <b>N<\/b> uint (32-\u0431\u0438\u0442\u043d\u044b\u0445) \u0447\u0438\u0441\u0435\u043b.<\/p>\n<p>  \u041a\u0435\u0440\u043d\u0435\u043b <b>vector_add<\/b> \u0432\u044b\u0433\u043b\u044f\u0434\u0438\u0442 <a href=\"https:\/\/github.com\/johan92\/altera_opencl_sandbox\/blob\/master\/vector_add\/device\/vector_add.cl\">\u043e\u0447\u0435\u043d\u044c \u043f\u0440\u043e\u0441\u0442\u043e<\/a>:  <\/p>\n<pre><code>\/\/ ACL kernel for adding two input vectors __kernel void vector_add( __global const uint *restrict x,                             __global const uint *restrict y,                             __global       uint *restrict z ) {     \/\/ get index of the work item     int index = get_global_id(0);       \/\/ add the vector elements     z[index] = x[index] + y[index]; } <\/code><\/pre>\n<p>  \u041f\u043e\u043b\u043d\u043e\u0441\u0442\u044c\u044e \u043a\u043e\u0434 \u0434\u043b\u044f \u0445\u043e\u0441\u0442\u0430 \u043f\u0440\u0438\u0432\u043e\u0434\u0438\u0442\u044c \u043d\u0435 \u0431\u0443\u0434\u0443: \u0435\u0433\u043e \u043c\u043e\u0436\u043d\u043e \u0433\u043b\u044f\u043d\u0443\u0442\u044c \u0432\u043e\u0442 <a href=\"https:\/\/github.com\/johan92\/altera_opencl_sandbox\/blob\/master\/vector_add\/host\/src\/main.cpp\">\u0442\u0443\u0442<\/a>.<\/p>\n<p>  \u0427\u0442\u043e \u043e\u043d \u0434\u0435\u043b\u0430\u0435\u0442:  <\/p>\n<ul>\n<li>\u043f\u044b\u0442\u0430\u0435\u0442\u0441\u044f \u0440\u0430\u0441\u043f\u043e\u0437\u043d\u0430\u0442\u044c, \u043a\u0430\u043a\u0438\u0435 \u0435\u0441\u0442\u044c OpenCL \u0434\u0435\u0432\u0430\u0439\u0441\u044b<\/li>\n<li>\u043f\u0435\u0440\u0435\u043f\u0440\u043e\u0433\u0440\u0430\u043c\u043c\u0438\u0440\u0443\u0435\u0442 FPGA, \u0438\u0441\u043f\u043e\u043b\u044c\u0437\u0443\u044f aocx-\u0444\u0430\u0439\u043b<\/li>\n<li>\u0438\u043d\u0438\u0446\u0438\u0430\u043b\u0438\u0437\u0438\u0440\u0443\u0435\u0442 \u0431\u0443\u0444\u0435\u0440\u0430 \u0434\u043b\u044f \u043c\u0430\u0441\u0441\u0438\u0432\u043e\u0432 X, Y, Z<\/li>\n<li>\u0433\u0435\u043d\u0435\u0440\u0438\u0440\u0443\u0435\u0442 \u0434\u0430\u043d\u043d\u044b\u0435 \u0432 \u043c\u0430\u0441\u0441\u0438\u0432\u0430\u0445 X \u0438 Y, \u0430 \u0442\u0430\u043a \u0436\u0435 \u0432\u044b\u0447\u0438\u0441\u043b\u044f\u0435\u0442 (\u043d\u0430 \u043f\u0440\u043e\u0446\u0435\u0441\u0441\u043e\u0440\u0435) \u0440\u0435\u0444\u0435\u0440\u0435\u043d\u0441\u043d\u044b\u0439 \u043e\u0442\u0432\u0435\u0442<\/li>\n<li>\u043f\u0435\u0440\u0435\u0434\u0430\u0435\u0442 \u0443\u043a\u0430\u0437\u0430\u0442\u0435\u043b\u0438 \u043d\u0430 \u043c\u0430\u0441\u0441\u0438\u0432\u044b \u0432 \u043a\u0435\u0440\u043d\u0435\u043b<\/li>\n<li>\u0437\u0430\u043f\u0443\u0441\u043a\u0430\u0435\u0442 \u043e\u0431\u0440\u0430\u0431\u043e\u0442\u043a\u0443<\/li>\n<li>\u0434\u043e\u0436\u0438\u0434\u0430\u0435\u0442\u0441\u044f \u0435\u0451 \u043e\u043a\u043e\u043d\u0447\u0430\u043d\u0438\u044f<\/li>\n<li>\u0441\u0440\u0430\u0432\u043d\u0438\u0432\u0430\u0435\u0442 \u0440\u0435\u0444\u0435\u0440\u0435\u043d\u0441\u043d\u044b\u0439 \u043e\u0442\u0432\u0435\u0442 \u0441 \u0442\u0435\u043c, \u0447\u0442\u043e \u043f\u043e\u0441\u0447\u0438\u0442\u0430\u043b \u043a\u0435\u0440\u043d\u0435\u043b<\/li>\n<\/ul>\n<p>  \u0421\u0431\u043e\u0440\u043a\u0430 \u0435\u0433\u043e \u0442\u0440\u0438\u0432\u0438\u0430\u043b\u044c\u043d\u0430: \u0437\u0430\u043f\u0443\u0441\u043a\u0430\u0435\u043c \u043e\u0447\u0435\u043d\u044c \u043f\u0440\u043e\u0441\u0442\u043e\u0439 <a href=\"https:\/\/github.com\/johan92\/altera_opencl_sandbox\/blob\/master\/vector_add\/Makefile\">Makefile<\/a>, \u043a\u043e\u0442\u043e\u0440\u044b\u0439 \u0438\u0441\u043f\u043e\u043b\u044c\u0437\u0443\u0435\u0442 ARM-\u043e\u0432\u0441\u043a\u0438\u0439 \u043a\u0440\u043e\u0441\u0441 \u043a\u043e\u043c\u043f\u0438\u043b\u044f\u0442\u043e\u0440. (\u0425\u043e\u0441\u0442\u043e\u043c \u0436\u0435 \u0432 \u043d\u0430\u0448\u0435\u043c \u0441\u043b\u0443\u0447\u0430\u0435 \u0431\u0443\u0434\u0435\u0442 \u044f\u0432\u043b\u044f\u0442\u044c\u0441\u044f ARM, \u043a\u043e\u0442\u043e\u0440\u044b\u0439 \u043d\u0430\u0445\u043e\u0434\u0438\u0442\u0441\u044f \u0432 SoC&#8217;e).<\/p>\n<p>  \u041f\u043e\u043b\u0443\u0447\u0430\u0435\u043c <b>aocx<\/b>:  <\/p>\n<pre><code>ish@xmr:~\/tmp\/cl\/vector_add$ aoc device\/vector_add.cl -o bin\/vector_add.aocx --board de1soc_sharedonly --profile -v aoc: Environment checks are completed successfully. You are now compiling the full flow!! aoc: Selected target board de1soc_sharedonly aoc: Running OpenCL parser.... aoc: OpenCL parser completed successfully. aoc: Compiling.... aoc: Linking with IP library ... aoc: First stage compilation completed successfully. aoc: Hardware generation completed successfully. <\/code><\/pre>\n<p>  \u041d\u0430\u043f\u043e\u043c\u043d\u044e, \u0447\u0442\u043e \u0444\u043b\u0430\u0433 <b>&#8212;profile<\/b> \u0434\u043e\u0431\u0430\u0432\u043b\u044f\u0435\u0442 \u0432 \u043f\u0440\u043e\u0448\u0438\u0432\u043a\u0443 \u0441\u0447\u0435\u0442\u0447\u0438\u043a\u0438 \u0434\u043b\u044f \u043f\u0440\u043e\u0444\u0438\u043b\u0438\u0440\u043e\u0432\u0430\u043d\u0438\u044f, \u0430 <b>-v<\/b> \u043f\u0440\u043e\u0441\u0442\u043e \u0434\u043b\u044f verbose.<\/p>\n<p>  \u042d\u0442\u043e \u0437\u0430\u0439\u043c\u0435\u0442 \u043c\u0438\u043d\u0443\u0442 \u0434\u0435\u0441\u044f\u0442\u044c-\u043f\u044f\u0442\u043d\u0430\u0434\u0446\u0430\u0442\u044c.<\/p>\n<p>  \u0412 \u0434\u0438\u0440\u0435\u043a\u0442\u043e\u0440\u0438\u0438 <b>bin<\/b> \u043f\u043e\u044f\u0432\u0438\u043b\u0441\u044f <b>vector_add.aocx<\/b>, \u0430 \u0432 <b>bin_vector_add<\/b> \u043a\u0432\u0430\u0440\u0442\u0443\u0441\u043e\u0432\u0441\u043a\u0438\u0439 \u043f\u0440\u043e\u0435\u043a\u0442, \u043a\u043e\u0442\u043e\u0440\u044b\u0439 \u0438 \u0441\u043e\u0431\u0438\u0440\u0430\u043b\u0441\u044f \u0432\u0441\u0451 \u044d\u0442\u043e \u0432\u0440\u0435\u043c\u044f.<\/p>\n<p>  \u041e\u0442\u0447\u0451\u0442 \u043e \u0441\u0431\u043e\u0440\u043a\u0435:  <\/p>\n<pre><code>+-------------------------------------------------------------------------------+ ; Fitter Summary                                                                ; +---------------------------------+---------------------------------------------+ ; Fitter Status                   ; Successful - Sat Oct 17 21:36:01 2015       ; ; Quartus II 64-Bit Version       ; 14.1.0 Build 186 12\/03\/2014 SJ Full Version ; ; Revision Name                   ; top                                         ; ; Top-level Entity Name           ; top                                         ; ; Family                          ; Cyclone V                                   ; ; Device                          ; 5CSEMA5F31C6                                ; ; Timing Models                   ; Final                                       ; ; Logic utilization (in ALMs)     ; 5,570 \/ 32,070 ( 17 % )                     ; ; Total registers                 ; 9685                                        ; ; Total pins                      ; 103 \/ 457 ( 23 % )                          ; ; Total virtual pins              ; 0                                           ; ; Total block memory bits         ; 127,344 \/ 4,065,280 ( 3 % )                 ; ; Total DSP Blocks                ; 0 \/ 87 ( 0 % )                              ; ; Total HSSI RX PCSs              ; 0                                           ; ; Total HSSI PMA RX Deserializers ; 0                                           ; ; Total HSSI TX PCSs              ; 0                                           ; ; Total HSSI PMA TX Serializers   ; 0                                           ; ; Total PLLs                      ; 2 \/ 6 ( 33 % )                              ; ; Total DLLs                      ; 1 \/ 4 ( 25 % )                              ; +---------------------------------+---------------------------------------------+ <\/code><\/pre>\n<p>  \u0411\u043e\u043b\u044c\u0448\u0435 \u0432\u0441\u0435\u0433\u043e \u0437\u0434\u0435\u0441\u044c \u0438\u043d\u0442\u0435\u0440\u0435\u0441\u0443\u0435\u0442 \u0434\u0432\u0435 \u0441\u0442\u0440\u043e\u0447\u043a\u0438: <b>Logic utilization<\/b> \u0438 <b>Total block memory bits<\/b>.<\/p>\n<p>  \u042d\u0442\u043e\u0442 \u043f\u0440\u043e\u0441\u0442\u043e\u0439 \u043f\u0440\u0438\u043c\u0435\u0440 \u0437\u0430\u043d\u044f\u043b 5570 ALM. \u041d\u0430 \u0441\u0430\u043c\u043e\u043c \u0434\u0435\u043b\u0435 \u043e\u043f\u0435\u0440\u0430\u0446\u0438\u044f \u0441\u043b\u043e\u0436\u0435\u043d\u0438\u044f \u0437\u0430\u043d\u0438\u043c\u0430\u0435\u0442 \u043c\u0435\u043d\u044c\u0448\u0435 1% \u043e\u0442 \u044d\u0442\u043e\u0433\u043e \u0447\u0438\u0441\u043b\u0430: \u0432\u0441\u0451 \u043e\u0441\u0442\u0430\u043b\u044c\u043d\u043e\u0435 \u0437\u0430\u043d\u044f\u043b\u0430 \u00ab\u0438\u043d\u0444\u0440\u0430\u0441\u0442\u0440\u0443\u043a\u0442\u0443\u0440\u0430\u00bb, \u043a\u043e\u0442\u043e\u0440\u0430\u044f \u0447\u0438\u0442\u0430\u0435\u0442 \u0438 \u0437\u0430\u043f\u0438\u0441\u044b\u0432\u0430\u0435\u0442 \u0434\u0430\u043d\u043d\u044b\u0435 \u0438\u0437 DDR (\u0430 \u0442\u0430\u043a \u0436\u0435 \u043f\u0440\u043e\u0444\u0438\u043b\u0438\u0440\u0443\u044e\u0449\u0438\u0435 \u0441\u0447\u0435\u0442\u0447\u0438\u043a\u0438). \u0415\u0449\u0435 \u0432\u0430\u0436\u043d\u043e \u043e\u0442\u043c\u0435\u0442\u0438\u0442\u044c, \u0447\u0442\u043e \u043f\u0440\u043e\u0435\u043a\u0442 \u0432 \u041a\u0432\u0430\u0440\u0442\u0443\u0441\u0435 \u0441\u043e\u0431\u0438\u0440\u0430\u043b\u0441\u044f \u0441 \u0434\u0435\u0444\u043e\u043b\u0442\u043d\u044b\u043c\u0438 \u043d\u0430\u0441\u0442\u0440\u043e\u0439\u043a\u0430\u043c\u0438, \u043a\u043e\u0442\u043e\u0440\u044b\u0435 \u043d\u0435 \u0432\u043a\u043b\u044e\u0447\u0430\u043b\u0438 \u043d\u0438\u043a\u0430\u043a\u0443\u044e \u043e\u043f\u0442\u0438\u043c\u0438\u0437\u0430\u0446\u0438\u0438 \u043f\u043e \u0440\u0435\u0441\u0443\u0440\u0441\u0430\u043c\/\u0447\u0430\u0441\u0442\u043e\u0442\u0435.<\/p>\n<p>  \u0422\u0430\u043a \u0436\u0435 \u0438\u043d\u0442\u0435\u0440\u0435\u0441\u043d\u043e, \u0447\u0442\u043e \u0430\u0432\u0442\u043e\u043c\u0430\u0442\u0438\u0447\u0435\u0441\u043a\u0438 \u00ab\u0433\u0434\u0435-\u0442\u043e\u00bb \u043f\u043e\u044f\u0432\u0438\u043b\u0430\u0441\u044c \u043f\u0430\u043c\u044f\u0442\u044c \u0441 \u0441\u0443\u043c\u0430\u0440\u043d\u044b\u043c \u043e\u0431\u044a\u0435\u043c\u043e\u043c \u043d\u0430 ~128 \u041a\u0431\u0438\u0442. <\/p>\n<p>  \u041a\u0441\u0442\u0430\u0442\u0438, \u043c\u043e\u0436\u043d\u043e \u0433\u043b\u044f\u043d\u0443\u0442\u044c, \u043a\u0430\u043a\u0438\u0435 \u043f\u043e\u044f\u0432\u0438\u043b\u0438\u0441\u044c \u0441\u0435\u043a\u0446\u0438\u0438 \u0432 <b>vector_add.aocx<\/b>:  <\/p>\n<div class=\"spoiler\"><b class=\"spoiler_title\">\u0421\u043a\u0440\u044b\u0442\u044b\u0439 \u0442\u0435\u043a\u0441\u0442<\/b><\/p>\n<div class=\"spoiler_text\">\n<pre><code>ish@xmr:~\/tmp\/cl\/vector_add$ readelf -a bin\/vector_add.aocx  ELF Header:   Magic:   7f 45 4c 46 01 01 01 00 00 00 00 00 00 00 00 00    Class:                             ELF32   Data:                              2's complement, little endian   Version:                           1 (current)   OS\/ABI:                            UNIX - System V   ABI Version:                       0   Type:                              NONE (None)   Machine:                           Advanced Micro Devices X86-64   Version:                           0x1   Entry point address:               0x0   Start of program headers:          0 (bytes into file)   Start of section headers:          2370388 (bytes into file)   Flags:                             0x0   Size of this header:               52 (bytes)   Size of program headers:           0 (bytes)   Number of program headers:         0   Size of section headers:           40 (bytes)   Number of section headers:         20   Section header string table index: 1  Section Headers:   [Nr] Name              Type            Addr     Off    Size   ES Flg Lk Inf Al   [ 0]                   NULL            00000000 000000 000000 00      0   0  0   [ 1] .shstrtab         STRTAB          00000000 000080 00011c 00   S  0   0 128   [ 2]                   PROGBITS        00000000 000200 001000 00      0   0 128   [ 3] .acl.board        PROGBITS        00000000 001200 000011 00      0   0 128   [ 4] .acl.compileoptio PROGBITS        00000000 001280 000002 00      0   0 128   [ 5] .acl.version      PROGBITS        00000000 001300 00000a 00      0   0 128   [ 6] .acl.file.0       PROGBITS        00000000 001380 000030 00      0   0 128   [ 7] .acl.source.0     PROGBITS        00000000 001400 0006c2 00      0   0 128   [ 8] .acl.nfiles       PROGBITS        00000000 001b00 000001 00      0   0 128   [ 9] .acl.source       PROGBITS        00000000 001b80 0006c2 00      0   0 128   [10] .acl.opt.rpt.xml  PROGBITS        00000000 002280 000019 00      0   0 128   [11] .acl.mav.json     PROGBITS        00000000 002300 00107f 00      0   0 128   [12] .acl.area.json    PROGBITS        00000000 003380 0009da 00      0   0 128   [13] .acl.profiler.xml PROGBITS        00000000 003d80 002f08 00      0   0 128   [14] .acl.profile_base PROGBITS        00000000 006d00 0009c8 00      0   0 128   [15] .acl.autodiscover PROGBITS        00000000 007700 000071 00      0   0 128   [16] .acl.autodiscover PROGBITS        00000000 007780 00021e 00      0   0 128   [17] .acl.board_spec.x PROGBITS        00000000 007a00 0003eb 00      0   0 128   [18] .acl.fpga.bin     PROGBITS        00000000 007e00 23ab98 00      0   0 128   [19] .acl.quartus_repo PROGBITS        00000000 242a00 000151 00      0   0 128 Key to Flags:   W (write), A (alloc), X (execute), M (merge), S (strings), l (large)   I (info), L (link order), G (group), T (TLS), E (exclude), x (unknown)   O (extra OS processing required) o (OS specific), p (processor specific)  There are no section groups in this file.  There are no program headers in this file.  There are no relocations in this file.  There are no unwind sections in this file.  No version information found in this file. <\/code><\/pre>\n<p>  <\/div>\n<\/div>\n<p>  <a name=\"execute_on_fpga\"><\/a>  <\/p>\n<h2>\u0417\u0430\u043f\u0443\u0441\u043a\u0430\u0435\u043c \u043a\u0435\u0440\u043d\u0435\u043b<\/h2>\n<p>  \u041a\u043e\u043f\u0438\u0440\u0443\u0435\u043c \u0447\u0435\u0440\u0435\u0437 scp <b>vector_add<\/b> \u0438 <b>vector_add.ao\u0441x<\/b> \u043d\u0430 \u043f\u043b\u0430\u0442\u0443 \u0438 \u0437\u0430\u043f\u0443\u0441\u043a\u0430\u0435\u043c:  <\/p>\n<pre><code>root@socfpga:~\/myvectoradduint# ls -l -rwxr-xr-x    1 root     root         42525 Apr 16 06:57 vector_add -rw-r--r--    1 root     root       2371188 Apr 16 06:58 vector_add.aocx  root@socfpga:~\/myvectoradduint# .\/vector_add  Initializing OpenCL Platform: Altera SDK for OpenCL Using 1 device(s)   de1soc_sharedonly : Cyclone V SoC Development Kit Using AOCX: vector_add.aocx Launching for device 0 (1000000 elements)  Time: 112.475 ms Kernel time (device 0): 7.270 ms  Verification: PASS <\/code><\/pre>\n<p>  \u041d\u0430\u043c \u0443\u0434\u0430\u043b\u043e\u0441\u044c \u0441\u043b\u043e\u0436\u0438\u0442\u044c 1 \u043c\u0438\u043b\u043b\u0438\u043e\u043d \u043f\u0430\u0440 32-\u0431\u0438\u0442\u043d\u044b\u0445 \u0447\u0438\u0441\u0435\u043b \u0437\u0430 7.270 ms \u0438\u043b\u0438 \u043e\u0434\u043d\u0443 \u043f\u0430\u0440\u0443 \u0437\u0430 7.27 ns. \u041d\u0430 \u0441\u0430\u043c\u043e\u043c \u0434\u0435\u043b\u0435 \u044d\u0442\u043e\u0442 \u043f\u043e\u043a\u0430\u0437\u0430\u0442\u0435\u043b\u044c \u043f\u0440\u044f\u043c\u043e \u0441\u0435\u0439\u0447\u0430\u0441 \u043d\u0435 \u0442\u0430\u043a \u0438\u043d\u0442\u0435\u0440\u0435\u0441\u0435\u043d: \u043f\u0440\u0438\u043c\u0435\u0440 \u043d\u0435 \u0431\u044b\u043b \u043e\u043f\u0442\u0438\u043c\u0438\u0437\u0438\u0440\u043e\u0432\u0430\u043d \u043f\u043e \u043f\u0440\u043e\u0438\u0437\u0432\u043e\u0434\u0438\u0442\u0435\u043b\u044c\u043d\u043e\u0441\u0442\u0438. (\u0421\u043f\u043e\u0439\u043b\u0435\u0440: \u0438\u0441\u043f\u043e\u043b\u044c\u0437\u043e\u0432\u0430\u043b\u0441\u044f \u0442\u043e\u043b\u044c\u043a\u043e \u043e\u0434\u0438\u043d \u0441\u0443\u043c\u043c\u0430\u0442\u043e\u0440: \u0440\u0430\u0441\u043f\u0430\u0440\u0430\u043b\u043b\u0435\u043b\u0438\u0432\u0430\u043d\u0438\u044f \u0432\u044b\u0447\u0438\u0441\u043b\u0435\u043d\u0438\u0439 \u043d\u0435 \u0431\u044b\u043b\u043e).<\/p>\n<p>  \u041f\u043e\u0441\u043b\u0435 \u0432\u044b\u043f\u043e\u043b\u043d\u0435\u043d\u0438\u044f \u0432 \u0434\u0438\u0440\u0435\u043a\u0442\u043e\u0440\u0438\u0438 \u043f\u043e\u044f\u0432\u0438\u043b\u0441\u044f <b>profile.mon<\/b>:  <\/p>\n<pre><code>root@socfpga:~\/myvectoradduint# ls -l -rw-r--r--    1 root     root           170 Apr 16 06:58 profile.mon -rwxr-xr-x    1 root     root         42525 Apr 16 06:57 vector_add -rw-r--r--    1 root     root       2371188 Apr 16 06:58 vector_add.aocx <\/code><\/pre>\n<p>  \u041a\u043e\u043f\u0438\u0440\u0443\u0435\u043c \u0435\u0433\u043e \u043e\u0431\u0440\u0430\u0442\u043d\u043e \u043a \u0441\u0435\u0431\u0435 \u043d\u0430 \u043a\u043e\u043c\u043f\u044c\u044e\u0442\u0435\u0440 \u0438 \u0441\u043c\u043e\u0442\u0440\u0438\u043c \u0440\u0435\u0437\u0443\u043b\u044c\u0442\u0430\u0442 \u043f\u0440\u043e\u0444\u0438\u043b\u0438\u0440\u043e\u0432\u0430\u043d\u0438\u044f:  <\/p>\n<pre><code>ish@xmr:~\/tmp\/cl\/vector_add$ aocl report bin\/vector_add.aocx profile.mon <\/code><\/pre>\n<p>  <a href=\"https:\/\/habrastorage.org\/files\/c8f\/b62\/907\/c8fb629071844e2eb796e8b5e1aa4db0.png\"><img decoding=\"async\" src=\"https:\/\/habrastorage.org\/files\/c8f\/b62\/907\/c8fb629071844e2eb796e8b5e1aa4db0.png\"\/><\/a><\/p>\n<p>  <a href=\"https:\/\/habrastorage.org\/files\/f41\/091\/f78\/f41091f782794e438a8d5080a63fbff0.png\"><img decoding=\"async\" src=\"https:\/\/habrastorage.org\/files\/f41\/091\/f78\/f41091f782794e438a8d5080a63fbff0.png\"\/><\/a><\/p>\n<p>  <a href=\"https:\/\/habrastorage.org\/files\/d4f\/62e\/12f\/d4f62e12f84c485e8420bbc3d19da9e3.png\"><img decoding=\"async\" src=\"https:\/\/habrastorage.org\/files\/d4f\/62e\/12f\/d4f62e12f84c485e8420bbc3d19da9e3.png\"\/><\/a><\/p>\n<p>  \u041f\u0440\u043e\u0444\u0438\u043b\u0438\u0440\u043e\u0432\u0449\u0438\u043a \u043f\u043e\u043a\u0430\u0437\u0430\u043b, \u0447\u0442\u043e \u043c\u044b \u0438\u0441\u043f\u043e\u043b\u044c\u0437\u043e\u0432\u0430\u043b\u0438 \u0442\u043e\u043b\u044c\u043a\u043e \u0442\u0440\u0435\u0442\u044c \u043f\u0440\u043e\u043f\u0443\u0441\u043a\u043d\u043e\u0439 \u0441\u043f\u043e\u0441\u043e\u0431\u043d\u043e\u0441\u0442\u0438 \u0434\u043e \u0433\u043b\u043e\u0431\u0430\u043b\u044c\u043d\u043e\u0439 \u043f\u0430\u043c\u044f\u0442\u0438.<\/p>\n<p>  \u0415\u0441\u0442\u044c \u0432\u043e\u0437\u043c\u043e\u0436\u043d\u043e\u0441\u0442\u044c \u0437\u0430\u043f\u0443\u0441\u043a\u0430 \u0432\u0438\u0437\u0443\u0430\u043b\u0438\u0437\u0430\u0442\u043e\u0440\u0430:  <\/p>\n<pre><code>ish@xmr:~\/tmp\/cl\/vector_add$ aocl vis bin\/vector_add.aocx  <\/code><\/pre>\n<p>  <a href=\"https:\/\/habrastorage.org\/files\/500\/4f5\/9a3\/5004f59a35144fd785d963e434dea1a9.png\"><img decoding=\"async\" src=\"https:\/\/habrastorage.org\/files\/500\/4f5\/9a3\/5004f59a35144fd785d963e434dea1a9.png\"\/><\/a><br \/>  <a href=\"https:\/\/habrastorage.org\/getpro\/habr\/post_images\/005\/65f\/c08\/00565fc08e6d7e10466f6a4c3c18286c.png\"><img decoding=\"async\" src=\"https:\/\/habrastorage.org\/getpro\/habr\/post_images\/005\/65f\/c08\/00565fc08e6d7e10466f6a4c3c18286c.png\" alt=\"image\"\/><\/a><\/p>\n<p>  \u0412\u0438\u0437\u0443\u0430\u043b\u0438\u0437\u0430\u0442\u043e\u0440 \u043f\u043e\u043a\u0430\u0437\u0430\u043b, \u0447\u0442\u043e \u0435\u0441\u0442\u044c \u0442\u0440\u0438 \u0431\u043b\u043e\u043a\u0430, \u043a\u043e\u0442\u043e\u0440\u044b\u0435 \u043e\u0431\u0449\u0430\u044e\u0442\u0441\u044f \u0441 \u0433\u043b\u043e\u0431\u0430\u043b\u044c\u043d\u043e\u0439 \u043f\u0430\u043c\u044f\u0442\u044c\u044e: \u0434\u0432\u0430 \u043d\u0430 \u0447\u0442\u0435\u043d\u0438\u0435, \u043e\u0434\u0438\u043d \u043d\u0430 \u0437\u0430\u043f\u0438\u0441\u044c. \u0414\u043e\u0441\u0442\u0443\u043f \u043a \u0433\u043b\u043e\u0431\u0430\u043b\u044c\u043d\u043e\u0439 \u043f\u0430\u043c\u044f\u0442\u0438 \u0432 \u0434\u0430\u043d\u043d\u043e\u043c \u0441\u043b\u0443\u0447\u0430\u0435 \u043c\u043e\u0436\u0435\u0442 \u043e\u043a\u0430\u0437\u0430\u0442\u044c\u0441\u044f \u0443\u0437\u043a\u0438\u043c \u0437\u0432\u0435\u043d\u043e\u043c. \u0412 <b>Area report<\/b> \u0434\u043b\u044f \u043a\u0430\u0436\u0434\u043e\u0439 \u0441\u0442\u0440\u043e\u0447\u043a\u0438 \u043c\u043e\u0436\u043d\u043e \u0443\u0432\u0438\u0434\u0435\u0442\u044c \u043a\u043e\u043b\u0438\u0447\u0435\u0441\u0442\u0432\u043e \u0440\u0435\u0441\u0443\u0440\u0441\u043e\u0432, \u043a\u043e\u0442\u043e\u0440\u043e\u0435 \u0442\u0440\u0430\u0442\u0438\u0442\u0441\u044f \u0432 FPGA \u043d\u0430 \u0440\u0435\u0430\u043b\u0438\u0437\u0430\u0446\u0438\u044e. \u041a\u043e\u043d\u0435\u0447\u043d\u043e, \u043f\u0440\u0438\u043c\u0435\u0440 \u0438\u0437 \u043e\u0434\u043d\u043e\u0439 \u0441\u0442\u0440\u043e\u0447\u043a\u0438 \u043d\u0435 \u043f\u043e\u043a\u0430\u0437\u0430\u0442\u0435\u043b\u0435\u043d.<\/p>\n<p>  \u041d\u0430 youtube-\u043a\u0430\u043d\u0430\u043b\u0435 \u0410\u043b\u044c\u0442\u0435\u0440\u044b \u0435\u0441\u0442\u044c \u0432\u0438\u0434\u0435\u043e, \u0433\u0434\u0435 \u043f\u043e\u0434\u0440\u043e\u0431\u043d\u043e \u043f\u043e\u043a\u0430\u0437\u044b\u0432\u0430\u044e\u0442\u0441\u044f \u0432\u0441\u0435 \u0448\u0430\u0433\u0438, \u043e \u043a\u043e\u0442\u043e\u0440\u044b\u0445 \u044f \u0433\u043e\u0432\u043e\u0440\u0438\u043b \u0432\u044b\u0448\u0435:<\/p>\n<p>  <iframe loading=\"lazy\" width=\"560\" height=\"315\" src=\"https:\/\/www.youtube.com\/embed\/4PUKzI14mLY?feature=oembed\" frameborder=\"0\" allowfullscreen><\/iframe><\/p>\n<p>  \u041e\u0441\u0442\u0430\u043b\u044c\u043d\u044b\u0435 \u0432\u0438\u0434\u0435\u043e\u0437\u0430\u043f\u0438\u0441\u0438 \u0438\u0437 \u044d\u0442\u043e\u0433\u043e \u0446\u0438\u043a\u043b\u0430 \u043c\u043e\u0436\u043d\u043e \u043d\u0430\u0439\u0442\u0438 \u043f\u043e\u0434 \u0441\u043f\u043e\u0439\u043b\u0435\u0440\u043e\u043c:  <\/p>\n<div class=\"spoiler\"><b class=\"spoiler_title\">\u0421\u043a\u0440\u044b\u0442\u044b\u0439 \u0442\u0435\u043a\u0441\u0442<\/b><\/p>\n<div class=\"spoiler_text\"><iframe loading=\"lazy\" width=\"560\" height=\"315\" src=\"https:\/\/www.youtube.com\/embed\/WpcIYvQuvvo?feature=oembed\" frameborder=\"0\" allowfullscreen><\/iframe><br \/>  <iframe loading=\"lazy\" width=\"560\" height=\"315\" src=\"https:\/\/www.youtube.com\/embed\/npEUaj-MfVY?feature=oembed\" frameborder=\"0\" allowfullscreen><\/iframe><br \/>  <iframe loading=\"lazy\" width=\"560\" height=\"315\" src=\"https:\/\/www.youtube.com\/embed\/SKJR6PPeDFg?feature=oembed\" frameborder=\"0\" allowfullscreen><\/iframe>  <\/div>\n<\/div>\n<p>  <a name=\"the_end\"><\/a>  <\/p>\n<h2>\u0417\u0430\u043a\u043b\u044e\u0447\u0435\u043d\u0438\u0435<\/h2>\n<p>  \u0412 \u044d\u0442\u043e\u0439 \u0441\u0442\u0430\u0442\u044c\u0435 \u044f \u043f\u043e\u043f\u0440\u043e\u0431\u043e\u0432\u0430\u043b \u0438\u043d\u0441\u0442\u0440\u0443\u043c\u0435\u043d\u0442, \u043a\u043e\u0442\u043e\u0440\u044b\u0439 \u043f\u043e\u0437\u0432\u043e\u043b\u044f\u0435\u0442 \u043f\u0438\u0441\u0430\u0442\u044c \u043f\u043e\u0434 FPGA \u043d\u0430 \u0432\u044b\u0441\u043e\u043a\u043e\u043c \u0443\u0440\u043e\u0432\u043d\u0435 \u0431\u0435\u0437 \u0437\u043d\u0430\u043d\u0438\u044f HDL-\u044f\u0437\u044b\u043a\u043e\u0432. \u041a\u0430\u043a \u0432\u0438\u0434\u0438\u043c, \u043e\u043d \u0440\u0430\u0431\u043e\u0442\u0430\u0435\u0442 (\u043d\u0430 \u043f\u0440\u043e\u0441\u0442\u043e\u043c \u043f\u0440\u0438\u043c\u0435\u0440\u0435), \u0438 \u043d\u0430\u043c \u043f\u0440\u0430\u0432\u0434\u0430 \u043d\u0438\u0447\u0435\u0433\u043e \u043d\u0435 \u043f\u0440\u0438\u0448\u043b\u043e\u0441\u044c \u0434\u043e\u043f\u043e\u043b\u043d\u0438\u0442\u0435\u043b\u044c\u043d\u043e \u0434\u0435\u043b\u0430\u0442\u044c. <\/p>\n<p>  OpenCL \u043f\u043e\u0434 FPGA \u043d\u0435 \u0431\u0443\u0434\u0435\u0442 \u0437\u043e\u043b\u043e\u0442\u044b\u043c \u043c\u043e\u043b\u043e\u0442\u043a\u043e\u043c:   <\/p>\n<ul>\n<li>\u041d\u0435 \u043f\u043e\u0437\u0432\u043e\u043b\u044f\u0435\u0442 \u043e\u043f\u0438\u0441\u044b\u0432\u0430\u0442\u044c \u043f\u0440\u043e\u0446\u0435\u0441\u0441\u044b \u0441 \u0442\u043e\u0447\u043d\u043e\u0441\u0442\u044c\u044e \u0434\u043e \u0442\u0430\u043a\u0442\u0430 (\u043d\u043e \u0432\u0435\u0434\u044c \u043e\u0442 \u044d\u0442\u043e\u0433\u043e \u043c\u044b \u0438 \u0445\u043e\u0442\u0435\u043b\u0438 \u0443\u0439\u0442\u0438!)<\/li>\n<li>\u041d\u0435\u043f\u0440\u0438\u043c\u0435\u043d\u0438\u043c \u043d\u0430 \u043c\u0430\u043b\u0435\u043d\u044c\u043a\u0438\u0445 \u0447\u0438\u043f\u0430\u0445: \u0438\u043d\u0444\u0440\u0430\u0441\u0442\u0440\u0443\u043a\u0442\u0443\u0440\u0430 \u043e\u0442\u044a\u0435\u0434\u0430\u0435\u0442 \u043e\u0433\u0440\u043e\u043c\u043d\u043e\u0435 \u043a\u043e\u043b\u0438\u0447\u0435\u0441\u0442\u0432\u043e \u0440\u0435\u0441\u0443\u0440\u0441\u043e\u0432.<\/li>\n<\/ul>\n<p>  \u041e\u0434\u043d\u0430\u043a\u043e \u0441 \u043f\u043e\u043c\u043e\u0449\u044c\u044e \u043d\u0435\u0433\u043e FPGA \u043c\u043e\u0436\u0435\u0442 \u0441\u043e\u0441\u0442\u0430\u0432\u0438\u0442\u044c \u043e\u0447\u0435\u043d\u044c \u0440\u0435\u0430\u043b\u044c\u043d\u0443\u044e \u043a\u043e\u043d\u043a\u0443\u0440\u0435\u043d\u0446\u0438\u044e GPU \u0432 \u0442\u0430\u043a\u0438\u0445 \u043e\u0431\u043b\u0430\u0441\u0442\u044f\u0445 \u043a\u0430\u043a \u0432\u0438\u0434\u0435\u043e\u043e\u0431\u0440\u0430\u0431\u043e\u0442\u043a\u0430 (\u043c\u0430\u0448\u0438\u043d\u043d\u043e\u0435 \u0437\u0440\u0435\u043d\u0438\u0435), \u0448\u0438\u0444\u0440\u043e\u0432\u0430\u043d\u0438\u0435, \u0426\u041e\u0421, \u0441\u0438\u043c\u0443\u043b\u0438\u0440\u043e\u0432\u0430\u043d\u0438\u0435 (\u043c\u043e\u0434\u0435\u043b\u0438\u0440\u043e\u0432\u0430\u043d\u0438\u0435) \u0440\u0430\u0437\u043b\u0438\u0447\u043d\u044b\u0445 \u043f\u0440\u043e\u0446\u0435\u0441\u0441\u043e\u0432. \u0415\u0441\u043b\u0438 \u0433\u043e\u0432\u043e\u0440\u0438\u0442\u044c \u043f\u0440\u043e \u0442\u0435 \u043e\u0431\u043b\u0430\u0441\u0442\u0438, \u0433\u0434\u0435 \u044f \u0440\u0430\u0431\u043e\u0442\u0430\u044e (\u0433\u0435\u043d\u0435\u0440\u0430\u0446\u0438\u044f, \u0444\u0438\u043b\u044c\u0442\u0440\u0430\u0446\u0438\u044f, \u043a\u043e\u043c\u043c\u0443\u0442\u0430\u0446\u0438\u044f Ethernet-\u043f\u0430\u043a\u0435\u0442\u043e\u0432), \u0433\u0434\u0435 \u0432\u044b\u0436\u0438\u043c\u0430\u043d\u0438\u0435 \u043c\u0430\u043a\u0441\u0438\u043c\u0430\u043b\u044c\u043d\u043e\u0439 \u043f\u0440\u043e\u0438\u0437\u0432\u043e\u0434\u0438\u0442\u0435\u043b\u044c\u043d\u043e\u0441\u0442\u0438 \u043a\u0430\u043a \u0440\u0430\u0437 \u043f\u0440\u043e\u0438\u0441\u0445\u043e\u0434\u0438\u0442 \u0431\u043b\u0430\u0433\u043e\u0434\u0430\u0440\u044f \u0443\u043f\u0440\u0430\u0432\u043b\u0435\u043d\u0438\u044e \u0441\u0430\u043c\u044b\u043c \u043d\u0438\u0437\u043a\u0438\u043c \u0443\u0440\u043e\u0432\u043d\u0435\u043c, \u0442\u043e \u043f\u043e\u043d\u0438\u043c\u0430\u043d\u0438\u044f, \u043a\u0430\u043a \u0438\u0441\u043f\u043e\u043b\u044c\u0437\u043e\u0432\u0430\u0442\u044c OpenCL (\u0438 \u043f\u043e\u043b\u0443\u0447\u0430\u0442\u044c \u0430\u043d\u0430\u043b\u043e\u0433\u0438\u0447\u043d\u044b\u0439 \u0440\u0435\u0437\u0443\u043b\u044c\u0442\u0430\u0442) \u0443 \u043c\u0435\u043d\u044f \u043d\u0435\u0442.<\/p>\n<p>  \u0415\u0441\u043b\u0438 \u0435\u0441\u0442\u044c \u043f\u043e\u0442\u0440\u0435\u0431\u043d\u043e\u0441\u0442\u044c \u0432 \u043c\u0430\u043a\u0441\u0438\u043c\u0430\u043b\u044c\u043d\u043e\u0439 \u043f\u0440\u043e\u0438\u0437\u0432\u043e\u0434\u0438\u0442\u0435\u043b\u044c\u043d\u043e\u0441\u0442\u0438, \u0442\u043e \u043d\u0430\u0434\u043e \u043e\u0447\u0435\u043d\u044c \u0445\u043e\u0440\u043e\u0448\u043e \u043f\u043e\u043d\u0438\u043c\u0430\u0442\u044c \u0432\u043e \u0447\u0442\u043e \u043f\u043e\u043b\u0443\u0447\u0430\u0435\u0442\u0441\u044f \u0442\u0430 \u0438\u043b\u0438 \u0438\u043d\u0430\u044f \u043a\u043e\u043d\u0441\u0442\u0440\u0443\u043a\u0446\u0438\u044f \u044f\u0437\u044b\u043a\u0430. \u041f\u043e\u044d\u0442\u043e\u043c\u0443, \u043c\u043d\u0435 \u043a\u0430\u0436\u0435\u0442\u0441\u044f, \u0442\u0435\u043c, \u043a\u0442\u043e \u0437\u0430\u0445\u043e\u0447\u0435\u0442 \u0447\u0442\u043e-\u0442\u043e \u0431\u043e\u043b\u0435\u0435 \u043c\u0435\u043d\u0435\u0435 \u0441\u0435\u0440\u044c\u0435\u0437\u043d\u043e\u0435 \u043f\u0438\u0441\u0430\u0442\u044c \u043d\u0430 OpenCL \u043f\u043e\u0434 FPGA \u043f\u0440\u0438\u0434\u0435\u0442\u0441\u044f \u043d\u0430 \u0431\u0430\u0437\u043e\u0432\u043e\u043c \u0443\u0440\u043e\u0432\u043d\u0435 \u0438\u0437\u0443\u0447\u0438\u0442\u044c Quartus, Qsys \u0438 Verilog (\u043d\u0430 \u0443\u0440\u043e\u0432\u043d\u0435 \u0447\u0442\u0435\u043d\u0438\u044f). \u0412\u043e\u0437\u043c\u043e\u0436\u043d\u043e, \u0432\u0438\u0437\u0443\u0430\u043b\u0438\u0437\u0430\u0442\u043e\u0440\u0430 \u0438 \u043f\u0440\u043e\u0444\u0438\u043b\u0438\u0440\u043e\u0432\u0449\u0438\u043a\u0430 \u0431\u0443\u0434\u0435\u0442 \u0445\u0432\u0430\u0442\u0430\u0442\u044c, \u043d\u043e \u043f\u043e\u043a\u0430 \u043e\u043d\u0438 \u0432\u044b\u0433\u043b\u044f\u0434\u044f\u0442 \u043a\u0430\u043a \u0441\u0442\u0443\u0434\u0435\u043d\u0447\u0435\u043d\u0441\u043a\u0438\u0435 \u043f\u043e\u0434\u0434\u0435\u043b\u043a\u0438, \u043d\u0430\u0434\u0435\u044e\u0441\u044c, \u0432 \u043d\u043e\u0432\u044b\u0445 \u0440\u0435\u043b\u0438\u0437\u0430\u0445 \u043a\u0432\u0430\u0440\u0442\u0443\u0441\u0430 \u044d\u0442\u043e \u0438\u0441\u043f\u0440\u0430\u0432\u044f\u0442.<\/p>\n<p>  \u0415\u0441\u043b\u0438 \u0433\u043e\u0432\u043e\u0440\u0438\u0442\u044c \u043e \u0440\u0435\u0430\u043b\u0442\u0430\u0439\u043c\u043e\u0432\u043e\u0439 \u043e\u0431\u0440\u0430\u0431\u043e\u0442\u043a\u0435 \u0432\u0438\u0434\u0435\u043e, \u0442\u043e \u0440\u0435\u043a\u043e\u043c\u0435\u043d\u0434\u0443\u044e \u0433\u043b\u044f\u043d\u0443\u0442\u044c \u0432\u043e\u0442 \u044d\u0442\u0443 \u0434\u0435\u043c\u043a\u0443:<br \/>  <iframe loading=\"lazy\" width=\"560\" height=\"315\" src=\"https:\/\/www.youtube.com\/embed\/ythPvAPB4iI?feature=oembed\" frameborder=\"0\" allowfullscreen><\/iframe><br \/>  \u0420\u0435\u0431\u044f\u0442\u0430 \u0438\u0437 iABRA \u0438\u0437\u043d\u0430\u0447\u0430\u043b\u044c\u043d\u043e \u0434\u0435\u043b\u0430\u043b\u0438 \u043c\u0430\u0448\u0438\u043d\u043d\u043e\u0435 \u0437\u0440\u0435\u043d\u0438\u0435 \u043d\u0430 OpenCL \u043f\u043e\u0434 AMD GPU, \u043d\u043e \u0437\u0430\u0442\u0435\u043c \u043f\u0435\u0440\u0435\u0435\u0445\u0430\u043b\u0438 \u043d\u0430 Altera. \u041f\u0440\u043e\u0433\u0440\u0430\u043c\u043c\u0438\u0441\u0442 \u043f\u043e\u0434\u0447\u0435\u0440\u043a\u0438\u0432\u0430\u0435\u0442, \u0447\u0442\u043e \u0438\u0441\u043f\u043e\u043b\u044c\u0437\u043e\u0432\u0430\u043d\u0438\u0435 OpenCL \u043f\u043e\u0437\u0432\u043e\u043b\u0438\u043b\u043e \u00ab\u043d\u0435 \u0440\u0430\u0437\u0431\u0438\u0440\u0430\u0442\u044c\u0441\u044f \u0432 VHDL, \u0442.\u043a. \u0443 \u043d\u0438\u0445 \u0432 \u044d\u0442\u043e\u043c \u043e\u043f\u044b\u0442\u0430 \u043d\u0435\u0442, \u0430 \u043f\u0438\u0441\u0430\u0442\u044c \u043d\u0430 \u0442\u043e\u043c, \u0447\u0442\u043e \u043e\u043d\u0438 \u0443\u043c\u0435\u044e\u0442\u00bb.<\/p>\n<p>  \u0412 \u043d\u0435\u043a\u043e\u0442\u043e\u0440\u044b\u0445 \u0434\u043e\u043a\u043b\u0430\u0434\u0430\u0445, \u0433\u0434\u0435 \u0441\u0440\u0430\u0432\u043d\u0438\u0432\u0430\u044e\u0442\u0441\u044f \u0440\u0435\u0430\u043b\u0438\u0437\u0430\u0446\u0438\u0438 \u0430\u043b\u0433\u043e\u0440\u0438\u0442\u043c\u043e\u0432 (\u0448\u0438\u0444\u0440\u043e\u0432\u0430\u043d\u0438\u0435, \u0432\u0438\u0434\u0435\u043e\u043e\u0431\u0440\u0430\u0431\u043e\u0442\u043a\u0430) \u043d\u0430 GPU \u0438 OpenCL FPGA \u0443\u0442\u0432\u0435\u0440\u0436\u0434\u0430\u0435\u0442\u0441\u044f, \u0447\u0442\u043e \u043a\u043e\u043b\u0438\u0447\u0435\u0441\u0442\u0432\u043e \u0432\u044b\u043f\u043e\u043b\u043d\u0435\u043d\u043d\u044b\u0445 \u043e\u043f\u0435\u0440\u0430\u0446\u0438\u0439 \u0432 \u0441\u0435\u043a\u0443\u043d\u0434\u0443 \u0443 \u043d\u0438\u0445 \u043f\u0440\u0438\u043c\u0435\u0440\u043d\u043e \u043e\u0434\u0438\u043d\u0430\u043a\u043e\u0432\u043e\u0435, \u043d\u043e FPGA \u043f\u043e\u0442\u0440\u0435\u0431\u043b\u044f\u0435\u0442 \u0432 10 \u0440\u0430\u0437 \u043c\u0435\u043d\u044c\u0448\u0435 \u044d\u043b\u0435\u043a\u0442\u0440\u043e\u044d\u043d\u0435\u0440\u0433\u0438\u0438. \u042f \u0432\u0441\u0435\u0433\u0434\u0430 \u043a \u0442\u0430\u043a\u0438\u043c \u0431\u0435\u043d\u0447\u043c\u0430\u0440\u043a\u0430\u043c \u043e\u0442\u043d\u043e\u0448\u0443\u0441\u044c \u043d\u0435\u043c\u043d\u043e\u0433\u043e \u0441\u043a\u0435\u043f\u0442\u0438\u0447\u0435\u0441\u043a\u0438, \u043f\u043e\u0442\u043e\u043c\u0443 \u0447\u0442\u043e \u0441\u0430\u043c \u0438\u0445 \u043d\u0435 \u043f\u0440\u043e\u0431\u043e\u0432\u0430\u043b)<\/p>\n<p>  \u0421 \u0432\u044b\u0445\u043e\u0434\u043e\u043c \u043d\u043e\u0432\u044b\u0445 \u0441\u0435\u043c\u0435\u0439\u0441\u0442\u0432 <b>Arria 10<\/b> \u0438 <b>Stratix 10<\/b> \u044f \u0434\u043e\u043f\u0443\u0441\u043a\u0430\u044e, \u0447\u0442\u043e \u0432\u0441\u0451 \u0431\u043e\u043b\u044c\u0448\u0435 \u043f\u0430\u0440\u0430\u043b\u043b\u0435\u043b\u044c\u043d\u044b\u0445 \u0432\u044b\u0447\u0438\u0441\u043b\u0435\u043d\u0438\u0439 \u043f\u0435\u0440\u0435\u0439\u0434\u0435\u0442 \u043d\u0430 \u0438\u0441\u043f\u043e\u043b\u044c\u0437\u043e\u0432\u0430\u043d\u0438\u0435 FPGA: \u043c\u044b \u044d\u0442\u0438 \u0447\u0438\u043f\u044b \u0443\u0432\u0438\u0434\u0438\u043c \u0432 \u0441\u0443\u043f\u0435\u0440\u043a\u043e\u043c\u043f\u044c\u044e\u0442\u0435\u0440\u0430\u0445 \u0438 \u0432 \u0434\u0430\u0442\u0430\u0446\u0435\u043d\u0442\u0440\u0430\u0445.<\/p>\n<p>  \u0418 \u0435\u0449\u0435 \u043e\u0434\u043d\u043e \u0432\u0438\u0434\u0435\u043e \u043e \u0440\u0435\u0430\u043b\u044c\u043d\u043e\u043c \u0438\u0441\u043f\u043e\u043b\u044c\u0437\u043e\u0432\u0430\u043d\u0438\u0438 Altera SDK for OpenCL:<br \/>  <iframe loading=\"lazy\" width=\"560\" height=\"315\" src=\"https:\/\/www.youtube.com\/embed\/ObqtwoVy5RQ?feature=oembed\" frameborder=\"0\" allowfullscreen><\/iframe><\/p>\n<p>  \u0421\u043f\u0430\u0441\u0438\u0431\u043e \u0437\u0430 \u0432\u043d\u0438\u043c\u0430\u043d\u0438\u0435! \u0411\u0443\u0434\u0443 \u0440\u0430\u0434 \u0432\u043e\u043f\u0440\u043e\u0441\u0430\u043c \u0438 \u0437\u0430\u043c\u0435\u0447\u0430\u043d\u0438\u044f\u043c \u0432 \u043a\u043e\u043c\u043c\u0435\u043d\u0442\u0430\u0440\u0438\u044f\u0445 \u0438\u043b\u0438 \u0432 \u043b\u0438\u0447\u043a\u0435)<\/p>\n<p>  <b>\u041f\u043e\u043b\u0435\u0437\u043d\u044b\u0435 \u0441\u0441\u044b\u043b\u043a\u0438<\/b>:  <\/p>\n<ul>\n<li><a href=\"https:\/\/github.com\/johan92\/altera_opencl_sandbox\/tree\/master\/vector_add\">\u0418\u0441\u0445\u043e\u0434\u043d\u0438\u043a\u0438 \u043f\u0440\u0438\u043c\u0435\u0440\u0430 \u0438 \u0430\u0432\u0442\u043e\u0441\u0433\u0435\u0440\u0435\u043d\u0435\u0440\u0435\u043d\u043d\u044b\u0439 Verilog-\u043a\u043e\u0434<\/a><\/li>\n<li><a href=\"https:\/\/www.altera.com\/products\/design-software\/embedded-software-developers\/opencl\/overview.html\">Altera SDK for OpenCL: Overview<\/a><\/li>\n<li><a href=\"http:\/\/www.altera.com\/literature\/hb\/opencl-sdk\/aocl_getting_started.pdf\">Altera SDK for OpenCL: Getting Started Guide <\/a><\/li>\n<li><a href=\"http:\/\/tcfpga.org\/fpga2013\/openCL_tutorial.pdf\"> <b>Harnessing the Power of FPGAs using Altera\u2019s OpenCL Compiler<\/b><\/a>: \u043e\u0447\u0435\u043d\u044c \u0431\u043e\u043b\u044c\u0448\u0430\u044f \u043f\u0440\u0435\u0437\u0435\u043d\u0442\u0430\u0446\u0438\u044f (&gt;100 \u0441\u043b\u0430\u0439\u0434\u043e\u0432) \u0434\u043b\u044f \u0442\u0435\u0445 \u043a\u0442\u043e \u043b\u044e\u0431\u0438\u0442 \u043a\u0430\u0440\u0442\u0438\u043d\u043a\u0438 \u0441\u043c\u043e\u0442\u0440\u0435\u0442\u044c \ud83d\ude42<\/li>\n<li><a href=\"http:\/\/www.altera.com\/literature\/hb\/opencl-sdk\/aocl_programming_guide.pdf\">Altera SDK for OpenCL: Programming Guide <\/a><\/li>\n<li><a href=\"http:\/\/www.altera.com\/literature\/hb\/opencl-sdk\/aocl_optimization_guide.pdf\">Altera SDK for OpenCL: Optimization Guide<\/a><\/li>\n<li><a href=\"https:\/\/www.altera.com\/en_US\/pdfs\/literature\/hb\/opencl-sdk\/aocl-best-practices-guide.pdf\">Altera SDK for OpenCL: Best Practices Guide<\/a><\/li>\n<\/ul>\n<div class=\"clear\"><\/div>\n<p> \u0441\u0441\u044b\u043b\u043a\u0430 \u043d\u0430 \u043e\u0440\u0438\u0433\u0438\u043d\u0430\u043b \u0441\u0442\u0430\u0442\u044c\u0438 <a href=\"http:\/\/habrahabr.ru\/post\/269009\/\"> http:\/\/habrahabr.ru\/post\/269009\/<\/a><\/p>\n","protected":false},"excerpt":{"rendered":"<p>       <img decoding=\"async\" src=\"https:\/\/habrastorage.org\/getpro\/habr\/post_images\/4cb\/21d\/43d\/4cb21d43df4b00dac92ec93d29c15488.gif\" alt=\"image\"\/><\/p>\n<p>  \u0412\u0441\u0435\u043c \u043f\u0440\u0438\u0432\u0435\u0442!<\/p>\n<p>  <b>Altera SDK for OpenCL<\/b> \u2014 \u044d\u0442\u043e \u043d\u0430\u0431\u043e\u0440 \u0431\u0438\u0431\u043b\u0438\u043e\u0442\u0435\u043a \u0438 \u043f\u0440\u0438\u043b\u043e\u0436\u0435\u043d\u0438\u0439, \u043a\u043e\u0442\u043e\u0440\u044b\u0439 \u043f\u043e\u0437\u0432\u043e\u043b\u044f\u0435\u0442 \u043a\u043e\u043c\u043f\u0438\u043b\u0438\u0440\u043e\u0432\u0430\u0442\u044c \u043a\u043e\u0434, \u043d\u0430\u043f\u0438\u0441\u0430\u043d\u043d\u044b\u0439 \u043d\u0430 <b>OpenCL<\/b>, \u0432 \u043f\u0440\u043e\u0448\u0438\u0432\u043a\u0443 \u0434\u043b\u044f \u041f\u041b\u0418\u0421 \u0444\u0438\u0440\u043c\u044b <b>Altera<\/b>. \u042d\u0442\u043e \u0434\u0430\u0451\u0442 \u0432\u043e\u0437\u043c\u043e\u0436\u043d\u043e\u0441\u0442\u044c \u043f\u0440\u043e\u0433\u0440\u0430\u043c\u043c\u0438\u0441\u0442\u0443 \u0438\u0441\u043f\u043e\u043b\u044c\u0437\u043e\u0432\u0430\u0442\u044c FPGA \u043a\u0430\u043a \u0443\u0441\u043a\u043e\u0440\u0438\u0442\u0435\u043b\u044c \u0432\u044b\u0441\u043e\u043a\u043e\u043f\u0440\u043e\u0438\u0437\u0432\u043e\u0434\u0438\u0442\u0435\u043b\u044c\u043d\u044b\u0445 \u0432\u044b\u0447\u0438\u0441\u043b\u0435\u043d\u0438\u0439 \u0431\u0435\u0437 \u0437\u043d\u0430\u043d\u0438\u044f HDL-\u044f\u0437\u044b\u043a\u043e\u0432, \u0430 \u043f\u0438\u0441\u0430\u0442\u044c \u043d\u0430 \u0442\u043e\u043c, \u0447\u0442\u043e \u043e\u043d \u043f\u0440\u0438\u0432\u044b\u043a, \u043a\u043e\u0433\u0434\u0430 \u044d\u0442\u043e \u0434\u0435\u043b\u0430\u0435\u0442 \u043f\u043e\u0434 GPU.<\/p>\n<p>  \u042f \u043f\u043e\u0438\u0433\u0440\u0430\u043b\u0441\u044f \u0441 \u044d\u0442\u0438\u043c \u0438\u043d\u0441\u0442\u0440\u0443\u043c\u0435\u043d\u0442\u043e\u043c \u043d\u0430 \u043f\u0440\u043e\u0441\u0442\u043e\u043c \u043f\u0440\u0438\u043c\u0435\u0440\u0435 \u0438 \u0445\u043e\u0447\u0443 \u043e\u0431 \u044d\u0442\u043e\u043c \u0432\u0430\u043c \u0440\u0430\u0441\u0441\u043a\u0430\u0437\u0430\u0442\u044c.<\/p>\n<p>  \u041f\u043b\u0430\u043d:  <\/p>\n<ul>\n<li><a href=\"#fpga\">\u041f\u0430\u0440\u0443 \u0441\u043b\u043e\u0432 \u043e\u0431 FPGA<\/a><\/li>\n<li><a href=\"#where_to_run\">\u041d\u0430 \u0447\u0451\u043c \u0437\u0430\u043f\u0443\u0441\u043a\u0430\u0442\u044c?<\/a><\/li>\n<li><a href=\"#workflow\">\u041f\u0440\u043e\u0446\u0435\u0441\u0441 \u0440\u0430\u0437\u0440\u0430\u0431\u043e\u0442\u043a\u0438 (workflow)<\/a><\/li>\n<li><a href=\"#opencl_bsp\">OpenCL BSP<\/a><\/li>\n<li><a href=\"#compile\">\u041a\u043e\u043c\u043f\u0438\u043b\u0438\u0440\u0443\u0435\u043c \u043a\u0435\u0440\u043d\u0435\u043b<\/a><\/li>\n<li><a href=\"#execute_on_fpga\">\u2026 \u0438 \u0437\u0430\u043f\u0443\u0441\u043a\u0430\u0435\u043c<\/a><\/li>\n<li><a href=\"#the_end\">\u0417\u0430\u043a\u043b\u044e\u0447\u0435\u043d\u0438\u0435<\/a><\/li>\n<\/ul>\n<p>  \u0414\u043e\u0431\u0440\u043e \u043f\u043e\u0436\u0430\u043b\u043e\u0432\u0430\u0442\u044c \u043f\u043e\u0434 \u043a\u0430\u0442! <b>\u041e\u0441\u0442\u043e\u0440\u043e\u0436\u043d\u043e<\/b>, \u0431\u0443\u0434\u0443\u0442 \u043a\u0430\u0440\u0442\u0438\u043d\u043a\u0438!  <\/p>\n","protected":false},"author":1,"featured_media":0,"comment_status":"open","ping_status":"open","sticky":false,"template":"","format":"standard","meta":{"footnotes":""},"categories":[],"tags":[],"class_list":["post-267709","post","type-post","status-publish","format-standard","hentry"],"_links":{"self":[{"href":"https:\/\/savepearlharbor.com\/index.php?rest_route=\/wp\/v2\/posts\/267709","targetHints":{"allow":["GET"]}}],"collection":[{"href":"https:\/\/savepearlharbor.com\/index.php?rest_route=\/wp\/v2\/posts"}],"about":[{"href":"https:\/\/savepearlharbor.com\/index.php?rest_route=\/wp\/v2\/types\/post"}],"author":[{"embeddable":true,"href":"https:\/\/savepearlharbor.com\/index.php?rest_route=\/wp\/v2\/users\/1"}],"replies":[{"embeddable":true,"href":"https:\/\/savepearlharbor.com\/index.php?rest_route=%2Fwp%2Fv2%2Fcomments&post=267709"}],"version-history":[{"count":0,"href":"https:\/\/savepearlharbor.com\/index.php?rest_route=\/wp\/v2\/posts\/267709\/revisions"}],"wp:attachment":[{"href":"https:\/\/savepearlharbor.com\/index.php?rest_route=%2Fwp%2Fv2%2Fmedia&parent=267709"}],"wp:term":[{"taxonomy":"category","embeddable":true,"href":"https:\/\/savepearlharbor.com\/index.php?rest_route=%2Fwp%2Fv2%2Fcategories&post=267709"},{"taxonomy":"post_tag","embeddable":true,"href":"https:\/\/savepearlharbor.com\/index.php?rest_route=%2Fwp%2Fv2%2Ftags&post=267709"}],"curies":[{"name":"wp","href":"https:\/\/api.w.org\/{rel}","templated":true}]}}