当前位置: 首页 > news >正文

【存储】ZYNQ+NVMe小型化全国产存储解决方案

文章目录

  • 1、背景
  • 2、基础理论
  • 3、设计方案
    • 3.1、FPGA设计方案
      • 3.1.1、NVMe控制器实现
      • 3.1.2、NVMe控制器实现
    • 3.2 驱动软件设计方案
      • 3.2.1 读写NVMe磁盘软件驱动
      • 3.2.2 NVMe磁盘驱动设计
      • 3.2.3 标准EXT4文件系统设计
    • 3.3 上位机控制软件设计方案
  • 4、测试结果
    • 4.1 硬件测试平台说明
    • 4.2 测试结果说明
      • 4.2 .1、基于PCIe Gen2 软核,裸机测试
      • 4.2.2基于PCIe Gen3 软核,裸机测试
      • 4.2.3基于PCIe Gen2软核,带ext4文件系统测试
  • 5、总结


1、背景

  针对机载或其他对体积空间、成本有高要求的存储场景,使用单片ZYNQ7045/7100(复旦微FMQL45T900/FMQL100TAI) FPGA,实现数据接口、存储、文件系统管理、导入导出等功能。

实现规格:
1)2盘可组成RAID阵列,双盘最大能实现8TB容量
2)实现EXT4标准文件系统
3)EXT4文件系统下2GB/s的写、读速度;自定义文件系统4GB/s的写、读速度。
4)能支持万兆网网盘导出、千兆网盘导出、FTP导出

2、基础理论

  ZYNQ的相关使用请参见Xilinx的官方手册/复旦微的官方手册。NVMe的实现原理需要参见NVMe的具体协议。

NVMe协议下载链接:
NVMe协议下载
请添加图片描述

3、设计方案

3.1、FPGA设计方案

3.1.1、NVMe控制器实现

  NVME控制器主要由PCIE接口适配器、AXI交换桥、PRP计算模块以及命令/文件系统通道模块构成。
  PCIE接口适配器通过逻辑实现AXI的Master接口以及Slave接口到PCIE的接口转换。由AXI的Master接口实现盘主动读写内存的功能,由AXI的Slave接口实现PS对盘的SQ/CQ队列的读写。
  PRP计算模块实现解析盘请求的PRP2地址,计算、传送内存页地址给盘,从而实现大于4KB的读写请求的内存地址传送功能。
  命令通过通过解析PS传送过来的SQ指令,填充RPR1、PRP2地址,使数据通道始终指向PL DDR,以及文件系统数据始终指向PS DDR,文件系统通道由盘主动读写PS DDR实现。数据通道通过盘解析SQ指令,通过AXI桥,主动访问PL DDR实现。
在这里插入图片描述

3.1.2、NVMe控制器实现

  PCIE控制器主要完成PCIE协议传输层以及数据链路层协议。组TLP包发送给PHY控制器;对PHY层数据解析成TLP、LCRC、Sequence number等字段;实现ACK/NCK协议保证报文的可靠性;流控制管理,根据链路层报文更新credit值。
  PHY控制器主要实现PMA/PCS层协议,实现高速串行总线的串并转换以及8B/10B编码等功能。
  接口适配功能将TL层自定义接口转换成标准的AXI Stream总线接口。
在这里插入图片描述

3.2 驱动软件设计方案

3.2.1 读写NVMe磁盘软件驱动

  SOC处理器PL和PS协同工作,共同完成数据高速实时记录、传输、存储、加卸载和文件管理等功能。 SOC内部采用异构的架构,PL完成带宽要求高、实时性要求高的底层协议转换处理,如以太网UDP协议处理、NVMe协议处理等,PS完成数据量比较小的处理,如文件系统管理、以太网L3以上的相关处理等。同时,PS还负责单板管理、版本在线升级、温度、电源电压等健康检测。
  FPGA内部实现接口处理,包解析处理,对于要记录和加载的数据,经过包解析后会送到核心交换模块,进行存储接口的调配以及和PS的文件系统管理的交互。
  软件驱动方案如下:
在这里插入图片描述

3.2.2 NVMe磁盘驱动设计

  Linux应用层接受相关读写NVMe磁盘指令,通过PCIe硬核驱动将控制命令队列发送给自定义NVMe磁盘驱动,自定义驱动程序根据数据类型不同,然后将队列存放于PS端的DDR中,并通过门铃告知NVMe磁盘。磁盘接收到门铃通知后,去相应地址读取指令并解码,然后执行相关读写流程。
在这里插入图片描述

