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

    基于“嵩山”超級(jí)計(jì)算機(jī)系統(tǒng)的大規(guī)模管網(wǎng)仿真

    2022-09-15 06:59:14楊周凡李冰洋謝景明劉勇杰
    計(jì)算機(jī)工程 2022年9期
    關(guān)鍵詞:嵩山模擬計(jì)算超級(jí)計(jì)算機(jī)

    楊周凡,韓 林,李冰洋,謝景明,韓 璞,劉勇杰

    (1.鄭州大學(xué) 信息工程學(xué)院,鄭州 450000;2.鄭州大學(xué) 國(guó)家超級(jí)計(jì)算鄭州中心,鄭州 450000)

    0 概述

    隨著世界各國(guó)對(duì)清潔能源需求的不斷增長(zhǎng),供水管道在能源結(jié)構(gòu)中發(fā)揮著重要的作用[1-2]。由于供水管道規(guī)模的擴(kuò)大,導(dǎo)致拓?fù)浣Y(jié)構(gòu)也越來(lái)越復(fù)雜[3-4]。供水管道中數(shù)值的準(zhǔn)確預(yù)測(cè)對(duì)整個(gè)管道建設(shè)和管道安全至關(guān)重要,供水管道系統(tǒng)的高效仿真是解決上述問(wèn)題的重要手段[5]。初期人們可通過(guò)對(duì)數(shù)值方法進(jìn)行改進(jìn),也可以使用更好的計(jì)算設(shè)備提升模擬計(jì)算效率,但是隨著管網(wǎng)拓?fù)浣Y(jié)構(gòu)大規(guī)模的擴(kuò)大以及CPU 功耗墻的出現(xiàn),該方法性能逐漸降低。

    近年來(lái),GPU 加速器開(kāi)始廣泛用于科學(xué)計(jì)算,其提供了優(yōu)越的計(jì)算處理能力和內(nèi)存帶寬,并提高了計(jì)算效率[6-8]。文獻(xiàn)[8]提出一種加速單GPU 芯片上開(kāi)放通道和管道組合流瞬態(tài)模擬的方法。在計(jì)算統(tǒng)一設(shè)備架構(gòu)(CUDA)的線(xiàn)程級(jí)并行結(jié)構(gòu)中,GPU 可以很好地利用其固有的并行性[9-10]。但是,對(duì)大規(guī)模管道網(wǎng)絡(luò)仿真計(jì)算時(shí),仿真計(jì)算粒度密集,而傳統(tǒng)計(jì)算機(jī)受限于計(jì)算粒度密集的程序,可能會(huì)影響供水管網(wǎng)大規(guī)模數(shù)值模擬時(shí)的效率?!搬陨健背?jí)計(jì)算機(jī)是我國(guó)自主研發(fā)的新一代E 級(jí)超級(jí)計(jì)算機(jī),其采用符合超算國(guó)際主流趨勢(shì)的海光1 號(hào)CPU+海光1 號(hào)DCU 加速器的異構(gòu)體系結(jié)構(gòu),所配備的DCU 加速器件使得該平臺(tái)更適合于部署高度密集型計(jì)算應(yīng)用。因此,供水管網(wǎng)模擬系統(tǒng)在“嵩山”超級(jí)計(jì)算機(jī)平臺(tái)上進(jìn)行模擬計(jì)算,可以進(jìn)一步突破瓶頸提升計(jì)算性能。

    盡管管網(wǎng)在超級(jí)計(jì)算機(jī)平臺(tái)上比傳統(tǒng)CPU 具有更高的計(jì)算效率,但單個(gè)DCU 節(jié)點(diǎn)的極限存儲(chǔ)和計(jì)算能力可能會(huì)影響管網(wǎng)在超擴(kuò)展尺度上處理計(jì)算系統(tǒng)時(shí)的效率。在這種情況下,如果在多塊DCU 中進(jìn)行計(jì)算,則需大幅擴(kuò)展管網(wǎng)模擬計(jì)算的規(guī)模。

    本文提出一種有效的并行化方案來(lái)提高管網(wǎng)的計(jì)算效率。面向“嵩山”超級(jí)計(jì)算機(jī)平臺(tái),利用HIP-C 語(yǔ)言修改程序完成程序跨平臺(tái)移植,在單DCU 中實(shí)現(xiàn)計(jì)算的并發(fā)。針對(duì)管網(wǎng)中管道元件中數(shù)據(jù)依賴(lài)問(wèn)題,對(duì)其進(jìn)行數(shù)據(jù)劃分,并結(jié)合HIP 編程模型和消息傳遞接口,將多個(gè)DCU 加速器集成到網(wǎng)絡(luò)體系結(jié)構(gòu)中,通過(guò)高效的混合并行化方案對(duì)管網(wǎng)進(jìn)行優(yōu)化[11]。

    1 相關(guān)工作

    本節(jié)主要介紹管網(wǎng)管道拓?fù)浣Y(jié)構(gòu),并描述HIP+MPI 混合編程。

    1.1 管道網(wǎng)絡(luò)模型

    管道運(yùn)輸是各種清潔能源開(kāi)發(fā)與輸送過(guò)程中一項(xiàng)重要的技術(shù)[12-13]。目前,管道運(yùn)輸技術(shù)已有很多成熟的理論和模型,隨著計(jì)算機(jī)技術(shù)和網(wǎng)絡(luò)通信的飛速發(fā)展,能源運(yùn)輸技術(shù)也逐漸實(shí)現(xiàn)了信息化,運(yùn)輸管道仿真模擬系統(tǒng)應(yīng)運(yùn)而生。模擬仿真通過(guò)把數(shù)據(jù)訪(fǎng)問(wèn)接口連接到系統(tǒng),及時(shí)更新數(shù)據(jù),將實(shí)時(shí)數(shù)據(jù)傳入到系統(tǒng)中進(jìn)行計(jì)算,實(shí)現(xiàn)管網(wǎng)的動(dòng)態(tài)模擬仿真[14-16]。

    首先以管網(wǎng)實(shí)際拓?fù)鋱D為基礎(chǔ)來(lái)考慮管網(wǎng)模型,為清晰地描述管網(wǎng)的模擬計(jì)算過(guò)程,本文通過(guò)以下簡(jiǎn)單管網(wǎng)進(jìn)行說(shuō)明。圖1 所示是一根獨(dú)立管道的兩個(gè)邊界節(jié)點(diǎn)。圖2 所示是一個(gè)簡(jiǎn)單的管道系統(tǒng),中間用一個(gè)非管道元件連接兩根管道,共有4 個(gè)臨界點(diǎn)。圖3 所示為擴(kuò)大管道規(guī)模后構(gòu)建一個(gè)閉環(huán)的管道系統(tǒng),管道內(nèi)由方程計(jì)算的值與非管道元件內(nèi)由方程計(jì)算得出的結(jié)果通過(guò)邊界值計(jì)算進(jìn)行數(shù)值交互,模擬仿真得出需要的數(shù)值。

    圖1 單個(gè)管道圖Fig.1 Single pipeline diagram

    圖2 簡(jiǎn)單的管道系統(tǒng)Fig.2 Simple pipeline system

    圖3 閉環(huán)的管道系統(tǒng)Fig.3 Closed-loop pipeline system

    1.2 MPI+HIP 混合編程

    并行計(jì)算在不同的粒度層次優(yōu)化,粒度一般分為粗粒度和細(xì)粒度。在集群上多個(gè)進(jìn)程進(jìn)行計(jì)算,進(jìn)程間通過(guò)消息傳遞的方式進(jìn)行通信[17-18]。由于MPI 的通信占用成本較高,因此更適合任務(wù)劃分清晰、通信不頻繁的粗粒度并行[19-20]。與MPI 相比,DCU 擅長(zhǎng)大規(guī)模密集計(jì)算,可在細(xì)粒度上進(jìn)行并行計(jì)算。本文結(jié)合MPI和DCU 的優(yōu)點(diǎn),通過(guò)MPI 消息傳遞機(jī)制控制多進(jìn)程計(jì)算,實(shí)現(xiàn)粗粒度上的并發(fā),并在每個(gè)進(jìn)程中使用DCU實(shí)現(xiàn)線(xiàn)程級(jí)計(jì)算和細(xì)粒度上的并發(fā)[21]。

    “嵩山”超級(jí)計(jì)算機(jī)一個(gè)節(jié)點(diǎn)內(nèi)共有4 塊DCU,如果只在單DCU 中進(jìn)行計(jì)算,每個(gè)節(jié)點(diǎn)的計(jì)算能力沒(méi)有被充分利用。為擴(kuò)展DCU 計(jì)算規(guī)模,在實(shí)現(xiàn)多DCU 計(jì)算時(shí),MPI+HIP 混合編程可以發(fā)揮優(yōu)勢(shì),為每一個(gè)DCU分別分配一個(gè)進(jìn)程,使用MPI 控制多進(jìn)程計(jì)算并進(jìn)行通信[22-23]。進(jìn)程之間使用消息傳遞接口傳輸數(shù)據(jù),進(jìn)程內(nèi)采用HIP 技術(shù)進(jìn)行線(xiàn)程級(jí)優(yōu)化,實(shí)現(xiàn)粗粒度和細(xì)粒度的結(jié)合,提升科學(xué)計(jì)算的性能。HIP+MPI 混合編程結(jié)構(gòu)如圖4 所示。

    圖4 MPI+HIP 混合編程結(jié)構(gòu)Fig.4 MPI+HIP mixed programming structure

    2 管網(wǎng)仿真計(jì)算的異構(gòu)實(shí)現(xiàn)

    2.1 管網(wǎng)計(jì)算的并行性

    管網(wǎng)模擬仿真系統(tǒng)在進(jìn)行數(shù)值模擬時(shí),大量的數(shù)據(jù)增加了計(jì)算時(shí)間,影響數(shù)值模擬的時(shí)間和精度。根據(jù)上文的內(nèi)容可以了解到DCU 的計(jì)算能力,這可以解決目前模擬計(jì)算中所遇到的問(wèn)題。下面將詳細(xì)介紹管網(wǎng)拓?fù)浣Y(jié)構(gòu)中管道與非管道的并行特性。參照?qǐng)D3 結(jié)構(gòu)中各元件計(jì)算的流程如圖5 所示。

    圖5 管網(wǎng)元件計(jì)算流程Fig.5 Calculation procedure of pipeline network components

    本文管道網(wǎng)絡(luò)仿真計(jì)算基于王海[13]提出的立體管網(wǎng)建模方法。將管網(wǎng)“對(duì)象化”,然后把管網(wǎng)元件的對(duì)象屬性賦予具體數(shù)值,得到每個(gè)元件與相鄰元件的連接屬性以及每個(gè)元件的初始狀態(tài)和邊界條件。管道元件和非管道元件在初始化后,可開(kāi)始第1 個(gè)時(shí)間步長(zhǎng)的計(jì)算,每次計(jì)算完成后,需要進(jìn)行收斂分析,如果計(jì)算精度達(dá)到0.000 1%,則結(jié)束循環(huán)。這時(shí)能夠得到穩(wěn)態(tài)時(shí)管道元件與非管道元件的流量、壓力和水力工況等數(shù)值。

    在分析該程序代碼進(jìn)行數(shù)值模擬計(jì)算時(shí),首先需要設(shè)置循環(huán)條件,直到計(jì)算結(jié)果不發(fā)散才可計(jì)算結(jié)束。在外循環(huán)中先對(duì)非管道元件進(jìn)行計(jì)算,在邏輯上將數(shù)組進(jìn)行切分,數(shù)組不同的分段執(zhí)行不同的非管道元件,使用hipDeviceSynchronize()函數(shù)進(jìn)行同步,直到所有非管道元件計(jì)算完畢,才能對(duì)管道元件進(jìn)行計(jì)算,然后同步直到所有管道元件計(jì)算完成。以上所有步驟在內(nèi)循環(huán)每5 000 次后進(jìn)行數(shù)值更新,并對(duì)計(jì)算結(jié)果進(jìn)行收斂計(jì)算,直到計(jì)算結(jié)果收斂或達(dá)到最大循環(huán)次數(shù),整個(gè)循環(huán)計(jì)算結(jié)束。在此過(guò)程中,各個(gè)非管道元件之間的計(jì)算是獨(dú)立的,管道元件之間的計(jì)算也沒(méi)有依賴(lài),管道和管道、非管道與非管道之間有較高的并行度。因此,可以考慮在粗粒度上把各管道和非管道元件作為求解任務(wù),將其傳輸?shù)皆O(shè)備端進(jìn)行并行計(jì)算。

    2.2 異構(gòu)實(shí)現(xiàn)

    供水管網(wǎng)仿真系統(tǒng)代碼是由C/C++語(yǔ)言編寫(xiě)的,本文通過(guò)使用HIP-C 對(duì)代碼進(jìn)行改寫(xiě),改寫(xiě)后的代碼可以在“嵩山”超級(jí)計(jì)算機(jī)上運(yùn)行并進(jìn)行測(cè)試。通過(guò)測(cè)試可以發(fā)現(xiàn),管道和非管道中水力計(jì)算部分耗時(shí)較長(zhǎng),一定程度上影響了模擬仿真計(jì)算的效率。因此,在工作中把管道和非管道中的計(jì)算部分在DCU 中進(jìn)行并行計(jì)算,因?yàn)镈CU 加速器對(duì)數(shù)據(jù)量較大、運(yùn)算復(fù)雜的密集性計(jì)算有顯著優(yōu)勢(shì),所以對(duì)于供水管網(wǎng)模擬計(jì)算時(shí)把計(jì)算耗時(shí)較長(zhǎng)的部分傳輸?shù)紻CU 中,計(jì)算效率有了顯著的提升。供水管網(wǎng)仿真系統(tǒng)在異構(gòu)架構(gòu)中的模擬實(shí)現(xiàn)流程如圖6 所示。

    結(jié)合圖6 分析在程序中需要讀取管道和非管道元件中的數(shù)據(jù),并寫(xiě)入不同的結(jié)構(gòu)體數(shù)組,然后定義結(jié)構(gòu)體指針,動(dòng)態(tài)分配各個(gè)管道和非管道結(jié)構(gòu)體指針的內(nèi)存,將主機(jī)端內(nèi)存的管道元件和非管道元件的結(jié)構(gòu)體數(shù)組傳輸?shù)紻CU 加速器設(shè)備內(nèi)存中,并對(duì)其進(jìn)行初始化。管網(wǎng)中管道元件和非管道元件需循環(huán)計(jì)算,直到達(dá)到收斂條件或最大循環(huán)次數(shù)方可跳出循環(huán)結(jié)束計(jì)算。在外循環(huán)中,對(duì)管網(wǎng)中各元件循環(huán)計(jì)算時(shí),管道元件和非管道元件將DCU 加速器映射到block 塊中,每個(gè)block 中可以根據(jù)實(shí)際應(yīng)用分配線(xiàn)程,非管道元件和管道元件計(jì)算時(shí)按順序計(jì)算。首先計(jì)算非管道元件并同步,當(dāng)所有非管道元件計(jì)算完畢之后開(kāi)始管道的計(jì)算,同理,管道計(jì)算后也需要同步。以上操作以5 000 次為基準(zhǔn),開(kāi)啟內(nèi)循環(huán),每循環(huán)計(jì)算5 000 次,所有元件進(jìn)行一次更新,并對(duì)其中的二通、三通、四通進(jìn)行收斂條件判斷,若達(dá)到收斂條件,則跳出循環(huán);否則再次重復(fù)上述步驟對(duì)非管道和管道進(jìn)行并行操作,直到外循環(huán)結(jié)束,跳出循環(huán),將最終的計(jì)算結(jié)果從設(shè)備端傳回到主機(jī)端,重新關(guān)聯(lián)非管道元件和管道,直至模擬計(jì)算結(jié)束。

    圖6 異構(gòu)版本供水管網(wǎng)仿真系統(tǒng)模擬流程Fig.6 Simulation procedure of water supply pipeline network simulation system of heterogeneous versions

    對(duì)于小規(guī)模的管道網(wǎng)絡(luò),可以實(shí)現(xiàn)在單DCU 中計(jì)算,當(dāng)管道網(wǎng)絡(luò)規(guī)模逐漸擴(kuò)大時(shí),單DCU 中計(jì)算規(guī)模不能滿(mǎn)足仿真計(jì)算的需求,因此將單DCU 擴(kuò)展到多DCU 中進(jìn)行模擬計(jì)算。

    3 DCU 多卡的實(shí)現(xiàn)

    供水管網(wǎng)模擬仿真系統(tǒng)在多DCU 中的實(shí)現(xiàn),合理的管道劃分方式和數(shù)據(jù)通信傳輸尤其重要。

    3.1 管道數(shù)據(jù)劃分

    管網(wǎng)數(shù)據(jù)必須根據(jù)DCU 節(jié)點(diǎn)處理管道數(shù)據(jù),并將這些數(shù)據(jù)逐個(gè)寫(xiě)入DCU,而不是計(jì)算整個(gè)過(guò)程中的所有管道數(shù)據(jù)。在程序優(yōu)化過(guò)程中直接將管道數(shù)據(jù)分成兩個(gè)部分,并將這兩個(gè)部分的數(shù)據(jù)分別寫(xiě)入到兩塊DCU 內(nèi)存中進(jìn)行計(jì)算,但在計(jì)算過(guò)程中程序運(yùn)行到一半發(fā)生了中斷,測(cè)試調(diào)試發(fā)現(xiàn)在對(duì)管道數(shù)據(jù)循環(huán)讀取時(shí),讀到一部分管道數(shù)據(jù)后循環(huán)中斷,發(fā)生數(shù)據(jù)缺失的情況。經(jīng)過(guò)分析,管道之間數(shù)據(jù)交互密切,各個(gè)DCU 中一部分管道和非管道元件之間存在數(shù)據(jù)依賴(lài)問(wèn)題。在對(duì)管道數(shù)據(jù)進(jìn)行讀取時(shí),無(wú)法實(shí)現(xiàn)跨進(jìn)程讀取操作,DCU 之間也無(wú)法進(jìn)行跨設(shè)備的數(shù)據(jù)訪(fǎng)問(wèn)。為解決該問(wèn)題,需要使用消息傳遞接口(MPI)使相關(guān)進(jìn)程之間進(jìn)行通信,實(shí)現(xiàn)數(shù)據(jù)跨進(jìn)程通信交互。

    使用MPI 控制兩進(jìn)程計(jì)算并進(jìn)行通信時(shí),將管道元件分成兩部分,同時(shí)需要找到一部分管道元件作為兩進(jìn)程中的公有部分,傳回到主機(jī)端通信傳遞。在此項(xiàng)目組的成員提出一種一維分割方法,該方法將整個(gè)管道和非管道數(shù)據(jù)分成兩個(gè)部分,管道數(shù)據(jù)按組號(hào)被分割為三部分:GroupId=0,GroupId=1 和GroupId=2。把分組GroupId=1 的管道數(shù)據(jù)寫(xiě)入到DCU0 中,然后將分組GroupId=2 的管道數(shù)據(jù)寫(xiě)入到DCU1 中,管道分割圖如圖7 所示。從圖7 可以看出,管道數(shù)據(jù)被相對(duì)均勻地分配到了兩塊DCU 加速器中,在兩塊DCU 中有一部分管道數(shù)據(jù)GroupId=0屬于兩塊DCU 中的公有部分。這一部分?jǐn)?shù)據(jù)需要同時(shí)寫(xiě)入到兩塊DCU 中,GroupId=0 的管道數(shù)據(jù)作為連接兩部分管道數(shù)據(jù)的橋梁,在管道元件和非管道元件計(jì)算5 000 次后,將GroupId=0 的管道數(shù)據(jù)從DCU0 中傳回到主機(jī)端進(jìn)行通信,然后再傳回到DCU1中,最后對(duì)管道元件刷新,代表一次通信完成。

    圖7 管道分割圖Fig.7 Pipeline segmentation diagram

    3.2 MPI 優(yōu)化

    本節(jié)主要描寫(xiě)MPI 的具體實(shí)現(xiàn)以及在實(shí)現(xiàn)過(guò)程中遇到的問(wèn)題。

    3.2.1 數(shù)據(jù)類(lèi)型重定義

    數(shù)據(jù)類(lèi)型在數(shù)據(jù)結(jié)構(gòu)中的定義是一組性質(zhì)相同的值的集合以及定義在這個(gè)值集合上的一組操作的總稱(chēng)。變量用來(lái)存儲(chǔ)值,它們有名字和數(shù)據(jù)類(lèi)型。結(jié)合供水管網(wǎng)仿真模擬的代碼,管道和非管道元件被封裝成結(jié)構(gòu)體,MPI 需要知道結(jié)構(gòu)體的數(shù)據(jù)類(lèi)型才能實(shí)現(xiàn)通信傳輸。因此,需要對(duì)結(jié)構(gòu)體實(shí)現(xiàn)數(shù)據(jù)類(lèi)型重定義。

    本文對(duì)程序中管道接口和管道的結(jié)構(gòu)體進(jìn)行重定義。首先程序中使用MPI_Datatype 定義新的數(shù)據(jù)類(lèi)型名稱(chēng),通過(guò)blocklens 數(shù)組定義管道接口和管道中每個(gè)數(shù)據(jù)類(lèi)型的長(zhǎng)度,并根據(jù)oldTypes 數(shù)組描述管道接口和管道舊數(shù)據(jù)的類(lèi)型,通過(guò)MPI_Address指定數(shù)組中每個(gè)塊中的偏移量。然后運(yùn)用MPI_Type_struct 生成新的管道接口和管道數(shù)據(jù)類(lèi)型。最后采用MPI_Type_commit 提交注冊(cè)新的數(shù)據(jù)類(lèi)型&PipeStruct 和&PipePortStruct。

    3.2.2 MPI 實(shí)現(xiàn)過(guò)程

    在MPI 信息傳遞接口進(jìn)行通信前,應(yīng)先對(duì)分割好的管道元件和非管道元件實(shí)現(xiàn)讀取和寫(xiě)入操作。利用一維分割方法對(duì)各個(gè)元件進(jìn)行分割后,通過(guò)MPI_Comm_rank()獲取進(jìn)程號(hào),進(jìn)程號(hào)控制各個(gè)進(jìn)程對(duì)非管道元件和管道的讀取,將各自的數(shù)據(jù)分別讀取到各進(jìn)程的結(jié)構(gòu)體數(shù)組中。本文主要使用數(shù)組指針進(jìn)行讀寫(xiě)操作,數(shù)組指針是動(dòng)態(tài)分配空間,使用更加靈活,相比直接使用數(shù)組,其代碼擴(kuò)展性更好。在讀寫(xiě)完成之后,再由hipMemcpy()將其分別傳入到各自的DCU 進(jìn)行計(jì)算。由于MPI 的通信是在主機(jī)端進(jìn)行的,需要使用hipMemcpy()來(lái)控制設(shè)備端與主機(jī)端之間數(shù)據(jù)的傳輸。圖8 所示為MPI 通信時(shí)數(shù)據(jù)傳輸?shù)倪^(guò)程。

    圖8 MPI 通信過(guò)程Fig.8 MPI communication process

    MPI 在實(shí)現(xiàn)過(guò)程中,主機(jī)端使用MPI_Comm_rank()獲取當(dāng)前的進(jìn)程號(hào),調(diào)用hipGetDevice()獲取DCU 加速器的設(shè)備編號(hào),以此確定進(jìn)程編號(hào)和設(shè)備編號(hào)的對(duì)應(yīng)關(guān)系。每個(gè)進(jìn)程控制一個(gè)DCU,在對(duì)應(yīng)的設(shè)備上進(jìn)行數(shù)據(jù)顯存的劃分,完成主機(jī)端向設(shè)備端計(jì)算數(shù)據(jù)的傳輸,并各自啟動(dòng)內(nèi)核函數(shù);每個(gè)進(jìn)程設(shè)置自己私有的主機(jī)端和設(shè)備端的數(shù)據(jù)指針,其中管道元件的數(shù)據(jù)被分為三部分,GroupId=0 是公有部分,這一部分管道元件數(shù)據(jù)使用hipMemcpy(DTH)從設(shè)備端傳輸?shù)街鳈C(jī)端被單獨(dú)寫(xiě)入到Host_PublicPipeArray 數(shù)組中,MPI 在管道和非管道分別計(jì)算5 000 次后,將共有數(shù)據(jù)通過(guò)DCU 私有的設(shè)備端數(shù)據(jù)指針拷貝回私有主機(jī)端,在私有主機(jī)端進(jìn)行數(shù)據(jù)的通信及更新,并進(jìn)行收斂性檢查,在主機(jī)端中結(jié)束通信后分別拷貝到私有設(shè)備端中,之后對(duì)所有非管道元件更新一次。在外循環(huán)進(jìn)程中,進(jìn)程對(duì)各自的管道和非管道元件每進(jìn)行5 000 次密集計(jì)算都會(huì)使用MPI 通信接口進(jìn)行傳輸通信并更新所有元件,直至供水管網(wǎng)模擬計(jì)算結(jié)果收斂,計(jì)算結(jié)束通信完成。圖9 所示為MPI 通信傳遞實(shí)現(xiàn)過(guò)程。

    圖9 MPI 通信實(shí)現(xiàn)過(guò)程Fig.9 MPI communication realization process

    從單DCU 加速器擴(kuò)展到多DCU 加速器,由MPI控制多進(jìn)程計(jì)算的實(shí)現(xiàn)解決了DCU 自身的偽并行,完成了大規(guī)模數(shù)據(jù)多進(jìn)程的并發(fā)實(shí)現(xiàn)。多DCU 的實(shí)現(xiàn)擴(kuò)大了密集計(jì)算的規(guī)模,突破了單DCU 加速器計(jì)算資源的限制,對(duì)以后大規(guī)模程序的計(jì)算需求具有重要意義。

    4 實(shí)驗(yàn)測(cè)試

    “嵩山”超級(jí)計(jì)算機(jī)系統(tǒng)的操作系統(tǒng)為Centos-6.7,集群作業(yè)管理系統(tǒng)為Gridview,CPU 編譯器為gcc/g++-7.3.1,DCU 加速器編譯器為hipcc-2.9.6,MPI 版本為hpcx-2.4.1,CPU 處理器為英特爾?酷睿?i9-9980XE。

    4.1 功能性測(cè)試

    本文在“嵩山”超級(jí)計(jì)算機(jī)平臺(tái)單節(jié)點(diǎn)單DCU上進(jìn)行正確性驗(yàn)證。首先對(duì)CPU+DCU 異構(gòu)實(shí)現(xiàn)的供水管網(wǎng)模擬仿真計(jì)算進(jìn)行小規(guī)模數(shù)據(jù)測(cè)試,將記錄模擬出的數(shù)值與管網(wǎng)串行實(shí)現(xiàn)的模擬仿真結(jié)果進(jìn)行比較,經(jīng)對(duì)比發(fā)現(xiàn),兩者計(jì)算結(jié)果的數(shù)值變化在允許范圍內(nèi),通過(guò)了正確性驗(yàn)證。

    4.1.1 異構(gòu)實(shí)現(xiàn)結(jié)果對(duì)比

    將供水管網(wǎng)模擬實(shí)現(xiàn)的異構(gòu)版本與在CPU 處理器英特爾?酷睿?i9-9980XE 上的運(yùn)行結(jié)果進(jìn)行對(duì)比,為使描述清晰簡(jiǎn)潔,將在單DCU 內(nèi)優(yōu)化方法簡(jiǎn)稱(chēng)為方法1,在多DCU 內(nèi)優(yōu)化方法簡(jiǎn)稱(chēng)為方法2。通過(guò)輸入小規(guī)模器件數(shù)量和大規(guī)模器件數(shù)量,并在不同的計(jì)算平臺(tái)上進(jìn)行仿真計(jì)算測(cè)試。如表1 所示,選取器件規(guī)模數(shù)分別為10 000、30 000。

    表1 不同規(guī)模器件在CPU 和方法1 下的結(jié)果對(duì)比Table 1 Comparison of results of different scale devices in CPU and method 1

    由表1 數(shù)據(jù)可以看出,在器件數(shù)為10 000 時(shí),在DCU 加速器上的加速比為5.065,隨著計(jì)算規(guī)模的增加,當(dāng)輸入器件數(shù)為30 000 時(shí),加速比達(dá)到了9.833。分析其原因,是因?yàn)樵谛∫?guī)模數(shù)據(jù)計(jì)算時(shí),不能充分利用DCU 加速器的并行資源,計(jì)算性能有一定幅度的提升,但不能達(dá)到最優(yōu)。當(dāng)器件數(shù)量增多時(shí),DCU加速器在大規(guī)模密集計(jì)算的計(jì)算優(yōu)勢(shì)突出,加速效果明顯提升。實(shí)驗(yàn)結(jié)果證明了CPU+DCU 異構(gòu)實(shí)現(xiàn)的供水管網(wǎng)模擬計(jì)算在“嵩山”超級(jí)計(jì)算機(jī)平臺(tái)的單DCU 加速器環(huán)境中,加速效果十分顯著,在保證相同計(jì)算精度的前提下,計(jì)算速度提升5~10 倍,且管網(wǎng)模型規(guī)模越大,DCU 加速效果則越顯著。

    表2 所示是GPU 異構(gòu)平臺(tái)上的運(yùn)行結(jié)果與方法1進(jìn)行對(duì)比,加速比提升了2~3 倍??梢钥闯觯凇搬陨健背?jí)計(jì)算機(jī)上的移植相比顯卡為GT 730 的GPU異構(gòu)平臺(tái)仍有顯著的優(yōu)勢(shì)。

    表2 不同規(guī)模器件在GPU 和方法1 下的結(jié)果對(duì)比Table 2 Comparison of results of different scale devices in GPU and method 1

    本節(jié)實(shí)驗(yàn)驗(yàn)證了供水管網(wǎng)模擬仿真系統(tǒng)在不同平臺(tái)的測(cè)試結(jié)果,表明“嵩山”超級(jí)計(jì)算機(jī)更適合于大規(guī)模仿真計(jì)算,且其相對(duì)于以往實(shí)施x86 平臺(tái)或GPU 異構(gòu)平臺(tái),計(jì)算性能都有明顯提升。

    4.1.2 多DCU(方法2)實(shí)現(xiàn)測(cè)試分析

    由于越來(lái)越多管道的建立,管網(wǎng)拓?fù)鋸?fù)雜,計(jì)算量大,單DCU 的計(jì)算規(guī)模已經(jīng)不能滿(mǎn)足龐大的管網(wǎng)數(shù)據(jù)計(jì)算量。本節(jié)基于MPI+HIP 模型選擇供水管網(wǎng)仿真計(jì)算在多DCU 上的實(shí)現(xiàn)進(jìn)行實(shí)驗(yàn),將在單DCU 上管網(wǎng)模擬仿真運(yùn)行的時(shí)間作為基準(zhǔn),測(cè)試該模擬程序在單節(jié)點(diǎn)內(nèi)多個(gè)DCU 上運(yùn)行的并行效率,如表3 所示。

    表3 不同規(guī)模器件在方法1 和方法2 下的結(jié)果對(duì)比Table 3 Comparison of results of different scale devices under method 1 and method 2 s

    在輸入管器件數(shù)量分別為10 000、30 000 時(shí),DCU 單卡加速與DCU 多卡加速速度相當(dāng),多卡加速效果略?xún)?yōu)于單卡,但當(dāng)面對(duì)超大規(guī)模管網(wǎng)模型時(shí),多卡加速效果將明顯優(yōu)于單卡環(huán)境。原因是由于在MPI 進(jìn)行通信傳輸時(shí),需要將管網(wǎng)中管道和非管道元件從設(shè)備端傳輸?shù)街鳈C(jī)端進(jìn)行數(shù)據(jù)通信,然后再傳回到設(shè)備端。在輸入規(guī)模少的管道和非管道數(shù)據(jù)進(jìn)行計(jì)算時(shí),使用hipMemcpy()進(jìn)行傳輸所占用的時(shí)間較長(zhǎng),核函數(shù)內(nèi)密集計(jì)算占比較小,性能提升不明顯,但是隨著輸入管網(wǎng)規(guī)模的增大,在核函數(shù)內(nèi)計(jì)算占比遠(yuǎn)超過(guò)傳輸占比時(shí),加速比取得大幅提升。

    表4 所示是將在CPU 加速器上的運(yùn)行結(jié)果與DCU 多卡加速結(jié)果進(jìn)行對(duì)比,加速比提升了5~10 倍。從表4 可以看出,將數(shù)據(jù)規(guī)模擴(kuò)展到多塊DCU 中測(cè)試結(jié)果取得較優(yōu)的性能,隨著規(guī)模的擴(kuò)大,加速比與規(guī)模的擴(kuò)大成正比。

    表4 不同規(guī)模器件在CPU 和方法2 下的結(jié)果對(duì)比Table 4 Comparison of results of different scale devices under CPU and method 2

    實(shí)驗(yàn)結(jié)果證明了基于HIP 編程模型和MPI 實(shí)現(xiàn)的供水管網(wǎng)模擬仿真計(jì)算在“嵩山”超級(jí)計(jì)算機(jī)系統(tǒng)的多DCU 上具有良好的可拓展性,對(duì)供水管網(wǎng)在“嵩山”超級(jí)計(jì)算機(jī)平臺(tái)上實(shí)現(xiàn)規(guī)模擴(kuò)展具有重要的意義。

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

    本文利用HIP-C 語(yǔ)言實(shí)現(xiàn)供水管網(wǎng)模擬仿真計(jì)算在“嵩山”超級(jí)計(jì)算機(jī)平臺(tái)的移植,通過(guò)對(duì)管道和非管道元件的數(shù)據(jù)進(jìn)行劃分,并基于CPU+DCU 異構(gòu)架構(gòu),利用HIP 編程模型和消息傳遞接口控制DCU 的并發(fā)和多進(jìn)程之間數(shù)據(jù)的通信傳遞,擴(kuò)展管網(wǎng)仿真計(jì)算的規(guī)模,同時(shí)提升模擬實(shí)現(xiàn)的效率。實(shí)驗(yàn)結(jié)果驗(yàn)證了本文優(yōu)化方法的有效性。下一步將進(jìn)行管網(wǎng)內(nèi)核函數(shù)計(jì)算部分的優(yōu)化工作,研究擴(kuò)展核函數(shù)內(nèi)管道和非管道元件的并行特性,以達(dá)到提升管網(wǎng)仿真計(jì)算性能的目標(biāo)。

    猜你喜歡
    嵩山模擬計(jì)算超級(jí)計(jì)算機(jī)
    超級(jí)計(jì)算機(jī)
    R1234ze PVTx熱物性模擬計(jì)算
    能源工程(2022年1期)2022-03-29 01:06:26
    超級(jí)計(jì)算機(jī)及其在航空航天領(lǐng)域中的應(yīng)用
    科技傳播(2019年22期)2020-01-14 03:06:36
    我愛(ài)我家
    美國(guó)制造出全球最快超級(jí)計(jì)算機(jī)
    每秒100億億次 中國(guó)超級(jí)計(jì)算機(jī)
    尹朝陽(yáng):嵩山高
    鄭州嵩山地磁臺(tái)站建站可行性分析
    擠出發(fā)泡片材褶皺分析及模擬計(jì)算
    實(shí)際發(fā)射工況下底排藥柱結(jié)構(gòu)完整性的模擬計(jì)算
    淫妇啪啪啪对白视频| 成年女人看的毛片在线观看| 日韩欧美 国产精品| 1000部很黄的大片| 国产午夜福利久久久久久| 久久久久国产精品人妻aⅴ院| 亚洲va日本ⅴa欧美va伊人久久| 搡老熟女国产l中国老女人| 亚洲欧美日韩高清在线视频| 熟女少妇亚洲综合色aaa.| 老司机午夜十八禁免费视频| 在线观看午夜福利视频| 十八禁人妻一区二区| 亚洲七黄色美女视频| 色综合站精品国产| 天堂动漫精品| 在线观看一区二区三区| 国产一区在线观看成人免费| 亚洲乱码一区二区免费版| 国产精品久久久久久亚洲av鲁大| 国产野战对白在线观看| 久久亚洲精品不卡| 美女高潮喷水抽搐中文字幕| 免费人成视频x8x8入口观看| 成年女人毛片免费观看观看9| 看黄色毛片网站| 999久久久精品免费观看国产| 亚洲片人在线观看| 丝袜美腿在线中文| 一卡2卡三卡四卡精品乱码亚洲| 在线播放无遮挡| 国产免费一级a男人的天堂| 亚洲精品成人久久久久久| 有码 亚洲区| 高清毛片免费观看视频网站| 熟女少妇亚洲综合色aaa.| 一本综合久久免费| 国产真实伦视频高清在线观看 | 国产精品国产高清国产av| 好男人电影高清在线观看| 亚洲av免费在线观看| 男女视频在线观看网站免费| 欧美日韩亚洲国产一区二区在线观看| 久久精品国产亚洲av涩爱 | 一进一出好大好爽视频| 欧美成人a在线观看| 99久久综合精品五月天人人| 成人国产综合亚洲| 色噜噜av男人的天堂激情| 国产精品精品国产色婷婷| 操出白浆在线播放| 看片在线看免费视频| 国内精品美女久久久久久| 一进一出好大好爽视频| 免费观看的影片在线观看| 国产精品永久免费网站| 岛国在线观看网站| eeuss影院久久| 亚洲无线在线观看| 一进一出抽搐动态| 看黄色毛片网站| 日韩免费av在线播放| 亚洲精品美女久久久久99蜜臀| 俺也久久电影网| 内地一区二区视频在线| 黄色成人免费大全| 美女黄网站色视频| 国产精品嫩草影院av在线观看 | 久久久精品欧美日韩精品| 男插女下体视频免费在线播放| 免费看日本二区| 91在线观看av| 女人高潮潮喷娇喘18禁视频| 国产伦人伦偷精品视频| 成年免费大片在线观看| 两性午夜刺激爽爽歪歪视频在线观看| 久久国产乱子伦精品免费另类| 天天添夜夜摸| 国产69精品久久久久777片| 少妇的逼水好多| 久久精品人妻少妇| 日本成人三级电影网站| 美女免费视频网站| 免费观看人在逋| 国产日本99.免费观看| 黑人欧美特级aaaaaa片| 国产极品精品免费视频能看的| 亚洲成人中文字幕在线播放| 夜夜爽天天搞| 在线观看免费午夜福利视频| 18+在线观看网站| 97碰自拍视频| 亚洲av美国av| 成人性生交大片免费视频hd| 亚洲午夜理论影院| 国产av在哪里看| 露出奶头的视频| 很黄的视频免费| 在线播放无遮挡| 日本与韩国留学比较| 国产精品精品国产色婷婷| 成年免费大片在线观看| 一本综合久久免费| 男女下面进入的视频免费午夜| 黄色视频,在线免费观看| 久久久久性生活片| 757午夜福利合集在线观看| 97人妻精品一区二区三区麻豆| 超碰av人人做人人爽久久 | 精品国产亚洲在线| 久久精品综合一区二区三区| 欧美丝袜亚洲另类 | 亚洲av不卡在线观看| 又黄又爽又免费观看的视频| 少妇丰满av| 欧美一区二区国产精品久久精品| 性色av乱码一区二区三区2| 中亚洲国语对白在线视频| 狂野欧美白嫩少妇大欣赏| 国产成人欧美在线观看| 黄色丝袜av网址大全| 一级毛片高清免费大全| 亚洲欧美日韩东京热| 国产黄片美女视频| 日本黄大片高清| 亚洲国产高清在线一区二区三| 国内精品美女久久久久久| 国产三级在线视频| 少妇丰满av| 亚洲18禁久久av| 亚洲av一区综合| 一本久久中文字幕| bbb黄色大片| 成人亚洲精品av一区二区| 日本一本二区三区精品| 一区二区三区国产精品乱码| 日本熟妇午夜| 亚洲 国产 在线| 极品教师在线免费播放| 国产成人啪精品午夜网站| h日本视频在线播放| 欧美午夜高清在线| 国产成人aa在线观看| 久久久久久久久中文| 2021天堂中文幕一二区在线观| 男女之事视频高清在线观看| 天堂影院成人在线观看| 国产极品精品免费视频能看的| 19禁男女啪啪无遮挡网站| 非洲黑人性xxxx精品又粗又长| 国产亚洲精品一区二区www| 少妇人妻一区二区三区视频| 免费看十八禁软件| 亚洲在线自拍视频| 色在线成人网| 国产精品 国内视频| xxx96com| 97碰自拍视频| 亚洲精品影视一区二区三区av| 尤物成人国产欧美一区二区三区| 色老头精品视频在线观看| 99视频精品全部免费 在线| 久久久色成人| 久久久国产成人精品二区| 亚洲人成网站高清观看| 夜夜看夜夜爽夜夜摸| 人人妻人人澡欧美一区二区| www.999成人在线观看| 最近最新免费中文字幕在线| 色av中文字幕| 免费看光身美女| av中文乱码字幕在线| 久久久久久国产a免费观看| 在线观看午夜福利视频| 亚洲不卡免费看| 国产精品乱码一区二三区的特点| 国产三级中文精品| 3wmmmm亚洲av在线观看| 免费看美女性在线毛片视频| 欧美日韩福利视频一区二区| www.熟女人妻精品国产| 欧美日韩精品网址| 午夜福利欧美成人| 日本免费a在线| 免费在线观看成人毛片| 欧美一级毛片孕妇| 欧美+日韩+精品| 亚洲欧美日韩无卡精品| 亚洲精品粉嫩美女一区| 免费大片18禁| 久久久国产成人免费| 高清在线国产一区| 亚洲精品一卡2卡三卡4卡5卡| 色在线成人网| 国产黄a三级三级三级人| 嫩草影院入口| 黄片大片在线免费观看| 国产精品亚洲av一区麻豆| 欧美一级a爱片免费观看看| 可以在线观看毛片的网站| 久久国产精品影院| 波多野结衣高清无吗| 久久久久久久久久黄片| 天美传媒精品一区二区| 国产精品自产拍在线观看55亚洲| 欧美成人性av电影在线观看| 在线观看日韩欧美| 亚洲精品乱码久久久v下载方式 | 日本免费一区二区三区高清不卡| 男女做爰动态图高潮gif福利片| 欧美日韩乱码在线| av黄色大香蕉| 亚洲国产精品999在线| 日韩欧美精品免费久久 | 成年版毛片免费区| 亚洲av日韩精品久久久久久密| 老司机福利观看| 久久精品91蜜桃| 深爱激情五月婷婷| 啦啦啦观看免费观看视频高清| av中文乱码字幕在线| 最近最新免费中文字幕在线| 一本综合久久免费| 亚洲内射少妇av| 亚洲欧美精品综合久久99| 一区二区三区激情视频| 亚洲av第一区精品v没综合| 九色国产91popny在线| 免费看a级黄色片| 国模一区二区三区四区视频| 在线观看舔阴道视频| 香蕉av资源在线| 非洲黑人性xxxx精品又粗又长| 欧美日韩精品网址| 亚洲狠狠婷婷综合久久图片| 国产精品一区二区免费欧美| 亚洲欧美日韩无卡精品| 国产精品美女特级片免费视频播放器| 一级黄色大片毛片| 一个人免费在线观看电影| 亚洲人成网站高清观看| 搡女人真爽免费视频火全软件 | 国产精品一区二区三区四区免费观看 | 制服丝袜大香蕉在线| 男女那种视频在线观看| 18禁黄网站禁片免费观看直播| 美女cb高潮喷水在线观看| 特级一级黄色大片| 午夜福利免费观看在线| 久久久久久久亚洲中文字幕 | 叶爱在线成人免费视频播放| 免费观看精品视频网站| 91麻豆精品激情在线观看国产| 国产中年淑女户外野战色| 国产精品1区2区在线观看.| 久久久久久国产a免费观看| 桃色一区二区三区在线观看| 亚洲无线观看免费| 亚洲精品一区av在线观看| 国产精品女同一区二区软件 | 久久久久久九九精品二区国产| 他把我摸到了高潮在线观看| 欧美区成人在线视频| 亚洲18禁久久av| 久9热在线精品视频| 国产成人av激情在线播放| 动漫黄色视频在线观看| 在线免费观看的www视频| 在线观看免费午夜福利视频| 国产亚洲精品一区二区www| 中文字幕av成人在线电影| 亚洲内射少妇av| 午夜激情福利司机影院| 欧美乱色亚洲激情| 97人妻精品一区二区三区麻豆| 俺也久久电影网| 啦啦啦韩国在线观看视频| 亚洲成人免费电影在线观看| 亚洲国产欧洲综合997久久,| www国产在线视频色| 白带黄色成豆腐渣| 高清日韩中文字幕在线| 一本一本综合久久| 成人精品一区二区免费| 亚洲精品一区av在线观看| 亚洲av熟女| av黄色大香蕉| 婷婷亚洲欧美| 久久精品夜夜夜夜夜久久蜜豆| av在线天堂中文字幕| 在线免费观看不下载黄p国产 | 日韩精品青青久久久久久| 亚洲精品国产精品久久久不卡| 亚洲精华国产精华精| 国产在视频线在精品| 手机成人av网站| 久久精品国产亚洲av香蕉五月| 啪啪无遮挡十八禁网站| 熟女少妇亚洲综合色aaa.| 无限看片的www在线观看| 欧美av亚洲av综合av国产av| 69人妻影院| 法律面前人人平等表现在哪些方面| 白带黄色成豆腐渣| 波多野结衣高清作品| bbb黄色大片| 婷婷亚洲欧美| 亚洲精品国产精品久久久不卡| 一卡2卡三卡四卡精品乱码亚洲| av在线蜜桃| 欧美日韩乱码在线| 天堂影院成人在线观看| 婷婷亚洲欧美| 亚洲av成人av| 免费看日本二区| 三级国产精品欧美在线观看| 免费搜索国产男女视频| 少妇的逼水好多| 国产精品香港三级国产av潘金莲| 18禁裸乳无遮挡免费网站照片| 午夜视频国产福利| 亚洲美女黄片视频| 免费观看人在逋| 国产av一区在线观看免费| 成年女人看的毛片在线观看| 亚洲内射少妇av| 别揉我奶头~嗯~啊~动态视频| 成人18禁在线播放| 又黄又爽又免费观看的视频| 91av网一区二区| 亚洲性夜色夜夜综合| 一进一出抽搐动态| 国产乱人伦免费视频| ponron亚洲| 极品教师在线免费播放| 国产精品av视频在线免费观看| www.999成人在线观看| 国产91精品成人一区二区三区| 男女下面进入的视频免费午夜| 精品久久久久久久毛片微露脸| 欧美丝袜亚洲另类 | 综合色av麻豆| 国产单亲对白刺激| 日本成人三级电影网站| 国产亚洲欧美在线一区二区| 女警被强在线播放| 久久久久国内视频| 可以在线观看的亚洲视频| 成人精品一区二区免费| 91av网一区二区| 老鸭窝网址在线观看| 麻豆一二三区av精品| 亚洲中文字幕一区二区三区有码在线看| 国产黄a三级三级三级人| 久9热在线精品视频| 在线观看舔阴道视频| eeuss影院久久| 好男人在线观看高清免费视频| 波多野结衣巨乳人妻| 啦啦啦免费观看视频1| 精品久久久久久久末码| 欧美极品一区二区三区四区| 久久久久免费精品人妻一区二区| 在线视频色国产色| 制服丝袜大香蕉在线| 午夜久久久久精精品| 亚洲人成网站在线播放欧美日韩| 啦啦啦免费观看视频1| 女人十人毛片免费观看3o分钟| 精品人妻一区二区三区麻豆 | 亚洲人成网站在线播| 亚洲精品一卡2卡三卡4卡5卡| 国产精品一区二区三区四区久久| 麻豆成人午夜福利视频| 国产色婷婷99| 亚洲成人精品中文字幕电影| 国产黄色小视频在线观看| 在线免费观看不下载黄p国产 | 搡老岳熟女国产| 一区二区三区免费毛片| 啦啦啦观看免费观看视频高清| 此物有八面人人有两片| 听说在线观看完整版免费高清| 亚洲欧美精品综合久久99| 亚洲一区二区三区色噜噜| 麻豆国产97在线/欧美| 成年免费大片在线观看| 亚洲av五月六月丁香网| 男人舔女人下体高潮全视频| 亚洲国产色片| 99久久99久久久精品蜜桃| 久久久成人免费电影| 18禁黄网站禁片午夜丰满| 熟妇人妻久久中文字幕3abv| 日韩成人在线观看一区二区三区| 日韩亚洲欧美综合| 99国产精品一区二区三区| 搡女人真爽免费视频火全软件 | 亚洲激情在线av| 欧美色视频一区免费| 国产探花极品一区二区| 3wmmmm亚洲av在线观看| 美女 人体艺术 gogo| 欧美三级亚洲精品| 亚洲黑人精品在线| 亚洲国产欧美网| 久久精品国产自在天天线| 麻豆成人午夜福利视频| 变态另类成人亚洲欧美熟女| 欧美一区二区国产精品久久精品| 中亚洲国语对白在线视频| 一本一本综合久久| 少妇的逼水好多| 欧美黄色片欧美黄色片| 欧美日韩一级在线毛片| 亚洲国产日韩欧美精品在线观看 | 熟女人妻精品中文字幕| 9191精品国产免费久久| 亚洲国产精品999在线| 99久久无色码亚洲精品果冻| 级片在线观看| 免费在线观看影片大全网站| 成人特级av手机在线观看| 国产视频内射| 国产精品一区二区三区四区免费观看 | 人人妻人人看人人澡| 亚洲乱码一区二区免费版| 69av精品久久久久久| 精品人妻一区二区三区麻豆 | 色综合婷婷激情| 美女免费视频网站| 成人无遮挡网站| 啦啦啦韩国在线观看视频| 久久精品人妻少妇| 舔av片在线| 欧美黄色淫秽网站| 一进一出抽搐gif免费好疼| 嫩草影院入口| 熟女少妇亚洲综合色aaa.| 99视频精品全部免费 在线| 男女之事视频高清在线观看| 亚洲中文日韩欧美视频| 国产一区在线观看成人免费| 嫁个100分男人电影在线观看| 可以在线观看毛片的网站| 日韩欧美精品v在线| 欧美xxxx黑人xx丫x性爽| 午夜精品一区二区三区免费看| 亚洲真实伦在线观看| 国产麻豆成人av免费视频| 怎么达到女性高潮| 在线视频色国产色| 欧美色视频一区免费| 18+在线观看网站| 3wmmmm亚洲av在线观看| 日本黄色片子视频| 麻豆成人av在线观看| 亚洲性夜色夜夜综合| 日韩一区二区视频免费看| 欧美三级亚洲精品| 毛片一级片免费看久久久久| 男女那种视频在线观看| 亚洲欧美成人综合另类久久久| 亚洲av免费高清在线观看| 亚洲在久久综合| 国产亚洲最大av| 乱码一卡2卡4卡精品| 久久久亚洲精品成人影院| 99久国产av精品国产电影| 三级经典国产精品| 一级片'在线观看视频| 国产色爽女视频免费观看| 亚洲熟女精品中文字幕| 51国产日韩欧美| 亚洲欧美一区二区三区黑人 | 亚洲最大成人中文| 久久久久久久久久黄片| 干丝袜人妻中文字幕| 国产高清不卡午夜福利| 精品久久久久久久久av| 成年av动漫网址| 22中文网久久字幕| 天天躁日日操中文字幕| 国产成人午夜福利电影在线观看| 天堂√8在线中文| 久久精品国产亚洲网站| 久久久亚洲精品成人影院| 欧美zozozo另类| 成人午夜高清在线视频| 亚洲精品影视一区二区三区av| 老司机影院毛片| 97热精品久久久久久| 插逼视频在线观看| 春色校园在线视频观看| 免费观看av网站的网址| 亚洲四区av| 国产午夜福利久久久久久| 午夜老司机福利剧场| 99视频精品全部免费 在线| 91久久精品国产一区二区成人| 不卡视频在线观看欧美| 国产综合精华液| 亚洲,欧美,日韩| 亚洲av一区综合| 久久精品国产亚洲av涩爱| 国产黄片视频在线免费观看| 国产一区二区三区综合在线观看 | 国产精品一二三区在线看| 免费高清在线观看视频在线观看| 久久99热6这里只有精品| 亚洲欧美日韩无卡精品| 18禁动态无遮挡网站| 日韩中字成人| 如何舔出高潮| 久久精品久久久久久噜噜老黄| 色尼玛亚洲综合影院| 日韩不卡一区二区三区视频在线| 蜜桃久久精品国产亚洲av| 亚洲av男天堂| 尤物成人国产欧美一区二区三区| 精品国产三级普通话版| 日日啪夜夜爽| 亚洲综合色惰| 免费黄频网站在线观看国产| 亚洲av福利一区| 99久久精品一区二区三区| 91久久精品国产一区二区三区| kizo精华| 国产精品精品国产色婷婷| 久久久久久久久久成人| 91在线精品国自产拍蜜月| 亚洲在久久综合| 欧美性感艳星| 日韩成人伦理影院| 日本爱情动作片www.在线观看| 国产成人freesex在线| 天美传媒精品一区二区| 精品久久久噜噜| 亚洲欧洲国产日韩| 直男gayav资源| 免费不卡的大黄色大毛片视频在线观看 | 免费av观看视频| 18禁在线播放成人免费| 免费大片黄手机在线观看| 午夜福利视频精品| 在线a可以看的网站| 亚洲最大成人手机在线| 我的老师免费观看完整版| 三级毛片av免费| 亚洲精品日韩av片在线观看| 晚上一个人看的免费电影| av国产免费在线观看| 国产久久久一区二区三区| 日韩欧美三级三区| 亚洲在线观看片| 亚洲精品色激情综合| 精品久久久噜噜| 精品一区在线观看国产| 国产精品人妻久久久久久| 久久综合国产亚洲精品| 国产精品99久久久久久久久| 青青草视频在线视频观看| 少妇熟女aⅴ在线视频| 国产成人a∨麻豆精品| 国产午夜福利久久久久久| 欧美xxxx性猛交bbbb| 免费看a级黄色片| 特大巨黑吊av在线直播| 最新中文字幕久久久久| videos熟女内射| 国产国拍精品亚洲av在线观看| 精品国内亚洲2022精品成人| 亚洲av成人av| 国产欧美日韩精品一区二区| av在线天堂中文字幕| 中国美白少妇内射xxxbb| 最近中文字幕高清免费大全6| 色综合色国产| 天天躁日日操中文字幕| 国产熟女欧美一区二区| 男人舔奶头视频| 免费看av在线观看网站| 深夜a级毛片| 日韩欧美国产在线观看| 国产精品三级大全| 国产精品不卡视频一区二区| 日本爱情动作片www.在线观看| 99久久九九国产精品国产免费| 国产 亚洲一区二区三区 | 免费观看av网站的网址| 久久久久九九精品影院| 国产精品久久久久久久电影| 国产成人a∨麻豆精品| 在线a可以看的网站| 国产精品一区www在线观看| 少妇高潮的动态图| 日韩av在线大香蕉| 国内精品美女久久久久久| 啦啦啦啦在线视频资源| 亚洲欧洲国产日韩| 真实男女啪啪啪动态图| 欧美另类一区| 精品酒店卫生间| 亚洲欧美中文字幕日韩二区| 久久国产乱子免费精品| 直男gayav资源| 亚洲18禁久久av| 联通29元200g的流量卡| 国产老妇女一区| 最后的刺客免费高清国语| 国产永久视频网站| 中文字幕制服av| 亚州av有码| 精品国内亚洲2022精品成人| 搡老乐熟女国产|