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

    基于Intel Xeon Phi的激光等離子體粒子模擬研究*

    2014-03-23 06:03:00姚文科杜云飛楊燦群
    關(guān)鍵詞:異構(gòu)等離子體粒子

    姚文科,杜云飛,吳 強(qiáng),楊燦群

    (1.國(guó)防科學(xué)技術(shù)大學(xué)并行與分布處理國(guó)家重點(diǎn)實(shí)驗(yàn)室,湖南長(zhǎng)沙410073;2.國(guó)防科學(xué)技術(shù)大學(xué)計(jì)算機(jī)學(xué)院,湖南長(zhǎng)沙410073)

    1 引言

    激光等離子體粒子模擬通常用于描述強(qiáng)激光與等離子體相互作用的非線性過(guò)程,從而預(yù)測(cè)、設(shè)計(jì)、解釋實(shí)驗(yàn)結(jié)果[1,2]。它對(duì)于解釋激光等離子體多種耦合過(guò)程的物理圖像細(xì)節(jié),發(fā)現(xiàn)新的物理現(xiàn)象具有重要的意義[1~4]。在實(shí)際應(yīng)用中,模擬迭代的時(shí)間步通??蛇_(dá)數(shù)千萬(wàn)步,模擬的粒子數(shù)目超過(guò)數(shù)百萬(wàn)個(gè)[5,6],為了在有效的時(shí)間內(nèi)獲得模擬結(jié)果,模擬對(duì)計(jì)算性能有著極高的要求。因此,使用高性能計(jì)算領(lǐng)域的最新成果加速激光等離子體粒子模擬具有重要的現(xiàn)實(shí)意義。

    近年來(lái),異構(gòu)系統(tǒng)已經(jīng)成為高性能計(jì)算領(lǐng)域的一種主流系統(tǒng)[2,7]。通過(guò)集成通用CPU和加速器單元如GPU等,異構(gòu)系統(tǒng)在功耗和性能方面占有優(yōu)勢(shì)。針對(duì)GPU等加速單元與CPU體系結(jié)構(gòu)差異大、編程模型不兼容的問題[7],Intel發(fā)布了支持X86指令架構(gòu)的Intel Xeon Phi協(xié)處理器[8]。Intel Xeon Phi一方面可以兼容原CPU上的程序庫(kù)、開發(fā)工具以及應(yīng)用程序,另一方面對(duì)于特定類型的計(jì)算任務(wù),可以提供極高的計(jì)算性能,如Intel Xeon PhiTMCoprocessor 5110P單卡雙精度浮點(diǎn)性能可達(dá)1.01 Tflops[2]。在2013年5月Top 500排名中,采用了CPU-Intel Xeon Phi異構(gòu)結(jié)構(gòu)的TH-2超級(jí)計(jì)算機(jī)排名榜首??梢灶A(yù)見,基于CPU-Intel Xeon Phi的異構(gòu)系統(tǒng)將在未來(lái)高性能計(jì)算領(lǐng)域中發(fā)揮重要的作用。

    基于這一背景,本文研究了三維等離子體粒子模擬程序LARED-P到Intel Xeon Phi的移植。首先采用Native模式對(duì)LARED-P程序中熱點(diǎn)計(jì)算任務(wù)進(jìn)行優(yōu)化研究,通過(guò)采用SIMD擴(kuò)展指令進(jìn)行手工向量化以及數(shù)據(jù)預(yù)取、循環(huán)展開的優(yōu)化,使該計(jì)算任務(wù)獲得了4.61倍的加速。隨后采用Offload模式將程序移植到CPU-Intel Xeon Phi異構(gòu)系統(tǒng)上,并通過(guò)使用異步數(shù)據(jù)傳輸和雙緩沖技術(shù)提升了程序性能。

    本文結(jié)構(gòu)如下:第2節(jié)介紹了Intel Xeon Phi的結(jié)構(gòu)特點(diǎn)和LARED-P算法,回顧了相關(guān)工作;第3節(jié)描述了Native模式下LARED-P在Intel Xeon Phi上的SIMD優(yōu)化;第4節(jié)展現(xiàn)了Offload模式下粒子運(yùn)動(dòng)方程的優(yōu)化過(guò)程;第5節(jié)給出了性能測(cè)評(píng)結(jié)果;第6節(jié)對(duì)全文進(jìn)行了簡(jiǎn)要總結(jié)。

    2 背景介紹

    本節(jié)主要對(duì)Intel Xeon Phi加速器的結(jié)構(gòu)和LARED-P程序結(jié)構(gòu)進(jìn)行簡(jiǎn)單介紹;同時(shí),對(duì)其他學(xué)者的類似研究工作進(jìn)行總結(jié)。

    2.1 Intel Xeon Phi的結(jié)構(gòu)

    Intel在2012年11月發(fā)布了Intel Xeon PhiTM協(xié)處理器,它基于Intel MIC(Many Integrated Core)架構(gòu)。每片Intel Xeon Phi可以提供62個(gè)x86兼容的計(jì)算核心[8],每個(gè)核包含一個(gè)支持512位SIMD的向量處理單元(VPU)。通過(guò)使用VPU,每個(gè)核可同時(shí)處理8路雙精度或16路單精度浮點(diǎn)運(yùn)算[8],目前,Intel通過(guò)提供Intel向量化庫(kù)、Intel Intrinsic函數(shù)等方式使用VPU。Intel Xeon Phi的每個(gè)核擁有32 KB的L1數(shù)據(jù)Cache和32 KB的L1指令Cache。此外,每個(gè)核還可以使用512 KB的L2 Cache。不同核的L2 Cache通過(guò)雙向內(nèi)存控制器相連。

    Intel提供了多種模式來(lái)使用Intel Xeon Phi,例如Native模式、Offload模式等。

    Native模式將Intel Xeon Phi作為一個(gè)獨(dú)立的處理節(jié)點(diǎn),其上運(yùn)行有微Linux操作系統(tǒng),內(nèi)存空間作為全部的存儲(chǔ)空間。

    Offload模式則將Intel Xeon Phi作為CPU的加速單元。CPU作為主控端,將計(jì)算密集部分傳送到Intel Xeon Phi上進(jìn)行計(jì)算,然后再將計(jì)算結(jié)果返回給CPU。

    2.2 LARED-P簡(jiǎn)介

    LARED-P程序是北京應(yīng)用物理與數(shù)學(xué)研究所采用粒子云網(wǎng)格法[3,4]實(shí)現(xiàn)的三維等離子體粒子模擬程序。它適應(yīng)于二維和三維Cartesian坐標(biāo)系,本文主要針對(duì)三維模擬進(jìn)行研究。它采用均勻矩形結(jié)構(gòu)網(wǎng)格離散整個(gè)模擬空間,等離子體采用粒子云近似。

    LARED-P程序流程如圖1所示,其中主要的三個(gè)任務(wù)為求解電磁場(chǎng)Maxwell方程、靜電勢(shì)Poisson方程和粒子運(yùn)動(dòng)方程。在計(jì)算過(guò)程中,LARED-P以有限差分方法離散Maxwell方程,然后采用蛙跳格式離散粒子運(yùn)動(dòng)方程,最后采用粒子云網(wǎng)格方法(PIC)耦合粒子和電磁場(chǎng)。這三個(gè)方程中粒子運(yùn)動(dòng)方程占據(jù)了計(jì)算時(shí)間的31.8%,粒子云方程占34.7%,粒子重排過(guò)程占27%。

    Figure 1 Flow chart of LARED-P圖1 LARED-P程序流程圖

    2.3 相關(guān)工作

    莫?jiǎng)t堯等人[4]在所開發(fā)的串行LARED-P程序的基礎(chǔ)上引進(jìn)網(wǎng)格與粒子的關(guān)系鏈表,重排粒子位置,消除了性能遷移,提高了單機(jī)性能。而后又開發(fā)了基于MPI環(huán)境的三維粒子模擬程序LARED-P,并采取三維分割、合理安排通信結(jié)構(gòu),設(shè)置虛網(wǎng)格等手段進(jìn)行優(yōu)化。

    劉來(lái)國(guó)等人[6]完成了基于GPU的LARED-P加速技術(shù)的研究與實(shí)現(xiàn)。加速后的LARED-P程序在NVIDIA Tesla S1070的單個(gè)GPU上獲得了相當(dāng)于主頻2.4 GHz的Intel(R)Core(TM)2 Quad CPU Q6600單核的6倍加速比。

    石志才等人[9]則針對(duì)LARED-P中粒子運(yùn)動(dòng)方程在GPU上的實(shí)現(xiàn)提出八色分解方案,消除并行訪問的讀寫依賴,擴(kuò)大了并行度,在NVIDIA Tesla M2090上獲得了相對(duì)于Intel Xeon X5670 CPU單核的20.08倍的加速比。

    3 Native模式下基于SIMD的優(yōu)化

    本節(jié)介紹在Native模式下針對(duì)LARED-P所做的優(yōu)化工作。該算法的實(shí)現(xiàn)部分見文獻(xiàn)[9]。運(yùn)動(dòng)方程的運(yùn)行時(shí)間占整個(gè)算法運(yùn)行時(shí)間的31.8%,在移植過(guò)程中為了提高其數(shù)據(jù)級(jí)并行,對(duì)它進(jìn)行了向量化。在使用編譯器選項(xiàng)-O3-mmic與-O3-novec-mmic對(duì)比中,發(fā)現(xiàn)兩者運(yùn)行時(shí)間沒明顯區(qū)別;加編譯指導(dǎo)#pragma vector命令后也沒太大提升。所以,我們選擇了手工向量化。

    3.1 基于SIMD擴(kuò)展指令的手工向量化

    通過(guò)調(diào)用Intel提供的Intrinsic接口函數(shù)對(duì)粒子運(yùn)動(dòng)方程的求解進(jìn)行手工向量化,該過(guò)程主要包括數(shù)據(jù)打包、向量計(jì)算以及數(shù)據(jù)解包等過(guò)程。以更新粒子位置為例,如圖2所示。其中,x、y、z三個(gè)數(shù)組分別存放粒子的x坐標(biāo)、y坐標(biāo)以及z坐標(biāo),vxj、vyj、vzj三個(gè)數(shù)組則存放粒子新速度的三個(gè)分量。

    這樣經(jīng)過(guò)SIMD向量化,程序局部性增強(qiáng),性能得到可觀的提升。

    在更新粒子新速度時(shí),涉及許多乘、加操作,為了提高效率可以使用乘加指令:_mm512_fmadd_pd(_mm512d,_mm512d,_mm512d)。乘加指令的使用帶來(lái)了可觀的性能提升。

    3.2 預(yù)取優(yōu)化

    Figure 2 Sketch map of vectorization圖2 向量化示意圖

    512位寬度的向量處理給訪存帶來(lái)了巨大挑戰(zhàn),為了降低訪問延遲,本文采用了預(yù)取指令mm_prefetch(),減少Cache失效。

    每次迭代訪問八個(gè)網(wǎng)格,這種訪問模式可預(yù)測(cè)性給預(yù)取帶來(lái)了便利。本文測(cè)試了幾組不同預(yù)取距離的運(yùn)行結(jié)果,如圖3所示。從圖3可以看出預(yù)取距離為一個(gè)迭代時(shí)性能最好。

    Figure 3 Result of prefetch圖3 預(yù)取效果圖

    4 基于Offload模式的程序移植

    隨后我們利用offload模式將LARED-P移植到CPU-Intel Xeon Phi異構(gòu)系統(tǒng)上。我們將熱點(diǎn)計(jì)算任務(wù)—運(yùn)動(dòng)方程的求解使用Intel Xeon Phi進(jìn)行加速,程序的其余部分仍然在CPU上完成。在移植的過(guò)程中發(fā)現(xiàn),CPU和Intel Xeon Phi之間的數(shù)據(jù)傳輸是程序性能瓶頸,占總時(shí)間60%。因此,如何降低傳輸開銷成為了本節(jié)工作的重點(diǎn)。我們主要采用了兩種優(yōu)化方法:異步數(shù)據(jù)傳輸和雙緩沖。

    4.1 異步數(shù)據(jù)傳輸

    當(dāng)使用Offload模式時(shí),CPU在將數(shù)據(jù)傳給Intel Xeon Phi之后,由于數(shù)據(jù)依賴的原因,需要等待其計(jì)算完畢并將結(jié)果傳送回CPU以后,CPU才能繼續(xù)執(zhí)行。為了減少CPU的空轉(zhuǎn)時(shí)間,我們采用了異步數(shù)據(jù)傳輸?shù)姆绞綄?duì)其進(jìn)行優(yōu)化。

    首先采用一種CPU提前計(jì)算的方式減少CPU的空轉(zhuǎn)時(shí)間。當(dāng)需要調(diào)用Intel Xeon Phi進(jìn)行粒子運(yùn)動(dòng)方程加速時(shí),CPU以異步方式將數(shù)據(jù)傳輸?shù)絀ntel Xeon Phi上,并提前進(jìn)行與粒子運(yùn)動(dòng)方程計(jì)算結(jié)果無(wú)關(guān)的任務(wù)的處理,如圖4所示。然而,由于大部分的計(jì)算任務(wù)都與運(yùn)動(dòng)方程相關(guān),因此這種方式取得的效果并不明顯。

    隨后采用了一種提前傳輸?shù)姆绞絹?lái)減少數(shù)據(jù)拷貝時(shí)CPU的等待時(shí)間。當(dāng)粒子運(yùn)動(dòng)方程相關(guān)的數(shù)據(jù)已經(jīng)準(zhǔn)備完畢時(shí),CPU立刻以異步的方式將數(shù)據(jù)傳給Intel Xeon Phi后,繼續(xù)以正常流程進(jìn)行任務(wù)處理,這樣增加了CPU和Intel Xeon Phi并行執(zhí)行的時(shí)間,從而隱藏了部分?jǐn)?shù)據(jù)傳輸時(shí)間。

    Figure 4 Sketch map of asynchronous mode圖4 異步傳輸示意圖

    4.2 雙緩沖

    為了進(jìn)一步減少數(shù)據(jù)傳輸開銷,我們采用了雙緩沖技術(shù),在CPU端開辟兩個(gè)發(fā)送緩沖區(qū)和兩個(gè)接收緩沖區(qū)。所需數(shù)據(jù)分組傳輸,相比之前MIC端需要接收全部數(shù)據(jù)之后才開始計(jì)算,在使用了雙緩沖之后,帶來(lái)的明顯好處是:以流水線方式執(zhí)行傳輸和計(jì)算,可以將絕大部分?jǐn)?shù)據(jù)傳輸時(shí)間隱藏,如圖5所示。

    Figure 5 Sketch map of double buffer圖5 雙緩沖示意圖

    5 性能評(píng)測(cè)

    本節(jié)對(duì)LARED-P算法進(jìn)行性能測(cè)試,測(cè)試平臺(tái)的具體配置如表1所示。我們采用的編譯器為Intel C++Compiler 13.0,MPI版本為3.0。

    Table 1 Configuration of the test platform表1 測(cè)試平臺(tái)的配置

    首先測(cè)試了手動(dòng)向量化和數(shù)據(jù)預(yù)取取得的性能提升。測(cè)試網(wǎng)格數(shù)為64*128*128,平均每個(gè)網(wǎng)格包含10個(gè)粒子。圖6為沒有向量化、只有向量化和向量化加預(yù)取三種情況下程序的運(yùn)行時(shí)間,從圖6中可以看出,向量化加速效果不錯(cuò),加速比可達(dá)到4.61,而預(yù)取的加速效果沒有向量化明顯,但是仍有19.7%的性能提升。因?yàn)镸IC卡內(nèi)存有限,無(wú)法再擴(kuò)大規(guī)模,而當(dāng)線程數(shù)接近64時(shí),運(yùn)行時(shí)間占整個(gè)程序時(shí)間的比例已經(jīng)非常小了,所以只測(cè)試到了64線程。CPU上運(yùn)行16線程時(shí)總時(shí)間為1.058 s,而MIC上64線程運(yùn)行時(shí)間為0.717 s,所以在MIC上每個(gè)核運(yùn)行一個(gè)線程的情況下,相對(duì)單塊CPU有1.48倍的加速。

    Figure 6 Result in native mode圖6 Native模式下實(shí)驗(yàn)結(jié)果

    接著測(cè)試了Offload模式下的異步輸入和雙緩沖的效果,如圖7所示。從圖7中可以看出,異步輸入和雙緩沖都對(duì)運(yùn)動(dòng)方程產(chǎn)生了一定的性能提升,相比于傳統(tǒng)Offload分別有9.8%和21.8%的性能提升。

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

    本文基于Intel Xeon Phi協(xié)處理器實(shí)現(xiàn)了LARED-P程序的移植。在移植的過(guò)程中,本文綜合運(yùn)用了Native和Offload兩種編程模式:首先運(yùn)用Native模式對(duì)LARED-P程序中熱點(diǎn)計(jì)算任務(wù)進(jìn)行優(yōu)化研究,通過(guò)采用SIMD擴(kuò)展指令使該計(jì)算任務(wù)獲得了4.61倍的加速;然后運(yùn)用Offload模式將程序移植到CPU-Intel Xeon Phi異構(gòu)系統(tǒng)上,并通過(guò)使用異步數(shù)據(jù)傳輸和雙緩沖技術(shù)分別獲得9.8%和21.8%的性能提升。

    Figure 7 Result in Offload mode圖7 Offload模式下實(shí)驗(yàn)結(jié)果

    [1] Zhu Shao-ping,Zhang Wei-yan.Overview of computer simulation on laser fusion in China[J].Journal of the Korean Physical Society,2006,49:33-38.

    [2] Chang Tie-qiang.Laser-plasma interaction and laser fusion[M].Changsha:Hunan Science and Technology Press,1998.(in Chinese)

    [3] Ma Yan-yun,Chang Wen-wei,Yin Yan,et al.An object-oriented 3D parallel simulation program PLASIM3D[J].Chinese Journal of Computation Physics,2004,21(3):305-311.(in Chinese)

    [4] Mo Ze-yao,Xu Lin-bao,Zhang Bao-lin,et al.Parallel computing and performance analysis for 2D plasma simulation with particle clouds in cells method[J].Chinese Journal of Computation Physics,1999,16(5)496-504.(in Chinese)

    [5] Cao Xiao-lin,Zheng Chun-yang,Zhang Ai-qing,et al.Program development of 3D plasma simulation oriented thousands of processors[J].Chinese Journal of Progress in Natural Science,2009,1(5):544-550.(in Chinese)

    [6] Liu Lai-guo,Xu Wei-xia,Yang Can-qun,et al.Accelerating LARED-P algorithm based on GPU[J].Computer Engineering &Science,2009,31(A01):59-63.(in Chinese)

    [7] Stantchev G,Dorland W,Gumerov N.Fast parallel particleto-grid interpolation for plasma PIC simulations on the GPU[J].Journal of Parallel and Distributed Computing,2008,68(10):1339-1349.

    [8] Intel?Xeon PhiTMCoprocessor System Software Developers Guide[R].SKU#328207-001EN,2012.

    [9] Yang Can-qun,Wu Qiang,Hu Hui-li,et al.Fast weighting method for plasma PIC simulation on the GPU-accelerated heterogeneous systems[J].Journal of Central South University,2013,20(6):1527-1535.

    [10] MPI-2:Extensions to the message-passing interface[EB/OL].[2012-05-16].http://micro.ustc.edu.cn/Linux/MPI/mpi-20.pdf.

    [11] Schulz K W,Ulerich R,Malaya N,et al.Early experiences porting scientific applications to the many integrated core(MIC)platform[C]∥Proc of the 2012 Highly Parallel Computing Symposium,2012:1.

    附中文參考文獻(xiàn):

    [2] 常鐵強(qiáng).激光等離子體相互作用與激光聚變[M].長(zhǎng)沙:湖南科學(xué)技術(shù)出版社,1998.

    [3] 馬燕云,常文蔚,銀燕,等.三維面向?qū)ο蟮牟⑿辛W幽M程序PLASIM3D[J].計(jì)算物理,2004,21(3):305-311.

    [4] 莫?jiǎng)t堯,許林寶,張寶琳,等.二維等離子體模擬粒子云網(wǎng)格方法的并行計(jì)算與性能分析[J].計(jì)算物理,1999,16(5):496-504.

    [5] 曹小林,鄭春陽(yáng),張愛清,等.面向數(shù)千處理器的三維等離子體粒子模擬程序研制[J].自然科學(xué)進(jìn)展,2009,19(5):544-550.

    [6] 劉來(lái)國(guó),徐煒遐,楊燦群,等.基于GPU的LARED-P算法加速[J].計(jì)算機(jī)工程與科學(xué),2009,31(A01):59-63.

    猜你喜歡
    異構(gòu)等離子體粒子
    試論同課異構(gòu)之“同”與“異”
    連續(xù)磁活動(dòng)對(duì)等離子體層演化的影響
    基于低溫等離子體修飾的PET/PVC浮選分離
    基于粒子群優(yōu)化的橋式起重機(jī)模糊PID控制
    基于粒子群優(yōu)化極點(diǎn)配置的空燃比輸出反饋控制
    等離子體種子處理技術(shù)介紹
    overlay SDN實(shí)現(xiàn)異構(gòu)兼容的關(guān)鍵技術(shù)
    LTE異構(gòu)網(wǎng)技術(shù)與組網(wǎng)研究
    在新興異構(gòu)SoCs上集成多種系統(tǒng)
    等離子體聚合廢植物油及其潤(rùn)滑性能
    中文资源天堂在线| 午夜激情福利司机影院| 亚洲男人的天堂狠狠| 精品久久久久久久久久免费视频| 国产探花在线观看一区二区| 午夜精品久久久久久毛片777| 国产午夜精品论理片| 最新在线观看一区二区三区| 老司机福利观看| 99久久成人亚洲精品观看| 日韩大尺度精品在线看网址| 欧美高清成人免费视频www| 久久久久免费精品人妻一区二区| 成年版毛片免费区| 老汉色∧v一级毛片| 亚洲乱码一区二区免费版| 久久久成人免费电影| 天堂√8在线中文| 国产精品女同一区二区软件 | 婷婷六月久久综合丁香| 中亚洲国语对白在线视频| 特大巨黑吊av在线直播| 老熟妇乱子伦视频在线观看| 婷婷六月久久综合丁香| 国产精华一区二区三区| 亚洲天堂国产精品一区在线| 国产一区二区三区视频了| 宅男免费午夜| 国产真实乱freesex| 久久久久久久亚洲中文字幕 | 午夜免费观看网址| 久久性视频一级片| 成人一区二区视频在线观看| 免费在线观看影片大全网站| 美女黄网站色视频| 99在线视频只有这里精品首页| 两个人看的免费小视频| 亚洲成人久久性| 五月玫瑰六月丁香| 亚洲人成电影免费在线| 在线观看舔阴道视频| 成人国产一区最新在线观看| 综合色av麻豆| 女人被狂操c到高潮| 欧美日韩国产亚洲二区| 中文字幕人成人乱码亚洲影| 国模一区二区三区四区视频| 久久久久久久亚洲中文字幕 | 一二三四社区在线视频社区8| 日韩av在线大香蕉| 亚洲中文字幕一区二区三区有码在线看| 草草在线视频免费看| 精品免费久久久久久久清纯| 欧美国产日韩亚洲一区| 欧美日韩黄片免| 中文字幕人妻丝袜一区二区| 久9热在线精品视频| 亚洲av成人精品一区久久| 久久精品91蜜桃| 国产精品免费一区二区三区在线| 日韩有码中文字幕| 欧美乱色亚洲激情| 又紧又爽又黄一区二区| 99热这里只有精品一区| 国产不卡一卡二| 99国产极品粉嫩在线观看| 亚洲乱码一区二区免费版| 日韩欧美三级三区| 亚洲性夜色夜夜综合| 亚洲精品影视一区二区三区av| bbb黄色大片| 国产精品 欧美亚洲| 久久久久久久久中文| 波野结衣二区三区在线 | www.色视频.com| 丰满乱子伦码专区| 嫩草影院精品99| 很黄的视频免费| 91在线观看av| 国产精品香港三级国产av潘金莲| 黄片大片在线免费观看| 窝窝影院91人妻| 日韩免费av在线播放| 国产精品日韩av在线免费观看| 可以在线观看的亚洲视频| 国产欧美日韩精品一区二区| 亚洲精品一区av在线观看| 叶爱在线成人免费视频播放| 熟女少妇亚洲综合色aaa.| 波野结衣二区三区在线 | 成年女人毛片免费观看观看9| 国产精品99久久久久久久久| 国产精品久久久人人做人人爽| 18美女黄网站色大片免费观看| 日本在线视频免费播放| 国产免费一级a男人的天堂| 国产成人福利小说| 午夜激情福利司机影院| 国产乱人伦免费视频| 日韩欧美一区二区三区在线观看| 国产淫片久久久久久久久 | 久久久久国产精品人妻aⅴ院| 少妇丰满av| 亚洲精品影视一区二区三区av| 午夜久久久久精精品| 欧美三级亚洲精品| 国产精品三级大全| 国产精品久久久久久久久免 | 国产高清视频在线播放一区| 欧美日韩乱码在线| 国产aⅴ精品一区二区三区波| 动漫黄色视频在线观看| 天堂动漫精品| 国产精品亚洲av一区麻豆| 岛国在线观看网站| 99热只有精品国产| 亚洲人成伊人成综合网2020| 国产精品98久久久久久宅男小说| 亚洲熟妇熟女久久| www国产在线视频色| 日韩精品中文字幕看吧| 床上黄色一级片| 国产亚洲av嫩草精品影院| 成年免费大片在线观看| 国产激情欧美一区二区| av专区在线播放| 欧美激情久久久久久爽电影| 亚洲成人久久性| 久久久久亚洲av毛片大全| 亚洲成av人片免费观看| a在线观看视频网站| 91字幕亚洲| 在线观看66精品国产| 国产精品1区2区在线观看.| 亚洲精品在线观看二区| 美女黄网站色视频| av视频在线观看入口| 亚洲成a人片在线一区二区| 可以在线观看毛片的网站| 日韩中文字幕欧美一区二区| 午夜福利欧美成人| 最近视频中文字幕2019在线8| 久久九九热精品免费| 欧美日韩亚洲国产一区二区在线观看| 久久精品国产综合久久久| 老熟妇仑乱视频hdxx| 国产高清视频在线播放一区| 18禁黄网站禁片免费观看直播| 九色成人免费人妻av| 无人区码免费观看不卡| 亚洲色图av天堂| 精品乱码久久久久久99久播| 亚洲人成伊人成综合网2020| 久久香蕉精品热| 国产成人福利小说| 亚洲国产中文字幕在线视频| 中文字幕av成人在线电影| 搡老妇女老女人老熟妇| 欧美一级a爱片免费观看看| 伊人久久大香线蕉亚洲五| 51午夜福利影视在线观看| 国产精品永久免费网站| 两个人的视频大全免费| 欧美激情在线99| 精品久久久久久久久久免费视频| 国产一区二区在线观看日韩 | 极品教师在线免费播放| 日韩人妻高清精品专区| 在线观看免费视频日本深夜| 女人高潮潮喷娇喘18禁视频| 淫妇啪啪啪对白视频| 男女那种视频在线观看| 无限看片的www在线观看| 99久久久亚洲精品蜜臀av| 国产三级中文精品| 精品国产三级普通话版| 狠狠狠狠99中文字幕| 欧美色欧美亚洲另类二区| 精品久久久久久久久久久久久| 国产伦在线观看视频一区| 91字幕亚洲| 一进一出好大好爽视频| 国产精品久久久久久人妻精品电影| 97超级碰碰碰精品色视频在线观看| 成人欧美大片| 全区人妻精品视频| 国产不卡一卡二| 超碰av人人做人人爽久久 | 亚洲第一欧美日韩一区二区三区| 国产激情偷乱视频一区二区| 国内精品美女久久久久久| 国产蜜桃级精品一区二区三区| 国内毛片毛片毛片毛片毛片| x7x7x7水蜜桃| 国产精品av视频在线免费观看| 12—13女人毛片做爰片一| 又爽又黄无遮挡网站| 老司机深夜福利视频在线观看| 在线视频色国产色| 日本免费a在线| 美女 人体艺术 gogo| 搞女人的毛片| 免费看a级黄色片| 嫩草影院精品99| 桃色一区二区三区在线观看| 亚洲一区二区三区不卡视频| 国产男靠女视频免费网站| 噜噜噜噜噜久久久久久91| 热99re8久久精品国产| 午夜日韩欧美国产| 久久欧美精品欧美久久欧美| 亚洲无线在线观看| 国产中年淑女户外野战色| 成人精品一区二区免费| 97碰自拍视频| 欧美性猛交╳xxx乱大交人| 久久久久性生活片| 欧美日韩国产亚洲二区| 国产成人系列免费观看| 岛国在线免费视频观看| 亚洲欧美日韩高清专用| 日本三级黄在线观看| 黄色丝袜av网址大全| 18+在线观看网站| 精品久久久久久,| 69人妻影院| 亚洲成av人片免费观看| 欧美另类亚洲清纯唯美| 日本a在线网址| 很黄的视频免费| 中文字幕av在线有码专区| 麻豆久久精品国产亚洲av| 亚洲,欧美精品.| 桃红色精品国产亚洲av| 级片在线观看| 久久国产精品影院| 搡女人真爽免费视频火全软件 | 久久精品国产亚洲av香蕉五月| 性色avwww在线观看| 精品久久久久久久久久免费视频| 国产成+人综合+亚洲专区| 又黄又爽又免费观看的视频| 1000部很黄的大片| 18禁黄网站禁片免费观看直播| 俄罗斯特黄特色一大片| 亚洲精华国产精华精| 欧美一区二区精品小视频在线| 日韩 欧美 亚洲 中文字幕| 一二三四社区在线视频社区8| 久9热在线精品视频| 美女被艹到高潮喷水动态| 精品电影一区二区在线| 露出奶头的视频| 狂野欧美白嫩少妇大欣赏| 狂野欧美白嫩少妇大欣赏| 亚洲无线在线观看| 久久午夜亚洲精品久久| 亚洲中文日韩欧美视频| 此物有八面人人有两片| 国产精品日韩av在线免费观看| 嫁个100分男人电影在线观看| 亚洲男人的天堂狠狠| 国产伦一二天堂av在线观看| 97人妻精品一区二区三区麻豆| 夜夜爽天天搞| 中文在线观看免费www的网站| av天堂中文字幕网| 美女高潮喷水抽搐中文字幕| 久久久久国内视频| 最近最新免费中文字幕在线| 午夜老司机福利剧场| 久久人妻av系列| 日本黄色视频三级网站网址| 国产精品免费一区二区三区在线| 男人和女人高潮做爰伦理| 真人做人爱边吃奶动态| 亚洲美女黄片视频| 欧美日韩中文字幕国产精品一区二区三区| 欧美日韩福利视频一区二区| 亚洲成av人片在线播放无| 日本五十路高清| 日韩av在线大香蕉| 久久久精品大字幕| 在线观看av片永久免费下载| 国产国拍精品亚洲av在线观看 | 亚洲不卡免费看| 国产三级在线视频| 欧美日韩一级在线毛片| 欧美三级亚洲精品| 男插女下体视频免费在线播放| 国产成人系列免费观看| 精品免费久久久久久久清纯| 日本在线视频免费播放| 国产99白浆流出| 18禁在线播放成人免费| 国产精品 欧美亚洲| 欧美一区二区精品小视频在线| 最近视频中文字幕2019在线8| 夜夜躁狠狠躁天天躁| 一区福利在线观看| 国产精品久久电影中文字幕| 久久国产乱子伦精品免费另类| 久99久视频精品免费| 精品一区二区三区视频在线观看免费| 午夜老司机福利剧场| 免费无遮挡裸体视频| 欧美一区二区亚洲| av专区在线播放| 久久精品国产亚洲av香蕉五月| 丝袜美腿在线中文| 日韩欧美一区二区三区在线观看| 亚洲性夜色夜夜综合| 女人被狂操c到高潮| 亚洲专区国产一区二区| 国产精品一区二区三区四区久久| 久久久国产成人免费| 亚洲欧美日韩东京热| 久久中文看片网| 精品无人区乱码1区二区| 老熟妇乱子伦视频在线观看| 亚洲国产欧美人成| 午夜视频国产福利| 久久精品综合一区二区三区| 天堂网av新在线| 国产精品一及| 两个人看的免费小视频| 欧美黑人欧美精品刺激| 亚洲第一电影网av| www.色视频.com| 欧美极品一区二区三区四区| 午夜福利欧美成人| 精品99又大又爽又粗少妇毛片 | 激情在线观看视频在线高清| 最近最新中文字幕大全免费视频| 国产亚洲精品一区二区www| 国产精品三级大全| 中文字幕av在线有码专区| 国产成人福利小说| 看片在线看免费视频| 国产黄a三级三级三级人| 欧美一级a爱片免费观看看| 国产精品,欧美在线| 亚洲国产精品久久男人天堂| 搡女人真爽免费视频火全软件 | 午夜福利在线在线| 国内精品久久久久久久电影| 免费看a级黄色片| 国产中年淑女户外野战色| 国产乱人视频| 亚洲欧美激情综合另类| 国产野战对白在线观看| 欧美3d第一页| 村上凉子中文字幕在线| 国产成人欧美在线观看| 啦啦啦免费观看视频1| 久久草成人影院| 日本与韩国留学比较| av片东京热男人的天堂| 91av网一区二区| 狂野欧美激情性xxxx| 久久国产乱子伦精品免费另类| 成年免费大片在线观看| 丁香欧美五月| 欧洲精品卡2卡3卡4卡5卡区| 午夜免费观看网址| 久久久精品大字幕| 亚洲国产欧美人成| 久久精品国产综合久久久| 嫩草影院精品99| 亚洲国产日韩欧美精品在线观看 | 精品福利观看| 国产精品久久视频播放| 亚洲 欧美 日韩 在线 免费| 午夜精品在线福利| ponron亚洲| 欧美日韩一级在线毛片| 午夜福利在线在线| 免费看日本二区| av国产免费在线观看| 特大巨黑吊av在线直播| 男女做爰动态图高潮gif福利片| 日本三级黄在线观看| 日韩欧美一区二区三区在线观看| 国产精品一区二区免费欧美| 亚洲熟妇中文字幕五十中出| 看片在线看免费视频| 午夜福利免费观看在线| 香蕉久久夜色| 最近最新中文字幕大全免费视频| 免费av不卡在线播放| 国产精品久久视频播放| 999久久久精品免费观看国产| 欧美乱妇无乱码| 色哟哟哟哟哟哟| 欧美日韩福利视频一区二区| 熟女电影av网| 露出奶头的视频| 91久久精品国产一区二区成人 | 一本一本综合久久| 国产伦一二天堂av在线观看| АⅤ资源中文在线天堂| 亚洲不卡免费看| 午夜影院日韩av| 一级作爱视频免费观看| 国产黄片美女视频| 久久久精品欧美日韩精品| 亚洲人成网站高清观看| 18禁黄网站禁片免费观看直播| 欧美日韩福利视频一区二区| 久久国产精品影院| 国产伦人伦偷精品视频| 可以在线观看毛片的网站| 黄片小视频在线播放| 欧美日韩亚洲国产一区二区在线观看| 波多野结衣高清无吗| 欧美成狂野欧美在线观看| 日本熟妇午夜| 俄罗斯特黄特色一大片| 人人妻人人看人人澡| 女生性感内裤真人,穿戴方法视频| 啦啦啦观看免费观看视频高清| 搡女人真爽免费视频火全软件 | 动漫黄色视频在线观看| 一进一出抽搐动态| 亚洲乱码一区二区免费版| 特大巨黑吊av在线直播| 国产91精品成人一区二区三区| 国产aⅴ精品一区二区三区波| 波多野结衣高清作品| 国产激情欧美一区二区| 最近视频中文字幕2019在线8| 久久国产精品人妻蜜桃| ponron亚洲| 精品一区二区三区视频在线观看免费| 国产精品三级大全| 老司机福利观看| 欧美最新免费一区二区三区 | 久久久久国产精品人妻aⅴ院| 精品乱码久久久久久99久播| 亚洲人与动物交配视频| 成人特级黄色片久久久久久久| 啪啪无遮挡十八禁网站| 内射极品少妇av片p| 国产亚洲欧美在线一区二区| 国产在线精品亚洲第一网站| 国内揄拍国产精品人妻在线| 免费观看精品视频网站| 天天一区二区日本电影三级| 国产av不卡久久| 国产在视频线在精品| 国产成人系列免费观看| 亚洲人成伊人成综合网2020| 人妻夜夜爽99麻豆av| 桃红色精品国产亚洲av| 久久精品人妻少妇| 国产精品久久久久久久久免 | 亚洲av成人av| 香蕉久久夜色| 午夜福利在线观看吧| 国产极品精品免费视频能看的| 黄片大片在线免费观看| 变态另类成人亚洲欧美熟女| 香蕉丝袜av| 人人妻人人看人人澡| 亚洲av日韩精品久久久久久密| 中文字幕久久专区| 久久精品91蜜桃| 成人国产一区最新在线观看| 亚洲av免费高清在线观看| 久久久久国产精品人妻aⅴ院| 乱人视频在线观看| 亚洲久久久久久中文字幕| 无遮挡黄片免费观看| 久久久久性生活片| 日韩人妻高清精品专区| tocl精华| 九九在线视频观看精品| 中亚洲国语对白在线视频| 老司机在亚洲福利影院| 国产亚洲av嫩草精品影院| 日韩免费av在线播放| 老司机午夜福利在线观看视频| 国产欧美日韩一区二区三| 丁香六月欧美| 男女之事视频高清在线观看| 女同久久另类99精品国产91| 中文字幕精品亚洲无线码一区| 成人三级黄色视频| 最近最新中文字幕大全电影3| 久久久国产精品麻豆| 欧美日韩瑟瑟在线播放| 嫁个100分男人电影在线观看| 日韩精品青青久久久久久| 成人亚洲精品av一区二区| 99精品欧美一区二区三区四区| 人人妻人人看人人澡| 亚洲欧美日韩卡通动漫| 我的老师免费观看完整版| 国产视频内射| 亚洲激情在线av| 国产激情偷乱视频一区二区| 丝袜美腿在线中文| 久久久久久人人人人人| 欧美极品一区二区三区四区| 老汉色av国产亚洲站长工具| 搞女人的毛片| 欧美乱妇无乱码| 亚洲乱码一区二区免费版| 国产高清videossex| 国产一区二区激情短视频| 两性午夜刺激爽爽歪歪视频在线观看| 久久性视频一级片| 精品久久久久久,| 国产aⅴ精品一区二区三区波| 淫秽高清视频在线观看| 黄色成人免费大全| 国产精品美女特级片免费视频播放器| 少妇丰满av| 国产激情欧美一区二区| 日韩av在线大香蕉| 日本免费一区二区三区高清不卡| 欧美成人免费av一区二区三区| 亚洲av美国av| 欧美日韩国产亚洲二区| 日本一二三区视频观看| 亚洲成人精品中文字幕电影| 国产精品一区二区免费欧美| 超碰av人人做人人爽久久 | 久久99热这里只有精品18| 天堂av国产一区二区熟女人妻| 亚洲欧美日韩卡通动漫| 一进一出抽搐gif免费好疼| 久久草成人影院| 亚洲国产欧洲综合997久久,| 亚洲最大成人中文| 国产真实乱freesex| 国产不卡一卡二| 国产精品电影一区二区三区| 亚洲国产精品成人综合色| 久久香蕉精品热| 久久久国产成人免费| 亚洲 国产 在线| 男人和女人高潮做爰伦理| 99久久成人亚洲精品观看| 日韩欧美三级三区| 国产伦精品一区二区三区四那| 90打野战视频偷拍视频| 欧美乱色亚洲激情| 91久久精品国产一区二区成人 | 男女午夜视频在线观看| 亚洲一区高清亚洲精品| 国产三级中文精品| 日本黄色片子视频| 国产真人三级小视频在线观看| 亚洲不卡免费看| 黄片小视频在线播放| 中文字幕久久专区| 90打野战视频偷拍视频| 国产午夜精品论理片| a在线观看视频网站| 亚洲自拍偷在线| 国产色婷婷99| 国产精品久久久久久人妻精品电影| 在线观看av片永久免费下载| 热99re8久久精品国产| 日韩成人在线观看一区二区三区| 日韩有码中文字幕| 国产精品 欧美亚洲| 国产精品久久久人人做人人爽| 最新美女视频免费是黄的| 国产亚洲欧美在线一区二区| 亚洲中文日韩欧美视频| 最近最新中文字幕大全免费视频| 亚洲成人免费电影在线观看| 狂野欧美白嫩少妇大欣赏| 国产三级中文精品| 中出人妻视频一区二区| 一进一出好大好爽视频| 最近最新中文字幕大全电影3| 欧美日韩国产亚洲二区| 男女之事视频高清在线观看| 欧美日韩综合久久久久久 | 国产视频一区二区在线看| 黄色片一级片一级黄色片| 成人三级黄色视频| xxx96com| 欧美一区二区国产精品久久精品| 国产精品亚洲美女久久久| 亚洲精华国产精华精| 日本黄大片高清| 午夜激情福利司机影院| 国内揄拍国产精品人妻在线| 国产精品一区二区免费欧美| 九色成人免费人妻av| 在线国产一区二区在线| 免费观看人在逋| 亚洲专区国产一区二区| 男插女下体视频免费在线播放| 免费在线观看影片大全网站| 色视频www国产| 男女做爰动态图高潮gif福利片| 人妻丰满熟妇av一区二区三区| 国产一区二区亚洲精品在线观看| 亚洲成av人片在线播放无| 啪啪无遮挡十八禁网站| 91久久精品电影网| 首页视频小说图片口味搜索| 久久99热这里只有精品18| 亚洲欧美日韩高清在线视频| 老熟妇乱子伦视频在线观看| 男女之事视频高清在线观看| 欧美区成人在线视频| 在线免费观看不下载黄p国产 | www国产在线视频色| 精品国产美女av久久久久小说|