3.2.3 标准EXT4文件系统设计

  Linux系统应用层接受读写磁盘命令。触发系统调用函数,进程由用户态转换到内核态,文件系统通过目录项检索缓存,如果没有则创建文件。通过虚拟文件系统接口调用具体文件系统读写函数,此处为ext4文件系统。经过文件系统的管理,创建磁盘管理的IO请求,此处IO请求分为,文件系统管理IO请求与原始数据读写请求。此时根据数据类型的不同,如果为原始数据读写请求,则将数据地址路由至系统指定缓存地址即可,否则原地址不变。将修改后的IO请求发送给磁盘驱动,磁盘解码命令,并执行相关IO请求。
  Linux ext4文件系统读写控制流程如下:
在这里插入图片描述

3.3 上位机控制软件设计方案

软件界面参考如图所示:
在这里插入图片描述

4、测试结果

4.1 硬件测试平台说明

使用XILINX的ZYNQ7100作为测试核心板,如下图所示:
在这里插入图片描述
在这里插入图片描述
在这里插入图片描述
在这里插入图片描述
在这里插入图片描述

整体硬件测试平台如下图:
在这里插入图片描述

4.2 测试结果说明

4.2 .1、基于PCIe Gen2 软核,裸机测试

不带文件系统,使用裸跑,PCIe使用两路Gen2 x4 的情况下,写可以达到 2.4GB/s ,读可以达到 2.8GB/s
在这里插入图片描述
在这里插入图片描述

4.2.2基于PCIe Gen3 软核,裸机测试

不带文件系统,使用裸跑,PCIe使用两路Gen3 x4 的情况下,写可以达到 4.2GB/s ,读可以达到 3.5GB/s
在这里插入图片描述
在这里插入图片描述

4.2.3基于PCIe Gen2软核,带ext4文件系统测试

标准的EXT4文件系统,PCIe使用两路Gen2 x4 的情况下,写可以达到 2GB/s ,读可以达到 2.2GB/s
在这里插入图片描述
在这里插入图片描述

5、总结

按照本文方式处理,使用ZYNQ标准的文件系统下可以达到2GB/s的存储带宽。该方案的文件系统采用标准的Linux内核系统,移植性好,成本低,运行也稳定。通过PCIE核的更换,PCIe核的增加,也能够适应不同的存储带宽核存储容量的需求。

文章引用:
https://blog.csdn.net/weixin_42549375/article/details/128168729

更多解决方案,请查看官网:
http://www.levelchip.com/

欢迎各位加入FPGA技术群聊,加群方式添加管理员weixin,请大家遵守群公告一起交流 FPGA相关技术方案
管理人员联系二维码:
请添加图片描述

相关文章:

【存储】ZYNQ+NVMe小型化全国产存储解决方案

文章目录 1、背景2、基础理论3、设计方案3.1、FPGA设计方案3.1.1、NVMe控制器实现3.1.2、NVMe控制器实现 3.2 驱动软件设计方案3.2.1 读写NVMe磁盘软件驱动3.2.2 NVMe磁盘驱动设计3.2.3 标准EXT4文件系统设计 3.3 上位机控制软件设计方案 4、测试结果4.1 硬件测试平台说明4.2 测…...

数据结构之栈详解(C语言手撕)

🎉个人名片: 🐼作者简介:一名乐于分享在学习道路上收获的大二在校生 🙈个人主页🎉:GOTXX 🐼个人WeChat:ILXOXVJE 🐼本文由GOTXX原创,首发CSDN&…...

Docker学习——Dock镜像

什么是Docker镜像 Docker 镜像类似于虚拟机镜像,可以将它理解为一个只读的模板。 一个镜像可以包含一个基本的操作系统环境,里面仅安装了 Apache 应用程序(或 用户需要的其他软件) 可以把它称为一个 Apache 镜像。镜像是创建 Do…...

CorelDRAW Graphics Suite2024专业图形设计软件Windows/Mac最新25.0.0.230版

CorelDRAW Graphics Suite 2024是一款专业的图形设计软件,它集成了CorelDRAW Standard 2024和其他高级图形处理工具,为用户提供了全面的图形设计和编辑解决方案。 该软件拥有强大的矢量编辑功能,用户可以轻松创建和编辑矢量图形,…...

el-form表单中,对非表单内字段增加校验的方法

1、问题说明: 在开发表单的时候,可能会遇到el-form-item中绑定的值不在表单绑定的数据对象中。 此时用prop绑定该字段名是无效的,需要单独对这个字段进行校验。 在el-form-item中有一个属性 error 。用于表单域验证错误信息,设…...

【VTKExamples::Points】第四期 ExtractEnclosedPoints

很高兴在雪易的CSDN遇见你 VTK技术爱好者 QQ:870202403 公众号:VTK忠粉 前言 本文分享VTK样例ExtractEnclosedPoints,并解析接口vtkExtractEnclosedPoints,希望对各位小伙伴有所帮助! 感谢各位小伙伴的点赞+关注,小易会继续努力分享,一起进步! 你的点赞就是我…...

