• <tr id="yyy80"></tr>
  • <sup id="yyy80"></sup>
  • <tfoot id="yyy80"><noscript id="yyy80"></noscript></tfoot>
  • 99热精品在线国产_美女午夜性视频免费_国产精品国产高清国产av_av欧美777_自拍偷自拍亚洲精品老妇_亚洲熟女精品中文字幕_www日本黄色视频网_国产精品野战在线观看 ?

    CPU-GPU 協(xié)同高性能衛(wèi)星數(shù)傳預(yù)處理方法

    2023-09-06 06:41:34張?chǎng)斡?/span>楊甲森陳志敏
    上海航天 2023年4期
    關(guān)鍵詞:數(shù)傳物理量線程

    張?chǎng)斡?,楊甲森,?聰,陳志敏,智 佳,陳 托

    (1.中國(guó)科學(xué)院國(guó)家空間科學(xué)中心,北京 100190;2.中國(guó)科學(xué)院大學(xué) 計(jì)算機(jī)科學(xué)與技術(shù)學(xué)院,北京 100049)

    0 引言

    數(shù)傳預(yù)處理是地面應(yīng)用系統(tǒng)生產(chǎn)數(shù)據(jù)產(chǎn)品、獲取探測(cè)成果的前提和基礎(chǔ)[1],其處理內(nèi)容包括傳輸幀同步、幀校驗(yàn)、分虛擬信道、源包同步、分應(yīng)用過(guò)程、工程遙測(cè)參數(shù)提取與物理量轉(zhuǎn)換、科學(xué)數(shù)據(jù)解壓縮等。高分辨率、高靈敏度、多頻段覆蓋的載荷探測(cè)趨勢(shì)下,Gbps 級(jí)數(shù)傳預(yù)處理需求日益迫切。

    我國(guó)航天器數(shù)傳大多采用的空間數(shù)據(jù)系統(tǒng)咨詢委員會(huì)(Consultative Committee for Space Data Systems,CCSDS)相關(guān)協(xié)議具有典型的分層特征[2],層間數(shù)據(jù)相互依賴,層內(nèi)不同虛擬信道、應(yīng)用過(guò)程數(shù)據(jù)相對(duì)獨(dú)立。因此,目前國(guó)內(nèi)外學(xué)者大多采用中央處理器(Central Processing Unit,CPU)單機(jī)、集群等同構(gòu)平臺(tái),以虛擬信道、應(yīng)用過(guò)程為任務(wù)劃分依據(jù),并行提高處理性能。包括基于消息傳遞接口(Message-Passing Interface,MPI)[3]、基于MPI+OpenMP[4]在分布式集群上實(shí)現(xiàn)衛(wèi)星遙感數(shù)據(jù)處理;基于Storm 流式計(jì)算框架實(shí)現(xiàn)遙感衛(wèi)星快視處理[5]、空間科學(xué)衛(wèi)星數(shù)據(jù)處理[6-7]。CPU 適用于處理復(fù)雜控制邏輯、較小數(shù)據(jù)規(guī)模問(wèn)題[8],限制了上述方法部分處理步驟性能提升。圖形處理器(Graphics Processing Unit,GPU)以 其TFLOPS 量級(jí)的計(jì)算能力,在信號(hào)處理[9-10]、譯碼[11-12]、遙感圖像處理[13-18]、衛(wèi)星軌道計(jì)算[19-20]等并行程度較大的數(shù)據(jù)密集型領(lǐng)域應(yīng)用中取得了良好的加速效果。

    本文面向高性能數(shù)傳預(yù)處理需求,在分析處理性能瓶頸的基礎(chǔ)上,針對(duì)預(yù)處理步驟層間依賴、各虛擬信道保序并行的特點(diǎn),提出一種層間流程CPU控制、層內(nèi)瓶頸步驟GPU 加速的協(xié)同處理新方法。對(duì)數(shù)傳數(shù)據(jù)預(yù)處理的CPU-GPU 協(xié)同任務(wù)劃分、GPU 線程分配進(jìn)行設(shè)計(jì),實(shí)現(xiàn)基于GPU 的幀校驗(yàn)、工程參數(shù)提取與物理量轉(zhuǎn)換的加速,為數(shù)傳預(yù)處理性能的提升提供一種新的解決途徑。

    1 數(shù)傳數(shù)據(jù)預(yù)處理分析

    1.1 數(shù)傳預(yù)處理內(nèi)容說(shuō)明

    如圖1 所示,在地面接收分系統(tǒng)完成譯碼后,數(shù)傳預(yù)處理完成高級(jí)在軌系統(tǒng)(Advanced Orbiting Systems,AOS)幀處理、源包處理,將結(jié)果分發(fā)至后續(xù)環(huán)節(jié)。涉及到CCSDS 協(xié)議包括空間包協(xié)議[21]、AOS 空間數(shù)據(jù)鏈路協(xié)議[22]、遙測(cè)同步和信道編碼協(xié)議[23]等,其中AOS 傳輸幀、空間包結(jié)構(gòu)見表1和表2。

    表1 AOS 傳輸幀格式Tab.1 AOS transfer frame format

    表2 空間包結(jié)構(gòu)Tab.2 Structural components of the space packet

    圖1 地面端數(shù)據(jù)處理的一般過(guò)程Fig.1 General process of ground data processing

    1.2 性能處理瓶頸及可并行性分析

    利用文件回放模擬數(shù)據(jù)輸入,測(cè)試CPU 單線程模式下預(yù)處理各操作速率見表3。

    表3 CPU 單線程熱點(diǎn)測(cè)試Tab.3 Hotpot test of the CPU single-threaded program

    其中幀校驗(yàn)和參數(shù)提取與物理量轉(zhuǎn)換計(jì)算量大,是處理瓶頸且可并行性高,作為本文主要研究對(duì)象。

    基于CCSDS 協(xié)議的分層模型和多路復(fù)用機(jī)制,預(yù)處理過(guò)程中數(shù)據(jù)結(jié)構(gòu)變化如圖2 所示。處理存在如下特點(diǎn):

    1)分層模型使各層數(shù)據(jù)的處理可任務(wù)并行;

    2)上層協(xié)議數(shù)據(jù)處理依賴下層輸出,不同層級(jí)數(shù)據(jù)間存在關(guān)聯(lián);

    3)多路復(fù)用機(jī)制使同一物理信道中分屬不同虛擬信道數(shù)據(jù)幀間、同一虛擬信道分屬不同應(yīng)用過(guò)程的源包間無(wú)依賴關(guān)系,可完全并行;

    4)存在保序約束,須保持各虛擬信道、各應(yīng)用過(guò)程內(nèi)數(shù)據(jù)的順序,發(fā)揮計(jì)數(shù)字段檢測(cè)數(shù)據(jù)丟失、重復(fù)、失序的作用,可保證源包及應(yīng)用過(guò)程數(shù)據(jù)正確拼接。

    2 CPU-GPU協(xié)同數(shù)傳數(shù)據(jù)預(yù)處理方法

    依據(jù)預(yù)處理步驟層間依賴、各虛擬信道保序并行的特點(diǎn),設(shè)計(jì)AOS 幀、源包處理步驟的CPU、GPU任務(wù)分劃,并基于GPU 統(tǒng)一計(jì)算設(shè)備架構(gòu)(Compute Unified Device Architecture,CUDA),實(shí)現(xiàn)幀校驗(yàn)、工程參數(shù)提取與物理量轉(zhuǎn)換步驟的加速。

    2.1 CPU-GPU 協(xié)同任務(wù)劃分

    GPU 含有上千個(gè)CUDA 核心,一次可支持幾萬(wàn)個(gè)線程并發(fā)。GPU 的寄存器帶寬為TB·s-1量級(jí),遠(yuǎn)高于GB·s-1量級(jí)的GPU 顯存帶寬。CPU 與GPU間傳輸數(shù)據(jù)的高速串行計(jì)算機(jī)擴(kuò)展總線(Peripheral Component Interconnect Express,PCIe)帶寬遠(yuǎn)又小于GPU 顯存帶寬。因此使用GPU 獲得良好加速效果,CPU、GPU 任務(wù)分劃要遵循以下原則[24]:

    1)增大核函數(shù)并行規(guī)模,避免核心空閑;

    2)提高GPU 中核函數(shù)算數(shù)強(qiáng)度,降低GPU 內(nèi)存讀寫占比;

    3)降低CPU-GPU 間數(shù)據(jù)傳輸量。

    2.1.1 AOS 幀處理流程設(shè)計(jì)

    分路分包前碼速率較高,而幀校驗(yàn)又為計(jì)算量較大的瓶頸步驟;各AOS 幀獨(dú)立校驗(yàn),幀間無(wú)依賴關(guān)系;高碼速率同時(shí)降低了等待數(shù)據(jù)積累到較大規(guī)模供GPU 處理的時(shí)延,基于上述考慮,如圖3 所示,設(shè)計(jì)GPU 加速幀校驗(yàn)與解析。使用CPU 對(duì)解擾后的碼流數(shù)據(jù)同步,得到AOS 幀寫入幀緩存,經(jīng)過(guò)PCIe 總線傳輸至GPU 全局內(nèi)存。GPU 處理完畢后不再向CPU 端傳回完整AOS 幀,而是傳回8 bit/幀的后續(xù)處理必須信息,數(shù)據(jù)傳輸量降低99.1%。傳回信息包括:幀格式符合性、VCID、虛擬信道幀計(jì)數(shù)、數(shù)據(jù)域有效數(shù)據(jù)結(jié)束地址。CPU 端異常幀報(bào)警器在檢測(cè)到幀格式不符合時(shí),重新解析該幀,生成異常幀報(bào)告;幀數(shù)據(jù)域提取處理器提取數(shù)據(jù),按VCID 寫入各源包碼流數(shù)據(jù)環(huán)形隊(duì)列存儲(chǔ)器,同步處理后得到源包(空間包)。

    圖3 CPU-GPU 協(xié)同的AOS 幀處理流程Fig.3 Processing flow of AOS frame parsing based on the CPU-GPU collaboration

    2.1.2 源包處理流程設(shè)計(jì)

    源包按裝載的數(shù)據(jù)類型,可分為業(yè)務(wù)數(shù)據(jù)源包、遙測(cè)參數(shù)源包、工程參數(shù)源包。空間科學(xué)衛(wèi)星的科學(xué)數(shù)據(jù)、遙感衛(wèi)星的圖像數(shù)據(jù)等業(yè)務(wù)數(shù)據(jù),數(shù)據(jù)量大、處理方法復(fù)雜、不同業(yè)務(wù)處理差異大。遙測(cè)數(shù)據(jù)是與航天器工作狀態(tài)有關(guān)的測(cè)量數(shù)據(jù)(如電壓、電流、溫度、壓力等),反映航天器的工作過(guò)程、工作結(jié)果和健康狀態(tài)[25],實(shí)時(shí)性要求高,數(shù)據(jù)量較小。工程參數(shù)主要是有效載荷的工作狀態(tài)數(shù)據(jù),相比遙測(cè)參數(shù),種類更多、數(shù)據(jù)量更大。

    根據(jù)不同類型的源包特點(diǎn),設(shè)計(jì)源包處理任務(wù)流程如圖4 所示。CPU 解析源包后生成異常源包報(bào)告,根據(jù)APID 將格式符合的源包寫入相應(yīng)的環(huán)形隊(duì)列存儲(chǔ)器。業(yè)務(wù)數(shù)據(jù)在預(yù)處理階段只做拼接處理,由CPU 完成。參數(shù)配置信息處理器讀取含有參數(shù)位置、源數(shù)據(jù)長(zhǎng)度、物理量轉(zhuǎn)換方法的配置文件,計(jì)算掩碼,在程序啟動(dòng)時(shí)向GPU 全局內(nèi)存?zhèn)鬏斠淮?。遙測(cè)參數(shù)數(shù)據(jù)量較小,為降低時(shí)延,由CPU完成提取與物理量轉(zhuǎn)換。工程參數(shù)由GPU 完成提取與物理量轉(zhuǎn)換。

    圖4 CPU-GPU 協(xié)同的源包處理流程Fig.4 Processing flow of space packet parsing based on the CPU-GPU collaboration

    2.2 基于GPU 的并行加速實(shí)現(xiàn)

    2.2.1 幀校驗(yàn)的CUDA 加速

    AOS 協(xié)議的差錯(cuò)控制使用生成多項(xiàng)式為C(x)=x16+x12+x5+1 的CRC 校 驗(yàn),CRC 校 驗(yàn)的基本思想是接收端的數(shù)據(jù)無(wú)誤碼則能被給定的生成多項(xiàng)式C(x)整除。CRC 校驗(yàn)以幀為基本單位,各幀之間不影響,設(shè)計(jì)每個(gè)GPU 線程校驗(yàn)一幀。從主機(jī)端緩存每次讀取N個(gè)長(zhǎng)度均為L(zhǎng)字節(jié)的AOS 幀至GPU 全局內(nèi)存中線性存儲(chǔ)。將網(wǎng)格內(nèi)的線程塊和線程塊內(nèi)的線程均組織成一維,線程塊數(shù)量為Nb;每個(gè)網(wǎng)格中線程數(shù)量Ng為

    每個(gè)線程在核函數(shù)中的唯一身份標(biāo)識(shí)idx為

    式 中:Tx∈[0,Db-1]為各線程在其線程塊中的索引。

    第idx個(gè)線程處理第i個(gè)傳輸幀,該幀的數(shù)據(jù)在全局內(nèi)存地址為:[idx?L,(idx+1)?L-1],每個(gè)線程完成校驗(yàn)后,解析幀主導(dǎo)頭各字段,提取所需信息寫入幀解析結(jié)果結(jié)構(gòu)體。所有線程計(jì)算完畢,使用cudaMemcpy()函數(shù)將幀解析結(jié)果結(jié)構(gòu)體數(shù)組傳輸至CPU 端內(nèi)存。

    2.2.2 工程參數(shù)提取與物理量轉(zhuǎn)換的CUDA 加速

    參數(shù)在源包中以二進(jìn)制信號(hào)形式存在,需要將參數(shù)提取、編碼、轉(zhuǎn)換后,才能直觀地用于載荷狀態(tài)監(jiān)視、參數(shù)判讀等任務(wù),可分為以下3 個(gè)步驟:

    步驟一參數(shù)提取。提取源包數(shù)據(jù)域碼流中各參數(shù)的二進(jìn)制信號(hào)源碼。

    參數(shù)位置由參數(shù)開始的字節(jié)地址Ab、開始字節(jié)的位地址Ab、比特長(zhǎng)度Lb唯一確定。某參數(shù)在源包中所占字節(jié)長(zhǎng)度Lb為

    將幀中第Ab至Ab+Lb-1 字節(jié)數(shù)據(jù)與位掩碼做按位與運(yùn)算并位移后得到參數(shù)源碼。

    步驟二參數(shù)編碼。將各參數(shù)的二進(jìn)制信號(hào)源碼編碼為實(shí)際數(shù)字或字符串。

    步驟三物理量轉(zhuǎn)換。參數(shù)經(jīng)某種方法的運(yùn)算后,轉(zhuǎn)換為直觀表達(dá)真實(shí)物理含義的值。常用的物理量轉(zhuǎn)換方法有源碼顯示、進(jìn)制轉(zhuǎn)換、含義映射、多項(xiàng)式變換、熱敏電阻分壓值轉(zhuǎn)換為溫度等。

    從CPU 端緩存每次讀取特定種類長(zhǎng)度為L(zhǎng)字節(jié),含M個(gè)參數(shù)的工程參數(shù)源包N個(gè),每個(gè)參數(shù)的處理結(jié)果使用R字節(jié)保存。將網(wǎng)格內(nèi)的線程塊和線程塊內(nèi)的線程均組織成一維,線程塊數(shù)量為Nb。設(shè)計(jì)了每個(gè)線程處理一個(gè)參數(shù)、每個(gè)線程處理一個(gè)源包2 種線程分配方案,通過(guò)實(shí)驗(yàn)分析2 種方案的特性。

    方案一每個(gè)線程處理一個(gè)參數(shù)。

    每個(gè)網(wǎng)格中x方向線程數(shù)量Ng為

    第idx個(gè)線程處理第個(gè)源包的第(idx%M)個(gè)參數(shù),將結(jié)果寫入GPU 全局內(nèi)存,內(nèi)存地址為[idx*R,(idx+1)*R-1]。

    方案二每個(gè)線程處理一個(gè)源包。

    每個(gè)網(wǎng)格中x方向線程數(shù)量Ng計(jì)算方法與公式(1)相同,第idx個(gè)線程處理第idx個(gè)源包的所有參數(shù),將結(jié)果寫入GPU 全局內(nèi)存,內(nèi)存地址為[idx*M*R,(idx+1)*M*R-1]。

    2.2.3 基于CUDA 流并發(fā)執(zhí)行核函數(shù)和數(shù)據(jù)傳輸

    CUDA 流是從主機(jī)發(fā)出在GPU 中執(zhí)行的一系列異步CUDA 操作,不同CUDA 流中的操作可能并發(fā)或交錯(cuò)執(zhí)行[14]。由于數(shù)據(jù)傳輸、計(jì)算分別通過(guò)GPU 的讀寫單元和流處理器進(jìn)行,如圖5 所示,主機(jī)向一個(gè)流發(fā)出數(shù)據(jù)傳輸命令后可立即獲得控制權(quán),到另一個(gè)流調(diào)用核函數(shù),從而重疊數(shù)據(jù)傳輸與核函數(shù)執(zhí)行[15]。在CUDA 操作完全并行執(zhí)行的理想情況下,數(shù)據(jù)傳輸時(shí)間可完全隱藏,隨著流數(shù)量增加,加速比趨近3。

    圖5 CUDA 流并發(fā)示意Fig.5 CUDA stream concurrency

    CUDA 流實(shí)現(xiàn)異步數(shù)據(jù)傳輸,需要在程序運(yùn)行期間將主機(jī)端數(shù)據(jù)緩存定義為不可分頁(yè)內(nèi)存,保持內(nèi)存物理地址不變。設(shè)創(chuàng)建NS個(gè)CUDA 流,將每次從緩存中讀取的N個(gè)AOS 幀或源包劃分NS個(gè)子集,平均分配到各個(gè)流中,使用cudaMemcpyAsync()函數(shù)異步傳輸數(shù)據(jù),使用循環(huán)調(diào)度各個(gè)流的數(shù)據(jù)傳輸和計(jì)算。

    3 實(shí)驗(yàn)驗(yàn)證與分析

    3.1 實(shí)驗(yàn)環(huán)境

    CPU 使用AMD Ryzen 5 2600X,基頻3.6 GHz。GPU 使用NVIDIA GeForce RTX 2080ti,顯卡為 圖靈架構(gòu),有68 個(gè)流多處理器,4 352 個(gè)CUDA 核心,11 GB GDDR6 顯存,顯存帶寬616 GB·s-1,單精度浮點(diǎn)數(shù)運(yùn)算峰值13TFLOPS,CUDA 版本10.1。CPU 與GPU 之間使用PCIe3.0 x16 總線連接,理 論帶寬15.754 GB·s-1。內(nèi)存使用48GB DDR4 雙通道內(nèi)存。硬盤使用512 GB NVMe 固態(tài)硬盤。

    由于不同型號(hào)CPU 物理核心數(shù)的差距,實(shí)踐中評(píng)價(jià)加速效果常使用CPU 單核與GPU 比較[9]。

    3.2 幀校驗(yàn)實(shí)驗(yàn)結(jié)果與分析

    傳輸幀幀長(zhǎng)898 字節(jié),前4 字節(jié)為同步碼,幀差錯(cuò)控制域2 字節(jié)。Nb設(shè)為256。如圖6 所示,使用單個(gè)CUDA 流,一次處理215個(gè)幀時(shí)達(dá)到最高處理速 率8.053 6 GB·s-1,加速比38.003;使 用16 個(gè)CUDA 流,一次處理219個(gè)幀時(shí)達(dá)到最高處理速率11.449 6 GB·s-1,加速比53.866。CPU 單線程方式,最高處理速率0.214 7 GB·s-1,串行計(jì)算性能基本與幀數(shù)量無(wú)關(guān)。

    圖6 速率隨AOS 幀個(gè)數(shù)的變化-CRCFig.6 Variation of the processing speed with the AOS frame number-CRC

    如圖7 所示,一次處理的幀數(shù)量少時(shí),GPU 沒(méi)有滿負(fù)荷工作,有空閑的計(jì)算資源,增加一次處理的幀數(shù)量,GPU 核函數(shù)耗時(shí)基本不變;當(dāng)一次處理的幀個(gè)數(shù)較大時(shí),GPU 滿負(fù)荷工作,GPU 核函數(shù)的耗時(shí)正比于一次處理的幀個(gè)數(shù)??筛鶕?jù)不同GPU性能,配置單次計(jì)算規(guī)模,達(dá)到最佳性能。

    圖7 GPU 核函數(shù)計(jì)算與數(shù)據(jù)傳輸耗時(shí)-CRCFig.7 Time of the kernel function and data transmission by GPU-CRC

    3.3 工程參數(shù)提取與物理量轉(zhuǎn)換實(shí)驗(yàn)結(jié)果與分析

    工程參數(shù)源包包長(zhǎng)390 字節(jié),含467 個(gè)參數(shù),每個(gè)參數(shù)轉(zhuǎn)換結(jié)果8 字節(jié)保存。Nb設(shè)為256。如圖8所 示,CPU 最高速 率0.004 4 GB·s-1。使用單 個(gè)CUDA 流,最高速率0.506 GB·s-1,加速比115.98;使用16 個(gè)CUDA 流,最高速率可達(dá)0.902 4 GB·s-1,加速比211.021。

    圖8 速率隨源包個(gè)數(shù)的變化Fig.8 Variation of the processing speed with the packet number

    如圖9 和圖10 所示,一次處理的源包個(gè)數(shù)小于215時(shí),每個(gè)線程處理一個(gè)源包的方案并行規(guī)模較小,速率比每個(gè)線程處理一個(gè)參數(shù)的方案低;源包個(gè)數(shù)大于215時(shí),兩方案均能使GPU 滿負(fù)荷工作,每個(gè)線程處理一個(gè)源包的算數(shù)強(qiáng)度更大,速率更高。在實(shí)際應(yīng)用中,可根據(jù)數(shù)據(jù)的時(shí)延性要求,配置一次處理的源包個(gè)數(shù),進(jìn)而確定線程分配方案。

    圖10 GPU 核函數(shù)計(jì)算與數(shù)據(jù)傳輸耗時(shí)-1 線程處理1 參數(shù)Fig.10 Time of the kernel function and data transmission by GPU-1 parameter for 1 thread

    4 結(jié)束語(yǔ)

    數(shù)傳數(shù)據(jù)預(yù)處理是衛(wèi)星數(shù)據(jù)處理的前置必須環(huán)節(jié),本文提出的CPU-GPU 協(xié)同的衛(wèi)星數(shù)傳數(shù)據(jù)預(yù)處理方法,利用GPU 并行計(jì)算加速處理過(guò)程的幀校驗(yàn)、參數(shù)提取與物理量轉(zhuǎn)換等耗時(shí)瓶頸步驟,實(shí)驗(yàn)結(jié)果表明,該方法可滿足Gbps 的衛(wèi)星數(shù)傳數(shù)據(jù)預(yù)處理需求。后續(xù)可開展的工作如下。

    1)增加處理深度,引入基于GPU 的數(shù)據(jù)解壓縮、科學(xué)數(shù)據(jù)快視、數(shù)據(jù)判讀,進(jìn)一步加速數(shù)據(jù)處理過(guò)程。

    2)研究適用于數(shù)傳數(shù)據(jù)處理的多CPU、多GPU 場(chǎng)景中有硬件和任務(wù)優(yōu)先級(jí)約束下的多目標(biāo)優(yōu)化調(diào)度算法。

    猜你喜歡
    數(shù)傳物理量線程
    基于數(shù)傳電臺(tái)的靶彈測(cè)控系統(tǒng)設(shè)計(jì)
    嫦娥衛(wèi)星數(shù)傳副瓣信號(hào)的干涉測(cè)量研究與精度驗(yàn)證
    載人航天(2019年1期)2019-03-07 01:41:02
    巧用求差法判斷電路中物理量大小
    淺談linux多線程協(xié)作
    電場(chǎng)中六個(gè)常見物理量的大小比較
    誰(shuí)、啥、怎樣、為什么——對(duì)幾個(gè)物理量的分析與綜合
    高速數(shù)傳電纜散射參數(shù)的測(cè)試及半實(shí)物仿真的分析與研究
    電子器件(2015年5期)2015-12-29 08:43:30
    頻率偏置對(duì)Ka頻段圓極化頻率復(fù)用數(shù)傳鏈路的影響
    航天器工程(2014年5期)2014-03-11 16:35:56
    關(guān)于圓盤狀物體的幾個(gè)物理量的計(jì)算
    物理與工程(2014年5期)2014-02-27 11:23:16
    Linux線程實(shí)現(xiàn)技術(shù)研究
    在线观看66精品国产| 成人av在线播放网站| 嫁个100分男人电影在线观看| av女优亚洲男人天堂| 很黄的视频免费| 欧美高清性xxxxhd video| 免费看日本二区| 校园春色视频在线观看| 日日摸夜夜添夜夜添小说| 亚洲欧美日韩东京热| 九九在线视频观看精品| 精品久久久久久久久亚洲 | 毛片女人毛片| 亚洲一区二区三区色噜噜| 丰满的人妻完整版| 18禁在线播放成人免费| av女优亚洲男人天堂| 精品久久久久久成人av| 中文字幕av在线有码专区| 色综合色国产| 亚洲成人久久性| 精品人妻1区二区| 男人舔女人下体高潮全视频| 一级毛片久久久久久久久女| 国产成人av教育| 中文字幕免费在线视频6| 欧美最黄视频在线播放免费| 久久香蕉精品热| 波多野结衣高清无吗| 亚洲美女视频黄频| 亚洲无线在线观看| 男人和女人高潮做爰伦理| 极品教师在线视频| 搡老熟女国产l中国老女人| 国产精品亚洲一级av第二区| eeuss影院久久| 国产高清视频在线观看网站| 俺也久久电影网| 精品日产1卡2卡| 国产精品电影一区二区三区| 少妇高潮的动态图| 国产高清视频在线播放一区| 国产91精品成人一区二区三区| 国产精品爽爽va在线观看网站| 午夜免费激情av| 欧美3d第一页| 久久久精品大字幕| 国产老妇女一区| av中文乱码字幕在线| 在线免费观看的www视频| 亚洲七黄色美女视频| www.www免费av| 美女cb高潮喷水在线观看| 久久草成人影院| 窝窝影院91人妻| 成年版毛片免费区| 一级a爱片免费观看的视频| 哪里可以看免费的av片| 桃红色精品国产亚洲av| 精品欧美国产一区二区三| 91精品国产九色| 成人亚洲精品av一区二区| 赤兔流量卡办理| 精品不卡国产一区二区三区| avwww免费| 中文字幕熟女人妻在线| 午夜爱爱视频在线播放| 国产色婷婷99| 日本-黄色视频高清免费观看| 一级a爱片免费观看的视频| 国产一区二区激情短视频| 国产精品久久视频播放| 无人区码免费观看不卡| 成人欧美大片| 国产爱豆传媒在线观看| 国产精品一区二区三区四区久久| 午夜免费激情av| 国产精品久久电影中文字幕| 欧美精品啪啪一区二区三区| 国产精品无大码| 精品乱码久久久久久99久播| 欧美黑人巨大hd| 成年免费大片在线观看| 韩国av一区二区三区四区| 国产精品一区二区性色av| 日韩欧美一区二区三区在线观看| 校园人妻丝袜中文字幕| 简卡轻食公司| 黄色欧美视频在线观看| 午夜福利在线观看免费完整高清在 | 欧美一区二区国产精品久久精品| 嫁个100分男人电影在线观看| 人妻久久中文字幕网| 波多野结衣巨乳人妻| 午夜福利在线观看免费完整高清在 | 国产精品美女特级片免费视频播放器| 啦啦啦观看免费观看视频高清| 国产精品1区2区在线观看.| 午夜福利18| 成人国产麻豆网| 哪里可以看免费的av片| 亚洲av熟女| xxxwww97欧美| 在线观看舔阴道视频| 我的老师免费观看完整版| 国产蜜桃级精品一区二区三区| 国产黄色小视频在线观看| 精品人妻熟女av久视频| 国产在线男女| 亚洲精品亚洲一区二区| 色哟哟·www| 亚洲欧美清纯卡通| 国内久久婷婷六月综合欲色啪| 国产探花极品一区二区| 成人三级黄色视频| 狂野欧美激情性xxxx在线观看| 最近在线观看免费完整版| 午夜福利在线观看吧| 国产69精品久久久久777片| 99精品在免费线老司机午夜| 中文亚洲av片在线观看爽| 亚洲av五月六月丁香网| 国内揄拍国产精品人妻在线| 久久午夜福利片| 国产精品久久久久久久久免| 国内精品一区二区在线观看| 91av网一区二区| 免费高清视频大片| 国产精品精品国产色婷婷| 久久久久久久久中文| 人妻夜夜爽99麻豆av| 久久久久久久久久黄片| 一边摸一边抽搐一进一小说| 级片在线观看| 亚洲中文字幕一区二区三区有码在线看| 国产伦精品一区二区三区视频9| 一夜夜www| 热99re8久久精品国产| 精品久久久久久成人av| 日韩,欧美,国产一区二区三区 | 精品午夜福利在线看| 中亚洲国语对白在线视频| 蜜桃久久精品国产亚洲av| 尾随美女入室| 国产一区二区在线观看日韩| 性插视频无遮挡在线免费观看| 国产视频内射| 日韩,欧美,国产一区二区三区 | 色吧在线观看| 亚洲va在线va天堂va国产| 直男gayav资源| 久久久久国产精品人妻aⅴ院| 无遮挡黄片免费观看| 我要看日韩黄色一级片| 免费看av在线观看网站| 两性午夜刺激爽爽歪歪视频在线观看| 色噜噜av男人的天堂激情| 69人妻影院| 干丝袜人妻中文字幕| 国产aⅴ精品一区二区三区波| 网址你懂的国产日韩在线| 3wmmmm亚洲av在线观看| 日韩欧美精品免费久久| 成人美女网站在线观看视频| 国产探花极品一区二区| 日韩欧美一区二区三区在线观看| 亚洲黑人精品在线| 日本一本二区三区精品| 色哟哟哟哟哟哟| 波多野结衣高清作品| 日本一二三区视频观看| 亚洲三级黄色毛片| 中文字幕av成人在线电影| 亚洲国产欧美人成| 成年人黄色毛片网站| 亚洲一区高清亚洲精品| 国产黄片美女视频| 亚州av有码| 禁无遮挡网站| 国产精品野战在线观看| 日本免费一区二区三区高清不卡| 亚洲av一区综合| 如何舔出高潮| 人妻制服诱惑在线中文字幕| 两个人的视频大全免费| a级毛片a级免费在线| 午夜激情欧美在线| 国产成人一区二区在线| av国产免费在线观看| 69人妻影院| 亚洲欧美精品综合久久99| 日韩国内少妇激情av| 欧美bdsm另类| 嫁个100分男人电影在线观看| 亚洲欧美日韩高清在线视频| 又粗又爽又猛毛片免费看| 91久久精品国产一区二区三区| 村上凉子中文字幕在线| 少妇裸体淫交视频免费看高清| 成人鲁丝片一二三区免费| 亚洲无线观看免费| 精品人妻1区二区| 亚洲七黄色美女视频| 九九爱精品视频在线观看| 欧美日韩综合久久久久久 | 久久久久久久精品吃奶| 国产综合懂色| 91午夜精品亚洲一区二区三区 | 真人一进一出gif抽搐免费| 色视频www国产| 欧美人与善性xxx| 久久欧美精品欧美久久欧美| 国产精品自产拍在线观看55亚洲| 亚洲欧美精品综合久久99| 免费无遮挡裸体视频| 免费av毛片视频| 最后的刺客免费高清国语| 国产 一区 欧美 日韩| 全区人妻精品视频| 床上黄色一级片| 成人性生交大片免费视频hd| 午夜视频国产福利| 18禁黄网站禁片免费观看直播| 天美传媒精品一区二区| 亚洲av电影不卡..在线观看| 中文亚洲av片在线观看爽| 床上黄色一级片| 韩国av在线不卡| 亚洲成av人片在线播放无| 亚洲成人精品中文字幕电影| 亚洲五月天丁香| 国产色爽女视频免费观看| 天天一区二区日本电影三级| 免费不卡的大黄色大毛片视频在线观看 | 如何舔出高潮| 夜夜看夜夜爽夜夜摸| 国产精品一区二区三区四区久久| 欧美中文日本在线观看视频| 欧美不卡视频在线免费观看| 99久久中文字幕三级久久日本| 美女cb高潮喷水在线观看| a级一级毛片免费在线观看| 欧美又色又爽又黄视频| 国产伦人伦偷精品视频| 欧美高清性xxxxhd video| 国产精品亚洲美女久久久| 男人舔女人下体高潮全视频| 亚洲五月天丁香| 中文字幕免费在线视频6| 色综合婷婷激情| 欧美日韩黄片免| 国国产精品蜜臀av免费| 成人鲁丝片一二三区免费| 天堂av国产一区二区熟女人妻| 男人舔奶头视频| 长腿黑丝高跟| 国产精品久久久久久久久免| 熟女电影av网| 丰满乱子伦码专区| 一级av片app| 99精品在免费线老司机午夜| 色在线成人网| 久久久色成人| 天天一区二区日本电影三级| 欧美精品国产亚洲| 性欧美人与动物交配| 精品不卡国产一区二区三区| 亚洲性夜色夜夜综合| 亚洲成人久久爱视频| 日本熟妇午夜| 久久久久久久久久黄片| 欧美xxxx性猛交bbbb| 特级一级黄色大片| 国产午夜精品久久久久久一区二区三区 | 99热这里只有精品一区| 日本-黄色视频高清免费观看| 久久久精品欧美日韩精品| 亚洲不卡免费看| 三级国产精品欧美在线观看| 在线观看美女被高潮喷水网站| 日韩欧美在线二视频| 国内精品美女久久久久久| 丰满人妻一区二区三区视频av| 熟女人妻精品中文字幕| 日韩,欧美,国产一区二区三区 | 女人十人毛片免费观看3o分钟| 99久久成人亚洲精品观看| 成人av一区二区三区在线看| 成人午夜高清在线视频| 亚洲图色成人| 99国产极品粉嫩在线观看| 亚洲自偷自拍三级| 一卡2卡三卡四卡精品乱码亚洲| 国产午夜福利久久久久久| 亚洲性夜色夜夜综合| 狂野欧美白嫩少妇大欣赏| 人妻制服诱惑在线中文字幕| 九色成人免费人妻av| 成人鲁丝片一二三区免费| 九九在线视频观看精品| 99在线人妻在线中文字幕| 久久草成人影院| 午夜福利在线观看免费完整高清在 | 精品人妻熟女av久视频| 三级男女做爰猛烈吃奶摸视频| 我的女老师完整版在线观看| 久久精品国产亚洲网站| h日本视频在线播放| 亚洲av日韩精品久久久久久密| 精品99又大又爽又粗少妇毛片 | www.www免费av| 中文字幕高清在线视频| www.色视频.com| 观看美女的网站| 乱码一卡2卡4卡精品| 91午夜精品亚洲一区二区三区 | 欧美区成人在线视频| 丝袜美腿在线中文| 成人高潮视频无遮挡免费网站| 狂野欧美激情性xxxx在线观看| 成人一区二区视频在线观看| 久久精品影院6| 乱码一卡2卡4卡精品| 国产精品av视频在线免费观看| 性欧美人与动物交配| av在线观看视频网站免费| 欧美xxxx性猛交bbbb| 悠悠久久av| 一本久久中文字幕| 日本-黄色视频高清免费观看| 日韩欧美精品免费久久| 亚洲国产日韩欧美精品在线观看| 美女高潮喷水抽搐中文字幕| 好男人在线观看高清免费视频| 天天一区二区日本电影三级| 亚洲最大成人av| 久久精品国产鲁丝片午夜精品 | 五月玫瑰六月丁香| 成人二区视频| 波多野结衣高清无吗| 制服丝袜大香蕉在线| 精品久久久久久久久久免费视频| 亚洲精品日韩av片在线观看| 日本欧美国产在线视频| 成人高潮视频无遮挡免费网站| avwww免费| 能在线免费观看的黄片| 国产黄片美女视频| 日本免费a在线| 精品久久久久久久久久免费视频| 草草在线视频免费看| 日韩 亚洲 欧美在线| 免费av不卡在线播放| 亚洲国产欧美人成| 精品久久久久久久久久免费视频| 久久精品国产自在天天线| 国产精品一区www在线观看 | 男女边吃奶边做爰视频| 国产在视频线在精品| 婷婷精品国产亚洲av在线| 最后的刺客免费高清国语| 欧美+日韩+精品| 国产成年人精品一区二区| 麻豆av噜噜一区二区三区| 国产免费一级a男人的天堂| 一区二区三区四区激情视频 | 91久久精品国产一区二区三区| 高清在线国产一区| 五月伊人婷婷丁香| 久99久视频精品免费| 精品不卡国产一区二区三区| 嫩草影院新地址| 大又大粗又爽又黄少妇毛片口| 一区福利在线观看| 麻豆精品久久久久久蜜桃| 黄色日韩在线| 亚洲性夜色夜夜综合| 精品久久久噜噜| 一a级毛片在线观看| 精品无人区乱码1区二区| 亚洲第一区二区三区不卡| 一区二区三区四区激情视频 | 国产成年人精品一区二区| 精品久久久久久成人av| av在线观看视频网站免费| 国内精品宾馆在线| 熟女电影av网| 一夜夜www| 看黄色毛片网站| 一级a爱片免费观看的视频| 久久久午夜欧美精品| 天美传媒精品一区二区| 成人一区二区视频在线观看| 一进一出好大好爽视频| 久久久久性生活片| 国产三级中文精品| 日韩亚洲欧美综合| 成年女人看的毛片在线观看| 亚洲黑人精品在线| 国产伦在线观看视频一区| 十八禁网站免费在线| 99热这里只有精品一区| 久久人人精品亚洲av| 亚洲四区av| 99久久九九国产精品国产免费| 九九热线精品视视频播放| 又爽又黄无遮挡网站| 欧美精品啪啪一区二区三区| 国内毛片毛片毛片毛片毛片| 18+在线观看网站| 麻豆国产97在线/欧美| 久久精品国产亚洲av天美| 亚洲精品成人久久久久久| 国产麻豆成人av免费视频| 在线观看66精品国产| 一个人免费在线观看电影| 日韩一区二区视频免费看| 日日撸夜夜添| 亚洲av免费高清在线观看| 一个人看的www免费观看视频| 99九九线精品视频在线观看视频| 国内精品久久久久精免费| 亚洲美女视频黄频| 中文字幕免费在线视频6| 欧美+亚洲+日韩+国产| 国产亚洲av嫩草精品影院| 成人国产综合亚洲| 校园人妻丝袜中文字幕| 看黄色毛片网站| 国产av不卡久久| 国产 一区 欧美 日韩| 日本 av在线| 三级毛片av免费| 欧美三级亚洲精品| 日韩av在线大香蕉| 日韩欧美在线乱码| 国产一区二区三区在线臀色熟女| 中文字幕久久专区| eeuss影院久久| 国产69精品久久久久777片| 亚洲精品亚洲一区二区| bbb黄色大片| 国产精品1区2区在线观看.| 日日干狠狠操夜夜爽| 特级一级黄色大片| 嫩草影院新地址| av在线亚洲专区| 亚洲无线在线观看| 久久人妻av系列| 国产免费av片在线观看野外av| 国产精品久久电影中文字幕| eeuss影院久久| 国产精品伦人一区二区| 国产午夜精品久久久久久一区二区三区 | 国产色爽女视频免费观看| 99久久精品热视频| 人妻夜夜爽99麻豆av| 中国美女看黄片| 亚洲三级黄色毛片| 色综合站精品国产| 熟妇人妻久久中文字幕3abv| 丝袜美腿在线中文| av在线蜜桃| 美女 人体艺术 gogo| 最好的美女福利视频网| 国产精品久久电影中文字幕| 十八禁网站免费在线| 国产激情偷乱视频一区二区| 91在线精品国自产拍蜜月| 99视频精品全部免费 在线| 国产精品一区www在线观看 | 蜜桃久久精品国产亚洲av| 88av欧美| 久久久久免费精品人妻一区二区| 中亚洲国语对白在线视频| 三级国产精品欧美在线观看| 免费看av在线观看网站| 国产精品一及| 麻豆一二三区av精品| 在线观看美女被高潮喷水网站| .国产精品久久| 别揉我奶头~嗯~啊~动态视频| 亚洲美女黄片视频| 午夜久久久久精精品| 变态另类丝袜制服| 国产精品99久久久久久久久| 中国美女看黄片| 久久热精品热| 国产精品久久久久久久久免| 美女高潮喷水抽搐中文字幕| 尾随美女入室| a在线观看视频网站| 精品人妻偷拍中文字幕| 一卡2卡三卡四卡精品乱码亚洲| 亚洲自偷自拍三级| 久久久久久久久久成人| 一边摸一边抽搐一进一小说| 男人舔奶头视频| 欧美高清性xxxxhd video| 久久精品影院6| 两性午夜刺激爽爽歪歪视频在线观看| 国产精华一区二区三区| 人人妻,人人澡人人爽秒播| 亚洲久久久久久中文字幕| 国产精品人妻久久久影院| 日日摸夜夜添夜夜添av毛片 | 两个人的视频大全免费| 如何舔出高潮| 国产欧美日韩精品亚洲av| 内射极品少妇av片p| 久久久久国内视频| 国产三级中文精品| 色尼玛亚洲综合影院| 久久精品综合一区二区三区| 日韩精品中文字幕看吧| 精品欧美国产一区二区三| 少妇人妻一区二区三区视频| 国产成人a区在线观看| 俄罗斯特黄特色一大片| 亚洲中文字幕日韩| 麻豆精品久久久久久蜜桃| 色综合亚洲欧美另类图片| 小蜜桃在线观看免费完整版高清| 久久久久久久精品吃奶| 国产爱豆传媒在线观看| 欧美高清性xxxxhd video| 精品久久国产蜜桃| 国产黄片美女视频| 午夜激情欧美在线| 他把我摸到了高潮在线观看| 91在线观看av| 97热精品久久久久久| 日韩一本色道免费dvd| 欧美高清性xxxxhd video| 久久久久久国产a免费观看| 免费无遮挡裸体视频| 亚洲成人久久爱视频| 日韩精品有码人妻一区| 欧美潮喷喷水| 性插视频无遮挡在线免费观看| 国产乱人视频| 欧美高清性xxxxhd video| 国产一区二区亚洲精品在线观看| 黄色一级大片看看| 国产美女午夜福利| 国产伦精品一区二区三区视频9| 亚洲中文日韩欧美视频| 久久久久国内视频| 村上凉子中文字幕在线| 久久久精品大字幕| 欧美zozozo另类| 免费在线观看影片大全网站| 亚洲欧美精品综合久久99| 少妇的逼好多水| 亚洲av五月六月丁香网| 少妇人妻精品综合一区二区 | 国产老妇女一区| 日本黄色片子视频| 国产男人的电影天堂91| 亚洲va日本ⅴa欧美va伊人久久| 精品一区二区三区视频在线| 美女免费视频网站| 亚洲在线观看片| 欧美激情在线99| 大型黄色视频在线免费观看| 直男gayav资源| 极品教师在线免费播放| 亚洲成人免费电影在线观看| 非洲黑人性xxxx精品又粗又长| 日日撸夜夜添| 中文资源天堂在线| 男人和女人高潮做爰伦理| 欧美bdsm另类| 日韩欧美在线乱码| 禁无遮挡网站| 久久精品国产自在天天线| 小蜜桃在线观看免费完整版高清| 性色avwww在线观看| 国产真实伦视频高清在线观看 | 亚洲av第一区精品v没综合| 我的老师免费观看完整版| 内地一区二区视频在线| 亚洲精品国产成人久久av| 亚洲中文字幕日韩| 欧美成人免费av一区二区三区| 久久久久久国产a免费观看| 又紧又爽又黄一区二区| 国产日本99.免费观看| 日本精品一区二区三区蜜桃| 天天一区二区日本电影三级| 一进一出抽搐动态| 最好的美女福利视频网| 中文字幕久久专区| 久久午夜福利片| 国产一区二区三区av在线 | 尤物成人国产欧美一区二区三区| 国内毛片毛片毛片毛片毛片| 国产女主播在线喷水免费视频网站 | 中文字幕人妻熟人妻熟丝袜美| 亚洲性夜色夜夜综合| 精品一区二区三区人妻视频| 亚洲国产精品久久男人天堂| 嫩草影院精品99| 三级国产精品欧美在线观看| 亚洲精品乱码久久久v下载方式| 俄罗斯特黄特色一大片| 亚洲成人久久性| 精品久久久久久久久久久久久| 超碰av人人做人人爽久久| 老熟妇仑乱视频hdxx| 亚洲天堂国产精品一区在线| 两个人视频免费观看高清| 人人妻,人人澡人人爽秒播| 人妻丰满熟妇av一区二区三区| 免费人成视频x8x8入口观看|