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

    基于SIMD 的并行傅里葉空間圖像相似度計算

    2021-11-18 02:19:18郭渝洛邊浩東董潤婷唐嘉豪王曉英黃建強(qiáng)
    計算機(jī)工程 2021年11期
    關(guān)鍵詞:矢量化傅里葉內(nèi)存

    郭渝洛,邊浩東,董潤婷,唐嘉豪,王曉英,黃建強(qiáng)

    (青海大學(xué) 計算機(jī)技術(shù)與應(yīng)用系,西寧 810016)

    0 概述

    二十世紀(jì)七十年代,TAYLOR 和GLAESER 研發(fā)了冷凍電鏡(cryo-Electron Microscopy,cryo-EM)。該項技術(shù)發(fā)展至今,已經(jīng)成為研究生物大分子結(jié)構(gòu)與功能強(qiáng)有力的手段,其簡化了生物細(xì)胞的成像過程,提高了成像質(zhì)量,將生物化學(xué)帶入一個新時代[1-3]。

    冷凍電鏡是在低溫下使用透射電子顯微鏡觀察樣品的顯微技術(shù),即把樣品保存在液氮或液氦溫度下,通過對其某方向的投影顯微像在時空中經(jīng)調(diào)整后進(jìn)行疊加,從而提高信噪比,最終將不同投影方向的顯微像在三維空間進(jìn)行重構(gòu),獲得大分子的三維結(jié)構(gòu)。

    實際上,基于2D 投影的3D 重構(gòu)具有挑戰(zhàn)性。首先,樣品中生物分子在隨機(jī)分布后具有不同的角度,很難確定它們正確的角度,因此,需要多次迭代步驟才能使最終的模型收斂;其次,為了避免損壞樣品,通常使用低劑量的電子束進(jìn)行輻照,而這樣獲得的電子顯微像具有高噪聲和低對比度,需要大量的電子顯微圖像來生成具有高分辨率的3D 模型。由此可見,冷凍電鏡模型重構(gòu)依賴于數(shù)以萬計的投影圖片進(jìn)行分析、組裝和優(yōu)化,冷凍電鏡三維重構(gòu)需要超過1 petaflops 的計算能力[4]。

    目前許多研究學(xué)者對冷凍電鏡三維重建計算的優(yōu)化提出了許多有效的解決方案,如文獻(xiàn)[5]基于分塊流模型的GPU 集群并行化冷凍電鏡三維重建,文獻(xiàn)[6]在CPU-GPU 異構(gòu)系統(tǒng)上并行化冷凍電鏡三維重建。

    在冷凍電鏡三維重構(gòu)過程中,傅里葉空間圖像相似度計算是調(diào)用最為頻繁的計算,其計算成本較高,存在應(yīng)用程序尚未充分利用并行化優(yōu)勢、編譯器自動對代碼進(jìn)行矢量化的優(yōu)化效果不佳和數(shù)據(jù)存儲架構(gòu)導(dǎo)致不必要內(nèi)存消耗等問題。隨著每個芯片處理核數(shù)的增加,負(fù)載均衡的重要性也在不斷提高,處理核的利用率是多核系統(tǒng)性能的一個關(guān)鍵指標(biāo)[7]。文獻(xiàn)[8-9]對經(jīng)典的負(fù)載平衡方法進(jìn)行了回顧和分類,基于此,本文對程序進(jìn)行手動負(fù)載均衡優(yōu)化操作,使各處理核對計算任務(wù)均衡處理,提高程序的并行效率。

    在現(xiàn)代微處理器中,單指令多數(shù)據(jù)流(Single Instruction Multiple Data,SIMD)作為一種利用通用核中數(shù)據(jù)級并行性的方法[10]得到了廣泛的認(rèn)可[11],SIMD 指令集允許程序員與編譯器通過CPU 實現(xiàn)數(shù)據(jù)級并行性,提高運(yùn)算效率。SIMD 矢量化在稀疏矩陣向量乘法上有著優(yōu)異的性能提升效果[12]。因此,本文借鑒SpMV 中用SIMD 矢量化對傅里葉空間圖像相似度計算進(jìn)行優(yōu)化。

    隨著CPU 計算速度越來越快,處理器速度與訪問主內(nèi)存速度差距日益增大,以至于程序?qū)⒋蟛糠諧PU時間花費(fèi)在等待內(nèi)存訪問上。緩存(cache)[13]技術(shù)能夠有效減少磁盤訪問次數(shù),提高數(shù)據(jù)訪問效率。但硬件緩存大多依賴于空間局部性來實現(xiàn)高效的內(nèi)存訪問,且多數(shù)內(nèi)存布局優(yōu)化算法都是基于深入理解程序的算法以及對原有數(shù)據(jù)結(jié)構(gòu)進(jìn)行調(diào)整。文獻(xiàn)[14]指出算法的內(nèi)存訪問模式已成為決定算法運(yùn)行時間的關(guān)鍵因素,文獻(xiàn)[15]則對大網(wǎng)格數(shù)據(jù)布局進(jìn)行優(yōu)化,提高了緩存的一致性,減少了緩存未命中率。

    更改數(shù)據(jù)存儲結(jié)構(gòu)能夠獲得更優(yōu)的存儲分配效果[16],但原程序中的數(shù)據(jù)結(jié)構(gòu)在地址空間中分散,不利于內(nèi)存訪問,因此,需要設(shè)計新的數(shù)據(jù)結(jié)構(gòu)實現(xiàn)對空間局部性的有效利用。本文提出一種基于SIMD的并行傅里葉空間圖像相似度算法。手動對任務(wù)進(jìn)行均勻分配操作,從而在多核處理器上實現(xiàn)負(fù)載均衡,同時使用AVX-512 指令集進(jìn)行高效的矢量化操作。此外,通過優(yōu)化原程序中的數(shù)據(jù)結(jié)構(gòu)并使其字節(jié)對齊,降低緩存缺失率。

    1 研究背景

    1.1 冷凍電鏡三維重建

    冷凍電鏡結(jié)構(gòu)解析的理論基礎(chǔ)是電鏡三維重構(gòu)原理[17],該原理基于數(shù)學(xué)中的中央截面定理和傅立葉變換的性質(zhì)。中央截面定理的含義是:一個函數(shù)沿某方向投影函數(shù)的傅立葉變換等于此函數(shù)的傅立葉變換通過原點(diǎn)且垂直于此投影方向的截面函數(shù),即一個生物樣品的電鏡圖像的傅里葉變換等于該三維物體的傅里葉變換通過樣品中心(設(shè)定為坐標(biāo)原點(diǎn))并垂直于攝像方向的截面,如圖1 所示。

    圖1 中央截面定理示意圖Fig.1 Schematic diagram of central section theorem

    由于一個函數(shù)的傅立葉變換的逆傅立葉變換等價于原來的函數(shù),因此利用傅里葉變換可以很容易地實現(xiàn)圖像的旋轉(zhuǎn)縮放和平移不變性。根據(jù)中央截面定理和傅里葉變換的性質(zhì),當(dāng)利用透射電子顯微鏡獲得的生物樣品多角度放大電子顯微圖像足夠多時,就能得到生物樣品在傅里葉空間的三維信息,再經(jīng)過傅里葉逆變換便能得到物體的三維結(jié)構(gòu),如圖2 所示[18]。

    圖2 冷凍電鏡三維重構(gòu)過程Fig.2 Three dimensional reconstruction process of cryo-EM

    在冷凍電鏡結(jié)構(gòu)解析的實踐中,可以根據(jù)生物樣品的性質(zhì)及其特點(diǎn),選擇不同的顯微鏡成像及三維重構(gòu)方法,目前主要使用單顆粒重構(gòu)、電子斷層掃描重構(gòu)等方法針對不同的生物大分子復(fù)合體及亞細(xì)胞結(jié)構(gòu)進(jìn)行解析[19]。

    冷凍電鏡單粒子法是獲得三維重構(gòu)圖像的重要辦法[20-21]。單粒子法就是對分離純化的顆粒分子分別成像,其適合的樣品分子量范圍為80~50 MD,最高分辨率約3 ?,其基本原理就是基于分子結(jié)構(gòu)同一性的假設(shè),利用不同投影角度的多個分子的顯微放大二維圖像進(jìn)行同一分析,通過對正、加和平均等圖像操作提高信噪比,最后將不同投影方向的單顆粒顯微像在三維空間進(jìn)行重構(gòu),獲得三維模型。

    1.2 傅里葉空間圖像相似度算法

    在冷凍電鏡數(shù)據(jù)分析處理中,傅里葉空間圖像相似度計算被頻繁調(diào)用,其主要使用計算樣品的二維真實圖像與空間中三維重構(gòu)模型的投影圖像之間的相似度,計算公式如下:

    傅里葉空間圖像相似度計算在程序中的實現(xiàn)代碼如算法1 所示,主要計算步驟如圖3 所示。

    圖3 傅里葉空間圖像相似度計算的主要步驟Fig.3 Main steps of Fourier space image similarity calculation

    首先將disturb0 與ctf 相乘,然后與復(fù)數(shù)pri 相乘,接著計算dat 與步驟2 結(jié)果相減后的范數(shù),與上一步的result 相加后,i加1,重復(fù)執(zhí)行步驟1,直至i=n-1。

    算法1串行傅里葉空間圖像相似度算法

    2 傅里葉空間圖像相似度計算優(yōu)化方法

    2.1 手動負(fù)載均衡

    經(jīng)過OpenMP 對程序進(jìn)行并行化處理后,程序具有良好的并行性。但是通過vtune 工具進(jìn)行分析后,有大量資源花費(fèi)在了Spin time 上。Spin time 是CPU 繁忙的等待時間,是等待其他同步資源處理的自旋等待時間。當(dāng)同步API 導(dǎo)致CPU 在軟件線程等待進(jìn)行輪詢時,通常會發(fā)生這種情況。對于并行程序,并行循環(huán)占大部分執(zhí)行時間。因此,減少并行循環(huán)的耗費(fèi)也是提升整個程序性能的關(guān)鍵,需要對其進(jìn)行手動負(fù)載均衡優(yōu)化。

    首先根據(jù)運(yùn)行環(huán)境CPU 的線程數(shù),盡可能將任務(wù)均分給每個線程上。如算法2 所示,本文用Begin與end 數(shù)組記錄下每個線程處理數(shù)據(jù)的起始點(diǎn)與終點(diǎn)。在函數(shù)logDataVSPrior 中將任務(wù)均勻地分給每個線程,盡可能使程序負(fù)載均衡。在并行循環(huán)計算完成后,再對每個線程計算的result 進(jìn)行累加,如算法3 所示。

    算法2根據(jù)線程數(shù)對任務(wù)進(jìn)行分配

    算法3手動負(fù)載均衡后的傅里葉空間圖像相似度算法

    2.2 SIMD 矢量化

    SIMD 矢量化操作在優(yōu)化稀疏矩陣向量乘法上表現(xiàn)優(yōu)異,其采用一個控制器來控制多個處理器,同時對一組數(shù)據(jù)中的每一個分別執(zhí)行相同操作,從而實現(xiàn)空間并行性。利用perf 工具分析特定程序后,編譯器已經(jīng)自動矢量化程序中主要的計算,但仍占據(jù)了大量的總體開銷。為了提高系統(tǒng)整體性能,需要在程序中手動添加SIMD 內(nèi)聯(lián)函數(shù)對其進(jìn)行矢量化優(yōu)化。從算法4 中可以看出,logDataVSPrior 函數(shù)中有大量數(shù)據(jù)執(zhí)行單個單元的運(yùn)算,如乘法、加法和減法,適合使用SIMD 向量化對其進(jìn)行優(yōu)化。因此,本文將SIMD 矢量化操作添加到logDataVSPrior 函數(shù)中。下文選擇INTEL 的AVX-512 指令集,并給出詳細(xì)優(yōu)化步驟。

    算法4更新數(shù)據(jù)結(jié)構(gòu)后傅里葉空間圖像相似度算法的實現(xiàn)

    為了方便使用SIMD 指令集,將復(fù)數(shù)數(shù)組拆分為實部數(shù)組和虛部數(shù)組,分別對復(fù)數(shù)的實部和虛部進(jìn)行計算,SIMD 優(yōu)化步驟如圖4 所示。首先利用_mm512_mul_pd 指令實現(xiàn)實數(shù)ctf 與實數(shù)disturb0 相乘的操作,并使用_mm512_fnmadd_pd 指令分別計算實部與虛部的值;然后利用_mm512_mul_pd 指令和_mm512_fmadd_pd 指令計算算法 4 中的“real*real+comp*comp”,通 過_mm512_fmadd_pd 指令將步驟4 的計算結(jié)果與sigRcp 相乘再與mark 進(jìn)行相加,并把結(jié)果存儲在mark 中;重復(fù)執(zhí)行上述步驟,直到本線程上的任務(wù)處理完畢;最后利用_mm512_add_pd 指令將每個線程上得到的計算結(jié)果進(jìn)行累加,得到二范數(shù)之和。

    圖4 SIMD 優(yōu)化步驟Fig.4 SIMD optimization step

    2.3 內(nèi)存訪問優(yōu)化

    目前CPU 計算速度遠(yuǎn)超內(nèi)存訪問速度,緩慢的內(nèi)存訪問速度成為限制系統(tǒng)整體性能的主要瓶頸。利用Linux 系統(tǒng)的Perf 工具進(jìn)行分析,根據(jù)分析結(jié)果可以推斷出,由于較高的LLC 缺失率,CPU 需耗費(fèi)時間等待從本地或遠(yuǎn)程DRAM 中獲取數(shù)據(jù)。由于原程序的數(shù)據(jù)存儲架構(gòu)不利于內(nèi)存訪問,導(dǎo)致不必要的內(nèi)存消耗,因此提高內(nèi)存訪問效率也是提升整個程序性能的關(guān)鍵。

    SIMD 矢量化中提出的數(shù)據(jù)結(jié)構(gòu),將復(fù)數(shù)分為實部向量與虛部向量,在logDataVSPrior 函數(shù)計算中存在大量的相對較長數(shù)據(jù)訪問操作,這對內(nèi)存訪問非常不利。如圖5 所示,對于需要計算的6 個數(shù)組,需要獲取6 個位置的數(shù)據(jù)值,然后進(jìn)行計算。假設(shè)每個數(shù)據(jù)之間的步長比當(dāng)前CPU 的緩存行大得多,那么需要執(zhí)行6 次高速緩存行替換操作才能獲得6 個不同位置的值。然而,多次替換高速緩存行的操作會影響緩存性能。

    圖5 SIMD 優(yōu)化后的數(shù)據(jù)結(jié)構(gòu)Fig.5 Data structure after SIMD optimization

    為解決這個問題,本文提出一種有效的數(shù)據(jù)結(jié)構(gòu)。如圖6 所示,將6 個不同的數(shù)組鄰接存放,這樣可以將一次循環(huán)內(nèi)需要使用的數(shù)據(jù)合并到新結(jié)構(gòu)向量中,僅需訪問一次索引位置,即可獲得需要計算的連續(xù)數(shù)據(jù)。與原來的數(shù)據(jù)結(jié)構(gòu)相比,合并后的數(shù)據(jù)結(jié)構(gòu)能夠更好地實現(xiàn)緩存數(shù)據(jù)的重用,提高緩存命中率。這是因為合并后的數(shù)據(jù)結(jié)構(gòu)使將來用到的數(shù)據(jù)與當(dāng)前正在使用的數(shù)據(jù)在空間地址上相鄰,從而減少了替換高速緩存行的操作。

    圖6 本文提出的數(shù)據(jù)存儲結(jié)構(gòu)Fig.6 Data storage structure proposed in this paper

    目前,計算機(jī)的內(nèi)存空間都是按照字節(jié)進(jìn)行劃分的,多數(shù)CPU 只從對齊的地址開始加載數(shù)據(jù),如果數(shù)據(jù)不按照一定的規(guī)則存儲,則會降低讀取速度,從而影響計算效率。因此,字節(jié)對齊在CPU 架構(gòu)中起著重要的作用。當(dāng)高速緩存行獲取未字節(jié)對齊的數(shù)據(jù)時,會發(fā)生圖7(a)所示的情況。從圖中可以看出,int 類型占用4 Byte 的內(nèi)存空間,當(dāng)一個變量int 的起始地址是1 時,那么CPU 需要進(jìn)行2 次數(shù)據(jù)讀取操作,這是因為僅一次讀取操作無法完全獲得所需的數(shù)據(jù),所以需要多次讀取來獲取剩余的數(shù)據(jù)。圖7(b)顯示了數(shù)據(jù)按照內(nèi)存對齊的方式存放后,只需要1 次讀取操作就能完全獲得所需數(shù)據(jù),提高了讀取速度。

    圖7 數(shù)據(jù)字節(jié)對齊操作Fig.7 Data byte alignment operation

    3 實驗與結(jié)果分析

    3.1 設(shè)備信息

    本文使用的實驗平臺是Intel 的Skylake 架構(gòu)CPU。對于SIMD 指令集,選擇CPU 支持的AVX-512 指令集??焖俑咝У腛penMP 并行語言用于多線程實現(xiàn)。硬件和軟件配置如表1 所示。

    表1 實驗平臺信息Table 1 Experimental platform information

    3.2 性能比較與分析

    如圖8 所示,本文演示了10 000、20 000、40 000、80 000、和100 000 張真實圖像與投影圖像的所有像素在傅里葉空間中的二范數(shù)之和的性能,并比較了4 種不同狀態(tài)下的加速比性能,即原代碼運(yùn)行時間/優(yōu)化后代碼運(yùn)行時間。

    圖8 不同大小數(shù)據(jù)集上的加速比Fig.8 Speedup on different size datasets

    在圖8 中,原代碼表示使用OenMP 進(jìn)行并行化處理的傅里葉空間圖像相似度計算的時間成本,優(yōu)化1 表示僅實現(xiàn)手動負(fù)載均衡優(yōu)化的時間成本,優(yōu)化2 表示在優(yōu)化1 的基礎(chǔ)上同時實現(xiàn)手動SIMD 矢量化優(yōu)化的時間成本,優(yōu)化3 表示實現(xiàn)第2 節(jié)提到的所有優(yōu)化方法。

    在同一實驗平臺上,可以發(fā)現(xiàn)優(yōu)化1 的時間成本相比原代碼有明顯的性能提升,主要有以下3 方面原因:

    1)在經(jīng)過手動負(fù)載均衡優(yōu)化后,各處理核對任務(wù)均衡處理,進(jìn)行負(fù)載均衡處理的時間成本可以忽略不計,并且能夠有效減少負(fù)載不均衡導(dǎo)致的回滾次數(shù),提高程序并行效率。

    2)實現(xiàn)SIMD 矢量化的優(yōu)化2 比優(yōu)化1 具有更快的計算速度,因為自動矢量化并不能充分利用機(jī)器中SIMD 的性能,經(jīng)過手動矢量化后達(dá)到了更好的并行效果。

    3)優(yōu)化3 中使用了創(chuàng)新的數(shù)據(jù)結(jié)構(gòu)以及字節(jié)對齊操作,使即將要用到的數(shù)據(jù)連續(xù)存儲,實現(xiàn)了優(yōu)秀的空間局部性,字節(jié)對齊操作提高了讀取速度。因此,優(yōu)化3 相較于之前的優(yōu)化有較明顯的性能提升。

    對于不同大小的數(shù)據(jù)集,性能影響會有所不同。從圖8 中可以看出,在不同大小的數(shù)據(jù)集上都有相同的性能優(yōu)化趨勢,在數(shù)據(jù)集規(guī)模為10 000 和20 000 時,程序具有更出色的性能提升效果,這是因為其空間開銷接近高速緩存空間大小,較小的內(nèi)存消耗更適合利用高速緩存的空間局部性。

    為更直觀地反映本文方法的優(yōu)化性能,對比不同數(shù)據(jù)集上的程序加速比性能。如表2 所示??梢钥闯觯c原程序相比,優(yōu)化后的程序運(yùn)行時間平均提高了5.132 倍加速比。隨著數(shù)據(jù)集增大,程序性能依舊得到穩(wěn)定的提高,這表明本文優(yōu)化方法不會因為數(shù)據(jù)集增大而導(dǎo)致性能下降。

    表2 在不同數(shù)據(jù)集上的程序加速比Table 2 Program speedup on different datasets

    4 結(jié)束語

    針對傅里葉空間圖像相似度算法,本文在單個節(jié)點(diǎn)上通過手動負(fù)載均衡、手動SIMD 矢量化和內(nèi)存訪問優(yōu)化這3 種優(yōu)化方法來獲得更高效的性能。測試結(jié)果表明,優(yōu)化后的程序具有更穩(wěn)定的性能。本文僅對單節(jié)點(diǎn)的傅里葉空間圖像相似度算法進(jìn)行優(yōu)化,下一步將針對多節(jié)點(diǎn)上的程序做優(yōu)化處理和測試。

    猜你喜歡
    矢量化傅里葉內(nèi)存
    “春夏秋冬”的內(nèi)存
    雙線性傅里葉乘子算子的量化加權(quán)估計
    基于小波降噪的稀疏傅里葉變換時延估計
    交互式矢量化技術(shù)在水文站網(wǎng)分布圖編繪中的應(yīng)用
    科技視界(2016年10期)2016-04-26 21:12:24
    基于傅里葉變換的快速TAMVDR算法
    基于VP Studio和CASS的柵格地形圖矢量化方法
    快速離散傅里葉變換算法研究與FPGA實現(xiàn)
    電測與儀表(2015年5期)2015-04-09 11:30:44
    遙感圖像多尺度分割算法與矢量化算法的集成
    基于內(nèi)存的地理信息訪問技術(shù)
    矢量化技術(shù)在檔案管理中的應(yīng)用
    河南科技(2013年3期)2013-04-10 14:34:43
    av福利片在线观看| 一级毛片久久久久久久久女| 欧美性感艳星| a 毛片基地| 久久久久久久大尺度免费视频| 日本欧美视频一区| 最近中文字幕2019免费版| av国产免费在线观看| 黄片wwwwww| 国产真实伦视频高清在线观看| 国产精品99久久99久久久不卡 | 国产老妇伦熟女老妇高清| 91久久精品国产一区二区三区| 视频中文字幕在线观看| 日韩亚洲欧美综合| 免费看av在线观看网站| 精品亚洲乱码少妇综合久久| 国产一区有黄有色的免费视频| 久久精品国产a三级三级三级| 中文字幕亚洲精品专区| 在线亚洲精品国产二区图片欧美 | 99久久精品热视频| 久久久久精品久久久久真实原创| 一区二区三区精品91| 精品国产露脸久久av麻豆| 亚洲成人av在线免费| 免费av不卡在线播放| 天堂中文最新版在线下载| 国产熟女欧美一区二区| 熟女av电影| 久久久久久久久久成人| 伊人久久精品亚洲午夜| 国产探花极品一区二区| 亚洲最大成人中文| 纵有疾风起免费观看全集完整版| 在线观看一区二区三区| 激情五月婷婷亚洲| 国产精品嫩草影院av在线观看| 18禁在线无遮挡免费观看视频| 免费观看的影片在线观看| 久热久热在线精品观看| 99久久人妻综合| 熟妇人妻不卡中文字幕| 欧美极品一区二区三区四区| 亚洲人成网站高清观看| 麻豆精品久久久久久蜜桃| 建设人人有责人人尽责人人享有的 | 欧美成人精品欧美一级黄| 精品一区二区三区视频在线| 国产视频内射| 国产视频内射| 五月天丁香电影| 麻豆成人午夜福利视频| 亚洲av综合色区一区| 观看免费一级毛片| 麻豆成人av视频| 肉色欧美久久久久久久蜜桃| 久久久午夜欧美精品| 成人国产av品久久久| 小蜜桃在线观看免费完整版高清| 国产精品偷伦视频观看了| 少妇的逼好多水| 亚洲国产欧美人成| 国产一区二区三区综合在线观看 | 国产精品嫩草影院av在线观看| 水蜜桃什么品种好| 成年av动漫网址| a级一级毛片免费在线观看| 国产黄片美女视频| 国产精品国产三级专区第一集| 精品久久久久久电影网| 嫩草影院入口| 成人综合一区亚洲| 国产极品天堂在线| 久久 成人 亚洲| 在线亚洲精品国产二区图片欧美 | 在线精品无人区一区二区三 | 久久精品国产亚洲网站| av在线app专区| 亚洲国产精品国产精品| 国产精品国产av在线观看| 人人妻人人爽人人添夜夜欢视频 | 妹子高潮喷水视频| 国产深夜福利视频在线观看| 99久久精品一区二区三区| 五月开心婷婷网| 久久久亚洲精品成人影院| 亚洲av成人精品一二三区| 成人影院久久| 国产乱来视频区| 亚洲久久久国产精品| 久久国产乱子免费精品| 性色avwww在线观看| 久久久久久久亚洲中文字幕| 久久精品人妻少妇| 18禁在线播放成人免费| 午夜激情福利司机影院| 中文在线观看免费www的网站| 一边亲一边摸免费视频| 一边亲一边摸免费视频| 亚洲色图综合在线观看| 久久97久久精品| 在线看a的网站| 久久鲁丝午夜福利片| 久久精品国产亚洲av涩爱| 欧美日韩综合久久久久久| 久久99热这里只有精品18| 成人18禁高潮啪啪吃奶动态图 | 女人久久www免费人成看片| 亚洲精品乱码久久久久久按摩| 91午夜精品亚洲一区二区三区| 男女下面进入的视频免费午夜| 在线观看三级黄色| 亚洲欧美日韩卡通动漫| 中文字幕精品免费在线观看视频 | 一级黄片播放器| 亚洲av不卡在线观看| 国产高清三级在线| 国产片特级美女逼逼视频| 一级av片app| 久久久久久久久久成人| 一区二区三区精品91| 国产欧美另类精品又又久久亚洲欧美| 伦理电影免费视频| 久久久久久久精品精品| 欧美xxxx性猛交bbbb| 久久精品国产亚洲av天美| 欧美激情国产日韩精品一区| 午夜福利在线观看免费完整高清在| 2022亚洲国产成人精品| 国产精品国产三级国产av玫瑰| 久久ye,这里只有精品| 一区二区三区免费毛片| 国产在视频线精品| 精品一区二区免费观看| 久久人人爽av亚洲精品天堂 | 午夜免费男女啪啪视频观看| 国产精品.久久久| 亚洲精品久久久久久婷婷小说| 亚洲自偷自拍三级| 免费观看的影片在线观看| 精品亚洲成国产av| 久久久久久久久久人人人人人人| 国产一区二区在线观看日韩| 天堂8中文在线网| 人妻系列 视频| 秋霞伦理黄片| 亚洲精华国产精华液的使用体验| 国产一区二区三区综合在线观看 | 永久网站在线| 国产黄频视频在线观看| 亚洲av国产av综合av卡| 国产精品偷伦视频观看了| 国国产精品蜜臀av免费| av一本久久久久| 免费观看无遮挡的男女| 在线免费观看不下载黄p国产| 中文字幕亚洲精品专区| 97超碰精品成人国产| 最近中文字幕2019免费版| 日本与韩国留学比较| 最近最新中文字幕免费大全7| 久久精品久久精品一区二区三区| 国产美女午夜福利| 97在线人人人人妻| 亚洲色图av天堂| 最黄视频免费看| 久久婷婷青草| 亚洲av不卡在线观看| 成人综合一区亚洲| 色网站视频免费| 草草在线视频免费看| 天天躁夜夜躁狠狠久久av| 亚洲第一区二区三区不卡| 久久热精品热| 日韩伦理黄色片| 青春草亚洲视频在线观看| 日本黄色片子视频| 国产探花极品一区二区| 国产午夜精品久久久久久一区二区三区| 亚洲av成人精品一二三区| 亚洲aⅴ乱码一区二区在线播放| 亚洲人成网站在线播| 夜夜爽夜夜爽视频| 插逼视频在线观看| 欧美bdsm另类| 亚洲,一卡二卡三卡| 狂野欧美白嫩少妇大欣赏| 国产在线一区二区三区精| 日韩国内少妇激情av| 免费观看a级毛片全部| 免费观看无遮挡的男女| 久久精品国产亚洲av天美| h日本视频在线播放| 日日啪夜夜撸| 91久久精品国产一区二区三区| 国产精品久久久久久精品电影小说 | 大又大粗又爽又黄少妇毛片口| 午夜福利在线观看免费完整高清在| 国产伦精品一区二区三区视频9| 色吧在线观看| 国产黄片美女视频| 欧美日韩精品成人综合77777| 欧美精品国产亚洲| 男女免费视频国产| 精品国产乱码久久久久久小说| 亚洲国产精品一区三区| 麻豆成人午夜福利视频| 性色av一级| 岛国毛片在线播放| 精品一区二区免费观看| 日韩大片免费观看网站| 亚洲国产色片| 亚洲人成网站高清观看| 欧美三级亚洲精品| 日韩不卡一区二区三区视频在线| 青春草亚洲视频在线观看| 国产成人aa在线观看| 国产亚洲av片在线观看秒播厂| 国产在线免费精品| 日本wwww免费看| 亚洲婷婷狠狠爱综合网| 国产无遮挡羞羞视频在线观看| av在线老鸭窝| 大香蕉久久网| av免费观看日本| 高清日韩中文字幕在线| 日本-黄色视频高清免费观看| 美女主播在线视频| 国产精品一区二区在线不卡| 国产淫片久久久久久久久| 午夜福利网站1000一区二区三区| 国产精品免费大片| 亚洲精品第二区| 精品少妇黑人巨大在线播放| 午夜福利网站1000一区二区三区| 色吧在线观看| 亚洲高清免费不卡视频| 特大巨黑吊av在线直播| 亚洲人成网站在线观看播放| 免费观看av网站的网址| 少妇人妻久久综合中文| 精品久久久精品久久久| 久久久a久久爽久久v久久| 夜夜看夜夜爽夜夜摸| 亚洲av男天堂| 99久久精品国产国产毛片| 成人一区二区视频在线观看| 免费观看av网站的网址| 亚洲内射少妇av| 日本欧美国产在线视频| 精品一品国产午夜福利视频| 亚洲av日韩在线播放| 国产男人的电影天堂91| 久久精品夜色国产| 亚洲国产精品999| 亚洲av中文av极速乱| 丰满乱子伦码专区| 婷婷色综合www| 蜜桃久久精品国产亚洲av| 国产成人精品福利久久| 国产伦精品一区二区三区视频9| 久久6这里有精品| av黄色大香蕉| 午夜福利在线观看免费完整高清在| 国国产精品蜜臀av免费| 国产精品蜜桃在线观看| 色网站视频免费| 中文精品一卡2卡3卡4更新| 日韩亚洲欧美综合| 欧美高清性xxxxhd video| .国产精品久久| 美女国产视频在线观看| 精品少妇久久久久久888优播| 国产亚洲av片在线观看秒播厂| 三级经典国产精品| 欧美精品国产亚洲| 晚上一个人看的免费电影| 性高湖久久久久久久久免费观看| 99热国产这里只有精品6| 欧美日韩国产mv在线观看视频 | 国产探花极品一区二区| 国产精品无大码| 王馨瑶露胸无遮挡在线观看| 高清毛片免费看| h日本视频在线播放| 久久久国产一区二区| 久久精品久久久久久久性| 免费看不卡的av| 欧美日韩在线观看h| 午夜福利视频精品| 亚洲国产毛片av蜜桃av| 免费观看av网站的网址| 丰满乱子伦码专区| 国产精品国产三级国产专区5o| 色综合色国产| 国产成人91sexporn| 亚洲国产色片| 日韩国内少妇激情av| av免费在线看不卡| 日韩亚洲欧美综合| 麻豆成人av视频| av免费观看日本| 国产精品久久久久久av不卡| 亚洲av成人精品一区久久| 天天躁夜夜躁狠狠久久av| 国产男女内射视频| 大香蕉97超碰在线| 99热这里只有是精品50| 边亲边吃奶的免费视频| 成人18禁高潮啪啪吃奶动态图 | 中国美白少妇内射xxxbb| 免费高清在线观看视频在线观看| 偷拍熟女少妇极品色| 蜜桃亚洲精品一区二区三区| 精品国产露脸久久av麻豆| 最黄视频免费看| 在线天堂最新版资源| 在线观看一区二区三区| 午夜免费鲁丝| 一个人免费看片子| 在线天堂最新版资源| 午夜福利在线在线| 一个人看的www免费观看视频| 亚州av有码| av不卡在线播放| 亚洲成人中文字幕在线播放| 18禁裸乳无遮挡动漫免费视频| 中文欧美无线码| av国产精品久久久久影院| 亚洲精品国产av蜜桃| 亚洲av欧美aⅴ国产| 亚洲成人手机| kizo精华| 亚洲成人中文字幕在线播放| 亚洲成人手机| 精品一区二区三卡| 黄片无遮挡物在线观看| 91精品国产国语对白视频| 新久久久久国产一级毛片| 汤姆久久久久久久影院中文字幕| 亚洲aⅴ乱码一区二区在线播放| 久久久久久久久久久丰满| 插逼视频在线观看| 亚洲精品色激情综合| 亚洲国产精品成人久久小说| 内射极品少妇av片p| 777米奇影视久久| 18禁动态无遮挡网站| 亚洲电影在线观看av| 男女边吃奶边做爰视频| 亚洲图色成人| 这个男人来自地球电影免费观看 | 热re99久久精品国产66热6| 联通29元200g的流量卡| 一区二区三区精品91| 高清欧美精品videossex| 亚洲性久久影院| 成人国产av品久久久| 夜夜看夜夜爽夜夜摸| 我的女老师完整版在线观看| 国产人妻一区二区三区在| 久久av网站| 亚洲成人中文字幕在线播放| 一本久久精品| 伦精品一区二区三区| 亚洲av男天堂| 啦啦啦啦在线视频资源| 亚洲精品自拍成人| av不卡在线播放| 欧美日韩综合久久久久久| 一二三四中文在线观看免费高清| 麻豆成人av视频| 久久ye,这里只有精品| 亚洲丝袜综合中文字幕| 日日撸夜夜添| 久久久久网色| 欧美激情极品国产一区二区三区 | 丰满乱子伦码专区| 老熟女久久久| 亚洲真实伦在线观看| 国产免费视频播放在线视频| 亚洲av成人精品一区久久| 免费高清在线观看视频在线观看| 欧美成人一区二区免费高清观看| 国产高清三级在线| 久久热精品热| 啦啦啦啦在线视频资源| av在线app专区| 自拍偷自拍亚洲精品老妇| 插阴视频在线观看视频| 十八禁网站网址无遮挡 | av国产精品久久久久影院| 九草在线视频观看| 国产精品爽爽va在线观看网站| 免费少妇av软件| 亚洲精品成人av观看孕妇| 成人高潮视频无遮挡免费网站| 日韩中字成人| 人妻少妇偷人精品九色| 秋霞伦理黄片| 日本vs欧美在线观看视频 | 精品少妇久久久久久888优播| 国产精品久久久久久久久免| 性高湖久久久久久久久免费观看| 伦理电影免费视频| 精品亚洲成国产av| 久久国产乱子免费精品| 精品一品国产午夜福利视频| 高清欧美精品videossex| 亚洲人成网站在线观看播放| 99热国产这里只有精品6| 狂野欧美激情性bbbbbb| 一级毛片黄色毛片免费观看视频| 日韩强制内射视频| 国产色婷婷99| 久久精品久久久久久噜噜老黄| 国产精品国产三级国产专区5o| 身体一侧抽搐| 国模一区二区三区四区视频| 久久久久久久久久成人| 欧美少妇被猛烈插入视频| 蜜桃久久精品国产亚洲av| 国产黄频视频在线观看| 水蜜桃什么品种好| 免费观看在线日韩| 亚洲高清免费不卡视频| 免费看光身美女| 多毛熟女@视频| tube8黄色片| 一区二区av电影网| 国产一级毛片在线| 欧美亚洲 丝袜 人妻 在线| 亚洲精品日本国产第一区| .国产精品久久| 国产av国产精品国产| 国产伦理片在线播放av一区| 男女边吃奶边做爰视频| 中文字幕久久专区| 久久久成人免费电影| 欧美日韩亚洲高清精品| 欧美精品一区二区免费开放| 午夜激情福利司机影院| 国产精品一区二区性色av| 18禁裸乳无遮挡免费网站照片| 国产亚洲午夜精品一区二区久久| a 毛片基地| 99精国产麻豆久久婷婷| 久久韩国三级中文字幕| 国产伦在线观看视频一区| 中文精品一卡2卡3卡4更新| videos熟女内射| 黄片wwwwww| 超碰97精品在线观看| 欧美亚洲 丝袜 人妻 在线| 中文乱码字字幕精品一区二区三区| 亚洲成人av在线免费| 亚洲aⅴ乱码一区二区在线播放| 日韩在线高清观看一区二区三区| 欧美另类一区| 亚洲精品中文字幕在线视频 | 一级片'在线观看视频| 尤物成人国产欧美一区二区三区| 久久热精品热| 亚洲av综合色区一区| 亚洲美女视频黄频| 精品一区二区三卡| 激情 狠狠 欧美| 亚洲精品亚洲一区二区| 欧美 日韩 精品 国产| 日日撸夜夜添| 人人妻人人看人人澡| 最近中文字幕高清免费大全6| 久久久久久久久久人人人人人人| 亚洲国产精品成人久久小说| 国产真实伦视频高清在线观看| 直男gayav资源| xxx大片免费视频| 国产精品国产av在线观看| 亚洲色图综合在线观看| 国产成人精品久久久久久| 最近的中文字幕免费完整| 亚洲欧美日韩无卡精品| 中文在线观看免费www的网站| 97在线视频观看| 99国产精品免费福利视频| 能在线免费看毛片的网站| 22中文网久久字幕| 欧美极品一区二区三区四区| 自拍欧美九色日韩亚洲蝌蚪91 | 人妻夜夜爽99麻豆av| 国产精品一二三区在线看| 在线观看一区二区三区| 日韩电影二区| 黄色怎么调成土黄色| 国产有黄有色有爽视频| 韩国av在线不卡| 欧美bdsm另类| 成年女人在线观看亚洲视频| 国产黄片视频在线免费观看| 你懂的网址亚洲精品在线观看| 最近2019中文字幕mv第一页| 久久久久精品久久久久真实原创| 久久精品熟女亚洲av麻豆精品| 日本av手机在线免费观看| 在线天堂最新版资源| 少妇 在线观看| 国产一区二区在线观看日韩| 联通29元200g的流量卡| 一区二区三区四区激情视频| 亚洲av日韩在线播放| 亚洲av综合色区一区| 99久久中文字幕三级久久日本| 18+在线观看网站| 国产精品久久久久久av不卡| 中文字幕av成人在线电影| 中文字幕亚洲精品专区| 一边亲一边摸免费视频| 日韩国内少妇激情av| 2021少妇久久久久久久久久久| 在线观看免费日韩欧美大片 | 超碰97精品在线观看| 最近最新中文字幕免费大全7| 在线播放无遮挡| 午夜老司机福利剧场| 91午夜精品亚洲一区二区三区| 中文字幕制服av| 大码成人一级视频| 麻豆成人av视频| 春色校园在线视频观看| 亚洲美女黄色视频免费看| 国产在线一区二区三区精| 麻豆国产97在线/欧美| 国产在线免费精品| 精品人妻熟女av久视频| 久久精品国产自在天天线| 男女无遮挡免费网站观看| 校园人妻丝袜中文字幕| av在线蜜桃| 女的被弄到高潮叫床怎么办| 一边亲一边摸免费视频| 女性生殖器流出的白浆| a 毛片基地| 日韩不卡一区二区三区视频在线| 成人午夜精彩视频在线观看| 天天躁日日操中文字幕| freevideosex欧美| 在线观看人妻少妇| 视频中文字幕在线观看| 亚洲av日韩在线播放| 如何舔出高潮| 国产亚洲91精品色在线| 国产精品一区二区三区四区免费观看| 欧美精品亚洲一区二区| 九九久久精品国产亚洲av麻豆| a级一级毛片免费在线观看| 美女福利国产在线 | av国产久精品久网站免费入址| 日日啪夜夜撸| 涩涩av久久男人的天堂| 综合色丁香网| 纵有疾风起免费观看全集完整版| 熟妇人妻不卡中文字幕| 国产精品爽爽va在线观看网站| 欧美区成人在线视频| 日韩一区二区三区影片| 黑人高潮一二区| 内射极品少妇av片p| 国产片特级美女逼逼视频| 99热国产这里只有精品6| 国产av一区二区精品久久 | 亚洲欧美日韩东京热| 精品一区二区三区视频在线| 少妇人妻 视频| 久久婷婷青草| 亚洲婷婷狠狠爱综合网| 午夜福利在线在线| 久久久久久久亚洲中文字幕| 舔av片在线| 又爽又黄a免费视频| 国产视频首页在线观看| 亚洲电影在线观看av| 蜜桃亚洲精品一区二区三区| 有码 亚洲区| 一个人看的www免费观看视频| 久久精品国产亚洲网站| 亚洲自偷自拍三级| 色综合色国产| 少妇 在线观看| 免费不卡的大黄色大毛片视频在线观看| 伦精品一区二区三区| 男人爽女人下面视频在线观看| 成人黄色视频免费在线看| 久久精品熟女亚洲av麻豆精品| 18禁在线无遮挡免费观看视频| av播播在线观看一区| 精品一区二区三卡| 亚洲婷婷狠狠爱综合网| 亚洲美女黄色视频免费看| 久久婷婷青草| 日韩欧美精品免费久久| 国产精品偷伦视频观看了| 免费少妇av软件| 嫩草影院入口| 国产一区二区三区av在线| 秋霞伦理黄片| 插阴视频在线观看视频| 亚洲熟女精品中文字幕| av视频免费观看在线观看| 精品久久久精品久久久| 婷婷色综合大香蕉| 日韩电影二区| 日韩一本色道免费dvd| 国产亚洲av片在线观看秒播厂| 一区二区三区四区激情视频|