bug--xxoobject has no attribute xxx

Python 创建类的实例后却不能调用写的方法,检查了半天原来是缩进的问题,def函数不应该和class并列 只能说这个英文空格太小了,看不出来。。。。...

7 BUILD.gn文件怎么写,Gn + Ninja编译一个Hello world程序的例子Demo

BUILD.gn文件怎么写,Gn Ninja编译一个Hello world程序的例子Demo 作者将狼才鲸创建日期2024-03-11 Ninja安装流程见:一个能直接运行的Ninja例子,build.ninja文件怎么写?Gn安装流程见:Ubuntu18.04下安装Gn软件 这是一…...

北京市行政村边界shp数据/北京市乡镇边界/北京市土地利用分类数据

北京是一座有着三千多年历史的古都,在不同的朝代有着不同的称谓,大致算起来有二十多个别称。北京地势西北高、东南低。西部、北部和东北部三面环山,东南部是一片缓缓向渤海倾斜的平原。境内流经的主要河流有:永定河、潮白河、北运…...

力扣--动态规划/深度优先算法/回溯算法93.复原IP地址

这题主要用了动态规划和回溯算法。 动态规划数组初始化(DP数组): 首先,创建一个二维数组dp,用于记录字符串中哪些部分是合法的IP地址。对字符串进行遍历,同时考虑每个可能的IP地址部分(每部分由1到3个字符组…...

第一次Python小练习题目

1.打印某学校的校训,具体内容如下所示: ****************************** 勤奋 严谨 求实 创新 ****************************** 注意: 第一行和最后一行各有 30 个*号。 答案: school_strs "勤奋 严谨 求实 创新&q…...

[BUG] docker运行Java程序时配置代理-Dhttp.proxyHost后启动报错

[BUG] docker运行Java程序时配置代理-Dhttp.proxyHost后启动报错 bug现象描述 版本:2.0.4(客户端和服务端都是) 环境:私有云环境,只有少量跳板机器可以访问公网,其他机器均通过配置代理方式访问公网 bug现…...

Python网站的搭建和html基础

1.Python网站代码及讲解 一般我们搭建小型的网站就用flask库就行了。 (1)安装flask库 安装完python后,按住windows徽标键和r,弹出“运行”,在里面输入cmd。 回车打开,输入“pip install flask”。 (2&am…...

SpringCloud(21)之SpringCloud Alibaba Nacos实战应用

一、Nacos安装 1.1 Nacos概述 Nacos是Alibaba微服务生态组件中的重要组件之一,主要用它实现应用的动态服务发现、配置管理、 服务管理。Nacos discovery alibaba/spring-cloud-alibaba Wiki GitHub Nacos 致力于帮助您发现、配置和管理微服务。Nacos 提供了一组简…...

Python 基础语法:基本数据类型(元组)

1 元组(Tuples)概述 1.1 元组的定义与特点 元组(Tuples)是Python中的一个内置数据类型,用于存储一系列有序的元素。元组中的元素可以是任何类型,包括数字、字符串、列表等,且元素之间用逗号…...

vuepress-theme-vdoing博客搭建教程

搭建流程 前言 这是笔者搭建个人博客所经历的流程,特附上笔记 笔者个人博客地址:沉梦听雨的编程指南 一、主题介绍 本博客使用的主题为:vuepress-theme-vdoing,相关介绍和使用方法可以参考该主题的官方文档 官方文档快速上手…...

ICC2:create terminal参考脚本

我正在「拾陆楼」和朋友们讨论有趣的话题,你⼀起来吧? 拾陆楼知识星球入口 set list "" set i 0 ; set length xx set width xx foreach port $list { if {$i == 0} { set startx 0 set starty 0 } else { set sta…...

并行计算CUDA DEMO

//并行计算CUDA DEMO #include "cuda_runtime.h" #include "device_launch_parameters.h" #include <stdio.h> cudaError_t addWithCuda(int *c, const int *a, const int *b, unsigned int size); __global__ void addKernel(int *c, const int …...

【linux线程(一)】什么是线程?怎样操作线程?

&#x1f493;博主CSDN主页:杭电码农-NEO&#x1f493;   ⏩专栏分类:Linux从入门到精通⏪   &#x1f69a;代码仓库:NEO的学习日记&#x1f69a;   &#x1f339;关注我&#x1faf5;带你学更多操作系统知识   &#x1f51d;&#x1f51d; Linux线程 1. 前言2. 什么是线…...

python-0002-linux安装pycharm

下载软件包 下载地址&#xff1a;https://download.csdn.net/download/qq_41833259/88944791 安装 # 解压 tar -zxvf 你的软件包 # 进入软件解压后的路径&#xff0c;如解压到了/home/soft/pycharm cd /home/soft/pycharm cd bin # 执行启动命令 sh pycharm.sh # 等待软件启…...

2026论文降AIGC保姆级指南:从80%降到10%,这5款降ai率工具亲测好用(附去AI味心法)

2026各校对AIGC越来越严格&#xff0c;但其实只要方法对&#xff0c;降下来也没那么难。 为了帮大家降低ai率&#xff0c;我把市面上的十几款主流降AI工具都试了一遍&#xff0c;今天这篇就给大家分享一下&#xff0c;如何在保留正常逻辑的前提下&#xff0c;将AI率降到学校要…...

Sabaki国际化与本地化:打造多语言围棋编辑环境

Sabaki国际化与本地化&#xff1a;打造多语言围棋编辑环境 【免费下载链接】Sabaki An elegant Go board and SGF editor for a more civilized age. 项目地址: https://gitcode.com/gh_mirrors/sa/Sabaki Sabaki是一款优雅的围棋棋盘和SGF编辑器&#xff0c;为全球围棋…...

喔去,litellm 竟然被投毒了,赶紧检查你的机器中招了没有送

一、什么是setuptools&#xff1f; setuptools 是一个用于创建、分发和安装 Python 包的核心库。 它可以帮助你&#xff1a; 定义 Python 包的元数据&#xff08;如名称、版本、作者等&#xff09;。 声明包的依赖项&#xff0c;确保你的包能够正确运行。 构建源代码分发包&…...

HTML函数在老旧浏览器运行慢是硬件问题吗_软硬协同分析【教程】

老旧浏览器HTML操作卡顿主因是渲染与JS引擎陈旧&#xff0c;如IE8不支持CSS3选择器致querySelectorAll遍历DOM&#xff1b;验证需看Performance面板中Recalculate Style/Layout占比超60%&#xff1b;兼容须降级&#xff1a;拆解选择器、用DocumentFragment批量插入、避免强制同…...

Flutter 三方库结合鸿蒙6.0+(API20+)开发实践案例教程

欢迎加入开源鸿蒙跨平台社区&#xff1a;https://openharmonycrossplatform.csdn.net 本文面向鸿蒙新手开发者&#xff0c;结合具体项目案例&#xff0c;详细讲解如何使用 Flutter 开发鸿蒙6.0以上&#xff08;API20及以上&#xff09;应用&#xff0c;并集成常用三方库实现核…...

AI报告审核驱动降本增效:IACheck助力电子电气检测机构优化合规成本结构

在电子电气行业快速发展的背景下&#xff0c;产品更新周期不断缩短&#xff0c;检测认证需求持续增长。无论是消费电子、工业设备&#xff0c;还是智能终端产品&#xff0c;在进入市场之前都需要通过严格的检测与认证流程。而检测报告&#xff0c;作为这一过程的核心输出&#…...

Harness Engineering:Agent工具生态扩展

Harness Engineering:Agent工具生态扩展 1. 引入与连接(唤起兴趣与建立关联) 1.1 引人入胜的开场:从「一次性Agent工具」到「永不落幕的Agent生产流水线」 想象一下这个场景:你是一家互联网金融公司的AI负责人,上周刚上线了一款「智能财报分析Agent」——它能调用行业…...

还在为充气泵电压波动导致MCU复位发愁吗?CSM53系列拥有40V宽压输入配合优秀的瞬态响应,轻松抵御电机启停浪涌,配合2.5μA微功耗,让你的便携充气泵续航提升30%!

CSM53系列LDO在充气泵中的详细应用分析一、先搞懂核心&#xff1a;CSM53系列LDO的关键特性&#xff08;适配充气泵的核心优势&#xff09;在分析应用前&#xff0c;先明确这款芯片的核心参数&#xff0c;这是适配充气泵场景的基础&#xff1a;* 二、充气泵的系统架构与LDO的定位…...

【JavaScript高级编程】拆解函数流水线 上雌

一、什么是setuptools&#xff1f; setuptools 是一个用于创建、分发和安装 Python 包的核心库。 它可以帮助你&#xff1a; 定义 Python 包的元数据&#xff08;如名称、版本、作者等&#xff09;。 声明包的依赖项&#xff0c;确保你的包能够正确运行。 构建源代码分发包&…...

Pebblebee Halo:追踪标签与个人安全的创新融合

兼具追踪与安全的多功能神器Pebblebee Halo 作为 Safe Haven 系列的首款产品&#xff0c;将追踪与个人安全功能完美融合。它不仅是一个传统的追踪标签&#xff0c;兼容 Apple 的 Find My 和 Google 的 Find Hub&#xff0c;能在地图上显示位置&#xff0c;蓝牙追踪范围在理想条…...